1936c5a86SJed Brown /* 2936c5a86SJed Brown A star forest (SF) describes a communication pattern 3936c5a86SJed Brown */ 46524c165SJacob Faibussowitsch #ifndef PETSCSF_H 526bd1501SBarry Smith #define PETSCSF_H 6ac09b921SBarry Smith 72c8e378dSBarry Smith #include <petscsys.h> 80c312b8eSJed Brown #include <petscsftypes.h> 997929ea7SJunchao Zhang #include <petscvec.h> /* for Vec, VecScatter etc */ 10936c5a86SJed Brown 11ac09b921SBarry Smith /* SUBMANSEC = PetscSF */ 12ac09b921SBarry Smith 13014dd563SJed Brown PETSC_EXTERN PetscClassId PETSCSF_CLASSID; 14936c5a86SJed Brown 15936c5a86SJed Brown /*E 1620662ed9SBarry Smith PetscSFPattern - Pattern of the `PetscSF` graph 17dd5b3ca6SJunchao Zhang 1820662ed9SBarry Smith Values: 1920662ed9SBarry Smith + `PETSCSF_PATTERN_GENERAL` - A general graph. One sets the graph with `PetscSFSetGraph()` and usually does not use this enum directly. 2020662ed9SBarry Smith . `PETSCSF_PATTERN_ALLGATHER` - A graph that every rank gathers all roots from all ranks (like `MPI_Allgather()`). One sets the graph with `PetscSFSetGraphWithPattern()`. 2120662ed9SBarry Smith . `PETSCSF_PATTERN_GATHER` - A graph that rank 0 gathers all roots from all ranks (like `MPI_Gatherv()` with root=0). One sets the graph with `PetscSFSetGraphWithPattern()`. 2220662ed9SBarry Smith - `PETSCSF_PATTERN_ALLTOALL` - A graph that every rank gathers different roots from all ranks (like `MPI_Alltoall()`). One sets the graph with `PetscSFSetGraphWithPattern()`. 23dd5b3ca6SJunchao Zhang In an ALLTOALL graph, we assume each process has <size> leaves and <size> roots, with each leaf connecting to a remote root. Here <size> is 24dd5b3ca6SJunchao Zhang the size of the communicator. This does not mean one can not communicate multiple data items between a pair of processes. One just needs to 2587497f52SBarry Smith create a new MPI datatype for the multiple data items, e.g., by `MPI_Type_contiguous`. 26dd5b3ca6SJunchao Zhang Level: beginner 27dd5b3ca6SJunchao Zhang 2820662ed9SBarry Smith .seealso: `PetscSF`, `PetscSFSetGraph()`, `PetscSFSetGraphWithPattern()` 29dd5b3ca6SJunchao Zhang E*/ 309371c9d4SSatish Balay typedef enum { 319371c9d4SSatish Balay PETSCSF_PATTERN_GENERAL = 0, 329371c9d4SSatish Balay PETSCSF_PATTERN_ALLGATHER, 339371c9d4SSatish Balay PETSCSF_PATTERN_GATHER, 349371c9d4SSatish Balay PETSCSF_PATTERN_ALLTOALL 359371c9d4SSatish Balay } PetscSFPattern; 36dd5b3ca6SJunchao Zhang 37dd5b3ca6SJunchao Zhang /*E 3887497f52SBarry Smith PetscSFWindowSyncType - Type of synchronization for `PETSCSFWINDOW` 39936c5a86SJed Brown 4020662ed9SBarry Smith Values: 4120662ed9SBarry Smith + `PETSCSF_WINDOW_SYNC_FENCE` - simplest model, synchronizing across communicator 4220662ed9SBarry Smith . `PETSCSF_WINDOW_SYNC_LOCK` - passive model, less synchronous, requires less setup than `PETSCSF_WINDOW_SYNC_ACTIVE`, but may require more handshakes 4320662ed9SBarry Smith - `PETSCSF_WINDOW_SYNC_ACTIVE` - active model, provides most information to MPI implementation, needs to construct 2-way process groups (more setup than `PETSCSF_WINDOW_SYNC_LOCK`) 44936c5a86SJed Brown 45e84a5f06SJed Brown Level: advanced 46936c5a86SJed Brown 4720662ed9SBarry Smith .seealso: `PetscSF`, `PetscSFWindowSetSyncType()`, `PetscSFWindowGetSyncType()` 48936c5a86SJed Brown E*/ 499371c9d4SSatish Balay typedef enum { 509371c9d4SSatish Balay PETSCSF_WINDOW_SYNC_FENCE, 519371c9d4SSatish Balay PETSCSF_WINDOW_SYNC_LOCK, 529371c9d4SSatish Balay PETSCSF_WINDOW_SYNC_ACTIVE 539371c9d4SSatish Balay } PetscSFWindowSyncType; 545af141bcSJed Brown PETSC_EXTERN const char *const PetscSFWindowSyncTypes[]; 55936c5a86SJed Brown 56e84a5f06SJed Brown /*E 5720662ed9SBarry Smith PetscSFWindowFlavorType - Flavor for the creation of MPI windows for `PETSCSFWINDOW` 585b0d146aSStefano Zampini 5920662ed9SBarry Smith Values: 6020662ed9SBarry Smith + `PETSCSF_WINDOW_FLAVOR_CREATE` - Use `MPI_Win_create()`, no reuse 6120662ed9SBarry Smith . `PETSCSF_WINDOW_FLAVOR_DYNAMIC` - Use `MPI_Win_create_dynamic()` and dynamically attach pointers 6220662ed9SBarry Smith . `PETSCSF_WINDOW_FLAVOR_ALLOCATE` - Use `MPI_Win_allocate()` 6320662ed9SBarry Smith - `PETSCSF_WINDOW_FLAVOR_SHARED` - Use `MPI_Win_allocate_shared()` 645b0d146aSStefano Zampini 655b0d146aSStefano Zampini Level: advanced 665b0d146aSStefano Zampini 6720662ed9SBarry Smith .seealso: `PetscSF`, `PetscSFWindowSetFlavorType()`, `PetscSFWindowGetFlavorType()` 685b0d146aSStefano Zampini E*/ 699371c9d4SSatish Balay typedef enum { 709371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_CREATE, 719371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_DYNAMIC, 729371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_ALLOCATE, 739371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_SHARED 749371c9d4SSatish Balay } PetscSFWindowFlavorType; 755b0d146aSStefano Zampini PETSC_EXTERN const char *const PetscSFWindowFlavorTypes[]; 765b0d146aSStefano Zampini 775b0d146aSStefano Zampini /*E 7887497f52SBarry Smith PetscSFDuplicateOption - Aspects to preserve when duplicating a `PetscSF` 79e84a5f06SJed Brown 8020662ed9SBarry Smith Values: 8120662ed9SBarry Smith + `PETSCSF_DUPLICATE_CONFONLY` - configuration only, user must call `PetscSFSetGraph()` 8220662ed9SBarry Smith . `PETSCSF_DUPLICATE_RANKS` - communication ranks preserved, but different graph (allows simpler setup after calling `PetscSFSetGraph()`) 8320662ed9SBarry Smith - `PETSCSF_DUPLICATE_GRAPH` - entire graph duplicated 84e84a5f06SJed Brown 85e84a5f06SJed Brown Level: beginner 86e84a5f06SJed Brown 8720662ed9SBarry Smith .seealso: `PetscSF`, `PetscSFDuplicate()` 88e84a5f06SJed Brown E*/ 899371c9d4SSatish Balay typedef enum { 909371c9d4SSatish Balay PETSCSF_DUPLICATE_CONFONLY, 919371c9d4SSatish Balay PETSCSF_DUPLICATE_RANKS, 929371c9d4SSatish Balay PETSCSF_DUPLICATE_GRAPH 939371c9d4SSatish Balay } PetscSFDuplicateOption; 94e84a5f06SJed Brown PETSC_EXTERN const char *const PetscSFDuplicateOptions[]; 95090c6444SJed Brown 961f40158dSVaclav Hapla /*E 9720662ed9SBarry Smith PetscSFConcatenateRootMode - Modes of root concatenation when concatenating `PetscSF`s 981f40158dSVaclav Hapla 9920662ed9SBarry Smith Values: 10020662ed9SBarry Smith + `PETSCSF_CONCATENATE_ROOTMODE_LOCAL` - concatenate root spaces locally (separately on each rank) 10120662ed9SBarry Smith . `PETSCSF_CONCATENATE_ROOTMODE_SHARED` - do not concatenate roots; root space is considered the same for each input `PetscSF` (checked in debug mode) 10220662ed9SBarry Smith - `PETSCSF_CONCATENATE_ROOTMODE_GLOBAL` - concatenate root spaces globally 1031f40158dSVaclav Hapla 1041f40158dSVaclav Hapla Level: advanced 1051f40158dSVaclav Hapla 10620662ed9SBarry Smith .seealso: `PetscSF`, `PetscSFConcatenate()` 1071f40158dSVaclav Hapla E*/ 1081f40158dSVaclav Hapla typedef enum { 1091f40158dSVaclav Hapla PETSCSF_CONCATENATE_ROOTMODE_LOCAL, 1101f40158dSVaclav Hapla PETSCSF_CONCATENATE_ROOTMODE_SHARED, 1111f40158dSVaclav Hapla PETSCSF_CONCATENATE_ROOTMODE_GLOBAL, 1121f40158dSVaclav Hapla } PetscSFConcatenateRootMode; 1131f40158dSVaclav Hapla PETSC_EXTERN const char *const PetscSFConcatenateRootModes[]; 1141f40158dSVaclav Hapla 115adc40e5bSBarry Smith PETSC_EXTERN PetscFunctionList PetscSFList; 116bdf89e91SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFRegister(const char[], PetscErrorCode (*)(PetscSF)); 1175af141bcSJed Brown 118607a6623SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFInitializePackage(void); 119014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFFinalizePackage(void); 12079c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFCreate(MPI_Comm, PetscSF *); 121014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFDestroy(PetscSF *); 1225af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetType(PetscSF, PetscSFType); 12329046d53SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFGetType(PetscSF, PetscSFType *); 124014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFView(PetscSF, PetscViewer); 125fe2efc57SMark PETSC_EXTERN PetscErrorCode PetscSFViewFromOptions(PetscSF, PetscObject, const char[]); 1265af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetUp(PetscSF); 127014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetFromOptions(PetscSF); 128e84a5f06SJed Brown PETSC_EXTERN PetscErrorCode PetscSFDuplicate(PetscSF, PetscSFDuplicateOption, PetscSF *); 1295af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFWindowSetSyncType(PetscSF, PetscSFWindowSyncType); 1305af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFWindowGetSyncType(PetscSF, PetscSFWindowSyncType *); 1315b0d146aSStefano Zampini PETSC_EXTERN PetscErrorCode PetscSFWindowSetFlavorType(PetscSF, PetscSFWindowFlavorType); 1325b0d146aSStefano Zampini PETSC_EXTERN PetscErrorCode PetscSFWindowGetFlavorType(PetscSF, PetscSFWindowFlavorType *); 1332eb0eadbSSatish Balay PETSC_EXTERN PetscErrorCode PetscSFWindowSetInfo(PetscSF, MPI_Info); 1342eb0eadbSSatish Balay PETSC_EXTERN PetscErrorCode PetscSFWindowGetInfo(PetscSF, MPI_Info *); 135014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetRankOrder(PetscSF, PetscBool); 136db2b9530SVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFSetGraph(PetscSF, PetscInt, PetscInt, PetscInt *, PetscCopyMode, PetscSFNode *, PetscCopyMode); 137dd5b3ca6SJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFSetGraphWithPattern(PetscSF, PetscLayout, PetscSFPattern); 13879c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFGetGraph(PetscSF, PetscInt *, PetscInt *, const PetscInt **, const PetscSFNode **); 139f723732fSJed Brown PETSC_EXTERN PetscErrorCode PetscSFGetLeafRange(PetscSF, PetscInt *, PetscInt *); 14072502a1fSJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFCreateEmbeddedRootSF(PetscSF, PetscInt, const PetscInt *, PetscSF *); 1412f5fb4c2SMatthew G. Knepley PETSC_EXTERN PetscErrorCode PetscSFCreateEmbeddedLeafSF(PetscSF, PetscInt, const PetscInt *, PetscSF *); 142014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFReset(PetscSF); 143b5a8e515SJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetUpRanks(PetscSF, MPI_Group); 144dec1416fSJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFGetRootRanks(PetscSF, PetscInt *, const PetscMPIInt **, const PetscInt **, const PetscInt **, const PetscInt **); 1458750ddebSJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFGetLeafRanks(PetscSF, PetscInt *, const PetscMPIInt **, const PetscInt **, const PetscInt **); 146014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFGetGroups(PetscSF, MPI_Group *, MPI_Group *); 147014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFGetMultiSF(PetscSF, PetscSF *); 148014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFCreateInverseSF(PetscSF, PetscSF *); 1491f40158dSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFConcatenate(MPI_Comm, PetscInt, PetscSF[], PetscSFConcatenateRootMode, PetscInt[], PetscSF *); 150936c5a86SJed Brown 1518fa9e22eSVaclav Hapla /* Build PetscSF from PetscLayout */ 152db2b9530SVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFSetGraphLayout(PetscSF, PetscLayout, PetscInt, PetscInt *, PetscCopyMode, const PetscInt *); 153eb58282aSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFGetGraphLayout(PetscSF, PetscLayout *, PetscInt *, const PetscInt *[], PetscInt *[]); 1548fa9e22eSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFCreateFromLayouts(PetscLayout, PetscLayout, PetscSF *); 155deffd5ebSksagiyam PETSC_EXTERN PetscErrorCode PetscSFCreateByMatchingIndices(PetscLayout, PetscInt, const PetscInt *, const PetscInt *, PetscInt, PetscInt, const PetscInt *, const PetscInt *, PetscInt, PetscSF *, PetscSF *); 156fbc7033fSJed Brown PETSC_EXTERN PetscErrorCode PetscSFMerge(PetscSF, PetscSF, PetscSF *); 1578b5d2d36SJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetGraphFromCoordinates(PetscSF, PetscInt, PetscInt, PetscInt, PetscReal, const PetscReal *, const PetscReal *); 1588fa9e22eSVaclav Hapla 1598fa9e22eSVaclav Hapla /* PetscSection interoperability */ 160b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFSetGraphSection(PetscSF, PetscSection, PetscSection); 161b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFCreateRemoteOffsets(PetscSF, PetscSection, PetscSection, PetscInt **); 162b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFDistributeSection(PetscSF, PetscSection, PetscInt **, PetscSection); 163b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFCreateSectionSF(PetscSF, PetscSection, PetscInt[], PetscSection, PetscSF *); 164b0c7db22SLisandro Dalcin 1653482bfa8SJunchao Zhang /* Reduce rootdata to leafdata using provided operation */ 16693d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFBcastBegin(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 16793d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFBcastEnd(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 16893d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFBcastWithMemTypeBegin(PetscSF, MPI_Datatype, PetscMemType, const void *, PetscMemType, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(6, 2); 169d0295fc0SJunchao Zhang 170936c5a86SJed Brown /* Reduce leafdata into rootdata using provided operation */ 17193d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFReduceBegin(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 17293d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFReduceEnd(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 17393d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFReduceWithMemTypeBegin(PetscSF, MPI_Datatype, PetscMemType, const void *, PetscMemType, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(6, 2); 174d3b3e55cSJunchao Zhang 175936c5a86SJed Brown /* Atomically modifies (using provided operation) rootdata using leafdata from each leaf, value at root at time of modification is returned in leafupdate. */ 17693d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFFetchAndOpBegin(PetscSF, MPI_Datatype, void *, const void *, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(5, 2); 17793d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFFetchAndOpEnd(PetscSF, MPI_Datatype, void *, const void *, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(5, 2); 178d3b3e55cSJunchao Zhang 17993d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFFetchAndOpWithMemTypeBegin(PetscSF, MPI_Datatype, PetscMemType, void *, PetscMemType, const void *, PetscMemType, void *, MPI_Op) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(6, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(8, 2); 180d3b3e55cSJunchao Zhang 181936c5a86SJed Brown /* Compute the degree of every root vertex (number of leaves in its star) */ 18279c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFComputeDegreeBegin(PetscSF, const PetscInt **); 18379c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFComputeDegreeEnd(PetscSF, const PetscInt **); 18466dfcd1aSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFComputeMultiRootOriginalNumbering(PetscSF, const PetscInt[], PetscInt *, PetscInt *[]); 185936c5a86SJed Brown /* Concatenate data from all leaves into roots */ 18693d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFGatherBegin(PetscSF, MPI_Datatype, const void *, void *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 18793d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFGatherEnd(PetscSF, MPI_Datatype, const void *, void *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 188936c5a86SJed Brown /* Distribute distinct values to each leaf from roots */ 18993d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFScatterBegin(PetscSF, MPI_Datatype, const void *, void *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 19093d501b3SJacob Faibussowitsch PETSC_EXTERN PetscErrorCode PetscSFScatterEnd(PetscSF, MPI_Datatype, const void *, void *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 2) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(4, 2); 191936c5a86SJed Brown 192a7b3aa13SAta Mesgarnejad PETSC_EXTERN PetscErrorCode PetscSFCompose(PetscSF, PetscSF, PetscSF *); 19304c0ada0SJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFComposeInverse(PetscSF, PetscSF, PetscSF *); 194a7b3aa13SAta Mesgarnejad 195*edd03b47SJacob Faibussowitsch #define MPIU_REPLACE MPI_REPLACE PETSC_DEPRECATED_MACRO(3, 15, 0, "MPI_REPLACE", ) 1968bfbc91cSJed Brown 197*edd03b47SJacob Faibussowitsch PETSC_DEPRECATED_FUNCTION(3, 12, 0, "PetscSFGetRootRanks()", ) 198d71ae5a4SJacob Faibussowitsch static inline PetscErrorCode PetscSFGetRanks(PetscSF sf, PetscInt *nranks, const PetscMPIInt **ranks, const PetscInt **roffset, const PetscInt **rmine, const PetscInt **rremote) 199d71ae5a4SJacob Faibussowitsch { 2009371c9d4SSatish Balay return PetscSFGetRootRanks(sf, nranks, ranks, roffset, rmine, rremote); 2019371c9d4SSatish Balay } 202e2652d4cSJunchao Zhang 203*edd03b47SJacob Faibussowitsch PETSC_DEPRECATED_FUNCTION(3, 15, 0, "PetscSFCreateEmbeddedRootSF()", ) 204d71ae5a4SJacob Faibussowitsch static inline PetscErrorCode PetscSFCreateEmbeddedSF(PetscSF sf, PetscInt nselected, const PetscInt *selected, PetscSF *esf) 205d71ae5a4SJacob Faibussowitsch { 2069371c9d4SSatish Balay return PetscSFCreateEmbeddedRootSF(sf, nselected, selected, esf); 2079371c9d4SSatish Balay } 208c73c85a0SVaclav Hapla 209*edd03b47SJacob Faibussowitsch PETSC_DEPRECATED_FUNCTION(3, 15, 0, "PetscSFBcastBegin()", ) 210d71ae5a4SJacob Faibussowitsch static inline PetscErrorCode PetscSFBcastAndOpBegin(PetscSF sf, MPI_Datatype unit, const void *rootdata, void *leafdata, MPI_Op op) 211d71ae5a4SJacob Faibussowitsch { 2129371c9d4SSatish Balay return PetscSFBcastBegin(sf, unit, rootdata, leafdata, op); 2139371c9d4SSatish Balay } 214c73c85a0SVaclav Hapla 215*edd03b47SJacob Faibussowitsch PETSC_DEPRECATED_FUNCTION(3, 15, 0, "PetscSFBcastEnd()", ) 216d71ae5a4SJacob Faibussowitsch static inline PetscErrorCode PetscSFBcastAndOpEnd(PetscSF sf, MPI_Datatype unit, const void *rootdata, void *leafdata, MPI_Op op) 217d71ae5a4SJacob Faibussowitsch { 2189371c9d4SSatish Balay return PetscSFBcastEnd(sf, unit, rootdata, leafdata, op); 2199371c9d4SSatish Balay } 220c73c85a0SVaclav Hapla 221*edd03b47SJacob Faibussowitsch PETSC_DEPRECATED_FUNCTION(3, 15, 0, "PetscSFBcastWithMemTypeBegin()", ) 222d71ae5a4SJacob Faibussowitsch static inline PetscErrorCode PetscSFBcastAndOpWithMemtypeBegin(PetscSF sf, MPI_Datatype unit, PetscMemType rootmtype, const void *rootdata, PetscMemType leafmtype, void *leafdata, MPI_Op op) 223d71ae5a4SJacob Faibussowitsch { 2249371c9d4SSatish Balay return PetscSFBcastWithMemTypeBegin(sf, unit, rootmtype, rootdata, leafmtype, leafdata, op); 2259371c9d4SSatish Balay } 226e2652d4cSJunchao Zhang 227936c5a86SJed Brown #endif 228