1936c5a86SJed Brown /* 2936c5a86SJed Brown A star forest (SF) describes a communication pattern 3936c5a86SJed Brown */ 426bd1501SBarry Smith #if !defined(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 15ac762476SJed Brown #define PETSCSFBASIC "basic" 16027eff8aSJunchao Zhang #define PETSCSFNEIGHBOR "neighbor" 17dd5b3ca6SJunchao Zhang #define PETSCSFALLGATHERV "allgatherv" 18dd5b3ca6SJunchao Zhang #define PETSCSFALLGATHER "allgather" 19dd5b3ca6SJunchao Zhang #define PETSCSFGATHERV "gatherv" 20dd5b3ca6SJunchao Zhang #define PETSCSFGATHER "gather" 21dd5b3ca6SJunchao Zhang #define PETSCSFALLTOALL "alltoall" 22ed658588SBarry Smith #define PETSCSFWINDOW "window" 235af141bcSJed Brown 24936c5a86SJed Brown /*E 25dd5b3ca6SJunchao Zhang PetscSFPattern - Pattern of the PetscSF graph 26dd5b3ca6SJunchao Zhang 2787497f52SBarry Smith $ `PETSCSF_PATTERN_GENERAL` - A general graph. One sets the graph with PetscSFSetGraph() and usually does not use this enum directly. 2887497f52SBarry Smith $ `PETSCSF_PATTERN_ALLGATHER` - A graph that every rank gathers all roots from all ranks (like `MPI_Allgather()`). One sets the graph with `PetscSFSetGraphWithPattern()`. 2987497f52SBarry 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()`. 3087497f52SBarry Smith $ `PETSCSF_PATTERN_ALLTOALL` - A graph that every rank gathers different roots from all ranks (like `MPI_Alltoall()`). One sets the graph with `PetscSFSetGraphWithPattern()`. 31dd5b3ca6SJunchao 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 32dd5b3ca6SJunchao 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 3387497f52SBarry Smith create a new MPI datatype for the multiple data items, e.g., by `MPI_Type_contiguous`. 34dd5b3ca6SJunchao Zhang Level: beginner 35dd5b3ca6SJunchao Zhang 36db781477SPatrick Sanan .seealso: `PetscSFSetGraph()`, `PetscSFSetGraphWithPattern()` 37dd5b3ca6SJunchao Zhang E*/ 389371c9d4SSatish Balay typedef enum { 399371c9d4SSatish Balay PETSCSF_PATTERN_GENERAL = 0, 409371c9d4SSatish Balay PETSCSF_PATTERN_ALLGATHER, 419371c9d4SSatish Balay PETSCSF_PATTERN_GATHER, 429371c9d4SSatish Balay PETSCSF_PATTERN_ALLTOALL 439371c9d4SSatish Balay } PetscSFPattern; 44dd5b3ca6SJunchao Zhang 45dd5b3ca6SJunchao Zhang /*E 4687497f52SBarry Smith PetscSFWindowSyncType - Type of synchronization for `PETSCSFWINDOW` 47936c5a86SJed Brown 4887497f52SBarry Smith $ `PETSCSF_WINDOW_SYNC_FENCE` - simplest model, synchronizing across communicator 4987497f52SBarry Smith $ `PETSCSF_WINDOW_SYNC_LOCK` - passive model, less synchronous, requires less setup than PETSCSF_WINDOW_SYNC_ACTIVE, but may require more handshakes 5087497f52SBarry 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) 51936c5a86SJed Brown 52e84a5f06SJed Brown Level: advanced 53936c5a86SJed Brown 54db781477SPatrick Sanan .seealso: `PetscSFWindowSetSyncType()`, `PetscSFWindowGetSyncType()` 55936c5a86SJed Brown E*/ 569371c9d4SSatish Balay typedef enum { 579371c9d4SSatish Balay PETSCSF_WINDOW_SYNC_FENCE, 589371c9d4SSatish Balay PETSCSF_WINDOW_SYNC_LOCK, 599371c9d4SSatish Balay PETSCSF_WINDOW_SYNC_ACTIVE 609371c9d4SSatish Balay } PetscSFWindowSyncType; 615af141bcSJed Brown PETSC_EXTERN const char *const PetscSFWindowSyncTypes[]; 62936c5a86SJed Brown 63e84a5f06SJed Brown /*E 645b0d146aSStefano Zampini PetscSFWindowFlavorType - Flavor for the creation of MPI windows for PETSCSFWINDOW 655b0d146aSStefano Zampini 6687497f52SBarry Smith $ `PETSCSF_WINDOW_FLAVOR_CREATE` - Use `MPI_Win_create()`, no reuse 6787497f52SBarry Smith $ `PETSCSF_WINDOW_FLAVOR_DYNAMIC` - Use `MPI_Win_create_dynamic()` and dynamically attach pointers 6887497f52SBarry Smith $ `PETSCSF_WINDOW_FLAVOR_ALLOCATE` - Use `MPI_Win_allocate()` 6987497f52SBarry Smith $ `PETSCSF_WINDOW_FLAVOR_SHARED` - Use `MPI_Win_allocate_shared()` 705b0d146aSStefano Zampini 715b0d146aSStefano Zampini Level: advanced 725b0d146aSStefano Zampini 73db781477SPatrick Sanan .seealso: `PetscSFWindowSetFlavorType()`, `PetscSFWindowGetFlavorType()` 745b0d146aSStefano Zampini E*/ 759371c9d4SSatish Balay typedef enum { 769371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_CREATE, 779371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_DYNAMIC, 789371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_ALLOCATE, 799371c9d4SSatish Balay PETSCSF_WINDOW_FLAVOR_SHARED 809371c9d4SSatish Balay } PetscSFWindowFlavorType; 815b0d146aSStefano Zampini PETSC_EXTERN const char *const PetscSFWindowFlavorTypes[]; 825b0d146aSStefano Zampini 835b0d146aSStefano Zampini /*E 8487497f52SBarry Smith PetscSFDuplicateOption - Aspects to preserve when duplicating a `PetscSF` 85e84a5f06SJed Brown 8687497f52SBarry Smith $ `PETSCSF_DUPLICATE_CONFONLY` - configuration only, user must call `PetscSFSetGraph()` 8787497f52SBarry Smith $ `PETSCSF_DUPLICATE_RANKS` - communication ranks preserved, but different graph (allows simpler setup after calling `PetscSFSetGraph()`) 8887497f52SBarry Smith $ `PETSCSF_DUPLICATE_GRAPH` - entire graph duplicated 89e84a5f06SJed Brown 90e84a5f06SJed Brown Level: beginner 91e84a5f06SJed Brown 92db781477SPatrick Sanan .seealso: `PetscSFDuplicate()` 93e84a5f06SJed Brown E*/ 949371c9d4SSatish Balay typedef enum { 959371c9d4SSatish Balay PETSCSF_DUPLICATE_CONFONLY, 969371c9d4SSatish Balay PETSCSF_DUPLICATE_RANKS, 979371c9d4SSatish Balay PETSCSF_DUPLICATE_GRAPH 989371c9d4SSatish Balay } PetscSFDuplicateOption; 99e84a5f06SJed Brown PETSC_EXTERN const char *const PetscSFDuplicateOptions[]; 100090c6444SJed Brown 101adc40e5bSBarry Smith PETSC_EXTERN PetscFunctionList PetscSFList; 102bdf89e91SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFRegister(const char[], PetscErrorCode (*)(PetscSF)); 1035af141bcSJed Brown 104607a6623SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFInitializePackage(void); 105014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFFinalizePackage(void); 10679c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFCreate(MPI_Comm, PetscSF *); 107014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFDestroy(PetscSF *); 1085af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetType(PetscSF, PetscSFType); 10929046d53SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFGetType(PetscSF, PetscSFType *); 110014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFView(PetscSF, PetscViewer); 111fe2efc57SMark PETSC_EXTERN PetscErrorCode PetscSFViewFromOptions(PetscSF, PetscObject, const char[]); 1125af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetUp(PetscSF); 113014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetFromOptions(PetscSF); 114e84a5f06SJed Brown PETSC_EXTERN PetscErrorCode PetscSFDuplicate(PetscSF, PetscSFDuplicateOption, PetscSF *); 1155af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFWindowSetSyncType(PetscSF, PetscSFWindowSyncType); 1165af141bcSJed Brown PETSC_EXTERN PetscErrorCode PetscSFWindowGetSyncType(PetscSF, PetscSFWindowSyncType *); 1175b0d146aSStefano Zampini PETSC_EXTERN PetscErrorCode PetscSFWindowSetFlavorType(PetscSF, PetscSFWindowFlavorType); 1185b0d146aSStefano Zampini PETSC_EXTERN PetscErrorCode PetscSFWindowGetFlavorType(PetscSF, PetscSFWindowFlavorType *); 1192eb0eadbSSatish Balay PETSC_EXTERN PetscErrorCode PetscSFWindowSetInfo(PetscSF, MPI_Info); 1202eb0eadbSSatish Balay PETSC_EXTERN PetscErrorCode PetscSFWindowGetInfo(PetscSF, MPI_Info *); 121014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetRankOrder(PetscSF, PetscBool); 122db2b9530SVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFSetGraph(PetscSF, PetscInt, PetscInt, PetscInt *, PetscCopyMode, PetscSFNode *, PetscCopyMode); 123dd5b3ca6SJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFSetGraphWithPattern(PetscSF, PetscLayout, PetscSFPattern); 12479c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFGetGraph(PetscSF, PetscInt *, PetscInt *, const PetscInt **, const PetscSFNode **); 125f723732fSJed Brown PETSC_EXTERN PetscErrorCode PetscSFGetLeafRange(PetscSF, PetscInt *, PetscInt *); 12672502a1fSJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFCreateEmbeddedRootSF(PetscSF, PetscInt, const PetscInt *, PetscSF *); 1272f5fb4c2SMatthew G. Knepley PETSC_EXTERN PetscErrorCode PetscSFCreateEmbeddedLeafSF(PetscSF, PetscInt, const PetscInt *, PetscSF *); 128014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFReset(PetscSF); 129b5a8e515SJed Brown PETSC_EXTERN PetscErrorCode PetscSFSetUpRanks(PetscSF, MPI_Group); 130dec1416fSJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFGetRootRanks(PetscSF, PetscInt *, const PetscMPIInt **, const PetscInt **, const PetscInt **, const PetscInt **); 1318750ddebSJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFGetLeafRanks(PetscSF, PetscInt *, const PetscMPIInt **, const PetscInt **, const PetscInt **); 132014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFGetGroups(PetscSF, MPI_Group *, MPI_Group *); 133014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFGetMultiSF(PetscSF, PetscSF *); 134014dd563SJed Brown PETSC_EXTERN PetscErrorCode PetscSFCreateInverseSF(PetscSF, PetscSF *); 135157edd7aSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFConcatenate(MPI_Comm, PetscInt, PetscSF[], PetscBool, PetscInt[], PetscSF *); 136936c5a86SJed Brown 1378fa9e22eSVaclav Hapla /* Build PetscSF from PetscLayout */ 138db2b9530SVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFSetGraphLayout(PetscSF, PetscLayout, PetscInt, PetscInt *, PetscCopyMode, const PetscInt *); 139*eb58282aSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFGetGraphLayout(PetscSF, PetscLayout *, PetscInt *, const PetscInt *[], PetscInt *[]); 1408fa9e22eSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFCreateFromLayouts(PetscLayout, PetscLayout, PetscSF *); 141deffd5ebSksagiyam PETSC_EXTERN PetscErrorCode PetscSFCreateByMatchingIndices(PetscLayout, PetscInt, const PetscInt *, const PetscInt *, PetscInt, PetscInt, const PetscInt *, const PetscInt *, PetscInt, PetscSF *, PetscSF *); 1428fa9e22eSVaclav Hapla 1438fa9e22eSVaclav Hapla /* PetscSection interoperability */ 144b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFSetGraphSection(PetscSF, PetscSection, PetscSection); 145b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFCreateRemoteOffsets(PetscSF, PetscSection, PetscSection, PetscInt **); 146b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFDistributeSection(PetscSF, PetscSection, PetscInt **, PetscSection); 147b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFCreateSectionSF(PetscSF, PetscSection, PetscInt[], PetscSection, PetscSF *); 148b0c7db22SLisandro Dalcin 1493482bfa8SJunchao Zhang /* Reduce rootdata to leafdata using provided operation */ 15093d501b3SJacob 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); 15193d501b3SJacob 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); 15293d501b3SJacob 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); 153d0295fc0SJunchao Zhang 154936c5a86SJed Brown /* Reduce leafdata into rootdata using provided operation */ 15593d501b3SJacob 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); 15693d501b3SJacob 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); 15793d501b3SJacob 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); 158d3b3e55cSJunchao Zhang 159936c5a86SJed Brown /* Atomically modifies (using provided operation) rootdata using leafdata from each leaf, value at root at time of modification is returned in leafupdate. */ 16093d501b3SJacob 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); 16193d501b3SJacob 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); 162d3b3e55cSJunchao Zhang 16393d501b3SJacob 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); 164d3b3e55cSJunchao Zhang 165936c5a86SJed Brown /* Compute the degree of every root vertex (number of leaves in its star) */ 16679c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFComputeDegreeBegin(PetscSF, const PetscInt **); 16779c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFComputeDegreeEnd(PetscSF, const PetscInt **); 16866dfcd1aSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFComputeMultiRootOriginalNumbering(PetscSF, const PetscInt[], PetscInt *, PetscInt *[]); 169936c5a86SJed Brown /* Concatenate data from all leaves into roots */ 17093d501b3SJacob 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); 17193d501b3SJacob 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); 172936c5a86SJed Brown /* Distribute distinct values to each leaf from roots */ 17393d501b3SJacob 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); 17493d501b3SJacob 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); 175936c5a86SJed Brown 176a7b3aa13SAta Mesgarnejad PETSC_EXTERN PetscErrorCode PetscSFCompose(PetscSF, PetscSF, PetscSF *); 17704c0ada0SJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFComposeInverse(PetscSF, PetscSF, PetscSF *); 178a7b3aa13SAta Mesgarnejad 17983df288dSJunchao Zhang #define MPIU_REPLACE MPI_REPLACE PETSC_DEPRECATED_MACRO("GCC warning \"MPIU_REPLACE macro is deprecated use MPI_REPLACE (since version 3.15)\"") 1808bfbc91cSJed Brown 181dec1416fSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFGetRootRanks (since v3.12)") 1829371c9d4SSatish Balay static inline PetscErrorCode PetscSFGetRanks(PetscSF sf, PetscInt *nranks, const PetscMPIInt **ranks, const PetscInt **roffset, const PetscInt **rmine, const PetscInt **rremote) { 1839371c9d4SSatish Balay return PetscSFGetRootRanks(sf, nranks, ranks, roffset, rmine, rremote); 1849371c9d4SSatish Balay } 185e2652d4cSJunchao Zhang 18672502a1fSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFCreateEmbeddedRootSF (since v3.15)") 1879371c9d4SSatish Balay static inline PetscErrorCode PetscSFCreateEmbeddedSF(PetscSF sf, PetscInt nselected, const PetscInt *selected, PetscSF *esf) { 1889371c9d4SSatish Balay return PetscSFCreateEmbeddedRootSF(sf, nselected, selected, esf); 1899371c9d4SSatish Balay } 190c73c85a0SVaclav Hapla 191ad227feaSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFBcastBegin (since v3.15)") 1929371c9d4SSatish Balay static inline PetscErrorCode PetscSFBcastAndOpBegin(PetscSF sf, MPI_Datatype unit, const void *rootdata, void *leafdata, MPI_Op op) { 1939371c9d4SSatish Balay return PetscSFBcastBegin(sf, unit, rootdata, leafdata, op); 1949371c9d4SSatish Balay } 195c73c85a0SVaclav Hapla 196ad227feaSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFBcastEnd (since v3.15)") 1979371c9d4SSatish Balay static inline PetscErrorCode PetscSFBcastAndOpEnd(PetscSF sf, MPI_Datatype unit, const void *rootdata, void *leafdata, MPI_Op op) { 1989371c9d4SSatish Balay return PetscSFBcastEnd(sf, unit, rootdata, leafdata, op); 1999371c9d4SSatish Balay } 200c73c85a0SVaclav Hapla 201ad227feaSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFBcastWithMemTypeBegin (since v3.15)") 2029371c9d4SSatish Balay static inline PetscErrorCode PetscSFBcastAndOpWithMemtypeBegin(PetscSF sf, MPI_Datatype unit, PetscMemType rootmtype, const void *rootdata, PetscMemType leafmtype, void *leafdata, MPI_Op op) { 2039371c9d4SSatish Balay return PetscSFBcastWithMemTypeBegin(sf, unit, rootmtype, rootdata, leafmtype, leafdata, op); 2049371c9d4SSatish Balay } 205e2652d4cSJunchao Zhang 206936c5a86SJed Brown #endif 207