xref: /petsc/src/dm/impls/moab/dmmbvec.cxx (revision db66d124cedba962fb8ceb469cd36885b3f01337)
1032b8ab6SVijay Mahadevan #include <petsc-private/dmmbimpl.h> /*I  "petscdm.h"   I*/
2032b8ab6SVijay Mahadevan #include <petsc-private/vecimpl.h> /*I  "petscdm.h"   I*/
3032b8ab6SVijay Mahadevan 
4032b8ab6SVijay Mahadevan #include <petscdmmoab.h>
5032b8ab6SVijay Mahadevan #include <MBTagConventions.hpp>
6032b8ab6SVijay Mahadevan 
7032b8ab6SVijay Mahadevan // declare for use later but before they're defined
8032b8ab6SVijay Mahadevan static PetscErrorCode DMMoab_VecUserDestroy(void *user);
9032b8ab6SVijay Mahadevan static PetscErrorCode DMMoab_VecDuplicate(Vec x,Vec *y);
10032b8ab6SVijay Mahadevan static PetscErrorCode DMMoab_VecCreateTagName_Private(moab::ParallelComm *pcomm,char** tag_name);
11032b8ab6SVijay Mahadevan 
12032b8ab6SVijay Mahadevan #undef __FUNCT__
13032b8ab6SVijay Mahadevan #define __FUNCT__ "DMMoab_CreateVector_Private"
14032b8ab6SVijay Mahadevan PetscErrorCode DMMoab_CreateVector_Private(DM dm,moab::Tag tag,PetscInt tag_size,moab::Range* userrange,PetscBool is_global_vec,PetscBool destroy_tag,Vec *vec)
15032b8ab6SVijay Mahadevan {
16032b8ab6SVijay Mahadevan   PetscErrorCode         ierr;
17032b8ab6SVijay Mahadevan   moab::ErrorCode        merr;
18032b8ab6SVijay Mahadevan   PetscBool              is_newtag;
19032b8ab6SVijay Mahadevan   moab::Range           *range;
20032b8ab6SVijay Mahadevan   PetscInt               *gindices,*gsindices;
21032b8ab6SVijay Mahadevan   PetscInt               i,count,icount,dof;
22032b8ab6SVijay Mahadevan   PetscInt               size,rank;
23032b8ab6SVijay Mahadevan   PetscScalar *data_ptr;
24032b8ab6SVijay Mahadevan 
25*db66d124SVijay Mahadevan   Vec_MOAB *vmoab;
26032b8ab6SVijay Mahadevan   DM_Moab *dmmoab = (DM_Moab*)dm->data;
27032b8ab6SVijay Mahadevan   moab::ParallelComm *pcomm = dmmoab->pcomm;
28032b8ab6SVijay Mahadevan   moab::Interface *mbiface = dmmoab->mbiface;
29032b8ab6SVijay Mahadevan   moab::Tag ltog_tag = dmmoab->ltog_tag;
30032b8ab6SVijay Mahadevan 
31032b8ab6SVijay Mahadevan   PetscFunctionBegin;
32032b8ab6SVijay Mahadevan   if(!userrange) range = dmmoab->vowned;
33032b8ab6SVijay Mahadevan   else range = userrange;
34*db66d124SVijay Mahadevan   if(!range) SETERRQ(PETSC_COMM_WORLD, PETSC_ERR_ARG_WRONG, "Input range cannot be empty or call DMSetUp first.");
35032b8ab6SVijay Mahadevan 
36032b8ab6SVijay Mahadevan   if (!tag) {
37*db66d124SVijay Mahadevan     /* get the new name for the anonymous MOABVec -> the tag_name will be destroyed along with Tag */
38032b8ab6SVijay Mahadevan     char *tag_name = PETSC_NULL;
39032b8ab6SVijay Mahadevan     ierr = DMMoab_VecCreateTagName_Private(pcomm,&tag_name);CHKERRQ(ierr);
40032b8ab6SVijay Mahadevan     is_newtag = PETSC_TRUE;
41032b8ab6SVijay Mahadevan 
42*db66d124SVijay Mahadevan     /* Create the default value for the tag (all zeros) */
43032b8ab6SVijay Mahadevan     std::vector<PetscScalar> default_value(tag_size, 0.0);
44032b8ab6SVijay Mahadevan 
45*db66d124SVijay Mahadevan     /* Create the tag */
46032b8ab6SVijay Mahadevan     merr = mbiface->tag_get_handle(tag_name,tag_size,moab::MB_TYPE_DOUBLE,tag,
47032b8ab6SVijay Mahadevan                                    moab::MB_TAG_DENSE|moab::MB_TAG_CREAT,default_value.data());MBERRNM(merr);
48032b8ab6SVijay Mahadevan     ierr = PetscFree(tag_name);CHKERRQ(ierr);
49032b8ab6SVijay Mahadevan   }
50032b8ab6SVijay Mahadevan   else {
51*db66d124SVijay Mahadevan     /* Make sure the tag data is of type "double" */
52032b8ab6SVijay Mahadevan     moab::DataType tag_type;
53032b8ab6SVijay Mahadevan     merr = mbiface->tag_get_data_type(tag, tag_type);MBERRNM(merr);
54032b8ab6SVijay Mahadevan     if(tag_type != moab::MB_TYPE_DOUBLE) SETERRQ(PETSC_COMM_SELF, PETSC_ERR_ARG_WRONG, "Tag data type must be MB_TYPE_DOUBLE");
55032b8ab6SVijay Mahadevan     is_newtag = destroy_tag;
56032b8ab6SVijay Mahadevan   }
57032b8ab6SVijay Mahadevan 
58*db66d124SVijay Mahadevan   /* Create the MOAB internal data object */
59032b8ab6SVijay Mahadevan   ierr = PetscNew(Vec_MOAB,&vmoab);CHKERRQ(ierr);
60032b8ab6SVijay Mahadevan   vmoab->tag = tag;
61032b8ab6SVijay Mahadevan   vmoab->mbiface = mbiface;
62032b8ab6SVijay Mahadevan   vmoab->pcomm = pcomm;
63032b8ab6SVijay Mahadevan   vmoab->new_tag = is_newtag;
64032b8ab6SVijay Mahadevan   vmoab->is_global_vec = is_global_vec;
65032b8ab6SVijay Mahadevan   merr = mbiface->tag_get_length(tag,vmoab->tag_size);MBERR("tag_get_size", merr);
66032b8ab6SVijay Mahadevan 
67*db66d124SVijay Mahadevan   /* set the reference for vector range */
68032b8ab6SVijay Mahadevan   vmoab->tag_range = new moab::Range(*range);
69032b8ab6SVijay Mahadevan 
70*db66d124SVijay Mahadevan   /* Call tag_iterate. This will cause MOAB to allocate memory for the
71*db66d124SVijay Mahadevan      tag data if it hasn't already happened */
72032b8ab6SVijay Mahadevan   merr = mbiface->tag_iterate(tag,range->begin(),range->end(),count,(void*&)data_ptr);MBERRNM(merr);
73032b8ab6SVijay Mahadevan 
74*db66d124SVijay Mahadevan   /* Check to make sure the tag data is in a single sequence */
75032b8ab6SVijay Mahadevan   if ((unsigned)count != range->size()) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SUP,"Can only create MOAB Vector for single sequence");
76032b8ab6SVijay Mahadevan 
77032b8ab6SVijay Mahadevan   ierr = MPI_Comm_size(((PetscObject)dm)->comm, &size);CHKERRQ(ierr);
78032b8ab6SVijay Mahadevan   ierr = MPI_Comm_rank(((PetscObject)dm)->comm, &rank);CHKERRQ(ierr);
79032b8ab6SVijay Mahadevan 
80*db66d124SVijay Mahadevan   /* Create the PETSc Vector
81*db66d124SVijay Mahadevan      Query MOAB mesh to check if there are any ghosted entities
82032b8ab6SVijay Mahadevan        -> if we do, create a ghosted vector to map correctly to the same layout
83032b8ab6SVijay Mahadevan        -> else, create a non-ghosted parallel vector */
84032b8ab6SVijay Mahadevan   if (!is_global_vec && (size>1) && dmmoab->nghost) {
85032b8ab6SVijay Mahadevan     moab::Range::iterator  iter;
86032b8ab6SVijay Mahadevan     ierr = PetscMalloc(dmmoab->nghost*sizeof(PetscInt), &gsindices);CHKERRQ(ierr);
87*db66d124SVijay Mahadevan 
88032b8ab6SVijay Mahadevan     for(iter = dmmoab->vghost->begin(),icount=0; iter != dmmoab->vghost->end(); iter++) {
89032b8ab6SVijay Mahadevan       merr = mbiface->tag_get_data(ltog_tag,&(*iter),1,&dof);MBERRNM(merr);
90032b8ab6SVijay Mahadevan       gsindices[icount++] = dof;
91032b8ab6SVijay Mahadevan     }
92032b8ab6SVijay Mahadevan 
93*db66d124SVijay Mahadevan     /* This is an MPI Vector with ghosted padding */
94032b8ab6SVijay Mahadevan     ierr = VecCreateGhostBlockWithArray(vmoab->pcomm->comm(),vmoab->tag_size,vmoab->tag_size*dmmoab->nloc,
95032b8ab6SVijay Mahadevan                               vmoab->tag_size*dmmoab->n,dmmoab->nghost,gsindices,data_ptr,vec);CHKERRQ(ierr);
96032b8ab6SVijay Mahadevan 
97032b8ab6SVijay Mahadevan     ierr = PetscFree(gsindices);CHKERRQ(ierr);
98032b8ab6SVijay Mahadevan   }
99032b8ab6SVijay Mahadevan   else if (size>1) {
100*db66d124SVijay Mahadevan     /* This is an MPI Vector without ghosted padding */
101032b8ab6SVijay Mahadevan     ierr = VecCreateMPIWithArray(vmoab->pcomm->comm(),vmoab->tag_size,vmoab->tag_size*range->size(),
102032b8ab6SVijay Mahadevan                               PETSC_DECIDE,data_ptr,vec);CHKERRQ(ierr);
103032b8ab6SVijay Mahadevan   }
104032b8ab6SVijay Mahadevan   else {
105*db66d124SVijay Mahadevan     /* This is a sequential vector - valid only for the single processor case since MOAB tags are always partitioned
106*db66d124SVijay Mahadevan        and we cannot define a Vec using the Tag array with size>1 will be of full length */
107032b8ab6SVijay Mahadevan     ierr = VecCreateSeqWithArray(PETSC_COMM_SELF,vmoab->tag_size,vmoab->tag_size*dmmoab->n,data_ptr,vec);CHKERRQ(ierr);
108032b8ab6SVijay Mahadevan   }
109032b8ab6SVijay Mahadevan 
110032b8ab6SVijay Mahadevan   PetscContainer moabdata;
111032b8ab6SVijay Mahadevan   ierr = PetscContainerCreate(PETSC_COMM_SELF,&moabdata);CHKERRQ(ierr);
112032b8ab6SVijay Mahadevan   ierr = PetscContainerSetPointer(moabdata,vmoab);CHKERRQ(ierr);
113032b8ab6SVijay Mahadevan   ierr = PetscContainerSetUserDestroy(moabdata,DMMoab_VecUserDestroy);CHKERRQ(ierr);
114032b8ab6SVijay Mahadevan   ierr = PetscObjectCompose((PetscObject)*vec,"MOABData",(PetscObject)moabdata);CHKERRQ(ierr);
115032b8ab6SVijay Mahadevan   (*vec)->ops->duplicate = DMMoab_VecDuplicate;
116032b8ab6SVijay Mahadevan   ierr = PetscContainerDestroy(&moabdata);CHKERRQ(ierr);
117032b8ab6SVijay Mahadevan 
118032b8ab6SVijay Mahadevan   if (!dmmoab->ltog_map) {
119*db66d124SVijay Mahadevan     /* Vector created, manually set local to global mapping */
120032b8ab6SVijay Mahadevan     ierr = PetscMalloc(range->size()*sizeof(PetscInt)*vmoab->tag_size, &gindices);CHKERRQ(ierr);
121032b8ab6SVijay Mahadevan     moab::Range::iterator  iter;
122032b8ab6SVijay Mahadevan     for(iter = range->begin(),count=0; iter != range->end(); iter++,count+=vmoab->tag_size) {
123032b8ab6SVijay Mahadevan       merr = mbiface->tag_get_data(ltog_tag,&(*iter),1,&dof);MBERRNM(merr);
124032b8ab6SVijay Mahadevan       for(i=0; i<vmoab->tag_size; ++i)
125032b8ab6SVijay Mahadevan         gindices[count+i] = (dof)*vmoab->tag_size+i;
126032b8ab6SVijay Mahadevan     }
127032b8ab6SVijay Mahadevan 
128032b8ab6SVijay Mahadevan     ierr = ISLocalToGlobalMappingCreate(PETSC_COMM_SELF,range->size(),gindices,
129032b8ab6SVijay Mahadevan                                         PETSC_COPY_VALUES,&dmmoab->ltog_map);CHKERRQ(ierr);
130032b8ab6SVijay Mahadevan 
131032b8ab6SVijay Mahadevan     ierr = VecSetLocalToGlobalMappingBlock(*vec,dmmoab->ltog_map);CHKERRQ(ierr);
132032b8ab6SVijay Mahadevan 
133*db66d124SVijay Mahadevan     /* Clean up */
134032b8ab6SVijay Mahadevan     ierr = PetscFree(gindices);CHKERRQ(ierr);
135032b8ab6SVijay Mahadevan   }
136032b8ab6SVijay Mahadevan   else {
137032b8ab6SVijay Mahadevan     ierr = VecSetLocalToGlobalMappingBlock(*vec,dmmoab->ltog_map);CHKERRQ(ierr);
138032b8ab6SVijay Mahadevan   }
139032b8ab6SVijay Mahadevan 
140032b8ab6SVijay Mahadevan   /* set the DM reference to the vector */
141032b8ab6SVijay Mahadevan   ierr = VecSetDM(*vec, dm);CHKERRQ(ierr);
142032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
143032b8ab6SVijay Mahadevan }
144032b8ab6SVijay Mahadevan 
145032b8ab6SVijay Mahadevan 
146032b8ab6SVijay Mahadevan #undef __FUNCT__
147032b8ab6SVijay Mahadevan #define __FUNCT__ "DMMoabCreateVector"
148032b8ab6SVijay Mahadevan /*@
149032b8ab6SVijay Mahadevan   DMMoabCreateVector - Create a Vec from either an existing tag, or a specified tag size, and a range of entities
150032b8ab6SVijay Mahadevan 
151032b8ab6SVijay Mahadevan   Collective on MPI_Comm
152032b8ab6SVijay Mahadevan 
153032b8ab6SVijay Mahadevan   Input Parameter:
154032b8ab6SVijay Mahadevan . dm              - The DMMoab object being set
155032b8ab6SVijay Mahadevan . tag             - If non-zero, block size will be taken from the tag size
156032b8ab6SVijay Mahadevan . tag_size        - If tag was zero, this parameter specifies the block size; unique tag name will be generated automatically
157032b8ab6SVijay Mahadevan . range           - If non-empty, Vec corresponds to these entities, otherwise to the entities set on the DMMoab
158032b8ab6SVijay Mahadevan . is_global_vec   - If true, this is a local representation of the Vec (including ghosts in parallel), otherwise a truly parallel one
159032b8ab6SVijay Mahadevan . destroy_tag     - If true, MOAB tag is destroyed with Vec, otherwise it is left on MOAB
160032b8ab6SVijay Mahadevan 
161032b8ab6SVijay Mahadevan   Output Parameter:
162032b8ab6SVijay Mahadevan . vec             - The created vector
163032b8ab6SVijay Mahadevan 
164032b8ab6SVijay Mahadevan   Level: beginner
165032b8ab6SVijay Mahadevan 
166032b8ab6SVijay Mahadevan .keywords: DMMoab, create
167032b8ab6SVijay Mahadevan @*/
168032b8ab6SVijay Mahadevan PetscErrorCode DMMoabCreateVector(DM dm,moab::Tag tag,PetscInt tag_size,moab::Range* range,PetscBool is_global_vec,PetscBool destroy_tag,Vec *vec)
169032b8ab6SVijay Mahadevan {
170032b8ab6SVijay Mahadevan   PetscErrorCode     ierr;
171032b8ab6SVijay Mahadevan 
172032b8ab6SVijay Mahadevan   PetscFunctionBegin;
173032b8ab6SVijay Mahadevan   if(!tag && !tag_size) SETERRQ(PETSC_COMM_SELF, PETSC_ERR_ARG_WRONG, "Both tag_size and tag cannot be null.");
174032b8ab6SVijay Mahadevan 
175032b8ab6SVijay Mahadevan   ierr = DMMoab_CreateVector_Private(dm,tag,tag_size,range,is_global_vec,destroy_tag,vec);CHKERRQ(ierr);
176032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
177032b8ab6SVijay Mahadevan }
178032b8ab6SVijay Mahadevan 
179032b8ab6SVijay Mahadevan 
180032b8ab6SVijay Mahadevan #undef __FUNCT__
181032b8ab6SVijay Mahadevan #define __FUNCT__ "DMCreateGlobalVector_Moab"
182032b8ab6SVijay Mahadevan PetscErrorCode DMCreateGlobalVector_Moab(DM dm,Vec *gvec)
183032b8ab6SVijay Mahadevan {
184032b8ab6SVijay Mahadevan   PetscErrorCode  ierr;
185032b8ab6SVijay Mahadevan   DM_Moab         *dmmoab = (DM_Moab*)dm->data;
186032b8ab6SVijay Mahadevan 
187032b8ab6SVijay Mahadevan   PetscFunctionBegin;
188032b8ab6SVijay Mahadevan   PetscValidHeaderSpecific(dm,DM_CLASSID,1);
189032b8ab6SVijay Mahadevan   PetscValidPointer(gvec,2);
190032b8ab6SVijay Mahadevan   ierr = DMMoab_CreateVector_Private(dm,PETSC_NULL,dmmoab->bs,dmmoab->vowned,PETSC_TRUE,PETSC_TRUE,gvec);CHKERRQ(ierr);
191032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
192032b8ab6SVijay Mahadevan }
193032b8ab6SVijay Mahadevan 
194032b8ab6SVijay Mahadevan 
195032b8ab6SVijay Mahadevan #undef __FUNCT__
196032b8ab6SVijay Mahadevan #define __FUNCT__ "DMCreateLocalVector_Moab"
197032b8ab6SVijay Mahadevan PetscErrorCode DMCreateLocalVector_Moab(DM dm,Vec *lvec)
198032b8ab6SVijay Mahadevan {
199032b8ab6SVijay Mahadevan   PetscErrorCode  ierr;
200032b8ab6SVijay Mahadevan   moab::Range     vlocal;
201032b8ab6SVijay Mahadevan   DM_Moab         *dmmoab = (DM_Moab*)dm->data;
202032b8ab6SVijay Mahadevan 
203032b8ab6SVijay Mahadevan   PetscFunctionBegin;
204032b8ab6SVijay Mahadevan   PetscValidHeaderSpecific(dm,DM_CLASSID,1);
205032b8ab6SVijay Mahadevan   PetscValidPointer(lvec,2);
206032b8ab6SVijay Mahadevan   vlocal = *dmmoab->vowned;
207032b8ab6SVijay Mahadevan   vlocal.merge(*dmmoab->vghost);
208032b8ab6SVijay Mahadevan   ierr = DMMoab_CreateVector_Private(dm,PETSC_NULL,dmmoab->bs,dmmoab->vowned,PETSC_FALSE,PETSC_TRUE,lvec);CHKERRQ(ierr);
209032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
210032b8ab6SVijay Mahadevan }
211032b8ab6SVijay Mahadevan 
212032b8ab6SVijay Mahadevan 
213032b8ab6SVijay Mahadevan #undef __FUNCT__
214032b8ab6SVijay Mahadevan #define __FUNCT__ "DMMoabGetVecTag"
215032b8ab6SVijay Mahadevan /*@
216032b8ab6SVijay Mahadevan   DMMoabGetVecTag - Get the MOAB tag associated with this Vec
217032b8ab6SVijay Mahadevan 
218032b8ab6SVijay Mahadevan   Collective on MPI_Comm
219032b8ab6SVijay Mahadevan 
220032b8ab6SVijay Mahadevan   Input Parameter:
221032b8ab6SVijay Mahadevan . vec - Vec being queried
222032b8ab6SVijay Mahadevan 
223032b8ab6SVijay Mahadevan   Output Parameter:
224032b8ab6SVijay Mahadevan . tag - Tag associated with this Vec
225032b8ab6SVijay Mahadevan 
226032b8ab6SVijay Mahadevan   Level: beginner
227032b8ab6SVijay Mahadevan 
228032b8ab6SVijay Mahadevan .keywords: DMMoab, create
229032b8ab6SVijay Mahadevan @*/
230032b8ab6SVijay Mahadevan PetscErrorCode DMMoabGetVecTag(Vec vec,moab::Tag *tag)
231032b8ab6SVijay Mahadevan {
232032b8ab6SVijay Mahadevan   PetscContainer  moabdata;
233032b8ab6SVijay Mahadevan   Vec_MOAB        *vmoab;
234032b8ab6SVijay Mahadevan   PetscErrorCode  ierr;
235032b8ab6SVijay Mahadevan 
236032b8ab6SVijay Mahadevan   PetscFunctionBegin;
237032b8ab6SVijay Mahadevan   PetscValidPointer(tag,2);
238032b8ab6SVijay Mahadevan 
239032b8ab6SVijay Mahadevan   // Get the MOAB private data:
240032b8ab6SVijay Mahadevan   ierr = PetscObjectQuery((PetscObject)vec,"MOABData", (PetscObject*) &moabdata);CHKERRQ(ierr);
241032b8ab6SVijay Mahadevan   ierr = PetscContainerGetPointer(moabdata, (void**) &vmoab);CHKERRQ(ierr);
242032b8ab6SVijay Mahadevan 
243032b8ab6SVijay Mahadevan   *tag = vmoab->tag;
244032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
245032b8ab6SVijay Mahadevan }
246032b8ab6SVijay Mahadevan 
247032b8ab6SVijay Mahadevan 
248032b8ab6SVijay Mahadevan #undef __FUNCT__
249032b8ab6SVijay Mahadevan #define __FUNCT__ "DMMoabGetVecRange"
250032b8ab6SVijay Mahadevan /*@
251032b8ab6SVijay Mahadevan   DMMoabGetVecRange - Get the MOAB entities associated with this Vec
252032b8ab6SVijay Mahadevan 
253032b8ab6SVijay Mahadevan   Collective on MPI_Comm
254032b8ab6SVijay Mahadevan 
255032b8ab6SVijay Mahadevan   Input Parameter:
256032b8ab6SVijay Mahadevan . vec   - Vec being queried
257032b8ab6SVijay Mahadevan 
258032b8ab6SVijay Mahadevan   Output Parameter:
259032b8ab6SVijay Mahadevan . range - Entities associated with this Vec
260032b8ab6SVijay Mahadevan 
261032b8ab6SVijay Mahadevan   Level: beginner
262032b8ab6SVijay Mahadevan 
263032b8ab6SVijay Mahadevan .keywords: DMMoab, create
264032b8ab6SVijay Mahadevan @*/
265032b8ab6SVijay Mahadevan PetscErrorCode DMMoabGetVecRange(Vec vec,moab::Range *range)
266032b8ab6SVijay Mahadevan {
267032b8ab6SVijay Mahadevan   PetscContainer  moabdata;
268032b8ab6SVijay Mahadevan   Vec_MOAB        *vmoab;
269032b8ab6SVijay Mahadevan   PetscErrorCode  ierr;
270032b8ab6SVijay Mahadevan 
271032b8ab6SVijay Mahadevan   PetscFunctionBegin;
272032b8ab6SVijay Mahadevan   PetscValidPointer(range,2);
273032b8ab6SVijay Mahadevan 
274032b8ab6SVijay Mahadevan   // Get the MOAB private data handle
275032b8ab6SVijay Mahadevan   ierr = PetscObjectQuery((PetscObject)vec,"MOABData", (PetscObject*) &moabdata);CHKERRQ(ierr);
276032b8ab6SVijay Mahadevan   ierr = PetscContainerGetPointer(moabdata, (void**) &vmoab);CHKERRQ(ierr);
277032b8ab6SVijay Mahadevan 
278032b8ab6SVijay Mahadevan   *range = *vmoab->tag_range;
279032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
280032b8ab6SVijay Mahadevan }
281032b8ab6SVijay Mahadevan 
282032b8ab6SVijay Mahadevan 
283032b8ab6SVijay Mahadevan #undef __FUNCT__
284032b8ab6SVijay Mahadevan #define __FUNCT__ "DMMoab_VecDuplicate"
285032b8ab6SVijay Mahadevan PetscErrorCode DMMoab_VecDuplicate(Vec x,Vec *y)
286032b8ab6SVijay Mahadevan {
287032b8ab6SVijay Mahadevan   PetscErrorCode ierr;
288032b8ab6SVijay Mahadevan   DM             dm;
289032b8ab6SVijay Mahadevan   PetscContainer  moabdata;
290032b8ab6SVijay Mahadevan   Vec_MOAB        *vmoab;
291032b8ab6SVijay Mahadevan 
292032b8ab6SVijay Mahadevan   PetscFunctionBegin;
293032b8ab6SVijay Mahadevan   PetscValidHeaderSpecific(x,VEC_CLASSID,1);
294032b8ab6SVijay Mahadevan   PetscValidPointer(y,2);
295032b8ab6SVijay Mahadevan 
296032b8ab6SVijay Mahadevan   // Get the Vec_MOAB struct for the original vector
297032b8ab6SVijay Mahadevan   ierr = PetscObjectQuery((PetscObject)x,"MOABData", (PetscObject*) &moabdata);CHKERRQ(ierr);
298032b8ab6SVijay Mahadevan   ierr = PetscContainerGetPointer(moabdata, (void**)&vmoab);CHKERRQ(ierr);
299032b8ab6SVijay Mahadevan 
300032b8ab6SVijay Mahadevan   ierr = VecGetDM(x, &dm);CHKERRQ(ierr);
301032b8ab6SVijay Mahadevan   PetscValidHeaderSpecific(dm,DM_CLASSID,1);
302032b8ab6SVijay Mahadevan 
303032b8ab6SVijay Mahadevan   ierr = DMMoab_CreateVector_Private(dm,PETSC_NULL,vmoab->tag_size,vmoab->tag_range,vmoab->is_global_vec,PETSC_TRUE,y);CHKERRQ(ierr);
304032b8ab6SVijay Mahadevan   ierr = VecSetDM(*y, dm);CHKERRQ(ierr);
305032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
306032b8ab6SVijay Mahadevan }
307032b8ab6SVijay Mahadevan 
308032b8ab6SVijay Mahadevan 
309032b8ab6SVijay Mahadevan #undef __FUNCT__
310032b8ab6SVijay Mahadevan #define __FUNCT__ "DMMoab_VecCreateTagName_Private"
311032b8ab6SVijay Mahadevan /*  DMMoab_VecCreateTagName_Private
312032b8ab6SVijay Mahadevan  *
313032b8ab6SVijay Mahadevan  *  Creates a unique tag name that will be shared across processes. If
314032b8ab6SVijay Mahadevan  *  pcomm is NULL, then this is a serial vector. A unique tag name
315032b8ab6SVijay Mahadevan  *  will be returned in tag_name in either case.
316032b8ab6SVijay Mahadevan  *
317032b8ab6SVijay Mahadevan  *  The tag names have the format _PETSC_VEC_N where N is some integer.
318032b8ab6SVijay Mahadevan  *
319032b8ab6SVijay Mahadevan  *  NOTE: The tag_name is allocated in this routine; The user needs to free
320032b8ab6SVijay Mahadevan  *        the character array.
321032b8ab6SVijay Mahadevan  */
322032b8ab6SVijay Mahadevan PetscErrorCode DMMoab_VecCreateTagName_Private(moab::ParallelComm *pcomm,char** tag_name)
323032b8ab6SVijay Mahadevan {
324032b8ab6SVijay Mahadevan   moab::ErrorCode mberr;
325032b8ab6SVijay Mahadevan   PetscErrorCode  ierr;
326032b8ab6SVijay Mahadevan   PetscInt        n,global_n;
327032b8ab6SVijay Mahadevan   moab::Tag indexTag;
328032b8ab6SVijay Mahadevan 
329032b8ab6SVijay Mahadevan   PetscFunctionBegin;
330032b8ab6SVijay Mahadevan   const char*       PVEC_PREFIX      = "__PETSC_VEC_";
331032b8ab6SVijay Mahadevan   ierr = PetscMalloc(PETSC_MAX_PATH_LEN, tag_name);CHKERRQ(ierr);
332032b8ab6SVijay Mahadevan 
333032b8ab6SVijay Mahadevan   // Check to see if there are any PETSc vectors defined:
334032b8ab6SVijay Mahadevan   moab::Interface  *mbiface = pcomm->get_moab();
335032b8ab6SVijay Mahadevan   moab::EntityHandle rootset = mbiface->get_root_set();
336032b8ab6SVijay Mahadevan 
337032b8ab6SVijay Mahadevan     // Create a tag in MOAB mesh to index and keep track of number of Petsc vec tags
338032b8ab6SVijay Mahadevan   mberr = mbiface->tag_get_handle("__PETSC_VECS__",1,moab::MB_TYPE_INTEGER,indexTag,
339032b8ab6SVijay Mahadevan                                   moab::MB_TAG_SPARSE | moab::MB_TAG_CREAT,0);MBERRNM(mberr);
340032b8ab6SVijay Mahadevan   mberr = mbiface->tag_get_data(indexTag, &rootset, 1, &n);
341032b8ab6SVijay Mahadevan   if (mberr == moab::MB_TAG_NOT_FOUND) n=0;  /* this is the first temporary vector */
342032b8ab6SVijay Mahadevan   else MBERRNM(mberr);
343032b8ab6SVijay Mahadevan 
344032b8ab6SVijay Mahadevan   /* increment the new value of n */
345032b8ab6SVijay Mahadevan   ++n;
346032b8ab6SVijay Mahadevan 
347032b8ab6SVijay Mahadevan   // Make sure that n is consistent across all processes:
348032b8ab6SVijay Mahadevan   ierr = MPI_Allreduce(&n,&global_n,1,MPI_INT,MPI_MAX,pcomm->comm());CHKERRQ(ierr);
349032b8ab6SVijay Mahadevan 
350032b8ab6SVijay Mahadevan   // Set the new name accordingly and return:
351032b8ab6SVijay Mahadevan   ierr = PetscSNPrintf(*tag_name, PETSC_MAX_PATH_LEN-1, "%s_%D", PVEC_PREFIX, global_n);CHKERRQ(ierr);
352032b8ab6SVijay Mahadevan   mberr = mbiface->tag_set_data(indexTag, &rootset, 1, (const void*)&global_n);MBERRNM(mberr);
353032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
354032b8ab6SVijay Mahadevan }
355032b8ab6SVijay Mahadevan 
356032b8ab6SVijay Mahadevan 
357032b8ab6SVijay Mahadevan #undef __FUNCT__
358032b8ab6SVijay Mahadevan #define __FUNCT__ "DMMoab_VecUserDestroy"
359032b8ab6SVijay Mahadevan PetscErrorCode DMMoab_VecUserDestroy(void *user)
360032b8ab6SVijay Mahadevan {
361032b8ab6SVijay Mahadevan   Vec_MOAB        *vmoab;
362032b8ab6SVijay Mahadevan   PetscErrorCode  ierr;
363032b8ab6SVijay Mahadevan   moab::ErrorCode merr;
364032b8ab6SVijay Mahadevan 
365032b8ab6SVijay Mahadevan   PetscFunctionBegin;
366032b8ab6SVijay Mahadevan   vmoab = (Vec_MOAB*)user;
367032b8ab6SVijay Mahadevan 
368032b8ab6SVijay Mahadevan   if(vmoab->new_tag && vmoab->tag) {
369032b8ab6SVijay Mahadevan     // Tag created via a call to VecDuplicate, delete the underlying tag in MOAB...
370032b8ab6SVijay Mahadevan     merr = vmoab->mbiface->tag_delete(vmoab->tag);MBERRNM(merr);
371032b8ab6SVijay Mahadevan   }
372032b8ab6SVijay Mahadevan   delete vmoab->tag_range;
373032b8ab6SVijay Mahadevan   vmoab->tag = PETSC_NULL;
374032b8ab6SVijay Mahadevan   vmoab->mbiface = PETSC_NULL;
375032b8ab6SVijay Mahadevan   vmoab->pcomm = PETSC_NULL;
376032b8ab6SVijay Mahadevan   ierr = PetscFree(vmoab);CHKERRQ(ierr);
377032b8ab6SVijay Mahadevan   PetscFunctionReturn(0);
378032b8ab6SVijay Mahadevan }
379032b8ab6SVijay Mahadevan 
380*db66d124SVijay Mahadevan #undef __FUNCT__
381*db66d124SVijay Mahadevan #define __FUNCT__ "DMGlobalToLocalBegin_Moab"
382*db66d124SVijay Mahadevan PetscErrorCode  DMGlobalToLocalBegin_Moab(DM dm,Vec g,InsertMode mode,Vec l)
383*db66d124SVijay Mahadevan {
384*db66d124SVijay Mahadevan   PetscErrorCode    ierr;
385*db66d124SVijay Mahadevan   DM_Moab         *dmmoab = (DM_Moab*)dm->data;
386*db66d124SVijay Mahadevan 
387*db66d124SVijay Mahadevan   PetscFunctionBegin;
388*db66d124SVijay Mahadevan   ierr = VecScatterBegin(dmmoab->ltog_sendrecv,g,l,mode,SCATTER_FORWARD);CHKERRQ(ierr);
389*db66d124SVijay Mahadevan   PetscFunctionReturn(0);
390*db66d124SVijay Mahadevan }
391*db66d124SVijay Mahadevan 
392*db66d124SVijay Mahadevan 
393*db66d124SVijay Mahadevan #undef __FUNCT__
394*db66d124SVijay Mahadevan #define __FUNCT__ "DMGlobalToLocalEnd_Moab"
395*db66d124SVijay Mahadevan PetscErrorCode  DMGlobalToLocalEnd_Moab(DM dm,Vec g,InsertMode mode,Vec l)
396*db66d124SVijay Mahadevan {
397*db66d124SVijay Mahadevan   PetscErrorCode    ierr;
398*db66d124SVijay Mahadevan   DM_Moab         *dmmoab = (DM_Moab*)dm->data;
399*db66d124SVijay Mahadevan 
400*db66d124SVijay Mahadevan   PetscFunctionBegin;
401*db66d124SVijay Mahadevan   ierr = VecScatterEnd(dmmoab->ltog_sendrecv,g,l,mode,SCATTER_FORWARD);CHKERRQ(ierr);
402*db66d124SVijay Mahadevan   PetscFunctionReturn(0);
403*db66d124SVijay Mahadevan }
404*db66d124SVijay Mahadevan 
405*db66d124SVijay Mahadevan 
406*db66d124SVijay Mahadevan #undef __FUNCT__
407*db66d124SVijay Mahadevan #define __FUNCT__ "DMLocalToGlobalBegin_Moab"
408*db66d124SVijay Mahadevan PetscErrorCode  DMLocalToGlobalBegin_Moab(DM dm,Vec l,InsertMode mode,Vec g)
409*db66d124SVijay Mahadevan {
410*db66d124SVijay Mahadevan   PetscErrorCode    ierr;
411*db66d124SVijay Mahadevan   DM_Moab         *dmmoab = (DM_Moab*)dm->data;
412*db66d124SVijay Mahadevan 
413*db66d124SVijay Mahadevan   PetscFunctionBegin;
414*db66d124SVijay Mahadevan   ierr = VecScatterBegin(dmmoab->ltog_sendrecv,l,g,mode,SCATTER_REVERSE);CHKERRQ(ierr);
415*db66d124SVijay Mahadevan   PetscFunctionReturn(0);
416*db66d124SVijay Mahadevan }
417*db66d124SVijay Mahadevan 
418*db66d124SVijay Mahadevan 
419*db66d124SVijay Mahadevan #undef __FUNCT__
420*db66d124SVijay Mahadevan #define __FUNCT__ "DMLocalToGlobalEnd_Moab"
421*db66d124SVijay Mahadevan PetscErrorCode  DMLocalToGlobalEnd_Moab(DM dm,Vec l,InsertMode mode,Vec g)
422*db66d124SVijay Mahadevan {
423*db66d124SVijay Mahadevan   PetscErrorCode    ierr;
424*db66d124SVijay Mahadevan   DM_Moab         *dmmoab = (DM_Moab*)dm->data;
425*db66d124SVijay Mahadevan 
426*db66d124SVijay Mahadevan   PetscFunctionBegin;
427*db66d124SVijay Mahadevan   ierr = VecScatterEnd(dmmoab->ltog_sendrecv,l,g,mode,SCATTER_REVERSE);CHKERRQ(ierr);
428*db66d124SVijay Mahadevan   PetscFunctionReturn(0);
429*db66d124SVijay Mahadevan }
430*db66d124SVijay Mahadevan 
431*db66d124SVijay Mahadevan 
432