xref: /petsc/src/dm/impls/plex/plexcheckinterface.c (revision 48a46eb9bd028bec07ec0f396b1a3abb43f14558)
1f84a5eb8SVaclav Hapla #include <petsc/private/dmpleximpl.h> /*I      "petscdmplex.h"   I*/
2f84a5eb8SVaclav Hapla 
3f84a5eb8SVaclav Hapla /* TODO PetscArrayExchangeBegin/End */
4f84a5eb8SVaclav Hapla /* TODO blocksize */
5f84a5eb8SVaclav Hapla /* TODO move to API ? */
69371c9d4SSatish Balay static PetscErrorCode ExchangeArrayByRank_Private(PetscObject obj, MPI_Datatype dt, PetscInt nsranks, const PetscMPIInt sranks[], PetscInt ssize[], const void *sarr[], PetscInt nrranks, const PetscMPIInt rranks[], PetscInt *rsize_out[], void **rarr_out[]) {
7f84a5eb8SVaclav Hapla   PetscInt     r;
8f84a5eb8SVaclav Hapla   PetscInt    *rsize;
9f84a5eb8SVaclav Hapla   void       **rarr;
10f84a5eb8SVaclav Hapla   MPI_Request *sreq, *rreq;
11f84a5eb8SVaclav Hapla   PetscMPIInt  tag, unitsize;
12f84a5eb8SVaclav Hapla   MPI_Comm     comm;
13f84a5eb8SVaclav Hapla 
14f84a5eb8SVaclav Hapla   PetscFunctionBegin;
159566063dSJacob Faibussowitsch   PetscCallMPI(MPI_Type_size(dt, &unitsize));
169566063dSJacob Faibussowitsch   PetscCall(PetscObjectGetComm(obj, &comm));
179566063dSJacob Faibussowitsch   PetscCall(PetscMalloc2(nrranks, &rsize, nrranks, &rarr));
189566063dSJacob Faibussowitsch   PetscCall(PetscMalloc2(nrranks, &rreq, nsranks, &sreq));
19f84a5eb8SVaclav Hapla   /* exchange array size */
209566063dSJacob Faibussowitsch   PetscCall(PetscObjectGetNewTag(obj, &tag));
21*48a46eb9SPierre Jolivet   for (r = 0; r < nrranks; r++) PetscCallMPI(MPI_Irecv(&rsize[r], 1, MPIU_INT, rranks[r], tag, comm, &rreq[r]));
22*48a46eb9SPierre Jolivet   for (r = 0; r < nsranks; r++) PetscCallMPI(MPI_Isend(&ssize[r], 1, MPIU_INT, sranks[r], tag, comm, &sreq[r]));
239566063dSJacob Faibussowitsch   PetscCallMPI(MPI_Waitall(nrranks, rreq, MPI_STATUSES_IGNORE));
249566063dSJacob Faibussowitsch   PetscCallMPI(MPI_Waitall(nsranks, sreq, MPI_STATUSES_IGNORE));
25f84a5eb8SVaclav Hapla   /* exchange array */
269566063dSJacob Faibussowitsch   PetscCall(PetscObjectGetNewTag(obj, &tag));
27f84a5eb8SVaclav Hapla   for (r = 0; r < nrranks; r++) {
289566063dSJacob Faibussowitsch     PetscCall(PetscMalloc(rsize[r] * unitsize, &rarr[r]));
299566063dSJacob Faibussowitsch     PetscCallMPI(MPI_Irecv(rarr[r], rsize[r], dt, rranks[r], tag, comm, &rreq[r]));
30f84a5eb8SVaclav Hapla   }
31*48a46eb9SPierre Jolivet   for (r = 0; r < nsranks; r++) PetscCallMPI(MPI_Isend(sarr[r], ssize[r], dt, sranks[r], tag, comm, &sreq[r]));
329566063dSJacob Faibussowitsch   PetscCallMPI(MPI_Waitall(nrranks, rreq, MPI_STATUSES_IGNORE));
339566063dSJacob Faibussowitsch   PetscCallMPI(MPI_Waitall(nsranks, sreq, MPI_STATUSES_IGNORE));
349566063dSJacob Faibussowitsch   PetscCall(PetscFree2(rreq, sreq));
35f84a5eb8SVaclav Hapla   *rsize_out = rsize;
36f84a5eb8SVaclav Hapla   *rarr_out  = rarr;
37f84a5eb8SVaclav Hapla   PetscFunctionReturn(0);
38f84a5eb8SVaclav Hapla }
39f84a5eb8SVaclav Hapla 
40f84a5eb8SVaclav Hapla /* TODO VecExchangeBegin/End */
41f84a5eb8SVaclav Hapla /* TODO move to API ? */
429371c9d4SSatish Balay static PetscErrorCode ExchangeVecByRank_Private(PetscObject obj, PetscInt nsranks, const PetscMPIInt sranks[], Vec svecs[], PetscInt nrranks, const PetscMPIInt rranks[], Vec *rvecs[]) {
43f84a5eb8SVaclav Hapla   PetscInt            r;
44f84a5eb8SVaclav Hapla   PetscInt           *ssize, *rsize;
45f84a5eb8SVaclav Hapla   PetscScalar       **rarr;
46f84a5eb8SVaclav Hapla   const PetscScalar **sarr;
47f84a5eb8SVaclav Hapla   Vec                *rvecs_;
48f84a5eb8SVaclav Hapla   MPI_Request        *sreq, *rreq;
49f84a5eb8SVaclav Hapla 
50f84a5eb8SVaclav Hapla   PetscFunctionBegin;
519566063dSJacob Faibussowitsch   PetscCall(PetscMalloc4(nsranks, &ssize, nsranks, &sarr, nrranks, &rreq, nsranks, &sreq));
52f84a5eb8SVaclav Hapla   for (r = 0; r < nsranks; r++) {
539566063dSJacob Faibussowitsch     PetscCall(VecGetLocalSize(svecs[r], &ssize[r]));
549566063dSJacob Faibussowitsch     PetscCall(VecGetArrayRead(svecs[r], &sarr[r]));
55f84a5eb8SVaclav Hapla   }
569566063dSJacob Faibussowitsch   PetscCall(ExchangeArrayByRank_Private(obj, MPIU_SCALAR, nsranks, sranks, ssize, (const void **)sarr, nrranks, rranks, &rsize, (void ***)&rarr));
579566063dSJacob Faibussowitsch   PetscCall(PetscMalloc1(nrranks, &rvecs_));
58f84a5eb8SVaclav Hapla   for (r = 0; r < nrranks; r++) {
59f84a5eb8SVaclav Hapla     /* set array in two steps to mimic PETSC_OWN_POINTER */
609566063dSJacob Faibussowitsch     PetscCall(VecCreateSeqWithArray(PETSC_COMM_SELF, 1, rsize[r], NULL, &rvecs_[r]));
619566063dSJacob Faibussowitsch     PetscCall(VecReplaceArray(rvecs_[r], rarr[r]));
62f84a5eb8SVaclav Hapla   }
63*48a46eb9SPierre Jolivet   for (r = 0; r < nsranks; r++) PetscCall(VecRestoreArrayRead(svecs[r], &sarr[r]));
649566063dSJacob Faibussowitsch   PetscCall(PetscFree2(rsize, rarr));
659566063dSJacob Faibussowitsch   PetscCall(PetscFree4(ssize, sarr, rreq, sreq));
66f84a5eb8SVaclav Hapla   *rvecs = rvecs_;
67f84a5eb8SVaclav Hapla   PetscFunctionReturn(0);
68f84a5eb8SVaclav Hapla }
69f84a5eb8SVaclav Hapla 
709371c9d4SSatish Balay static PetscErrorCode SortByRemote_Private(PetscSF sf, PetscInt *rmine1[], PetscInt *rremote1[]) {
71f84a5eb8SVaclav Hapla   PetscInt           nleaves;
72f84a5eb8SVaclav Hapla   PetscInt           nranks;
73f84a5eb8SVaclav Hapla   const PetscMPIInt *ranks;
74f84a5eb8SVaclav Hapla   const PetscInt    *roffset, *rmine, *rremote;
75f84a5eb8SVaclav Hapla   PetscInt           n, o, r;
76f84a5eb8SVaclav Hapla 
77f84a5eb8SVaclav Hapla   PetscFunctionBegin;
789566063dSJacob Faibussowitsch   PetscCall(PetscSFGetRootRanks(sf, &nranks, &ranks, &roffset, &rmine, &rremote));
79f84a5eb8SVaclav Hapla   nleaves = roffset[nranks];
809566063dSJacob Faibussowitsch   PetscCall(PetscMalloc2(nleaves, rmine1, nleaves, rremote1));
81f84a5eb8SVaclav Hapla   for (r = 0; r < nranks; r++) {
82f84a5eb8SVaclav Hapla     /* simultaneously sort rank-wise portions of rmine & rremote by values in rremote
83f84a5eb8SVaclav Hapla        - to unify order with the other side */
84f84a5eb8SVaclav Hapla     o = roffset[r];
85f84a5eb8SVaclav Hapla     n = roffset[r + 1] - o;
869566063dSJacob Faibussowitsch     PetscCall(PetscArraycpy(&(*rmine1)[o], &rmine[o], n));
879566063dSJacob Faibussowitsch     PetscCall(PetscArraycpy(&(*rremote1)[o], &rremote[o], n));
889566063dSJacob Faibussowitsch     PetscCall(PetscSortIntWithArray(n, &(*rremote1)[o], &(*rmine1)[o]));
89f84a5eb8SVaclav Hapla   }
90f84a5eb8SVaclav Hapla   PetscFunctionReturn(0);
91f84a5eb8SVaclav Hapla }
92f84a5eb8SVaclav Hapla 
939371c9d4SSatish Balay static PetscErrorCode GetRecursiveConeCoordinatesPerRank_Private(DM dm, PetscSF sf, PetscInt rmine[], Vec *coordinatesPerRank[]) {
94f84a5eb8SVaclav Hapla   IS                 pointsPerRank, conesPerRank;
95f84a5eb8SVaclav Hapla   PetscInt           nranks;
96f84a5eb8SVaclav Hapla   const PetscMPIInt *ranks;
97f84a5eb8SVaclav Hapla   const PetscInt    *roffset;
98f84a5eb8SVaclav Hapla   PetscInt           n, o, r;
99f84a5eb8SVaclav Hapla 
100f84a5eb8SVaclav Hapla   PetscFunctionBegin;
1019566063dSJacob Faibussowitsch   PetscCall(DMGetCoordinatesLocalSetUp(dm));
1029566063dSJacob Faibussowitsch   PetscCall(PetscSFGetRootRanks(sf, &nranks, &ranks, &roffset, NULL, NULL));
1039566063dSJacob Faibussowitsch   PetscCall(PetscMalloc1(nranks, coordinatesPerRank));
104f84a5eb8SVaclav Hapla   for (r = 0; r < nranks; r++) {
105f84a5eb8SVaclav Hapla     o = roffset[r];
106f84a5eb8SVaclav Hapla     n = roffset[r + 1] - o;
1079566063dSJacob Faibussowitsch     PetscCall(ISCreateGeneral(PETSC_COMM_SELF, n, &rmine[o], PETSC_USE_POINTER, &pointsPerRank));
1089566063dSJacob Faibussowitsch     PetscCall(DMPlexGetConeRecursiveVertices(dm, pointsPerRank, &conesPerRank));
1099566063dSJacob Faibussowitsch     PetscCall(DMGetCoordinatesLocalTuple(dm, conesPerRank, NULL, &(*coordinatesPerRank)[r]));
1109566063dSJacob Faibussowitsch     PetscCall(ISDestroy(&pointsPerRank));
1119566063dSJacob Faibussowitsch     PetscCall(ISDestroy(&conesPerRank));
112f84a5eb8SVaclav Hapla   }
113f84a5eb8SVaclav Hapla   PetscFunctionReturn(0);
114f84a5eb8SVaclav Hapla }
115f84a5eb8SVaclav Hapla 
1169371c9d4SSatish Balay static PetscErrorCode PetscSFComputeMultiRootOriginalNumberingByRank_Private(PetscSF sf, PetscSF imsf, PetscInt *irmine1[]) {
117f84a5eb8SVaclav Hapla   PetscInt       *mRootsOrigNumbering;
118f84a5eb8SVaclav Hapla   PetscInt        nileaves, niranks;
119f84a5eb8SVaclav Hapla   const PetscInt *iroffset, *irmine, *degree;
120f84a5eb8SVaclav Hapla   PetscInt        i, n, o, r;
121f84a5eb8SVaclav Hapla 
122f84a5eb8SVaclav Hapla   PetscFunctionBegin;
1239566063dSJacob Faibussowitsch   PetscCall(PetscSFGetGraph(imsf, NULL, &nileaves, NULL, NULL));
1249566063dSJacob Faibussowitsch   PetscCall(PetscSFGetRootRanks(imsf, &niranks, NULL, &iroffset, &irmine, NULL));
12508401ef6SPierre Jolivet   PetscCheck(nileaves == iroffset[niranks], PETSC_COMM_SELF, PETSC_ERR_PLIB, "nileaves != iroffset[niranks])");
1269566063dSJacob Faibussowitsch   PetscCall(PetscSFComputeDegreeBegin(sf, &degree));
1279566063dSJacob Faibussowitsch   PetscCall(PetscSFComputeDegreeEnd(sf, &degree));
1289566063dSJacob Faibussowitsch   PetscCall(PetscSFComputeMultiRootOriginalNumbering(sf, degree, NULL, &mRootsOrigNumbering));
1299566063dSJacob Faibussowitsch   PetscCall(PetscMalloc1(nileaves, irmine1));
130f84a5eb8SVaclav Hapla   for (r = 0; r < niranks; r++) {
131f84a5eb8SVaclav Hapla     o = iroffset[r];
132f84a5eb8SVaclav Hapla     n = iroffset[r + 1] - o;
133f84a5eb8SVaclav Hapla     for (i = 0; i < n; i++) (*irmine1)[o + i] = mRootsOrigNumbering[irmine[o + i]];
134f84a5eb8SVaclav Hapla   }
1359566063dSJacob Faibussowitsch   PetscCall(PetscFree(mRootsOrigNumbering));
136f84a5eb8SVaclav Hapla   PetscFunctionReturn(0);
137f84a5eb8SVaclav Hapla }
138f84a5eb8SVaclav Hapla 
139124f9872SVaclav Hapla /*@
140a8432d5bSVaclav Hapla   DMPlexCheckInterfaceCones - Check that points on inter-partition interfaces have conforming order of cone points.
141124f9872SVaclav Hapla 
142124f9872SVaclav Hapla   Input Parameters:
143124f9872SVaclav Hapla . dm - The DMPlex object
144124f9872SVaclav Hapla 
145a8432d5bSVaclav Hapla   Notes:
146a8432d5bSVaclav Hapla   For example, if there is an edge (rank,index)=(0,2) connecting points cone(0,2)=[(0,0),(0,1)] in this order, and the point SF containts connections 0 <- (1,0), 1 <- (1,1) and 2 <- (1,2),
147a8432d5bSVaclav Hapla   then this check would pass if the edge (1,2) has cone(1,2)=[(1,0),(1,1)]. By contrast, if cone(1,2)=[(1,1),(1,0)], then this check would fail.
148124f9872SVaclav Hapla 
149a8432d5bSVaclav Hapla   This is mainly intended for debugging/testing purposes. Does not check cone orientation, for this purpose use DMPlexCheckFaces().
150a8432d5bSVaclav Hapla 
15195eb5ee5SVaclav Hapla   For the complete list of DMPlexCheck* functions, see DMSetFromOptions().
15295eb5ee5SVaclav Hapla 
153a8432d5bSVaclav Hapla   Developer Note:
154a8432d5bSVaclav Hapla   Interface cones are expanded into vertices and then their coordinates are compared.
155124f9872SVaclav Hapla 
156124f9872SVaclav Hapla   Level: developer
157124f9872SVaclav Hapla 
158db781477SPatrick Sanan .seealso: `DMPlexGetCone()`, `DMPlexGetConeSize()`, `DMGetPointSF()`, `DMGetCoordinates()`, `DMSetFromOptions()`
159124f9872SVaclav Hapla @*/
1609371c9d4SSatish Balay PetscErrorCode DMPlexCheckInterfaceCones(DM dm) {
161f84a5eb8SVaclav Hapla   PetscSF            sf;
162f84a5eb8SVaclav Hapla   PetscInt           nleaves, nranks, nroots;
163f84a5eb8SVaclav Hapla   const PetscInt    *mine, *roffset, *rmine, *rremote;
164f84a5eb8SVaclav Hapla   const PetscSFNode *remote;
165f84a5eb8SVaclav Hapla   const PetscMPIInt *ranks;
166f84a5eb8SVaclav Hapla   PetscSF            msf, imsf;
167f84a5eb8SVaclav Hapla   PetscInt           nileaves, niranks;
168f84a5eb8SVaclav Hapla   const PetscMPIInt *iranks;
169f84a5eb8SVaclav Hapla   const PetscInt    *iroffset, *irmine, *irremote;
170f84a5eb8SVaclav Hapla   PetscInt          *rmine1, *rremote1; /* rmine and rremote copies simultaneously sorted by rank and rremote */
171f84a5eb8SVaclav Hapla   PetscInt          *mine_orig_numbering;
172f84a5eb8SVaclav Hapla   Vec               *sntCoordinatesPerRank;
173f84a5eb8SVaclav Hapla   Vec               *refCoordinatesPerRank;
174ea78f98cSLisandro Dalcin   Vec               *recCoordinatesPerRank = NULL;
175f84a5eb8SVaclav Hapla   PetscInt           r;
176f84a5eb8SVaclav Hapla   PetscMPIInt        commsize, myrank;
177f84a5eb8SVaclav Hapla   PetscBool          same;
1788f2c89e7SVaclav Hapla   PetscBool          verbose = PETSC_FALSE;
179f84a5eb8SVaclav Hapla   MPI_Comm           comm;
180f84a5eb8SVaclav Hapla 
181f84a5eb8SVaclav Hapla   PetscFunctionBegin;
18210b92ba9SVaclav Hapla   PetscValidHeaderSpecific(dm, DM_CLASSID, 1);
1839566063dSJacob Faibussowitsch   PetscCall(PetscObjectGetComm((PetscObject)dm, &comm));
1849566063dSJacob Faibussowitsch   PetscCallMPI(MPI_Comm_rank(comm, &myrank));
1859566063dSJacob Faibussowitsch   PetscCallMPI(MPI_Comm_size(comm, &commsize));
186f84a5eb8SVaclav Hapla   if (commsize < 2) PetscFunctionReturn(0);
1879566063dSJacob Faibussowitsch   PetscCall(DMGetPointSF(dm, &sf));
188f84a5eb8SVaclav Hapla   if (!sf) PetscFunctionReturn(0);
1899566063dSJacob Faibussowitsch   PetscCall(PetscSFGetGraph(sf, &nroots, &nleaves, &mine, &remote));
190f84a5eb8SVaclav Hapla   if (nroots < 0) PetscFunctionReturn(0);
1916858538eSMatthew G. Knepley   PetscCheck(dm->coordinates[0].x || dm->coordinates[0].xl, PetscObjectComm((PetscObject)dm), PETSC_ERR_ARG_WRONGSTATE, "DM coordinates must be set");
1929566063dSJacob Faibussowitsch   PetscCall(PetscSFSetUp(sf));
1939566063dSJacob Faibussowitsch   PetscCall(PetscSFGetRootRanks(sf, &nranks, &ranks, &roffset, &rmine, &rremote));
194f84a5eb8SVaclav Hapla 
195f84a5eb8SVaclav Hapla   /* Expand sent cones per rank */
1969566063dSJacob Faibussowitsch   PetscCall(SortByRemote_Private(sf, &rmine1, &rremote1));
1979566063dSJacob Faibussowitsch   PetscCall(GetRecursiveConeCoordinatesPerRank_Private(dm, sf, rmine1, &sntCoordinatesPerRank));
198f84a5eb8SVaclav Hapla 
199f84a5eb8SVaclav Hapla   /* Create inverse SF */
2009566063dSJacob Faibussowitsch   PetscCall(PetscSFGetMultiSF(sf, &msf));
2019566063dSJacob Faibussowitsch   PetscCall(PetscSFCreateInverseSF(msf, &imsf));
2029566063dSJacob Faibussowitsch   PetscCall(PetscSFSetUp(imsf));
2039566063dSJacob Faibussowitsch   PetscCall(PetscSFGetGraph(imsf, NULL, &nileaves, NULL, NULL));
2049566063dSJacob Faibussowitsch   PetscCall(PetscSFGetRootRanks(imsf, &niranks, &iranks, &iroffset, &irmine, &irremote));
205f84a5eb8SVaclav Hapla 
206f84a5eb8SVaclav Hapla   /* Compute original numbering of multi-roots (referenced points) */
2079566063dSJacob Faibussowitsch   PetscCall(PetscSFComputeMultiRootOriginalNumberingByRank_Private(sf, imsf, &mine_orig_numbering));
208f84a5eb8SVaclav Hapla 
209124f9872SVaclav Hapla   /* Expand coordinates of the referred cones per rank */
2109566063dSJacob Faibussowitsch   PetscCall(GetRecursiveConeCoordinatesPerRank_Private(dm, imsf, mine_orig_numbering, &refCoordinatesPerRank));
211f84a5eb8SVaclav Hapla 
212f84a5eb8SVaclav Hapla   /* Send the coordinates */
2139566063dSJacob Faibussowitsch   PetscCall(ExchangeVecByRank_Private((PetscObject)sf, nranks, ranks, sntCoordinatesPerRank, niranks, iranks, &recCoordinatesPerRank));
214f84a5eb8SVaclav Hapla 
2158f2c89e7SVaclav Hapla   /* verbose output */
2169566063dSJacob Faibussowitsch   PetscCall(PetscOptionsGetBool(((PetscObject)dm)->options, ((PetscObject)dm)->prefix, "-dm_plex_check_cones_conform_on_interfaces_verbose", &verbose, NULL));
2178f2c89e7SVaclav Hapla   if (verbose) {
2189f27a777SBarry Smith     PetscViewer sv, v = PETSC_VIEWER_STDOUT_WORLD;
2199566063dSJacob Faibussowitsch     PetscCall(PetscViewerASCIIPrintf(v, "============\nDMPlexCheckInterfaceCones output\n============\n"));
2209566063dSJacob Faibussowitsch     PetscCall(PetscViewerASCIIPushSynchronized(v));
2219566063dSJacob Faibussowitsch     PetscCall(PetscViewerASCIISynchronizedPrintf(v, "[%d] --------\n", myrank));
2228f2c89e7SVaclav Hapla     for (r = 0; r < nranks; r++) {
22363a3b9bcSJacob Faibussowitsch       PetscCall(PetscViewerASCIISynchronizedPrintf(v, "  r=%" PetscInt_FMT " ranks[r]=%d sntCoordinatesPerRank[r]:\n", r, ranks[r]));
2249566063dSJacob Faibussowitsch       PetscCall(PetscViewerASCIIPushTab(v));
2259566063dSJacob Faibussowitsch       PetscCall(PetscViewerGetSubViewer(v, PETSC_COMM_SELF, &sv));
2269566063dSJacob Faibussowitsch       PetscCall(VecView(sntCoordinatesPerRank[r], sv));
2279566063dSJacob Faibussowitsch       PetscCall(PetscViewerRestoreSubViewer(v, PETSC_COMM_SELF, &sv));
2289566063dSJacob Faibussowitsch       PetscCall(PetscViewerASCIIPopTab(v));
2298f2c89e7SVaclav Hapla     }
2309566063dSJacob Faibussowitsch     PetscCall(PetscViewerASCIISynchronizedPrintf(v, "  ----------\n"));
2318f2c89e7SVaclav Hapla     for (r = 0; r < niranks; r++) {
23263a3b9bcSJacob Faibussowitsch       PetscCall(PetscViewerASCIISynchronizedPrintf(v, "  r=%" PetscInt_FMT " iranks[r]=%d refCoordinatesPerRank[r]:\n", r, iranks[r]));
2339566063dSJacob Faibussowitsch       PetscCall(PetscViewerASCIIPushTab(v));
2349566063dSJacob Faibussowitsch       PetscCall(PetscViewerGetSubViewer(v, PETSC_COMM_SELF, &sv));
2359566063dSJacob Faibussowitsch       PetscCall(VecView(refCoordinatesPerRank[r], sv));
2369566063dSJacob Faibussowitsch       PetscCall(PetscViewerRestoreSubViewer(v, PETSC_COMM_SELF, &sv));
2379566063dSJacob Faibussowitsch       PetscCall(PetscViewerASCIIPopTab(v));
2388f2c89e7SVaclav Hapla     }
2399566063dSJacob Faibussowitsch     PetscCall(PetscViewerASCIISynchronizedPrintf(v, "  ----------\n"));
2408f2c89e7SVaclav Hapla     for (r = 0; r < niranks; r++) {
24163a3b9bcSJacob Faibussowitsch       PetscCall(PetscViewerASCIISynchronizedPrintf(v, "  r=%" PetscInt_FMT " iranks[r]=%d recCoordinatesPerRank[r]:\n", r, iranks[r]));
2429566063dSJacob Faibussowitsch       PetscCall(PetscViewerASCIIPushTab(v));
2439566063dSJacob Faibussowitsch       PetscCall(PetscViewerGetSubViewer(v, PETSC_COMM_SELF, &sv));
2449566063dSJacob Faibussowitsch       PetscCall(VecView(recCoordinatesPerRank[r], sv));
2459566063dSJacob Faibussowitsch       PetscCall(PetscViewerRestoreSubViewer(v, PETSC_COMM_SELF, &sv));
2469566063dSJacob Faibussowitsch       PetscCall(PetscViewerASCIIPopTab(v));
2478f2c89e7SVaclav Hapla     }
2489566063dSJacob Faibussowitsch     PetscCall(PetscViewerFlush(v));
2499566063dSJacob Faibussowitsch     PetscCall(PetscViewerASCIIPopSynchronized(v));
2508f2c89e7SVaclav Hapla   }
2518f2c89e7SVaclav Hapla 
252f84a5eb8SVaclav Hapla   /* Compare recCoordinatesPerRank with refCoordinatesPerRank */
253f84a5eb8SVaclav Hapla   for (r = 0; r < niranks; r++) {
2549566063dSJacob Faibussowitsch     PetscCall(VecEqual(refCoordinatesPerRank[r], recCoordinatesPerRank[r], &same));
25528b400f6SJacob Faibussowitsch     PetscCheck(same, PETSC_COMM_SELF, PETSC_ERR_PLIB, "interface cones do not conform for remote rank %d", iranks[r]);
256f84a5eb8SVaclav Hapla   }
257f84a5eb8SVaclav Hapla 
258f84a5eb8SVaclav Hapla   /* destroy sent stuff */
259*48a46eb9SPierre Jolivet   for (r = 0; r < nranks; r++) PetscCall(VecDestroy(&sntCoordinatesPerRank[r]));
2609566063dSJacob Faibussowitsch   PetscCall(PetscFree(sntCoordinatesPerRank));
2619566063dSJacob Faibussowitsch   PetscCall(PetscFree2(rmine1, rremote1));
2629566063dSJacob Faibussowitsch   PetscCall(PetscSFDestroy(&imsf));
263f84a5eb8SVaclav Hapla 
264f84a5eb8SVaclav Hapla   /* destroy referenced stuff */
265*48a46eb9SPierre Jolivet   for (r = 0; r < niranks; r++) PetscCall(VecDestroy(&refCoordinatesPerRank[r]));
2669566063dSJacob Faibussowitsch   PetscCall(PetscFree(refCoordinatesPerRank));
2679566063dSJacob Faibussowitsch   PetscCall(PetscFree(mine_orig_numbering));
268f84a5eb8SVaclav Hapla 
269f84a5eb8SVaclav Hapla   /* destroy received stuff */
270*48a46eb9SPierre Jolivet   for (r = 0; r < niranks; r++) PetscCall(VecDestroy(&recCoordinatesPerRank[r]));
2719566063dSJacob Faibussowitsch   PetscCall(PetscFree(recCoordinatesPerRank));
272f84a5eb8SVaclav Hapla   PetscFunctionReturn(0);
273f84a5eb8SVaclav Hapla }
274