xref: /petsc/src/dm/impls/swarm/data_bucket.c (revision 2eac95f8520d9ba12b3322b03606ec0954c54d13)
152849c42SDave May 
252849c42SDave May #include "data_bucket.h"
352849c42SDave May 
452849c42SDave May /* string helpers */
5*2eac95f8SDave May PetscErrorCode StringInList( const char name[], const PetscInt N, const DataField gfield[], PetscBool *val )
652849c42SDave May {
75c18a9d6SDave May 	PetscInt i;
852849c42SDave May 
952849c42SDave May 	*val = PETSC_FALSE;
1052849c42SDave May 	for( i=0; i<N; i++ ) {
1152849c42SDave May 		if( strcmp( name, gfield[i]->name ) == 0 ) {
1252849c42SDave May 			*val = PETSC_TRUE;
13*2eac95f8SDave May       PetscFunctionReturn(0);
1452849c42SDave May 		}
1552849c42SDave May 	}
16*2eac95f8SDave May   PetscFunctionReturn(0);
1752849c42SDave May }
1852849c42SDave May 
19*2eac95f8SDave May PetscErrorCode StringFindInList( const char name[], const PetscInt N, const DataField gfield[], PetscInt *index )
2052849c42SDave May {
215c18a9d6SDave May 	PetscInt i;
2252849c42SDave May 
2352849c42SDave May 	*index = -1;
2452849c42SDave May 	for( i=0; i<N; i++ ) {
2552849c42SDave May 		if( strcmp( name, gfield[i]->name ) == 0 ) {
2652849c42SDave May 			*index = i;
27*2eac95f8SDave May       PetscFunctionReturn(0);
2852849c42SDave May 		}
2952849c42SDave May 	}
30*2eac95f8SDave May   PetscFunctionReturn(0);
3152849c42SDave May }
3252849c42SDave May 
33*2eac95f8SDave May #undef __FUNCT__
34*2eac95f8SDave May #define __FUNCT__ "DataFieldCreate"
35*2eac95f8SDave May PetscErrorCode DataFieldCreate( const char registeration_function[], const char name[], const size_t size, const PetscInt L, DataField *DF )
3652849c42SDave May {
3752849c42SDave May 	DataField df;
3852849c42SDave May 
3952849c42SDave May 	df = malloc( sizeof(struct _p_DataField) );
4052849c42SDave May 	memset( df, 0, sizeof(struct _p_DataField) );
4152849c42SDave May 
4252849c42SDave May 
4352849c42SDave May 	asprintf( &df->registeration_function, "%s", registeration_function );
4452849c42SDave May 	asprintf( &df->name, "%s", name );
4552849c42SDave May 	df->atomic_size = size;
4652849c42SDave May 	df->L = L;
4752849c42SDave May 
4852849c42SDave May 	df->data = malloc( size * L ); /* allocate something so we don't have to reallocate */
4952849c42SDave May 	memset( df->data, 0, size * L );
5052849c42SDave May 
5152849c42SDave May 	*DF = df;
52*2eac95f8SDave May   PetscFunctionReturn(0);
5352849c42SDave May }
5452849c42SDave May 
55*2eac95f8SDave May #undef __FUNCT__
56*2eac95f8SDave May #define __FUNCT__ "DataFieldDestroy"
57*2eac95f8SDave May PetscErrorCode DataFieldDestroy( DataField *DF )
5852849c42SDave May {
5952849c42SDave May 	DataField df = *DF;
6052849c42SDave May 
6152849c42SDave May 	free( df->registeration_function );
6252849c42SDave May 	free( df->name );
6352849c42SDave May 	free( df->data );
6452849c42SDave May 	free(df);
6552849c42SDave May 
6652849c42SDave May 	*DF = NULL;
67*2eac95f8SDave May   PetscFunctionReturn(0);
6852849c42SDave May }
6952849c42SDave May 
7052849c42SDave May /* data bucket */
71*2eac95f8SDave May #undef __FUNCT__
72*2eac95f8SDave May #define __FUNCT__ "DataBucketCreate"
73*2eac95f8SDave May PetscErrorCode DataBucketCreate( DataBucket *DB )
7452849c42SDave May {
7552849c42SDave May 	DataBucket db;
7652849c42SDave May 
7752849c42SDave May 
7852849c42SDave May 	db = malloc( sizeof(struct _p_DataBucket) );
7952849c42SDave May 	memset( db, 0, sizeof(struct _p_DataBucket) );
8052849c42SDave May 
8152849c42SDave May 	db->finalised = PETSC_FALSE;
8252849c42SDave May 
8352849c42SDave May 	/* create empty spaces for fields */
8452849c42SDave May 	db->L         = 0;
8552849c42SDave May 	db->buffer    = 1;
8652849c42SDave May 	db->allocated = 1;
8752849c42SDave May 
8852849c42SDave May 	db->nfields   = 0;
8952849c42SDave May 	db->field     = malloc(sizeof(DataField));
9052849c42SDave May 
9152849c42SDave May 	*DB = db;
92*2eac95f8SDave May   PetscFunctionReturn(0);
9352849c42SDave May }
9452849c42SDave May 
95*2eac95f8SDave May #undef __FUNCT__
96*2eac95f8SDave May #define __FUNCT__ "DataBucketDestroy"
97*2eac95f8SDave May PetscErrorCode DataBucketDestroy( DataBucket *DB )
9852849c42SDave May {
9952849c42SDave May 	DataBucket db = *DB;
1005c18a9d6SDave May 	PetscInt f;
10152849c42SDave May 
10252849c42SDave May 	/* release fields */
10352849c42SDave May 	for( f=0; f<db->nfields; f++ ) {
10452849c42SDave May 		DataFieldDestroy(&db->field[f]);
10552849c42SDave May 	}
10652849c42SDave May 
10752849c42SDave May 	/* this will catch the initially allocated objects in the event that no fields are registered */
10852849c42SDave May 	if(db->field!=NULL) {
10952849c42SDave May 		free(db->field);
11052849c42SDave May 	}
11152849c42SDave May 
11252849c42SDave May 	free(db);
11352849c42SDave May 
11452849c42SDave May 	*DB = NULL;
115*2eac95f8SDave May   PetscFunctionReturn(0);
11652849c42SDave May }
11752849c42SDave May 
118*2eac95f8SDave May #undef __FUNCT__
119*2eac95f8SDave May #define __FUNCT__ "DataBucketRegisterField"
120*2eac95f8SDave May PetscErrorCode DataBucketRegisterField(
12152849c42SDave May                               DataBucket db,
12252849c42SDave May                               const char registeration_function[],
12352849c42SDave May                               const char field_name[],
12452849c42SDave May                               size_t atomic_size, DataField *_gfield )
12552849c42SDave May {
12652849c42SDave May 	PetscBool val;
12752849c42SDave May 	DataField *field,fp;
12852849c42SDave May 
12952849c42SDave May 	/* check we haven't finalised the registration of fields */
13052849c42SDave May 	/*
13152849c42SDave May    if(db->finalised==PETSC_TRUE) {
13252849c42SDave May    printf("ERROR: DataBucketFinalize() has been called. Cannot register more fields\n");
13352849c42SDave May    ERROR();
13452849c42SDave May    }
13552849c42SDave May    */
13652849c42SDave May 
13752849c42SDave May 	/* check for repeated name */
13852849c42SDave May 	StringInList( field_name, db->nfields, (const DataField*)db->field, &val );
139*2eac95f8SDave May 	if(val == PETSC_TRUE ) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_USER,"Field %s already exists. Cannot add same field twice",field_name);
14052849c42SDave May 
14152849c42SDave May 	/* create new space for data */
14252849c42SDave May 	field = realloc( db->field,     sizeof(DataField)*(db->nfields+1));
14352849c42SDave May 	db->field     = field;
14452849c42SDave May 
14552849c42SDave May 	/* add field */
14652849c42SDave May 	DataFieldCreate( registeration_function, field_name, atomic_size, db->allocated, &fp );
14752849c42SDave May 	db->field[ db->nfields ] = fp;
14852849c42SDave May 
14952849c42SDave May 	db->nfields++;
15052849c42SDave May 
15152849c42SDave May 	if(_gfield!=NULL){
15252849c42SDave May 		*_gfield = fp;
15352849c42SDave May 	}
154*2eac95f8SDave May   PetscFunctionReturn(0);
15552849c42SDave May }
15652849c42SDave May 
15752849c42SDave May /*
15852849c42SDave May  #define DataBucketRegisterField(db,name,size,k) {\
15952849c42SDave May  char *location;\
16052849c42SDave May  asprintf(&location,"Registered by %s() at line %d within file %s", __FUNCTION__, __LINE__, __FILE__);\
16152849c42SDave May  _DataBucketRegisterField( (db), location, (name), (size), (k) );\
16252849c42SDave May  free(location);\
16352849c42SDave May  }
16452849c42SDave May  */
16552849c42SDave May 
166*2eac95f8SDave May #undef __FUNCT__
167*2eac95f8SDave May #define __FUNCT__ "DataBucketGetDataFieldByName"
168*2eac95f8SDave May PetscErrorCode DataBucketGetDataFieldByName(DataBucket db,const char name[],DataField *gfield)
16952849c42SDave May {
1705c18a9d6SDave May 	PetscInt idx;
17152849c42SDave May 	PetscBool found;
17252849c42SDave May 
17352849c42SDave May 	StringInList(name,db->nfields,(const DataField*)db->field,&found);
174*2eac95f8SDave May 	if (!found) SETERRQ1(PETSC_COMM_SELF,PETSC_ERR_USER,"Cannot find DataField with name %s",name);
175*2eac95f8SDave May 
17652849c42SDave May 	StringFindInList(name,db->nfields,(const DataField*)db->field,&idx);
17752849c42SDave May 
17852849c42SDave May 	*gfield = db->field[idx];
179*2eac95f8SDave May   PetscFunctionReturn(0);
18052849c42SDave May }
18152849c42SDave May 
18252849c42SDave May void DataBucketQueryDataFieldByName(DataBucket db,const char name[],PetscBool *found)
18352849c42SDave May {
18452849c42SDave May 	*found = PETSC_FALSE;
18552849c42SDave May 	StringInList(name,db->nfields,(const DataField*)db->field,found);
18652849c42SDave May }
18752849c42SDave May 
18852849c42SDave May void DataBucketFinalize(DataBucket db)
18952849c42SDave May {
19052849c42SDave May 	db->finalised = PETSC_TRUE;
19152849c42SDave May }
19252849c42SDave May 
1935c18a9d6SDave May void DataFieldGetNumEntries(DataField df, PetscInt *sum)
19452849c42SDave May {
19552849c42SDave May 	*sum = df->L;
19652849c42SDave May }
19752849c42SDave May 
1985c18a9d6SDave May void DataFieldSetSize( DataField df, const PetscInt new_L )
19952849c42SDave May {
20052849c42SDave May 	void *tmp_data;
20152849c42SDave May 
20252849c42SDave May 	if( new_L <= 0 ) {
20352849c42SDave May 		printf("ERROR: Cannot set size of DataField to be <= 0 \n");
20452849c42SDave May 		ERROR();
20552849c42SDave May 	}
20652849c42SDave May 	if( new_L == df->L ) return;
20752849c42SDave May 
20852849c42SDave May 	if( new_L > df->L ) {
20952849c42SDave May 
21052849c42SDave May 		tmp_data = realloc( df->data, df->atomic_size * (new_L) );
21152849c42SDave May 		df->data = tmp_data;
21252849c42SDave May 
21352849c42SDave May 		/* init new contents */
21452849c42SDave May 		memset( ( ((char*)df->data)+df->L*df->atomic_size), 0, (new_L-df->L)*df->atomic_size );
21552849c42SDave May 
21652849c42SDave May 	}
21752849c42SDave May 	else {
21852849c42SDave May 		/* reallocate pointer list, add +1 in case new_L = 0 */
21952849c42SDave May 		tmp_data = realloc( df->data, df->atomic_size * (new_L+1) );
22052849c42SDave May 		df->data = tmp_data;
22152849c42SDave May 	}
22252849c42SDave May 
22352849c42SDave May 	df->L = new_L;
22452849c42SDave May }
22552849c42SDave May 
2265c18a9d6SDave May void DataFieldZeroBlock( DataField df, const PetscInt start, const PetscInt end )
22752849c42SDave May {
22852849c42SDave May 	if( start > end ) {
22952849c42SDave May 		printf("ERROR: Cannot zero a block of entries if start(%d) > end(%d) \n",start,end);
23052849c42SDave May 		ERROR();
23152849c42SDave May 	}
23252849c42SDave May 	if( start < 0 ) {
23352849c42SDave May 		printf("ERROR: Cannot zero a block of entries if start(%d) < 0 \n",start);
23452849c42SDave May 		ERROR();
23552849c42SDave May 	}
23652849c42SDave May 	if( end > df->L ) {
23752849c42SDave May 		printf("ERROR: Cannot zero a block of entries if end(%d) >= array size(%d) \n",end,df->L);
23852849c42SDave May 		ERROR();
23952849c42SDave May 	}
24052849c42SDave May 
24152849c42SDave May 	memset( ( ((char*)df->data)+start*df->atomic_size), 0, (end-start)*df->atomic_size );
24252849c42SDave May }
24352849c42SDave May 
24452849c42SDave May /*
24552849c42SDave May  A negative buffer value will simply be ignored and the old buffer value will be used.
24652849c42SDave May  */
2475c18a9d6SDave May void DataBucketSetSizes( DataBucket db, const PetscInt L, const PetscInt buffer )
24852849c42SDave May {
2495c18a9d6SDave May 	PetscInt current_allocated,new_used,new_unused,new_buffer,new_allocated,f;
25052849c42SDave May 
25152849c42SDave May 
25252849c42SDave May 	if( db->finalised == PETSC_FALSE ) {
25352849c42SDave May 		printf("ERROR: You must call DataBucketFinalize() before DataBucketSetSizes() \n");
25452849c42SDave May 		ERROR();
25552849c42SDave May 	}
25652849c42SDave May 
25752849c42SDave May 	current_allocated = db->allocated;
25852849c42SDave May 
25952849c42SDave May 	new_used   = L;
26052849c42SDave May 	new_unused = current_allocated - new_used;
26152849c42SDave May 	new_buffer = db->buffer;
26252849c42SDave May 	if( buffer >= 0 ) { /* update the buffer value */
26352849c42SDave May 		new_buffer = buffer;
26452849c42SDave May 	}
26552849c42SDave May 	new_allocated = new_used + new_buffer;
26652849c42SDave May 
26752849c42SDave May 	/* action */
26852849c42SDave May 	if ( new_allocated > current_allocated ) {
26952849c42SDave May 		/* increase size to new_used + new_buffer */
27052849c42SDave May 		for( f=0; f<db->nfields; f++ ) {
27152849c42SDave May 			DataFieldSetSize( db->field[f], new_allocated );
27252849c42SDave May 		}
27352849c42SDave May 
27452849c42SDave May 		db->L         = new_used;
27552849c42SDave May 		db->buffer    = new_buffer;
27652849c42SDave May 		db->allocated = new_used + new_buffer;
27752849c42SDave May 	}
27852849c42SDave May 	else {
27952849c42SDave May 		if( new_unused > 2 * new_buffer ) {
28052849c42SDave May 
28152849c42SDave May 			/* shrink array to new_used + new_buffer */
28252849c42SDave May 			for( f=0; f<db->nfields; f++ ) {
28352849c42SDave May 				DataFieldSetSize( db->field[f], new_allocated );
28452849c42SDave May 			}
28552849c42SDave May 
28652849c42SDave May 			db->L         = new_used;
28752849c42SDave May 			db->buffer    = new_buffer;
28852849c42SDave May 			db->allocated = new_used + new_buffer;
28952849c42SDave May 		}
29052849c42SDave May 		else {
29152849c42SDave May 			db->L      = new_used;
29252849c42SDave May 			db->buffer = new_buffer;
29352849c42SDave May 		}
29452849c42SDave May 	}
29552849c42SDave May 
29652849c42SDave May 	/* zero all entries from db->L to db->allocated */
29752849c42SDave May 	for( f=0; f<db->nfields; f++ ) {
29852849c42SDave May 		DataField field = db->field[f];
29952849c42SDave May 		DataFieldZeroBlock(field, db->L,db->allocated);
30052849c42SDave May 	}
30152849c42SDave May }
30252849c42SDave May 
3035c18a9d6SDave May void DataBucketSetInitialSizes( DataBucket db, const PetscInt L, const PetscInt buffer )
30452849c42SDave May {
3055c18a9d6SDave May 	PetscInt f;
30652849c42SDave May 	DataBucketSetSizes(db,L,buffer);
30752849c42SDave May 
30852849c42SDave May 	for( f=0; f<db->nfields; f++ ) {
30952849c42SDave May 		DataField field = db->field[f];
31052849c42SDave May 		DataFieldZeroBlock(field,0,db->allocated);
31152849c42SDave May 	}
31252849c42SDave May }
31352849c42SDave May 
3145c18a9d6SDave May void DataBucketGetSizes( DataBucket db, PetscInt *L, PetscInt *buffer, PetscInt *allocated )
31552849c42SDave May {
31652849c42SDave May 	if (L) { *L = db->L; }
31752849c42SDave May 	if (buffer) { *buffer = db->buffer; }
31852849c42SDave May 	if (allocated) { *allocated = db->allocated; }
31952849c42SDave May }
32052849c42SDave May 
3215c18a9d6SDave May void DataBucketGetGlobalSizes(MPI_Comm comm, DataBucket db, PetscInt *L, PetscInt *buffer, PetscInt *allocated )
32252849c42SDave May {
3235c18a9d6SDave May 	PetscInt _L,_buffer,_allocated;
3245c18a9d6SDave May 	PetscInt ierr;
32552849c42SDave May 
3265c18a9d6SDave May 	_L = db->L;
3275c18a9d6SDave May 	_buffer = db->buffer;
3285c18a9d6SDave May 	_allocated = db->allocated;
32952849c42SDave May 
3305c18a9d6SDave May 	if (L) {         ierr = MPI_Allreduce(&_L,L,1,MPIU_INT,MPI_SUM,comm); }
3315c18a9d6SDave May 	if (buffer) {    ierr = MPI_Allreduce(&_buffer,buffer,1,MPIU_INT,MPI_SUM,comm); }
3325c18a9d6SDave May 	if (allocated) { ierr = MPI_Allreduce(&_allocated,allocated,1,MPIU_INT,MPI_SUM,comm); }
33352849c42SDave May }
33452849c42SDave May 
3355c18a9d6SDave May void DataBucketGetDataFields( DataBucket db, PetscInt *L, DataField *fields[] )
33652849c42SDave May {
33752849c42SDave May 	if(L){      *L      = db->nfields; }
33852849c42SDave May 	if(fields){ *fields = db->field; }
33952849c42SDave May }
34052849c42SDave May 
34152849c42SDave May void DataFieldGetAccess( const DataField gfield )
34252849c42SDave May {
34352849c42SDave May 	if(gfield->active==PETSC_TRUE) {
34452849c42SDave May 		printf("ERROR: Field \"%s\" is already active. You must call DataFieldRestoreAccess()\n", gfield->name );
34552849c42SDave May 		ERROR();
34652849c42SDave May 	}
34752849c42SDave May 	gfield->active = PETSC_TRUE;
34852849c42SDave May }
34952849c42SDave May 
3505c18a9d6SDave May void DataFieldAccessPoint( const DataField gfield, const PetscInt pid, void **ctx_p )
35152849c42SDave May {
35252849c42SDave May #ifdef DATAFIELD_POINT_ACCESS_GUARD
35352849c42SDave May 	/* debug mode */
3545c18a9d6SDave May 	/* check poPetscInt is valid */
35552849c42SDave May 	if( pid < 0 ){ printf("ERROR: index must be >= 0\n"); ERROR();  }
35652849c42SDave May 	if( pid >= gfield->L ){ printf("ERROR: index must be < %d\n",gfield->L); ERROR(); }
35752849c42SDave May 
35852849c42SDave May 	if(gfield->active==PETSC_FALSE) {
3595c18a9d6SDave May 		printf("ERROR: Field \"%s\" is not active. You must call DataFieldGetAccess() before poPetscInt data can be retrivied\n",gfield->name);
36052849c42SDave May 		ERROR();
36152849c42SDave May 	}
36252849c42SDave May #endif
36352849c42SDave May 
36452849c42SDave May 	//*ctx_p  = (void*)( ((char*)gfield->data) + pid * gfield->atomic_size);
36552849c42SDave May 	*ctx_p = __DATATFIELD_point_access(gfield->data,pid,gfield->atomic_size);
36652849c42SDave May }
36752849c42SDave May 
3685c18a9d6SDave May void DataFieldAccessPointOffset( const DataField gfield, const size_t offset, const PetscInt pid, void **ctx_p )
36952849c42SDave May {
37052849c42SDave May #ifdef DATAFIELD_POINT_ACCESS_GUARD
37152849c42SDave May 	/* debug mode */
37252849c42SDave May 
3735c18a9d6SDave May 	/* check poPetscInt is valid */
3745c18a9d6SDave May 	/* if( offset < 0 ){ printf("ERROR: offset must be >= 0\n"); ERROR();  } *//* Note compiler realizes this can never happen with an unsigned PetscInt */
37552849c42SDave May 	if( offset >= gfield->atomic_size ){ printf("ERROR: offset must be < %zu\n",gfield->atomic_size); ERROR(); }
37652849c42SDave May 
3775c18a9d6SDave May 	/* check poPetscInt is valid */
37852849c42SDave May 	if( pid < 0 ){ printf("ERROR: index must be >= 0\n"); ERROR();  }
37952849c42SDave May 	if( pid >= gfield->L ){ printf("ERROR: index must be < %d\n",gfield->L); ERROR(); }
38052849c42SDave May 
38152849c42SDave May 	if(gfield->active==PETSC_FALSE) {
3825c18a9d6SDave May 		printf("ERROR: Field \"%s\" is not active. You must call DataFieldGetAccess() before poPetscInt data can be retrivied\n",gfield->name);
38352849c42SDave May 		ERROR();
38452849c42SDave May 	}
38552849c42SDave May #endif
38652849c42SDave May 
38752849c42SDave May 	*ctx_p = __DATATFIELD_point_access_offset(gfield->data,pid,gfield->atomic_size,offset);
38852849c42SDave May }
38952849c42SDave May 
39052849c42SDave May void DataFieldRestoreAccess( DataField gfield )
39152849c42SDave May {
39252849c42SDave May 	if(gfield->active==PETSC_FALSE) {
39352849c42SDave May 		printf("ERROR: Field \"%s\" is not active. You must call DataFieldGetAccess()\n", gfield->name );
39452849c42SDave May 		ERROR();
39552849c42SDave May 	}
39652849c42SDave May 	gfield->active = PETSC_FALSE;
39752849c42SDave May }
39852849c42SDave May 
39952849c42SDave May void DataFieldVerifyAccess( const DataField gfield, const size_t size)
40052849c42SDave May {
40152849c42SDave May #ifdef DATAFIELD_POINT_ACCESS_GUARD
40252849c42SDave May 	if(gfield->atomic_size != size ) {
40352849c42SDave May     printf("ERROR: Field \"%s\" must be mapped to %zu bytes, your intended structure is %zu bytes in length.\n",
40452849c42SDave May            gfield->name, gfield->atomic_size, size );
40552849c42SDave May 		ERROR();
40652849c42SDave May 	}
40752849c42SDave May #endif
40852849c42SDave May }
40952849c42SDave May 
41052849c42SDave May void DataFieldGetAtomicSize(const DataField gfield,size_t *size)
41152849c42SDave May {
41252849c42SDave May   if (size) { *size = gfield->atomic_size; }
41352849c42SDave May }
41452849c42SDave May 
41552849c42SDave May void DataFieldGetEntries(const DataField gfield,void **data)
41652849c42SDave May {
41752849c42SDave May   if (data) {
41852849c42SDave May     *data = gfield->data;
41952849c42SDave May   }
42052849c42SDave May }
42152849c42SDave May 
42252849c42SDave May void DataFieldRestoreEntries(const DataField gfield,void **data)
42352849c42SDave May {
42452849c42SDave May   if (data) {
42552849c42SDave May     *data = NULL;
42652849c42SDave May   }
42752849c42SDave May }
42852849c42SDave May 
42952849c42SDave May /* y = x */
4305c18a9d6SDave May void DataBucketCopyPoint( const DataBucket xb, const PetscInt pid_x,
4315c18a9d6SDave May                          const DataBucket yb, const PetscInt pid_y )
43252849c42SDave May {
4335c18a9d6SDave May 	PetscInt f;
43452849c42SDave May 	for( f=0; f<xb->nfields; f++ ) {
43552849c42SDave May 		void *dest;
43652849c42SDave May 		void *src;
43752849c42SDave May 
43852849c42SDave May 		DataFieldGetAccess( xb->field[f] );
43952849c42SDave May 		if (xb!=yb) { DataFieldGetAccess( yb->field[f] ); }
44052849c42SDave May 
44152849c42SDave May 		DataFieldAccessPoint( xb->field[f],pid_x, &src );
44252849c42SDave May 		DataFieldAccessPoint( yb->field[f],pid_y, &dest );
44352849c42SDave May 
44452849c42SDave May 		memcpy( dest, src, xb->field[f]->atomic_size );
44552849c42SDave May 
44652849c42SDave May 		DataFieldRestoreAccess( xb->field[f] );
44752849c42SDave May 		if (xb!=yb) { DataFieldRestoreAccess( yb->field[f] ); }
44852849c42SDave May 	}
44952849c42SDave May 
45052849c42SDave May }
45152849c42SDave May 
4525c18a9d6SDave May void DataBucketCreateFromSubset( DataBucket DBIn, const PetscInt N, const PetscInt list[], DataBucket *DB )
45352849c42SDave May {
4545c18a9d6SDave May 	PetscInt nfields;
45552849c42SDave May 	DataField *fields;
45652849c42SDave May 	DataBucketCreate(DB);
4575c18a9d6SDave May 	PetscInt f,L,buffer,allocated,p;
45852849c42SDave May 
45952849c42SDave May 	/* copy contents of DBIn */
46052849c42SDave May 	DataBucketGetDataFields(DBIn,&nfields,&fields);
46152849c42SDave May 	DataBucketGetSizes(DBIn,&L,&buffer,&allocated);
46252849c42SDave May 
46352849c42SDave May 	for(f=0;f<nfields;f++) {
464*2eac95f8SDave May 		DataBucketRegisterField(*DB,"DataBucketCreateFromSubset",fields[f]->name,fields[f]->atomic_size,NULL);
46552849c42SDave May 	}
46652849c42SDave May 	DataBucketFinalize(*DB);
46752849c42SDave May 
46852849c42SDave May 	DataBucketSetSizes(*DB,L,buffer);
46952849c42SDave May 
47052849c42SDave May 	/* now copy the desired guys from DBIn => DB */
47152849c42SDave May 	for( p=0; p<N; p++ ) {
47252849c42SDave May 		DataBucketCopyPoint(DBIn,list[p], *DB,p);
47352849c42SDave May 	}
47452849c42SDave May 
47552849c42SDave May }
47652849c42SDave May 
47752849c42SDave May // insert into an exisitng location
4785c18a9d6SDave May void DataFieldInsertPoint( const DataField field, const PetscInt index, const void *ctx )
47952849c42SDave May {
48052849c42SDave May 
48152849c42SDave May #ifdef DATAFIELD_POINT_ACCESS_GUARD
4825c18a9d6SDave May 	/* check poPetscInt is valid */
48352849c42SDave May 	if( index < 0 ){ printf("ERROR: index must be >= 0\n"); ERROR();  }
48452849c42SDave May 	if( index >= field->L ){ printf("ERROR: index must be < %d\n",field->L); ERROR(); }
48552849c42SDave May #endif
48652849c42SDave May 
48752849c42SDave May   //	memcpy( (void*)((char*)field->data + index*field->atomic_size), ctx, field->atomic_size );
48852849c42SDave May 	memcpy( __DATATFIELD_point_access(field->data,index,field->atomic_size), ctx, field->atomic_size );
48952849c42SDave May }
49052849c42SDave May 
49152849c42SDave May // remove data at index - replace with last point
4925c18a9d6SDave May void DataBucketRemovePointAtIndex( const DataBucket db, const PetscInt index )
49352849c42SDave May {
4945c18a9d6SDave May 	PetscInt f;
49552849c42SDave May 
49652849c42SDave May #ifdef DATAFIELD_POINT_ACCESS_GUARD
4975c18a9d6SDave May 	/* check poPetscInt is valid */
49852849c42SDave May 	if( index < 0 ){ printf("ERROR: index must be >= 0\n"); ERROR(); }
49952849c42SDave May 	if( index >= db->allocated ){ printf("ERROR: index must be < %d\n",db->L+db->buffer); ERROR(); }
50052849c42SDave May #endif
50152849c42SDave May 
5025c18a9d6SDave May 	if (index >= db->L) { /* this poPetscInt is not in the list - no need to error, but I will anyway */
5035c18a9d6SDave May 		printf("ERROR: You should not be trying to remove poPetscInt at index=%d since it's < db->L = %d \n", index, db->L );
50452849c42SDave May 		ERROR();
50552849c42SDave May 	}
50652849c42SDave May 
5075c18a9d6SDave May 	if (index != db->L-1) { /* not last poPetscInt in list */
50852849c42SDave May 		for( f=0; f<db->nfields; f++ ) {
50952849c42SDave May 			DataField field = db->field[f];
51052849c42SDave May 
51152849c42SDave May 			/* copy then remove */
51252849c42SDave May 			DataFieldCopyPoint( db->L-1,field, index,field );
51352849c42SDave May 
51452849c42SDave May 			//DataFieldZeroPoint(field,index);
51552849c42SDave May 		}
51652849c42SDave May 	}
51752849c42SDave May 
51852849c42SDave May 	/* decrement size */
51952849c42SDave May 	/* this will zero out an crap at the end of the list */
52052849c42SDave May 	DataBucketRemovePoint(db);
52152849c42SDave May 
52252849c42SDave May }
52352849c42SDave May 
52452849c42SDave May /* copy x into y */
5255c18a9d6SDave May void DataFieldCopyPoint( const PetscInt pid_x, const DataField field_x,
5265c18a9d6SDave May                         const PetscInt pid_y, const DataField field_y )
52752849c42SDave May {
52852849c42SDave May 
52952849c42SDave May #ifdef DATAFIELD_POINT_ACCESS_GUARD
5305c18a9d6SDave May 	/* check poPetscInt is valid */
53152849c42SDave May 	if( pid_x < 0 ){ printf("ERROR: (IN) index must be >= 0\n"); ERROR(); }
53252849c42SDave May 	if( pid_x >= field_x->L ){ printf("ERROR: (IN) index must be < %d\n",field_x->L); ERROR(); }
53352849c42SDave May 
53452849c42SDave May 	if( pid_y < 0 ){ printf("ERROR: (OUT) index must be >= 0\n"); ERROR(); }
53552849c42SDave May 	if( pid_y >= field_y->L ){ printf("ERROR: (OUT) index must be < %d\n",field_y->L); ERROR(); }
53652849c42SDave May 
53752849c42SDave May 	if( field_y->atomic_size != field_x->atomic_size ) {
53852849c42SDave May 		printf("ERROR: atomic size must match \n"); ERROR();
53952849c42SDave May 	}
54052849c42SDave May #endif
54152849c42SDave May 	/*
54252849c42SDave May    memcpy( (void*)((char*)field_y->data + pid_y*field_y->atomic_size),
54352849c42SDave May    (void*)((char*)field_x->data + pid_x*field_x->atomic_size),
54452849c42SDave May    field_x->atomic_size );
54552849c42SDave May    */
54652849c42SDave May 	memcpy(		__DATATFIELD_point_access(field_y->data,pid_y,field_y->atomic_size),
54752849c42SDave May          __DATATFIELD_point_access(field_x->data,pid_x,field_x->atomic_size),
54852849c42SDave May          field_y->atomic_size );
54952849c42SDave May 
55052849c42SDave May }
55152849c42SDave May 
55252849c42SDave May 
55352849c42SDave May // zero only the datafield at this point
5545c18a9d6SDave May void DataFieldZeroPoint( const DataField field, const PetscInt index )
55552849c42SDave May {
55652849c42SDave May #ifdef DATAFIELD_POINT_ACCESS_GUARD
5575c18a9d6SDave May 	/* check poPetscInt is valid */
55852849c42SDave May 	if( index < 0 ){ printf("ERROR: index must be >= 0\n"); ERROR(); }
55952849c42SDave May 	if( index >= field->L ){ printf("ERROR: index must be < %d\n",field->L); ERROR(); }
56052849c42SDave May #endif
56152849c42SDave May 
56252849c42SDave May   //	memset( (void*)((char*)field->data + index*field->atomic_size), 0, field->atomic_size );
56352849c42SDave May 	memset( __DATATFIELD_point_access(field->data,index,field->atomic_size), 0, field->atomic_size );
56452849c42SDave May }
56552849c42SDave May 
56652849c42SDave May // zero ALL data for this point
5675c18a9d6SDave May void DataBucketZeroPoint( const DataBucket db, const PetscInt index )
56852849c42SDave May {
5695c18a9d6SDave May 	PetscInt f;
57052849c42SDave May 
5715c18a9d6SDave May 	/* check poPetscInt is valid */
57252849c42SDave May 	if( index < 0 ){ printf("ERROR: index must be >= 0\n"); ERROR(); }
57352849c42SDave May 	if( index >= db->allocated ){ printf("ERROR: index must be < %d\n",db->allocated); ERROR(); }
57452849c42SDave May 
57552849c42SDave May 	for(f=0;f<db->nfields;f++){
57652849c42SDave May 		DataField field = db->field[f];
57752849c42SDave May 
57852849c42SDave May 		DataFieldZeroPoint(field,index);
57952849c42SDave May 	}
58052849c42SDave May }
58152849c42SDave May 
58252849c42SDave May /* increment */
58352849c42SDave May void DataBucketAddPoint( DataBucket db )
58452849c42SDave May {
58552849c42SDave May 	DataBucketSetSizes( db, db->L+1, -1 );
58652849c42SDave May }
58752849c42SDave May /* decrement */
58852849c42SDave May void DataBucketRemovePoint( DataBucket db )
58952849c42SDave May {
59052849c42SDave May 	DataBucketSetSizes( db, db->L-1, -1 );
59152849c42SDave May }
59252849c42SDave May 
59352849c42SDave May void _DataFieldViewBinary(DataField field, FILE *fp )
59452849c42SDave May {
59552849c42SDave May 	fprintf(fp,"<DataField>\n");
59652849c42SDave May 	fprintf(fp,"%d\n", field->L);
59752849c42SDave May 	fprintf(fp,"%zu\n",field->atomic_size);
59852849c42SDave May 	fprintf(fp,"%s\n", field->registeration_function);
59952849c42SDave May 	fprintf(fp,"%s\n", field->name);
60052849c42SDave May 
60152849c42SDave May 	fwrite(field->data, field->atomic_size, field->L, fp);
60252849c42SDave May   /*
60352849c42SDave May    printf("  ** wrote %zu bytes for DataField \"%s\" \n", field->atomic_size * field->L, field->name );
60452849c42SDave May    */
60552849c42SDave May 	fprintf(fp,"\n</DataField>\n");
60652849c42SDave May }
60752849c42SDave May 
60852849c42SDave May void _DataBucketRegisterFieldFromFile( FILE *fp, DataBucket db )
60952849c42SDave May {
61052849c42SDave May 	PetscBool val;
61152849c42SDave May 	DataField *field;
61252849c42SDave May 
61352849c42SDave May 	DataField gfield;
61452849c42SDave May 	char dummy[100];
61552849c42SDave May 	char registeration_function[5000];
61652849c42SDave May 	char field_name[5000];
6175c18a9d6SDave May 	PetscInt L;
61852849c42SDave May 	size_t atomic_size,strL;
61952849c42SDave May 
62052849c42SDave May 
62152849c42SDave May 	/* check we haven't finalised the registration of fields */
62252849c42SDave May 	/*
62352849c42SDave May    if(db->finalised==PETSC_TRUE) {
62452849c42SDave May    printf("ERROR: DataBucketFinalize() has been called. Cannot register more fields\n");
62552849c42SDave May    ERROR();
62652849c42SDave May    }
62752849c42SDave May    */
62852849c42SDave May 
62952849c42SDave May 
63052849c42SDave May 	/* read file contents */
63152849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
63252849c42SDave May 
63352849c42SDave May 	fscanf( fp, "%d\n",&L); //printf("read(L): %d\n", L);
63452849c42SDave May 
63552849c42SDave May 	fscanf( fp, "%zu\n",&atomic_size); //printf("read(size): %zu\n",atomic_size);
63652849c42SDave May 
63752849c42SDave May 	fgets(registeration_function,4999,fp); //printf("read(reg func): %s", registeration_function );
63852849c42SDave May 	strL = strlen(registeration_function);
63952849c42SDave May 	if(strL>1){
64052849c42SDave May 		registeration_function[strL-1] = 0;
64152849c42SDave May 	}
64252849c42SDave May 
64352849c42SDave May 	fgets(field_name,4999,fp); //printf("read(name): %s", field_name );
64452849c42SDave May 	strL = strlen(field_name);
64552849c42SDave May 	if(strL>1){
64652849c42SDave May 		field_name[strL-1] = 0;
64752849c42SDave May 	}
64852849c42SDave May 
6494b46c5e1SDave May #ifdef DATA_BUCKET_LOG
65052849c42SDave May 	printf("  ** read L=%d; atomic_size=%zu; reg_func=\"%s\"; name=\"%s\" \n", L,atomic_size,registeration_function,field_name);
65152849c42SDave May #endif
65252849c42SDave May 
65352849c42SDave May 
65452849c42SDave May 	/* check for repeated name */
65552849c42SDave May 	StringInList( field_name, db->nfields, (const DataField*)db->field, &val );
65652849c42SDave May 	if(val == PETSC_TRUE ) {
65752849c42SDave May 		printf("ERROR: Cannot add same field twice\n");
65852849c42SDave May 		ERROR();
65952849c42SDave May 	}
66052849c42SDave May 
66152849c42SDave May 	/* create new space for data */
66252849c42SDave May 	field = realloc( db->field,     sizeof(DataField)*(db->nfields+1));
66352849c42SDave May 	db->field     = field;
66452849c42SDave May 
66552849c42SDave May 	/* add field */
66652849c42SDave May 	DataFieldCreate( registeration_function, field_name, atomic_size, L, &gfield );
66752849c42SDave May 
66852849c42SDave May 	/* copy contents of file */
66952849c42SDave May 	fread(gfield->data, gfield->atomic_size, gfield->L, fp);
6704b46c5e1SDave May #ifdef DATA_BUCKET_LOG
67152849c42SDave May 	printf("  ** read %zu bytes for DataField \"%s\" \n", gfield->atomic_size * gfield->L, field_name );
67252849c42SDave May #endif
67352849c42SDave May 	/* finish reading meta data */
67452849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
67552849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
67652849c42SDave May 
67752849c42SDave May 	db->field[ db->nfields ] = gfield;
67852849c42SDave May 
67952849c42SDave May 	db->nfields++;
68052849c42SDave May 
68152849c42SDave May }
68252849c42SDave May 
68352849c42SDave May void _DataBucketViewAscii_HeaderWrite_v00(FILE *fp)
68452849c42SDave May {
68552849c42SDave May 	fprintf(fp,"<DataBucketHeader>\n");
68652849c42SDave May 	fprintf(fp,"type=DataBucket\n");
68752849c42SDave May 	fprintf(fp,"format=ascii\n");
68852849c42SDave May 	fprintf(fp,"version=0.0\n");
68952849c42SDave May 	fprintf(fp,"options=\n");
69052849c42SDave May 	fprintf(fp,"</DataBucketHeader>\n");
69152849c42SDave May }
69252849c42SDave May void _DataBucketViewAscii_HeaderRead_v00(FILE *fp)
69352849c42SDave May {
69452849c42SDave May 	char dummy[100];
69552849c42SDave May 	size_t strL;
69652849c42SDave May 
69752849c42SDave May 	// header open
69852849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
69952849c42SDave May 
70052849c42SDave May 	// type
70152849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
70252849c42SDave May 	strL = strlen(dummy);
70352849c42SDave May 	if(strL>1) { dummy[strL-1] = 0; }
70452849c42SDave May 	if(strcmp(dummy,"type=DataBucket")!=0) {
70552849c42SDave May 		printf("ERROR: Data file doesn't contain a DataBucket type\n");
70652849c42SDave May 		ERROR();
70752849c42SDave May 	}
70852849c42SDave May 
70952849c42SDave May 	// format
71052849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
71152849c42SDave May 
71252849c42SDave May 	// version
71352849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
71452849c42SDave May 	strL = strlen(dummy);
71552849c42SDave May 	if(strL>1) { dummy[strL-1] = 0; }
71652849c42SDave May 	if(strcmp(dummy,"version=0.0")!=0) {
71752849c42SDave May 		printf("ERROR: DataBucket file must be parsed with version=0.0 : You tried %s \n", dummy);
71852849c42SDave May 		ERROR();
71952849c42SDave May 	}
72052849c42SDave May 
72152849c42SDave May 	// options
72252849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
72352849c42SDave May 	// header close
72452849c42SDave May 	fgets(dummy,99,fp); //printf("read(header): %s", dummy );
72552849c42SDave May }
72652849c42SDave May 
72752849c42SDave May 
72852849c42SDave May void _DataBucketLoadFromFileBinary_SEQ(const char filename[], DataBucket *_db)
72952849c42SDave May {
73052849c42SDave May 	DataBucket db;
73152849c42SDave May 	FILE *fp;
7325c18a9d6SDave May 	PetscInt L,buffer,f,nfields;
73352849c42SDave May 
73452849c42SDave May 
7354b46c5e1SDave May #ifdef DATA_BUCKET_LOG
73652849c42SDave May 	printf("** DataBucketLoadFromFile **\n");
73752849c42SDave May #endif
73852849c42SDave May 
73952849c42SDave May 	/* open file */
74052849c42SDave May 	fp = fopen(filename,"rb");
74152849c42SDave May 	if(fp==NULL){
74252849c42SDave May 		printf("ERROR: Cannot open file with name %s \n", filename);
74352849c42SDave May 		ERROR();
74452849c42SDave May 	}
74552849c42SDave May 
74652849c42SDave May 	/* read header */
74752849c42SDave May 	_DataBucketViewAscii_HeaderRead_v00(fp);
74852849c42SDave May 
74952849c42SDave May 	fscanf(fp,"%d\n%d\n%d\n",&L,&buffer,&nfields);
75052849c42SDave May 
75152849c42SDave May 	DataBucketCreate(&db);
75252849c42SDave May 
75352849c42SDave May 	for( f=0; f<nfields; f++ ) {
75452849c42SDave May 		_DataBucketRegisterFieldFromFile(fp,db);
75552849c42SDave May 	}
75652849c42SDave May 	fclose(fp);
75752849c42SDave May 
75852849c42SDave May 	DataBucketFinalize(db);
75952849c42SDave May 
76052849c42SDave May 
76152849c42SDave May   /*
76252849c42SDave May    DataBucketSetSizes(db,L,buffer);
76352849c42SDave May    */
76452849c42SDave May 	db->L = L;
76552849c42SDave May 	db->buffer = buffer;
76652849c42SDave May 	db->allocated = L + buffer;
76752849c42SDave May 
76852849c42SDave May 	*_db = db;
76952849c42SDave May }
77052849c42SDave May 
77152849c42SDave May void DataBucketLoadFromFile(MPI_Comm comm,const char filename[], DataBucketViewType type, DataBucket *db)
77252849c42SDave May {
7735c18a9d6SDave May 	PetscMPIInt nproc,rank;
77452849c42SDave May 
77552849c42SDave May 	MPI_Comm_size(comm,&nproc);
77652849c42SDave May 	MPI_Comm_rank(comm,&rank);
77752849c42SDave May 
7784b46c5e1SDave May #ifdef DATA_BUCKET_LOG
77952849c42SDave May 	printf("** DataBucketLoadFromFile **\n");
78052849c42SDave May #endif
78152849c42SDave May 	if(type==DATABUCKET_VIEW_STDOUT) {
78252849c42SDave May 
78352849c42SDave May 	} else if(type==DATABUCKET_VIEW_ASCII) {
78452849c42SDave May 		printf("ERROR: Cannot be implemented as we don't know the underlying particle data structure\n");
78552849c42SDave May 		ERROR();
78652849c42SDave May 	} else if(type==DATABUCKET_VIEW_BINARY) {
78752849c42SDave May 		if (nproc==1) {
78852849c42SDave May 			_DataBucketLoadFromFileBinary_SEQ(filename,db);
78952849c42SDave May 		} else {
79052849c42SDave May 			char *name;
79152849c42SDave May 
79252849c42SDave May 			asprintf(&name,"%s_p%1.5d",filename, rank );
79352849c42SDave May 			_DataBucketLoadFromFileBinary_SEQ(name,db);
79452849c42SDave May 			free(name);
79552849c42SDave May 		}
79652849c42SDave May 	} else {
79752849c42SDave May 		printf("ERROR: Not implemented\n");
79852849c42SDave May 		ERROR();
79952849c42SDave May 	}
80052849c42SDave May }
80152849c42SDave May 
80252849c42SDave May 
80352849c42SDave May void _DataBucketViewBinary(DataBucket db,const char filename[])
80452849c42SDave May {
80552849c42SDave May 	FILE *fp = NULL;
8065c18a9d6SDave May 	PetscInt f;
80752849c42SDave May 
80852849c42SDave May 	fp = fopen(filename,"wb");
80952849c42SDave May 	if(fp==NULL){
81052849c42SDave May 		printf("ERROR: Cannot open file with name %s \n", filename);
81152849c42SDave May 		ERROR();
81252849c42SDave May 	}
81352849c42SDave May 
81452849c42SDave May 	/* db header */
81552849c42SDave May 	_DataBucketViewAscii_HeaderWrite_v00(fp);
81652849c42SDave May 
81752849c42SDave May 	/* meta-data */
81852849c42SDave May 	fprintf(fp,"%d\n%d\n%d\n", db->L,db->buffer,db->nfields);
81952849c42SDave May 
82052849c42SDave May 	for( f=0; f<db->nfields; f++ ) {
82152849c42SDave May     /* load datafields */
82252849c42SDave May 		_DataFieldViewBinary(db->field[f],fp);
82352849c42SDave May 	}
82452849c42SDave May 
82552849c42SDave May 	fclose(fp);
82652849c42SDave May }
82752849c42SDave May 
82852849c42SDave May void DataBucketView_SEQ(DataBucket db,const char filename[],DataBucketViewType type)
82952849c42SDave May {
83052849c42SDave May 	switch (type) {
83152849c42SDave May 		case DATABUCKET_VIEW_STDOUT:
83252849c42SDave May 		{
8335c18a9d6SDave May 			PetscInt f;
83452849c42SDave May 			double memory_usage_total = 0.0;
83552849c42SDave May 
83652849c42SDave May 			printf("DataBucketView(SEQ): (\"%s\")\n",filename);
83752849c42SDave May 			printf("  L                  = %d \n", db->L );
83852849c42SDave May 			printf("  buffer             = %d \n", db->buffer );
83952849c42SDave May 			printf("  allocated          = %d \n", db->allocated );
84052849c42SDave May 
84152849c42SDave May 			printf("  nfields registered = %d \n", db->nfields );
84252849c42SDave May 			for( f=0; f<db->nfields; f++ ) {
84352849c42SDave May 				double memory_usage_f = (double)(db->field[f]->atomic_size * db->allocated) * 1.0e-6;
84452849c42SDave May 
84552849c42SDave May 				printf("    [%3d]: field name  ==>> %30s : Mem. usage = %1.2e (MB) \n", f, db->field[f]->name, memory_usage_f  );
84652849c42SDave May 				memory_usage_total += memory_usage_f;
84752849c42SDave May 			}
84852849c42SDave May 			printf("  Total mem. usage                                                      = %1.2e (MB) \n", memory_usage_total );
84952849c42SDave May 		}
85052849c42SDave May 			break;
85152849c42SDave May 
85252849c42SDave May 		case DATABUCKET_VIEW_ASCII:
85352849c42SDave May 		{
85452849c42SDave May 			printf("ERROR: Cannot be implemented as we don't know the underlying particle data structure\n");
85552849c42SDave May 			ERROR();
85652849c42SDave May 		}
85752849c42SDave May 			break;
85852849c42SDave May 
85952849c42SDave May 		case DATABUCKET_VIEW_BINARY:
86052849c42SDave May 		{
86152849c42SDave May 			_DataBucketViewBinary(db,filename);
86252849c42SDave May 		}
86352849c42SDave May 			break;
86452849c42SDave May 
86552849c42SDave May 		case DATABUCKET_VIEW_HDF5:
86652849c42SDave May 		{
86752849c42SDave May 			printf("ERROR: Has not been implemented \n");
86852849c42SDave May 			ERROR();
86952849c42SDave May 		}
87052849c42SDave May 			break;
87152849c42SDave May 
87252849c42SDave May 		default:
87352849c42SDave May 			printf("ERROR: Unknown method requested \n");
87452849c42SDave May 			ERROR();
87552849c42SDave May 			break;
87652849c42SDave May 	}
87752849c42SDave May }
87852849c42SDave May 
87952849c42SDave May void DataBucketView_MPI(MPI_Comm comm,DataBucket db,const char filename[],DataBucketViewType type)
88052849c42SDave May {
88152849c42SDave May 	switch (type) {
88252849c42SDave May 		case DATABUCKET_VIEW_STDOUT:
88352849c42SDave May 		{
8845c18a9d6SDave May 			PetscInt f;
8855c18a9d6SDave May 			PetscInt L,buffer,allocated;
88652849c42SDave May 			double memory_usage_total,memory_usage_total_local = 0.0;
8875c18a9d6SDave May 			PetscMPIInt rank;
8885c18a9d6SDave May 			PetscInt ierr;
88952849c42SDave May 
89052849c42SDave May 			ierr = MPI_Comm_rank(comm,&rank);
89152849c42SDave May 
89252849c42SDave May 			DataBucketGetGlobalSizes(comm,db,&L,&buffer,&allocated);
89352849c42SDave May 
89452849c42SDave May 			for( f=0; f<db->nfields; f++ ) {
89552849c42SDave May 				double memory_usage_f = (double)(db->field[f]->atomic_size * db->allocated) * 1.0e-6;
89652849c42SDave May 
89752849c42SDave May 				memory_usage_total_local += memory_usage_f;
89852849c42SDave May 			}
89952849c42SDave May 			MPI_Allreduce(&memory_usage_total_local,&memory_usage_total,1,MPI_DOUBLE,MPI_SUM,comm);
90052849c42SDave May 
90152849c42SDave May 			if (rank==0) {
9025c18a9d6SDave May 				PetscPrintf(comm,"DataBucketView(MPI): (\"%s\")\n",filename);
9035c18a9d6SDave May 				PetscPrintf(comm,"  L                  = %D \n", L );
9045c18a9d6SDave May 				PetscPrintf(comm,"  buffer (max)       = %D \n", buffer );
9055c18a9d6SDave May 				PetscPrintf(comm,"  allocated          = %D \n", allocated );
90652849c42SDave May 
9075c18a9d6SDave May 				PetscPrintf(comm,"  nfields registered = %D \n", db->nfields );
90852849c42SDave May 				for( f=0; f<db->nfields; f++ ) {
90952849c42SDave May 					double memory_usage_f = (double)(db->field[f]->atomic_size * db->allocated) * 1.0e-6;
91052849c42SDave May 
91152849c42SDave May 					printf("    [%3d]: field name  ==>> %30s : Mem. usage = %1.2e (MB) : rank0\n", f, db->field[f]->name, memory_usage_f  );
91252849c42SDave May 				}
91352849c42SDave May 
91452849c42SDave May 				printf("  Total mem. usage                                                      = %1.2e (MB) : collective\n", memory_usage_total );
91552849c42SDave May 			}
91652849c42SDave May 
91752849c42SDave May 		}
91852849c42SDave May 			break;
91952849c42SDave May 
92052849c42SDave May 		case DATABUCKET_VIEW_ASCII:
92152849c42SDave May 		{
92252849c42SDave May 			printf("ERROR: Cannot be implemented as we don't know the underlying particle data structure\n");
92352849c42SDave May 			ERROR();
92452849c42SDave May 		}
92552849c42SDave May 			break;
92652849c42SDave May 
92752849c42SDave May 		case DATABUCKET_VIEW_BINARY:
92852849c42SDave May 		{
92952849c42SDave May 			char *name;
9305c18a9d6SDave May 			PetscMPIInt rank;
93152849c42SDave May 
93252849c42SDave May 			/* create correct extension */
93352849c42SDave May 			MPI_Comm_rank(comm,&rank);
93452849c42SDave May 			asprintf(&name,"%s_p%1.5d",filename, rank );
93552849c42SDave May 
93652849c42SDave May 			_DataBucketViewBinary(db,name);
93752849c42SDave May 
93852849c42SDave May 			free(name);
93952849c42SDave May 		}
94052849c42SDave May 			break;
94152849c42SDave May 
94252849c42SDave May 		case DATABUCKET_VIEW_HDF5:
94352849c42SDave May 		{
94452849c42SDave May 			printf("ERROR: Has not been implemented \n");
94552849c42SDave May 			ERROR();
94652849c42SDave May 		}
94752849c42SDave May 			break;
94852849c42SDave May 
94952849c42SDave May 		default:
95052849c42SDave May 			printf("ERROR: Unknown method requested \n");
95152849c42SDave May 			ERROR();
95252849c42SDave May 			break;
95352849c42SDave May 	}
95452849c42SDave May }
95552849c42SDave May 
95652849c42SDave May 
95752849c42SDave May void DataBucketView(MPI_Comm comm,DataBucket db,const char filename[],DataBucketViewType type)
95852849c42SDave May {
9595c18a9d6SDave May 	PetscMPIInt nproc;
96052849c42SDave May 
96152849c42SDave May 	MPI_Comm_size(comm,&nproc);
96252849c42SDave May 	if (nproc==1) {
96352849c42SDave May 		DataBucketView_SEQ(db,filename,type);
96452849c42SDave May 	} else {
96552849c42SDave May 		DataBucketView_MPI(comm,db,filename,type);
96652849c42SDave May 	}
96752849c42SDave May }
96852849c42SDave May 
96952849c42SDave May void DataBucketDuplicateFields(DataBucket dbA,DataBucket *dbB)
97052849c42SDave May {
97152849c42SDave May 	DataBucket db2;
9725c18a9d6SDave May 	PetscInt f;
97352849c42SDave May 
97452849c42SDave May 	DataBucketCreate(&db2);
97552849c42SDave May 
97652849c42SDave May 	/* copy contents from dbA into db2 */
97752849c42SDave May 	for (f=0; f<dbA->nfields; f++) {
97852849c42SDave May 		DataField field;
97952849c42SDave May 		size_t    atomic_size;
98052849c42SDave May 		char      *name;
98152849c42SDave May 
98252849c42SDave May 		field = dbA->field[f];
98352849c42SDave May 
98452849c42SDave May 		atomic_size = field->atomic_size;
98552849c42SDave May 		name        = field->name;
98652849c42SDave May 
987*2eac95f8SDave May 		DataBucketRegisterField(db2,"DataBucketDuplicateFields",name,atomic_size,NULL);
98852849c42SDave May 	}
98952849c42SDave May 	DataBucketFinalize(db2);
99052849c42SDave May 	DataBucketSetInitialSizes(db2,0,1000);
99152849c42SDave May 
99252849c42SDave May 	/* set pointer */
99352849c42SDave May 	*dbB = db2;
99452849c42SDave May }
99552849c42SDave May 
99652849c42SDave May /*
99752849c42SDave May  Insert points from db2 into db1
99852849c42SDave May  db1 <<== db2
99952849c42SDave May  */
100052849c42SDave May void DataBucketInsertValues(DataBucket db1,DataBucket db2)
100152849c42SDave May {
10025c18a9d6SDave May 	PetscInt n_mp_points1,n_mp_points2;
10035c18a9d6SDave May 	PetscInt n_mp_points1_new,p;
100452849c42SDave May 
100552849c42SDave May 	DataBucketGetSizes(db1,&n_mp_points1,0,0);
100652849c42SDave May 	DataBucketGetSizes(db2,&n_mp_points2,0,0);
100752849c42SDave May 
100852849c42SDave May 	n_mp_points1_new = n_mp_points1 + n_mp_points2;
100952849c42SDave May 	DataBucketSetSizes(db1,n_mp_points1_new,-1);
101052849c42SDave May 
101152849c42SDave May 	for (p=0; p<n_mp_points2; p++) {
101252849c42SDave May 		// db1 <<== db2 //
101352849c42SDave May 		DataBucketCopyPoint( db2,p, db1,(n_mp_points1 + p) );
101452849c42SDave May 	}
101552849c42SDave May }
101652849c42SDave May 
101752849c42SDave May /* helpers for parallel send/recv */
101852849c42SDave May void DataBucketCreatePackedArray(DataBucket db,size_t *bytes,void **buf)
101952849c42SDave May {
10205c18a9d6SDave May   PetscInt       f;
102152849c42SDave May   size_t    sizeof_marker_contents;
102252849c42SDave May   void      *buffer;
102352849c42SDave May 
102452849c42SDave May   sizeof_marker_contents = 0;
102552849c42SDave May   for (f=0; f<db->nfields; f++) {
102652849c42SDave May     DataField df = db->field[f];
102752849c42SDave May 
102852849c42SDave May     sizeof_marker_contents += df->atomic_size;
102952849c42SDave May   }
103052849c42SDave May 
103152849c42SDave May   buffer = malloc(sizeof_marker_contents);
103252849c42SDave May   memset(buffer,0,sizeof_marker_contents);
103352849c42SDave May 
103452849c42SDave May   if (bytes) { *bytes = sizeof_marker_contents; }
103552849c42SDave May   if (buf)   { *buf   = buffer; }
103652849c42SDave May }
103752849c42SDave May 
103852849c42SDave May void DataBucketDestroyPackedArray(DataBucket db,void **buf)
103952849c42SDave May {
104052849c42SDave May   if (buf) {
104152849c42SDave May     free(*buf);
104252849c42SDave May     *buf = NULL;
104352849c42SDave May   }
104452849c42SDave May }
104552849c42SDave May 
10465c18a9d6SDave May void DataBucketFillPackedArray(DataBucket db,const PetscInt index,void *buf)
104752849c42SDave May {
10485c18a9d6SDave May   PetscInt    f;
104952849c42SDave May   void   *data,*data_p;
105052849c42SDave May   size_t asize,offset;
105152849c42SDave May 
105252849c42SDave May   offset = 0;
105352849c42SDave May   for (f=0; f<db->nfields; f++) {
105452849c42SDave May     DataField df = db->field[f];
105552849c42SDave May 
105652849c42SDave May     asize = df->atomic_size;
105752849c42SDave May 
105852849c42SDave May     data = (void*)( df->data );
105952849c42SDave May     data_p = (void*)( (char*)data + index*asize );
106052849c42SDave May 
106152849c42SDave May     memcpy( (void*)((char*)buf + offset),  data_p,  asize);
106252849c42SDave May     offset = offset + asize;
106352849c42SDave May   }
106452849c42SDave May }
106552849c42SDave May 
10665c18a9d6SDave May void DataBucketInsertPackedArray(DataBucket db,const PetscInt idx,void *data)
106752849c42SDave May {
10685c18a9d6SDave May   PetscInt f;
106952849c42SDave May   void *data_p;
107052849c42SDave May   size_t offset;
107152849c42SDave May 
107252849c42SDave May   offset = 0;
107352849c42SDave May   for (f=0; f<db->nfields; f++) {
107452849c42SDave May     DataField df = db->field[f];
107552849c42SDave May 
107652849c42SDave May     data_p = (void*)( (char*)data + offset );
107752849c42SDave May 
107852849c42SDave May     DataFieldInsertPoint(df, idx, (void*)data_p );
107952849c42SDave May     offset = offset + df->atomic_size;
108052849c42SDave May   }
108152849c42SDave May }
1082