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