#include /*I "petscdm.h" I*/ #include /*I "petscdm.h" I*/ #include #include // declare for use later but before they're defined static PetscErrorCode DMMoab_VecUserDestroy(void *user); static PetscErrorCode DMMoab_VecDuplicate(Vec x,Vec *y); static PetscErrorCode DMMoab_VecCreateTagName_Private(moab::ParallelComm *pcomm,char** tag_name); #undef __FUNCT__ #define __FUNCT__ "DMMoab_CreateVector_Private" PetscErrorCode DMMoab_CreateVector_Private(DM dm,moab::Tag tag,PetscInt tag_size,moab::Range* userrange,PetscBool is_global_vec,PetscBool destroy_tag,Vec *vec) { PetscErrorCode ierr; moab::ErrorCode merr; PetscBool is_newtag; moab::Range *range; PetscInt *gindices,*gsindices; PetscInt i,count,icount,dof; PetscInt size,rank; PetscScalar *data_ptr; Vec_MOAB *vmoab; DM_Moab *dmmoab = (DM_Moab*)dm->data; moab::ParallelComm *pcomm = dmmoab->pcomm; moab::Interface *mbiface = dmmoab->mbiface; moab::Tag ltog_tag = dmmoab->ltog_tag; PetscFunctionBegin; if(!userrange) range = dmmoab->vowned; else range = userrange; if(!range) SETERRQ(PETSC_COMM_WORLD, PETSC_ERR_ARG_WRONG, "Input range cannot be empty or call DMSetUp first."); if (!tag) { /* get the new name for the anonymous MOABVec -> the tag_name will be destroyed along with Tag */ char *tag_name = PETSC_NULL; ierr = DMMoab_VecCreateTagName_Private(pcomm,&tag_name);CHKERRQ(ierr); is_newtag = PETSC_TRUE; /* Create the default value for the tag (all zeros) */ std::vector default_value(tag_size, 0.0); /* Create the tag */ merr = mbiface->tag_get_handle(tag_name,tag_size,moab::MB_TYPE_DOUBLE,tag, moab::MB_TAG_DENSE|moab::MB_TAG_CREAT,default_value.data());MBERRNM(merr); ierr = PetscFree(tag_name);CHKERRQ(ierr); } else { /* Make sure the tag data is of type "double" */ moab::DataType tag_type; merr = mbiface->tag_get_data_type(tag, tag_type);MBERRNM(merr); if(tag_type != moab::MB_TYPE_DOUBLE) SETERRQ(PETSC_COMM_SELF, PETSC_ERR_ARG_WRONG, "Tag data type must be MB_TYPE_DOUBLE"); is_newtag = destroy_tag; } /* Create the MOAB internal data object */ ierr = PetscNew(Vec_MOAB,&vmoab);CHKERRQ(ierr); vmoab->tag = tag; vmoab->mbiface = mbiface; vmoab->pcomm = pcomm; vmoab->new_tag = is_newtag; vmoab->is_global_vec = is_global_vec; merr = mbiface->tag_get_length(tag,vmoab->tag_size);MBERR("tag_get_size", merr); /* set the reference for vector range */ vmoab->tag_range = new moab::Range(*range); /* Call tag_iterate. This will cause MOAB to allocate memory for the tag data if it hasn't already happened */ merr = mbiface->tag_iterate(tag,range->begin(),range->end(),count,(void*&)data_ptr);MBERRNM(merr); /* Check to make sure the tag data is in a single sequence */ if ((unsigned)count != range->size()) SETERRQ(PETSC_COMM_SELF,PETSC_ERR_SUP,"Can only create MOAB Vector for single sequence"); ierr = MPI_Comm_size(((PetscObject)dm)->comm, &size);CHKERRQ(ierr); ierr = MPI_Comm_rank(((PetscObject)dm)->comm, &rank);CHKERRQ(ierr); /* Create the PETSc Vector Query MOAB mesh to check if there are any ghosted entities -> if we do, create a ghosted vector to map correctly to the same layout -> else, create a non-ghosted parallel vector */ if (!is_global_vec && (size>1) && dmmoab->nghost) { moab::Range::iterator iter; ierr = PetscMalloc(dmmoab->nghost*sizeof(PetscInt), &gsindices);CHKERRQ(ierr); for(iter = dmmoab->vghost->begin(),icount=0; iter != dmmoab->vghost->end(); iter++) { merr = mbiface->tag_get_data(ltog_tag,&(*iter),1,&dof);MBERRNM(merr); gsindices[icount++] = dof; } /* This is an MPI Vector with ghosted padding */ ierr = VecCreateGhostBlockWithArray(vmoab->pcomm->comm(),vmoab->tag_size,vmoab->tag_size*dmmoab->nloc, vmoab->tag_size*dmmoab->n,dmmoab->nghost,gsindices,data_ptr,vec);CHKERRQ(ierr); ierr = PetscFree(gsindices);CHKERRQ(ierr); } else if (size>1) { /* This is an MPI Vector without ghosted padding */ ierr = VecCreateMPIWithArray(vmoab->pcomm->comm(),vmoab->tag_size,vmoab->tag_size*range->size(), PETSC_DECIDE,data_ptr,vec);CHKERRQ(ierr); } else { /* This is a sequential vector - valid only for the single processor case since MOAB tags are always partitioned and we cannot define a Vec using the Tag array with size>1 will be of full length */ ierr = VecCreateSeqWithArray(PETSC_COMM_SELF,vmoab->tag_size,vmoab->tag_size*dmmoab->n,data_ptr,vec);CHKERRQ(ierr); } PetscContainer moabdata; ierr = PetscContainerCreate(PETSC_COMM_SELF,&moabdata);CHKERRQ(ierr); ierr = PetscContainerSetPointer(moabdata,vmoab);CHKERRQ(ierr); ierr = PetscContainerSetUserDestroy(moabdata,DMMoab_VecUserDestroy);CHKERRQ(ierr); ierr = PetscObjectCompose((PetscObject)*vec,"MOABData",(PetscObject)moabdata);CHKERRQ(ierr); (*vec)->ops->duplicate = DMMoab_VecDuplicate; ierr = PetscContainerDestroy(&moabdata);CHKERRQ(ierr); if (!dmmoab->ltog_map) { /* Vector created, manually set local to global mapping */ ierr = PetscMalloc(range->size()*sizeof(PetscInt)*vmoab->tag_size, &gindices);CHKERRQ(ierr); moab::Range::iterator iter; for(iter = range->begin(),count=0; iter != range->end(); iter++,count+=vmoab->tag_size) { merr = mbiface->tag_get_data(ltog_tag,&(*iter),1,&dof);MBERRNM(merr); for(i=0; itag_size; ++i) gindices[count+i] = (dof)*vmoab->tag_size+i; } ierr = ISLocalToGlobalMappingCreate(PETSC_COMM_SELF,range->size(),gindices, PETSC_COPY_VALUES,&dmmoab->ltog_map);CHKERRQ(ierr); ierr = VecSetLocalToGlobalMappingBlock(*vec,dmmoab->ltog_map);CHKERRQ(ierr); /* Clean up */ ierr = PetscFree(gindices);CHKERRQ(ierr); } else { ierr = VecSetLocalToGlobalMappingBlock(*vec,dmmoab->ltog_map);CHKERRQ(ierr); } /* set the DM reference to the vector */ ierr = VecSetDM(*vec, dm);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMMoabCreateVector" /*@ DMMoabCreateVector - Create a Vec from either an existing tag, or a specified tag size, and a range of entities Collective on MPI_Comm Input Parameter: . dm - The DMMoab object being set . tag - If non-zero, block size will be taken from the tag size . tag_size - If tag was zero, this parameter specifies the block size; unique tag name will be generated automatically . range - If non-empty, Vec corresponds to these entities, otherwise to the entities set on the DMMoab . is_global_vec - If true, this is a local representation of the Vec (including ghosts in parallel), otherwise a truly parallel one . destroy_tag - If true, MOAB tag is destroyed with Vec, otherwise it is left on MOAB Output Parameter: . vec - The created vector Level: beginner .keywords: DMMoab, create @*/ PetscErrorCode DMMoabCreateVector(DM dm,moab::Tag tag,PetscInt tag_size,moab::Range* range,PetscBool is_global_vec,PetscBool destroy_tag,Vec *vec) { PetscErrorCode ierr; PetscFunctionBegin; if(!tag && !tag_size) SETERRQ(PETSC_COMM_SELF, PETSC_ERR_ARG_WRONG, "Both tag_size and tag cannot be null."); ierr = DMMoab_CreateVector_Private(dm,tag,tag_size,range,is_global_vec,destroy_tag,vec);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMCreateGlobalVector_Moab" PetscErrorCode DMCreateGlobalVector_Moab(DM dm,Vec *gvec) { PetscErrorCode ierr; DM_Moab *dmmoab = (DM_Moab*)dm->data; PetscFunctionBegin; PetscValidHeaderSpecific(dm,DM_CLASSID,1); PetscValidPointer(gvec,2); ierr = DMMoab_CreateVector_Private(dm,PETSC_NULL,dmmoab->bs,dmmoab->vowned,PETSC_TRUE,PETSC_TRUE,gvec);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMCreateLocalVector_Moab" PetscErrorCode DMCreateLocalVector_Moab(DM dm,Vec *lvec) { PetscErrorCode ierr; moab::Range vlocal; DM_Moab *dmmoab = (DM_Moab*)dm->data; PetscFunctionBegin; PetscValidHeaderSpecific(dm,DM_CLASSID,1); PetscValidPointer(lvec,2); vlocal = *dmmoab->vowned; vlocal.merge(*dmmoab->vghost); ierr = DMMoab_CreateVector_Private(dm,PETSC_NULL,dmmoab->bs,dmmoab->vowned,PETSC_FALSE,PETSC_TRUE,lvec);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMMoabGetVecTag" /*@ DMMoabGetVecTag - Get the MOAB tag associated with this Vec Collective on MPI_Comm Input Parameter: . vec - Vec being queried Output Parameter: . tag - Tag associated with this Vec Level: beginner .keywords: DMMoab, create @*/ PetscErrorCode DMMoabGetVecTag(Vec vec,moab::Tag *tag) { PetscContainer moabdata; Vec_MOAB *vmoab; PetscErrorCode ierr; PetscFunctionBegin; PetscValidPointer(tag,2); // Get the MOAB private data: ierr = PetscObjectQuery((PetscObject)vec,"MOABData", (PetscObject*) &moabdata);CHKERRQ(ierr); ierr = PetscContainerGetPointer(moabdata, (void**) &vmoab);CHKERRQ(ierr); *tag = vmoab->tag; PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMMoabGetVecRange" /*@ DMMoabGetVecRange - Get the MOAB entities associated with this Vec Collective on MPI_Comm Input Parameter: . vec - Vec being queried Output Parameter: . range - Entities associated with this Vec Level: beginner .keywords: DMMoab, create @*/ PetscErrorCode DMMoabGetVecRange(Vec vec,moab::Range *range) { PetscContainer moabdata; Vec_MOAB *vmoab; PetscErrorCode ierr; PetscFunctionBegin; PetscValidPointer(range,2); // Get the MOAB private data handle ierr = PetscObjectQuery((PetscObject)vec,"MOABData", (PetscObject*) &moabdata);CHKERRQ(ierr); ierr = PetscContainerGetPointer(moabdata, (void**) &vmoab);CHKERRQ(ierr); *range = *vmoab->tag_range; PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMMoab_VecDuplicate" PetscErrorCode DMMoab_VecDuplicate(Vec x,Vec *y) { PetscErrorCode ierr; DM dm; PetscContainer moabdata; Vec_MOAB *vmoab; PetscFunctionBegin; PetscValidHeaderSpecific(x,VEC_CLASSID,1); PetscValidPointer(y,2); // Get the Vec_MOAB struct for the original vector ierr = PetscObjectQuery((PetscObject)x,"MOABData", (PetscObject*) &moabdata);CHKERRQ(ierr); ierr = PetscContainerGetPointer(moabdata, (void**)&vmoab);CHKERRQ(ierr); ierr = VecGetDM(x, &dm);CHKERRQ(ierr); PetscValidHeaderSpecific(dm,DM_CLASSID,1); ierr = DMMoab_CreateVector_Private(dm,PETSC_NULL,vmoab->tag_size,vmoab->tag_range,vmoab->is_global_vec,PETSC_TRUE,y);CHKERRQ(ierr); ierr = VecSetDM(*y, dm);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMMoab_VecCreateTagName_Private" /* DMMoab_VecCreateTagName_Private * * Creates a unique tag name that will be shared across processes. If * pcomm is NULL, then this is a serial vector. A unique tag name * will be returned in tag_name in either case. * * The tag names have the format _PETSC_VEC_N where N is some integer. * * NOTE: The tag_name is allocated in this routine; The user needs to free * the character array. */ PetscErrorCode DMMoab_VecCreateTagName_Private(moab::ParallelComm *pcomm,char** tag_name) { moab::ErrorCode mberr; PetscErrorCode ierr; PetscInt n,global_n; moab::Tag indexTag; PetscFunctionBegin; const char* PVEC_PREFIX = "__PETSC_VEC_"; ierr = PetscMalloc(PETSC_MAX_PATH_LEN, tag_name);CHKERRQ(ierr); // Check to see if there are any PETSc vectors defined: moab::Interface *mbiface = pcomm->get_moab(); moab::EntityHandle rootset = mbiface->get_root_set(); // Create a tag in MOAB mesh to index and keep track of number of Petsc vec tags mberr = mbiface->tag_get_handle("__PETSC_VECS__",1,moab::MB_TYPE_INTEGER,indexTag, moab::MB_TAG_SPARSE | moab::MB_TAG_CREAT,0);MBERRNM(mberr); mberr = mbiface->tag_get_data(indexTag, &rootset, 1, &n); if (mberr == moab::MB_TAG_NOT_FOUND) n=0; /* this is the first temporary vector */ else MBERRNM(mberr); /* increment the new value of n */ ++n; // Make sure that n is consistent across all processes: ierr = MPI_Allreduce(&n,&global_n,1,MPI_INT,MPI_MAX,pcomm->comm());CHKERRQ(ierr); // Set the new name accordingly and return: ierr = PetscSNPrintf(*tag_name, PETSC_MAX_PATH_LEN-1, "%s_%D", PVEC_PREFIX, global_n);CHKERRQ(ierr); mberr = mbiface->tag_set_data(indexTag, &rootset, 1, (const void*)&global_n);MBERRNM(mberr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMMoab_VecUserDestroy" PetscErrorCode DMMoab_VecUserDestroy(void *user) { Vec_MOAB *vmoab; PetscErrorCode ierr; moab::ErrorCode merr; PetscFunctionBegin; vmoab = (Vec_MOAB*)user; if(vmoab->new_tag && vmoab->tag) { // Tag created via a call to VecDuplicate, delete the underlying tag in MOAB... merr = vmoab->mbiface->tag_delete(vmoab->tag);MBERRNM(merr); } delete vmoab->tag_range; vmoab->tag = PETSC_NULL; vmoab->mbiface = PETSC_NULL; vmoab->pcomm = PETSC_NULL; ierr = PetscFree(vmoab);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMGlobalToLocalBegin_Moab" PetscErrorCode DMGlobalToLocalBegin_Moab(DM dm,Vec g,InsertMode mode,Vec l) { PetscErrorCode ierr; DM_Moab *dmmoab = (DM_Moab*)dm->data; PetscFunctionBegin; ierr = VecScatterBegin(dmmoab->ltog_sendrecv,g,l,mode,SCATTER_FORWARD);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMGlobalToLocalEnd_Moab" PetscErrorCode DMGlobalToLocalEnd_Moab(DM dm,Vec g,InsertMode mode,Vec l) { PetscErrorCode ierr; DM_Moab *dmmoab = (DM_Moab*)dm->data; PetscFunctionBegin; ierr = VecScatterEnd(dmmoab->ltog_sendrecv,g,l,mode,SCATTER_FORWARD);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMLocalToGlobalBegin_Moab" PetscErrorCode DMLocalToGlobalBegin_Moab(DM dm,Vec l,InsertMode mode,Vec g) { PetscErrorCode ierr; DM_Moab *dmmoab = (DM_Moab*)dm->data; PetscFunctionBegin; ierr = VecScatterBegin(dmmoab->ltog_sendrecv,l,g,mode,SCATTER_REVERSE);CHKERRQ(ierr); PetscFunctionReturn(0); } #undef __FUNCT__ #define __FUNCT__ "DMLocalToGlobalEnd_Moab" PetscErrorCode DMLocalToGlobalEnd_Moab(DM dm,Vec l,InsertMode mode,Vec g) { PetscErrorCode ierr; DM_Moab *dmmoab = (DM_Moab*)dm->data; PetscFunctionBegin; ierr = VecScatterEnd(dmmoab->ltog_sendrecv,l,g,mode,SCATTER_REVERSE);CHKERRQ(ierr); PetscFunctionReturn(0); }