xref: /petsc/include/petscsf.h (revision 9371c9d470a9602b6d10a8bf50c9b2280a79e45a)
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*/
38*9371c9d4SSatish Balay typedef enum {
39*9371c9d4SSatish Balay   PETSCSF_PATTERN_GENERAL = 0,
40*9371c9d4SSatish Balay   PETSCSF_PATTERN_ALLGATHER,
41*9371c9d4SSatish Balay   PETSCSF_PATTERN_GATHER,
42*9371c9d4SSatish Balay   PETSCSF_PATTERN_ALLTOALL
43*9371c9d4SSatish 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*/
56*9371c9d4SSatish Balay typedef enum {
57*9371c9d4SSatish Balay   PETSCSF_WINDOW_SYNC_FENCE,
58*9371c9d4SSatish Balay   PETSCSF_WINDOW_SYNC_LOCK,
59*9371c9d4SSatish Balay   PETSCSF_WINDOW_SYNC_ACTIVE
60*9371c9d4SSatish 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*/
75*9371c9d4SSatish Balay typedef enum {
76*9371c9d4SSatish Balay   PETSCSF_WINDOW_FLAVOR_CREATE,
77*9371c9d4SSatish Balay   PETSCSF_WINDOW_FLAVOR_DYNAMIC,
78*9371c9d4SSatish Balay   PETSCSF_WINDOW_FLAVOR_ALLOCATE,
79*9371c9d4SSatish Balay   PETSCSF_WINDOW_FLAVOR_SHARED
80*9371c9d4SSatish 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*/
94*9371c9d4SSatish Balay typedef enum {
95*9371c9d4SSatish Balay   PETSCSF_DUPLICATE_CONFONLY,
96*9371c9d4SSatish Balay   PETSCSF_DUPLICATE_RANKS,
97*9371c9d4SSatish Balay   PETSCSF_DUPLICATE_GRAPH
98*9371c9d4SSatish 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 *);
1398fa9e22eSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFCreateFromLayouts(PetscLayout, PetscLayout, PetscSF *);
1408fa9e22eSVaclav Hapla PETSC_DEPRECATED_FUNCTION("Use PetscSFCreateFromLayouts (since v3.15)")
141*9371c9d4SSatish Balay static inline PetscErrorCode PetscLayoutsCreateSF(PetscLayout rmap, PetscLayout lmap, PetscSF *sf) {
142*9371c9d4SSatish Balay   return PetscSFCreateFromLayouts(rmap, lmap, sf);
143*9371c9d4SSatish Balay }
144deffd5ebSksagiyam PETSC_EXTERN PetscErrorCode PetscSFCreateByMatchingIndices(PetscLayout, PetscInt, const PetscInt *, const PetscInt *, PetscInt, PetscInt, const PetscInt *, const PetscInt *, PetscInt, PetscSF *, PetscSF *);
1458fa9e22eSVaclav Hapla 
1468fa9e22eSVaclav Hapla /* PetscSection interoperability */
147b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFSetGraphSection(PetscSF, PetscSection, PetscSection);
148b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFCreateRemoteOffsets(PetscSF, PetscSection, PetscSection, PetscInt **);
149b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFDistributeSection(PetscSF, PetscSection, PetscInt **, PetscSection);
150b0c7db22SLisandro Dalcin PETSC_EXTERN PetscErrorCode PetscSFCreateSectionSF(PetscSF, PetscSection, PetscInt[], PetscSection, PetscSF *);
151b0c7db22SLisandro Dalcin 
1523482bfa8SJunchao Zhang /* Reduce rootdata to leafdata using provided operation */
153*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFBcastBegin(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
154*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFBcastEnd(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
155*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFBcastWithMemTypeBegin(PetscSF, MPI_Datatype, PetscMemType, const void *, PetscMemType, void *, MPI_Op) PetscAttrMPIPointerWithType(4, 2) PetscAttrMPIPointerWithType(6, 2);
156d0295fc0SJunchao Zhang 
157936c5a86SJed Brown /* Reduce leafdata into rootdata using provided operation */
158*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFReduceBegin(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
159*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFReduceEnd(PetscSF, MPI_Datatype, const void *, void *, MPI_Op) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
160*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFReduceWithMemTypeBegin(PetscSF, MPI_Datatype, PetscMemType, const void *, PetscMemType, void *, MPI_Op) PetscAttrMPIPointerWithType(4, 2) PetscAttrMPIPointerWithType(6, 2);
161d3b3e55cSJunchao Zhang 
162936c5a86SJed Brown /* Atomically modifies (using provided operation) rootdata using leafdata from each leaf, value at root at time of modification is returned in leafupdate. */
163*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFFetchAndOpBegin(PetscSF, MPI_Datatype, void *, const void *, void *, MPI_Op) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2) PetscAttrMPIPointerWithType(5, 2);
164*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFFetchAndOpEnd(PetscSF, MPI_Datatype, void *, const void *, void *, MPI_Op) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2) PetscAttrMPIPointerWithType(5, 2);
165d3b3e55cSJunchao Zhang 
166*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFFetchAndOpWithMemTypeBegin(PetscSF, MPI_Datatype, PetscMemType, void *, PetscMemType, const void *, PetscMemType, void *, MPI_Op) PetscAttrMPIPointerWithType(4, 2) PetscAttrMPIPointerWithType(6, 2) PetscAttrMPIPointerWithType(8, 2);
167d3b3e55cSJunchao Zhang 
168936c5a86SJed Brown /* Compute the degree of every root vertex (number of leaves in its star) */
16979c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFComputeDegreeBegin(PetscSF, const PetscInt **);
17079c40355SBarry Smith PETSC_EXTERN PetscErrorCode PetscSFComputeDegreeEnd(PetscSF, const PetscInt **);
17166dfcd1aSVaclav Hapla PETSC_EXTERN PetscErrorCode PetscSFComputeMultiRootOriginalNumbering(PetscSF, const PetscInt[], PetscInt *, PetscInt *[]);
172936c5a86SJed Brown /* Concatenate data from all leaves into roots */
173*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFGatherBegin(PetscSF, MPI_Datatype, const void *, void *) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
174*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFGatherEnd(PetscSF, MPI_Datatype, const void *, void *) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
175936c5a86SJed Brown /* Distribute distinct values to each leaf from roots */
176*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFScatterBegin(PetscSF, MPI_Datatype, const void *, void *) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
177*9371c9d4SSatish Balay PETSC_EXTERN PetscErrorCode PetscSFScatterEnd(PetscSF, MPI_Datatype, const void *, void *) PetscAttrMPIPointerWithType(3, 2) PetscAttrMPIPointerWithType(4, 2);
178936c5a86SJed Brown 
179a7b3aa13SAta Mesgarnejad PETSC_EXTERN PetscErrorCode PetscSFCompose(PetscSF, PetscSF, PetscSF *);
18004c0ada0SJunchao Zhang PETSC_EXTERN PetscErrorCode PetscSFComposeInverse(PetscSF, PetscSF, PetscSF *);
181a7b3aa13SAta Mesgarnejad 
18283df288dSJunchao Zhang #define MPIU_REPLACE MPI_REPLACE PETSC_DEPRECATED_MACRO("GCC warning \"MPIU_REPLACE macro is deprecated use MPI_REPLACE (since version 3.15)\"")
1838bfbc91cSJed Brown 
184dec1416fSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFGetRootRanks (since v3.12)")
185*9371c9d4SSatish Balay static inline PetscErrorCode PetscSFGetRanks(PetscSF sf, PetscInt *nranks, const PetscMPIInt **ranks, const PetscInt **roffset, const PetscInt **rmine, const PetscInt **rremote) {
186*9371c9d4SSatish Balay   return PetscSFGetRootRanks(sf, nranks, ranks, roffset, rmine, rremote);
187*9371c9d4SSatish Balay }
188e2652d4cSJunchao Zhang 
18972502a1fSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFCreateEmbeddedRootSF (since v3.15)")
190*9371c9d4SSatish Balay static inline PetscErrorCode PetscSFCreateEmbeddedSF(PetscSF sf, PetscInt nselected, const PetscInt *selected, PetscSF *esf) {
191*9371c9d4SSatish Balay   return PetscSFCreateEmbeddedRootSF(sf, nselected, selected, esf);
192*9371c9d4SSatish Balay }
193c73c85a0SVaclav Hapla 
194ad227feaSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFBcastBegin (since v3.15)")
195*9371c9d4SSatish Balay static inline PetscErrorCode PetscSFBcastAndOpBegin(PetscSF sf, MPI_Datatype unit, const void *rootdata, void *leafdata, MPI_Op op) {
196*9371c9d4SSatish Balay   return PetscSFBcastBegin(sf, unit, rootdata, leafdata, op);
197*9371c9d4SSatish Balay }
198c73c85a0SVaclav Hapla 
199ad227feaSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFBcastEnd (since v3.15)")
200*9371c9d4SSatish Balay static inline PetscErrorCode PetscSFBcastAndOpEnd(PetscSF sf, MPI_Datatype unit, const void *rootdata, void *leafdata, MPI_Op op) {
201*9371c9d4SSatish Balay   return PetscSFBcastEnd(sf, unit, rootdata, leafdata, op);
202*9371c9d4SSatish Balay }
203c73c85a0SVaclav Hapla 
204ad227feaSJunchao Zhang PETSC_DEPRECATED_FUNCTION("Use PetscSFBcastWithMemTypeBegin (since v3.15)")
205*9371c9d4SSatish Balay static inline PetscErrorCode PetscSFBcastAndOpWithMemtypeBegin(PetscSF sf, MPI_Datatype unit, PetscMemType rootmtype, const void *rootdata, PetscMemType leafmtype, void *leafdata, MPI_Op op) {
206*9371c9d4SSatish Balay   return PetscSFBcastWithMemTypeBegin(sf, unit, rootmtype, rootdata, leafmtype, leafdata, op);
207*9371c9d4SSatish Balay }
208e2652d4cSJunchao Zhang 
209936c5a86SJed Brown #endif
210