#include /*I "petscdm.h" I*/ #include /*I "petscdm.h" I*/ #include #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; DM_Moab *dmmoab = (DM_Moab*)dm->data; moab::ParallelComm *pcomm = dmmoab->pcomm; moab::Interface *mbiface = dmmoab->mbiface; moab::Tag ltog_tag = dmmoab->ltog_tag; Vec_MOAB *vmoab; PetscFunctionBegin; // if(!range) SETERRQ(PETSC_COMM_SELF, PETSC_ERR_ARG_WRONG, "Range cannot be empty."); if(!userrange) range = dmmoab->vowned; else range = userrange; 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); // VSM:: // TODO: Need to query MOAB mesh to see if we have ghosted entities -> then decide accordingly whether // to create a serial, parallel or ghosted vector // Also assert if the tag_range has the right count accordingly. // Create the PETSc Vector: /* check if we have ghosted entities in the mesh -> 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); // PetscPrintf(PETSC_COMM_SELF, "\n [%D] Setting ghost index for dof = %D, at count = [%D, %D] for new entry = %D", rank, dof, count, icount, dof*vmoab->tag_size); gsindices[icount++] = dof; } // ierr = PetscPrintf(PETSC_COMM_WORLD, "\n VecCreateGhostBlockWithArray: Creating Ghost MPI vector with array: Global=%D, Local=%D, Ghosted=%D", dmmoab->n, dmmoab->nloc, dmmoab->nghost); // ierr = PetscPrintf(PETSC_COMM_WORLD, "\n VecCreateGhostBlockWithArray: Creating Ghost MPI vector with array: Local=%D, Ghosted=%D", dmmoab->vowned->size(), dmmoab->vghost->size()); // 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 = PetscPrintf(PETSC_COMM_WORLD, "\n VecCreateMPIWithArray: Creating MPI vector with array"); ierr = VecCreateMPIWithArray(vmoab->pcomm->comm(),vmoab->tag_size,vmoab->tag_size*range->size(), PETSC_DECIDE,data_ptr,vec);CHKERRQ(ierr); // 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,<og);CHKERRQ(ierr); // ierr = VecSetLocalToGlobalMappingBlock(*vec,ltog);CHKERRQ(ierr); // // // Clean up: // ierr = ISLocalToGlobalMappingDestroy(<og);CHKERRQ(ierr); // ierr = PetscFree(gindices);CHKERRQ(ierr); } else { // ierr = PetscPrintf(PETSC_COMM_WORLD, "\n VecCreateSeqWithArray: Creating Serial vector with array"); // This is a serial 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 to 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; // DM_Moab *dmmoab; 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); // dmmoab = (DM_Moab*)dm->data; ierr = DMMoab_CreateVector_Private(dm,PETSC_NULL,vmoab->tag_size,vmoab->tag_range,vmoab->is_global_vec,PETSC_TRUE,y);CHKERRQ(ierr); // ierr = DMMoabCreateVector(dm,PETSC_NULL,dmmoab->bs,dmmoab->vowned,vmoab->is_global_vec,PETSC_TRUE,y);CHKERRQ(ierr); // ierr = DMMoabCreateVector(dm,PETSC_NULL,vmoab->tag_size,vmoab->tag_range,vmoab->is_global_vec,PETSC_TRUE,y);CHKERRQ(ierr); ierr = VecSetDM(*y, dm);CHKERRQ(ierr); // ierr = PetscObjectQuery((PetscObject)*y,"MOABData", (PetscObject*) &moabdata);CHKERRQ(ierr); // ierr = PetscContainerGetPointer(moabdata, (void**)&vmoab);CHKERRQ(ierr); // PetscPrintf(PETSC_COMM_WORLD, "\n In VecDuplicate: new tag range pointer = %u \n", vmoab->tag_range); // vmoab->tag_range->print("test"); 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); // ierr = PetscSNPrintf(*tag_name, PETSC_MAX_PATH_LEN-1, "%s_%D", PVEC_PREFIX, n);CHKERRQ(ierr); // mberr = mbiface->tag_set_data(indexTag, &rootset, 1, &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); }