xref: /petsc/include/petscsys.h (revision a29dfd43bb0c77e2653d3bfa2c953f902720a6d2)
1 /*
2    This is the main PETSc include file (for C and C++).  It is included by all
3    other PETSc include files, so it almost never has to be specifically included.
4    Portions of this code are under:
5    Copyright (c) 2022 Advanced Micro Devices, Inc. All rights reserved.
6 */
7 #pragma once
8 
9 /* ========================================================================== */
10 /*
11    petscconf.h is contained in ${PETSC_ARCH}/include/petscconf.h it is
12    found automatically by the compiler due to the -I${PETSC_DIR}/${PETSC_ARCH}/include that
13    PETSc's makefiles add to the compiler rules.
14    For --prefix installs the directory ${PETSC_ARCH} does not exist and petscconf.h is in the same
15    directory as the other PETSc include files.
16 */
17 #include <petscconf.h>
18 #include <petscpkg_version.h>
19 #include <petscconf_poison.h>
20 #include <petscfix.h>
21 #include <petscmacros.h>
22 
23 /* SUBMANSEC = Sys */
24 
25 #if defined(PETSC_DESIRE_FEATURE_TEST_MACROS)
26   /*
27    Feature test macros must be included before headers defined by IEEE Std 1003.1-2001
28    We only turn these in PETSc source files that require them by setting PETSC_DESIRE_FEATURE_TEST_MACROS
29 */
30   #if defined(PETSC__POSIX_C_SOURCE_200112L) && !defined(_POSIX_C_SOURCE)
31     #define _POSIX_C_SOURCE 200112L
32   #endif
33   #if defined(PETSC__BSD_SOURCE) && !defined(_BSD_SOURCE)
34     #define _BSD_SOURCE
35   #endif
36   #if defined(PETSC__DEFAULT_SOURCE) && !defined(_DEFAULT_SOURCE)
37     #define _DEFAULT_SOURCE
38   #endif
39   #if defined(PETSC__GNU_SOURCE) && !defined(_GNU_SOURCE)
40     #define _GNU_SOURCE
41   #endif
42 #endif
43 
44 #include <petscsystypes.h>
45 
46 /* ========================================================================== */
47 
48 /*
49     Defines the interface to MPI allowing the use of all MPI functions.
50 
51     PETSc does not use the C++ binding of MPI at ALL. The following flag
52     makes sure the C++ bindings are not included. The C++ bindings REQUIRE
53     putting mpi.h before ANY C++ include files, we cannot control this
54     with all PETSc users. Users who want to use the MPI C++ bindings can include
55     mpicxx.h directly in their code
56 */
57 #if !defined(MPICH_SKIP_MPICXX)
58   #define MPICH_SKIP_MPICXX 1
59 #endif
60 #if !defined(OMPI_SKIP_MPICXX)
61   #define OMPI_SKIP_MPICXX 1
62 #endif
63 #if defined(PETSC_HAVE_MPIUNI)
64   #include <petsc/mpiuni/mpi.h>
65 #else
66   #include <mpi.h>
67 #endif
68 
69 /*
70    Perform various sanity checks that the correct mpi.h is being included at compile time.
71    This usually happens because
72       * either an unexpected mpi.h is in the default compiler path (i.e. in /usr/include) or
73       * an extra include path -I/something (which contains the unexpected mpi.h) is being passed to the compiler
74 */
75 #if defined(PETSC_HAVE_MPIUNI)
76   #ifndef MPIUNI_H
77     #error "PETSc was configured with --with-mpi=0 but now appears to be compiling using a different mpi.h"
78   #endif
79 #elif defined(PETSC_HAVE_I_MPI)
80   #if !defined(I_MPI_NUMVERSION)
81     #error "PETSc was configured with I_MPI but now appears to be compiling using a non-I_MPI mpi.h"
82   #elif I_MPI_NUMVERSION != PETSC_PKG_I_MPI_NUMVERSION
83     #error "PETSc was configured with one I_MPI mpi.h version but now appears to be compiling using a different I_MPI mpi.h version"
84   #endif
85 #elif defined(PETSC_HAVE_MVAPICH2)
86   #if !defined(MVAPICH2_NUMVERSION)
87     #error "PETSc was configured with MVAPICH2 but now appears to be compiling using a non-MVAPICH2 mpi.h"
88   #elif MVAPICH2_NUMVERSION != PETSC_PKG_MVAPICH2_NUMVERSION
89     #error "PETSc was configured with one MVAPICH2 mpi.h version but now appears to be compiling using a different MVAPICH2 mpi.h version"
90   #endif
91 #elif defined(PETSC_HAVE_MPICH)
92   #if !defined(MPICH_NUMVERSION) || defined(MVAPICH2_NUMVERSION) || defined(I_MPI_NUMVERSION)
93     #error "PETSc was configured with MPICH but now appears to be compiling using a non-MPICH mpi.h"
94   #elif !PETSC_PKG_MPICH_VERSION_EQ(MPICH_NUMVERSION / 10000000, MPICH_NUMVERSION / 100000 % 100, MPICH_NUMVERSION / 1000 % 100)
95     #error "PETSc was configured with one MPICH mpi.h version but now appears to be compiling using a different MPICH mpi.h version"
96   #endif
97 #elif defined(PETSC_HAVE_OPENMPI)
98   #if !defined(OMPI_MAJOR_VERSION)
99     #error "PETSc was configured with Open MPI but now appears to be compiling using a non-Open MPI mpi.h"
100   #elif !PETSC_PKG_OPENMPI_VERSION_EQ(OMPI_MAJOR_VERSION, OMPI_MINOR_VERSION, OMPI_RELEASE_VERSION)
101     #error "PETSc was configured with one Open MPI mpi.h version but now appears to be compiling using a different Open MPI mpi.h version"
102   #endif
103 #elif defined(PETSC_HAVE_MSMPI_VERSION)
104   #if !defined(MSMPI_VER)
105     #error "PETSc was configured with MSMPI but now appears to be compiling using a non-MSMPI mpi.h"
106   #elif (MSMPI_VER != PETSC_HAVE_MSMPI_VERSION)
107     #error "PETSc was configured with one MSMPI mpi.h version but now appears to be compiling using a different MSMPI mpi.h version"
108   #endif
109 #elif defined(OMPI_MAJOR_VERSION) || defined(MPICH_NUMVERSION) || defined(MSMPI_VER)
110   #error "PETSc was configured with undetermined MPI - but now appears to be compiling using any of Open MPI, MS-MPI or a MPICH variant"
111 #endif
112 
113 /*
114     Need to put stdio.h AFTER mpi.h for MPICH2 with C++ compiler
115     see the top of mpicxx.h in the MPICH2 distribution.
116 */
117 #include <stdio.h>
118 
119 /* MSMPI on 32-bit Microsoft Windows requires this yukky hack - that breaks MPI standard compliance */
120 #if !defined(MPIAPI)
121   #define MPIAPI
122 #endif
123 
124 PETSC_EXTERN MPI_Datatype MPIU_ENUM PETSC_ATTRIBUTE_MPI_TYPE_TAG(PetscEnum);
125 PETSC_EXTERN MPI_Datatype MPIU_BOOL PETSC_ATTRIBUTE_MPI_TYPE_TAG(PetscBool);
126 
127 /*MC
128    MPIU_INT - Portable MPI datatype corresponding to `PetscInt` independent of the precision of `PetscInt`
129 
130    Level: beginner
131 
132    Note:
133    In MPI calls that require an MPI datatype that matches a `PetscInt` or array of `PetscInt` values, pass this value.
134 
135 .seealso: `PetscReal`, `PetscScalar`, `PetscComplex`, `PetscInt`, `MPIU_COUNT`, `MPIU_REAL`, `MPIU_SCALAR`, `MPIU_COMPLEX`
136 M*/
137 
138 PETSC_EXTERN MPI_Datatype MPIU_FORTRANADDR;
139 
140 #if defined(PETSC_USE_64BIT_INDICES)
141   #define MPIU_INT MPIU_INT64
142 #else
143   #define MPIU_INT MPI_INT
144 #endif
145 
146 /*MC
147    MPIU_COUNT - Portable MPI datatype corresponding to `PetscCount` independent of the precision of `PetscCount`
148 
149    Level: beginner
150 
151    Note:
152    In MPI calls that require an MPI datatype that matches a `PetscCount` or array of `PetscCount` values, pass this value.
153 
154   Developer Note:
155   It seems `MPI_AINT` is unsigned so this may be the wrong choice here since `PetscCount` is signed
156 
157 .seealso: `PetscReal`, `PetscScalar`, `PetscComplex`, `PetscInt`, `MPIU_INT`, `MPIU_REAL`, `MPIU_SCALAR`, `MPIU_COMPLEX`
158 M*/
159 #define MPIU_COUNT MPI_AINT
160 
161 /*
162     For the rare cases when one needs to send a size_t object with MPI
163 */
164 PETSC_EXTERN MPI_Datatype MPIU_SIZE_T PETSC_ATTRIBUTE_MPI_TYPE_TAG(size_t);
165 
166 /*
167       You can use PETSC_STDOUT as a replacement of stdout. You can also change
168     the value of PETSC_STDOUT to redirect all standard output elsewhere
169 */
170 PETSC_EXTERN FILE *PETSC_STDOUT;
171 
172 /*
173       You can use PETSC_STDERR as a replacement of stderr. You can also change
174     the value of PETSC_STDERR to redirect all standard error elsewhere
175 */
176 PETSC_EXTERN FILE *PETSC_STDERR;
177 
178 /*
179   Handle inclusion when using clang compiler with CUDA support
180   __float128 is not available for the device
181 */
182 #if defined(__clang__) && defined(__CUDA_ARCH__)
183   #define PETSC_SKIP_REAL___FLOAT128
184 #endif
185 
186 /*
187     Declare extern C stuff after including external header files
188 */
189 
190 PETSC_EXTERN PetscBool PETSC_RUNNING_ON_VALGRIND;
191 /*
192     Defines elementary mathematics functions and constants.
193 */
194 #include <petscmath.h>
195 
196 /*MC
197     PETSC_IGNORE - same as `NULL`, means PETSc will ignore this argument
198 
199    Level: beginner
200 
201    Note:
202    Accepted by many PETSc functions to not set a parameter and instead use a default value
203 
204    Fortran Note:
205    Use `PETSC_NULL_INTEGER`, `PETSC_NULL_DOUBLE_PRECISION` etc
206 
207 .seealso: `PETSC_DECIDE`, `PETSC_DEFAULT`, `PETSC_DETERMINE`
208 M*/
209 #define PETSC_IGNORE PETSC_NULLPTR
210 #define PETSC_NULL   PETSC_DEPRECATED_MACRO(3, 19, 0, "PETSC_NULLPTR", ) PETSC_NULLPTR
211 
212 /*MC
213    PETSC_UNLIMITED - standard way of passing an integer or floating point parameter to indicate PETSc there is no bound on the value allowed
214 
215    Level: beginner
216 
217    Example Usage:
218 .vb
219    KSPSetTolerances(ksp, PETSC_CURRENT, PETSC_CURRENT, PETSC_UNLIMITED, PETSC_UNLIMITED);
220 .ve
221   indicates that the solver is allowed to take any number of iterations and will not stop early no matter how the residual gets.
222 
223    Fortran Note:
224    Use `PETSC_UNLIMITED_INTEGER` or `PETSC_UNLIMITED_REAL`.
225 
226 .seealso: `PETSC_DEFAULT`, `PETSC_IGNORE`, `PETSC_DETERMINE`, `PETSC_DECIDE`
227 M*/
228 
229 /*MC
230    PETSC_DECIDE - standard way of passing an integer or floating point parameter to indicate PETSc should determine an appropriate value
231 
232    Level: beginner
233 
234    Example Usage:
235 .vb
236    VecSetSizes(ksp, PETSC_DECIDE, 10);
237 .ve
238   indicates that the global size of the vector is 10 and the local size will be automatically determined so that the sum of the
239   local sizes is the global size, see `PetscSplitOwnership()`.
240 
241    Fortran Note:
242    Use `PETSC_DECIDE_INTEGER` or `PETSC_DECIDE_REAL`.
243 
244 .seealso: `PETSC_DEFAULT`, `PETSC_IGNORE`, `PETSC_DETERMINE`, `PETSC_UNLIMITED'
245 M*/
246 
247 /*MC
248    PETSC_DETERMINE - standard way of passing an integer or floating point parameter to indicate PETSc should determine an appropriate value
249 
250    Level: beginner
251 
252     Example Usage:
253 .vb
254    VecSetSizes(ksp, 10, PETSC_DETERMINE);
255 .ve
256   indicates that the local size of the vector is 10 and the global size will be automatically summing up all the local sizes.
257 
258    Note:
259    Same as `PETSC_DECIDE`
260 
261    Fortran Note:
262    Use `PETSC_DETERMINE_INTEGER` or `PETSC_DETERMINE_REAL`.
263 
264    Developer Note:
265    I would like to use const `PetscInt` `PETSC_DETERMINE` = `PETSC_DECIDE`; but for
266    some reason this is not allowed by the standard even though `PETSC_DECIDE` is a constant value.
267 
268 .seealso: `PETSC_DECIDE`, `PETSC_DEFAULT`, `PETSC_IGNORE`, `VecSetSizes()`, `PETSC_UNLIMITED'
269 M*/
270 
271 /*MC
272    PETSC_CURRENT - standard way of indicating to an object not to change the current value of the parameter in the object
273 
274    Level: beginner
275 
276    Note:
277    Use `PETSC_DECIDE` to use the value that was set by PETSc when the object's type was set
278 
279    Fortran Note:
280    Use `PETSC_CURRENT_INTEGER` or `PETSC_CURRENT_REAL`.
281 
282 .seealso: `PETSC_DECIDE`, `PETSC_IGNORE`, `PETSC_DETERMINE`, `PETSC_DEFAULT`, `PETSC_UNLIMITED'
283 M*/
284 
285 /*MC
286    PETSC_DEFAULT - deprecated, see `PETSC_CURRENT` and `PETSC_DETERMINE`
287 
288    Level: beginner
289 
290    Note:
291    The name is confusing since it tells the object to continue to use the value it is using, not the default value when the object's type was set.
292 
293    Developer Note:
294    Unfortunately this was used for two different purposes in the past, to actually trigger the use of a default value or to continue the
295    use of currently set value (in, for example, `KSPSetTolerances()`.
296 
297 .seealso: `PETSC_DECIDE`, `PETSC_IGNORE`, `PETSC_DETERMINE`, `PETSC_CURRENT`, `PETSC_UNLIMITED'
298 M*/
299 
300 /* These MUST be preprocessor defines! see https://gitlab.com/petsc/petsc/-/issues/1370 */
301 #define PETSC_DECIDE    (-1)
302 #define PETSC_DETERMINE PETSC_DECIDE
303 #define PETSC_CURRENT   (-2)
304 #define PETSC_UNLIMITED (-3)
305 /*  PETSC_DEFAULT is deprecated in favor of PETSC_CURRENT for use in KSPSetTolerances() and similar functions */
306 #define PETSC_DEFAULT PETSC_CURRENT
307 
308 /*MC
309    PETSC_COMM_WORLD - the equivalent of the `MPI_COMM_WORLD` communicator which represents all the processes that PETSc knows about.
310 
311    Level: beginner
312 
313    Notes:
314    By default `PETSC_COMM_WORLD` and `MPI_COMM_WORLD` are identical unless you wish to
315    run PETSc on ONLY a subset of `MPI_COMM_WORLD`. In that case create your new (smaller)
316    communicator, call it, say comm, and set `PETSC_COMM_WORLD` = comm BEFORE calling
317    `PetscInitialize()`, but after `MPI_Init()` has been called.
318 
319    The value of `PETSC_COMM_WORLD` should never be used or accessed before `PetscInitialize()`
320    is called because it may not have a valid value yet.
321 
322 .seealso: `PETSC_COMM_SELF`
323 M*/
324 PETSC_EXTERN MPI_Comm PETSC_COMM_WORLD;
325 
326 /*MC
327    PETSC_COMM_SELF - This is always `MPI_COMM_SELF`
328 
329    Level: beginner
330 
331    Note:
332    Do not USE/access or set this variable before `PetscInitialize()` has been called.
333 
334 .seealso: `PETSC_COMM_WORLD`
335 M*/
336 #define PETSC_COMM_SELF MPI_COMM_SELF
337 
338 /*MC
339    PETSC_MPI_THREAD_REQUIRED - the required threading support used if PETSc initializes MPI with `MPI_Init_thread()`.
340 
341    No Fortran Support
342 
343    Level: beginner
344 
345    Note:
346    By default `PETSC_MPI_THREAD_REQUIRED` equals `MPI_THREAD_FUNNELED` when the MPI implementation provides `MPI_Init_thread()`, otherwise it equals `MPI_THREAD_SINGLE`
347 
348 .seealso: `PetscInitialize()`
349 M*/
350 PETSC_EXTERN PetscMPIInt PETSC_MPI_THREAD_REQUIRED;
351 
352 /*MC
353    PetscBeganMPI - indicates if PETSc initialized MPI during `PetscInitialize()` or if MPI was already initialized.
354 
355    Synopsis:
356    #include <petscsys.h>
357    PetscBool PetscBeganMPI;
358 
359    No Fortran Support
360 
361    Level: developer
362 
363 .seealso: `PetscInitialize()`, `PetscInitializeCalled`
364 M*/
365 PETSC_EXTERN PetscBool PetscBeganMPI;
366 
367 PETSC_EXTERN PetscBool PetscErrorHandlingInitialized;
368 PETSC_EXTERN PetscBool PetscInitializeCalled;
369 PETSC_EXTERN PetscBool PetscFinalizeCalled;
370 PETSC_EXTERN PetscBool PetscViennaCLSynchronize;
371 
372 PETSC_EXTERN PetscErrorCode PetscSetHelpVersionFunctions(PetscErrorCode (*)(MPI_Comm), PetscErrorCode (*)(MPI_Comm));
373 PETSC_EXTERN PetscErrorCode PetscCommDuplicate(MPI_Comm, MPI_Comm *, int *);
374 PETSC_EXTERN PetscErrorCode PetscCommDestroy(MPI_Comm *);
375 PETSC_EXTERN PetscErrorCode PetscCommGetComm(MPI_Comm, MPI_Comm *);
376 PETSC_EXTERN PetscErrorCode PetscCommRestoreComm(MPI_Comm, MPI_Comm *);
377 
378 #if defined(PETSC_HAVE_KOKKOS)
379 PETSC_EXTERN PetscErrorCode PetscKokkosInitializeCheck(void); /* Initialize Kokkos if not yet. */
380 #endif
381 
382 #if defined(PETSC_HAVE_NVSHMEM)
383 PETSC_EXTERN PetscBool      PetscBeganNvshmem;
384 PETSC_EXTERN PetscBool      PetscNvshmemInitialized;
385 PETSC_EXTERN PetscErrorCode PetscNvshmemFinalize(void);
386 #endif
387 
388 #if defined(PETSC_HAVE_ELEMENTAL)
389 PETSC_EXTERN PetscErrorCode PetscElementalInitializePackage(void);
390 PETSC_EXTERN PetscErrorCode PetscElementalInitialized(PetscBool *);
391 PETSC_EXTERN PetscErrorCode PetscElementalFinalizePackage(void);
392 #endif
393 
394 /*MC
395    PetscMalloc - Allocates memory, One should use `PetscNew()`, `PetscMalloc1()` or `PetscCalloc1()` usually instead of this
396 
397    Synopsis:
398     #include <petscsys.h>
399    PetscErrorCode PetscMalloc(size_t m,void **result)
400 
401    Not Collective
402 
403    Input Parameter:
404 .  m - number of bytes to allocate
405 
406    Output Parameter:
407 .  result - memory allocated
408 
409    Level: beginner
410 
411    Notes:
412    Memory is always allocated at least double aligned
413 
414    It is safe to allocate size 0 and pass the resulting pointer (which may or may not be `NULL`) to `PetscFree()`.
415 
416 .seealso: `PetscFree()`, `PetscNew()`
417 M*/
418 #define PetscMalloc(a, b) ((*PetscTrMalloc)((a), PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, (void **)(b)))
419 
420 /*MC
421    PetscRealloc - Reallocates memory
422 
423    Synopsis:
424     #include <petscsys.h>
425    PetscErrorCode PetscRealloc(size_t m,void **result)
426 
427    Not Collective
428 
429    Input Parameters:
430 +  m - number of bytes to allocate
431 -  result - previous memory
432 
433    Output Parameter:
434 .  result - new memory allocated
435 
436    Level: developer
437 
438    Note:
439    Memory is always allocated at least double aligned
440 
441 .seealso: `PetscMalloc()`, `PetscFree()`, `PetscNew()`
442 M*/
443 #define PetscRealloc(a, b) ((*PetscTrRealloc)((a), __LINE__, PETSC_FUNCTION_NAME, __FILE__, (void **)(b)))
444 
445 /*MC
446    PetscAddrAlign - Rounds up an address to `PETSC_MEMALIGN` alignment
447 
448    Synopsis:
449     #include <petscsys.h>
450    void *PetscAddrAlign(void *addr)
451 
452    Not Collective
453 
454    Input Parameter:
455 .  addr - address to align (any pointer type)
456 
457    Level: developer
458 
459 .seealso: `PetscMallocAlign()`
460 M*/
461 #define PetscAddrAlign(a) ((void *)((((PETSC_UINTPTR_T)(a)) + (PETSC_MEMALIGN - 1)) & ~(PETSC_MEMALIGN - 1)))
462 
463 /*MC
464    PetscCalloc - Allocates a cleared (zeroed) memory region aligned to `PETSC_MEMALIGN`
465 
466    Synopsis:
467     #include <petscsys.h>
468    PetscErrorCode PetscCalloc(size_t m,void **result)
469 
470    Not Collective
471 
472    Input Parameter:
473 .  m - number of bytes to allocate
474 
475    Output Parameter:
476 .  result - memory allocated
477 
478    Level: beginner
479 
480    Notes:
481    Memory is always allocated at least double aligned. This macro is useful in allocating memory pointed by void pointers
482 
483    It is safe to allocate size 0 and pass the resulting pointer (which may or may not be `NULL`) to `PetscFree()`.
484 
485 .seealso: `PetscFree()`, `PetscNew()`
486 M*/
487 #define PetscCalloc(m, result) PetscMallocA(1, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)m), (result))
488 
489 /*MC
490    PetscMalloc1 - Allocates an array of memory aligned to `PETSC_MEMALIGN`
491 
492    Synopsis:
493     #include <petscsys.h>
494    PetscErrorCode PetscMalloc1(size_t m1,type **r1)
495 
496    Not Collective
497 
498    Input Parameter:
499 .  m1 - number of elements to allocate  (may be zero)
500 
501    Output Parameter:
502 .  r1 - memory allocated
503 
504    Level: beginner
505 
506    Note:
507    This uses the sizeof() of the memory type requested to determine the total memory to be allocated, therefore you should not
508          multiply the number of elements requested by the `sizeof()` the type. For example use
509 .vb
510   PetscInt *id;
511   PetscMalloc1(10,&id);
512 .ve
513        not
514 .vb
515   PetscInt *id;
516   PetscMalloc1(10*sizeof(PetscInt),&id);
517 .ve
518 
519         Does not zero the memory allocated, use `PetscCalloc1()` to obtain memory that has been zeroed.
520 
521 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscCalloc1()`, `PetscMalloc2()`
522 M*/
523 #define PetscMalloc1(m1, r1) PetscMallocA(1, PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1))
524 
525 /*MC
526    PetscCalloc1 - Allocates a cleared (zeroed) array of memory aligned to `PETSC_MEMALIGN`
527 
528    Synopsis:
529     #include <petscsys.h>
530    PetscErrorCode PetscCalloc1(size_t m1,type **r1)
531 
532    Not Collective
533 
534    Input Parameter:
535 .  m1 - number of elements to allocate in 1st chunk  (may be zero)
536 
537    Output Parameter:
538 .  r1 - memory allocated
539 
540    Level: beginner
541 
542    Note:
543    See `PetsMalloc1()` for more details on usage.
544 
545 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc1()`, `PetscCalloc2()`
546 M*/
547 #define PetscCalloc1(m1, r1) PetscMallocA(1, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1))
548 
549 /*MC
550    PetscMalloc2 - Allocates 2 arrays of memory both aligned to `PETSC_MEMALIGN`
551 
552    Synopsis:
553     #include <petscsys.h>
554    PetscErrorCode PetscMalloc2(size_t m1,type **r1,size_t m2,type **r2)
555 
556    Not Collective
557 
558    Input Parameters:
559 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
560 -  m2 - number of elements to allocate in 2nd chunk  (may be zero)
561 
562    Output Parameters:
563 +  r1 - memory allocated in first chunk
564 -  r2 - memory allocated in second chunk
565 
566    Level: developer
567 
568 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc1()`, `PetscCalloc2()`
569 M*/
570 #define PetscMalloc2(m1, r1, m2, r2) PetscMallocA(2, PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2))
571 
572 /*MC
573    PetscCalloc2 - Allocates 2 cleared (zeroed) arrays of memory both aligned to `PETSC_MEMALIGN`
574 
575    Synopsis:
576     #include <petscsys.h>
577    PetscErrorCode PetscCalloc2(size_t m1,type **r1,size_t m2,type **r2)
578 
579    Not Collective
580 
581    Input Parameters:
582 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
583 -  m2 - number of elements to allocate in 2nd chunk  (may be zero)
584 
585    Output Parameters:
586 +  r1 - memory allocated in first chunk
587 -  r2 - memory allocated in second chunk
588 
589    Level: developer
590 
591 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscCalloc1()`, `PetscMalloc2()`
592 M*/
593 #define PetscCalloc2(m1, r1, m2, r2) PetscMallocA(2, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2))
594 
595 /*MC
596    PetscMalloc3 - Allocates 3 arrays of memory, all aligned to `PETSC_MEMALIGN`
597 
598    Synopsis:
599     #include <petscsys.h>
600    PetscErrorCode PetscMalloc3(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3)
601 
602    Not Collective
603 
604    Input Parameters:
605 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
606 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
607 -  m3 - number of elements to allocate in 3rd chunk  (may be zero)
608 
609    Output Parameters:
610 +  r1 - memory allocated in first chunk
611 .  r2 - memory allocated in second chunk
612 -  r3 - memory allocated in third chunk
613 
614    Level: developer
615 
616 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscCalloc3()`, `PetscFree3()`
617 M*/
618 #define PetscMalloc3(m1, r1, m2, r2, m3, r3) \
619   PetscMallocA(3, PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3))
620 
621 /*MC
622    PetscCalloc3 - Allocates 3 cleared (zeroed) arrays of memory, all aligned to `PETSC_MEMALIGN`
623 
624    Synopsis:
625     #include <petscsys.h>
626    PetscErrorCode PetscCalloc3(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3)
627 
628    Not Collective
629 
630    Input Parameters:
631 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
632 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
633 -  m3 - number of elements to allocate in 3rd chunk  (may be zero)
634 
635    Output Parameters:
636 +  r1 - memory allocated in first chunk
637 .  r2 - memory allocated in second chunk
638 -  r3 - memory allocated in third chunk
639 
640    Level: developer
641 
642 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscCalloc2()`, `PetscMalloc3()`, `PetscFree3()`
643 M*/
644 #define PetscCalloc3(m1, r1, m2, r2, m3, r3) \
645   PetscMallocA(3, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3))
646 
647 /*MC
648    PetscMalloc4 - Allocates 4 arrays of memory, all aligned to `PETSC_MEMALIGN`
649 
650    Synopsis:
651     #include <petscsys.h>
652    PetscErrorCode PetscMalloc4(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4)
653 
654    Not Collective
655 
656    Input Parameters:
657 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
658 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
659 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
660 -  m4 - number of elements to allocate in 4th chunk  (may be zero)
661 
662    Output Parameters:
663 +  r1 - memory allocated in first chunk
664 .  r2 - memory allocated in second chunk
665 .  r3 - memory allocated in third chunk
666 -  r4 - memory allocated in fourth chunk
667 
668    Level: developer
669 
670 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscCalloc4()`, `PetscFree4()`
671 M*/
672 #define PetscMalloc4(m1, r1, m2, r2, m3, r3, m4, r4) \
673   PetscMallocA(4, PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4))
674 
675 /*MC
676    PetscCalloc4 - Allocates 4 cleared (zeroed) arrays of memory, all aligned to `PETSC_MEMALIGN`
677 
678    Synopsis:
679     #include <petscsys.h>
680    PetscErrorCode PetscCalloc4(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4)
681 
682    Not Collective
683 
684    Input Parameters:
685 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
686 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
687 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
688 -  m4 - number of elements to allocate in 4th chunk  (may be zero)
689 
690    Output Parameters:
691 +  r1 - memory allocated in first chunk
692 .  r2 - memory allocated in second chunk
693 .  r3 - memory allocated in third chunk
694 -  r4 - memory allocated in fourth chunk
695 
696    Level: developer
697 
698 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscCalloc4()`, `PetscFree4()`
699 M*/
700 #define PetscCalloc4(m1, r1, m2, r2, m3, r3, m4, r4) \
701   PetscMallocA(4, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4))
702 
703 /*MC
704    PetscMalloc5 - Allocates 5 arrays of memory, all aligned to `PETSC_MEMALIGN`
705 
706    Synopsis:
707     #include <petscsys.h>
708    PetscErrorCode PetscMalloc5(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4,size_t m5,type **r5)
709 
710    Not Collective
711 
712    Input Parameters:
713 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
714 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
715 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
716 .  m4 - number of elements to allocate in 4th chunk  (may be zero)
717 -  m5 - number of elements to allocate in 5th chunk  (may be zero)
718 
719    Output Parameters:
720 +  r1 - memory allocated in first chunk
721 .  r2 - memory allocated in second chunk
722 .  r3 - memory allocated in third chunk
723 .  r4 - memory allocated in fourth chunk
724 -  r5 - memory allocated in fifth chunk
725 
726    Level: developer
727 
728 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscCalloc5()`, `PetscFree5()`
729 M*/
730 #define PetscMalloc5(m1, r1, m2, r2, m3, r3, m4, r4, m5, r5) \
731   PetscMallocA(5, PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4), ((size_t)((size_t)m5) * sizeof(**(r5))), (r5))
732 
733 /*MC
734    PetscCalloc5 - Allocates 5 cleared (zeroed) arrays of memory, all aligned to `PETSC_MEMALIGN`
735 
736    Synopsis:
737     #include <petscsys.h>
738    PetscErrorCode PetscCalloc5(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4,size_t m5,type **r5)
739 
740    Not Collective
741 
742    Input Parameters:
743 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
744 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
745 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
746 .  m4 - number of elements to allocate in 4th chunk  (may be zero)
747 -  m5 - number of elements to allocate in 5th chunk  (may be zero)
748 
749    Output Parameters:
750 +  r1 - memory allocated in first chunk
751 .  r2 - memory allocated in second chunk
752 .  r3 - memory allocated in third chunk
753 .  r4 - memory allocated in fourth chunk
754 -  r5 - memory allocated in fifth chunk
755 
756    Level: developer
757 
758 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc5()`, `PetscFree5()`
759 M*/
760 #define PetscCalloc5(m1, r1, m2, r2, m3, r3, m4, r4, m5, r5) \
761   PetscMallocA(5, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4), ((size_t)((size_t)m5) * sizeof(**(r5))), (r5))
762 
763 /*MC
764    PetscMalloc6 - Allocates 6 arrays of memory, all aligned to `PETSC_MEMALIGN`
765 
766    Synopsis:
767     #include <petscsys.h>
768    PetscErrorCode PetscMalloc6(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4,size_t m5,type **r5,size_t m6,type **r6)
769 
770    Not Collective
771 
772    Input Parameters:
773 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
774 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
775 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
776 .  m4 - number of elements to allocate in 4th chunk  (may be zero)
777 .  m5 - number of elements to allocate in 5th chunk  (may be zero)
778 -  m6 - number of elements to allocate in 6th chunk  (may be zero)
779 
780    Output Parameteasr:
781 +  r1 - memory allocated in first chunk
782 .  r2 - memory allocated in second chunk
783 .  r3 - memory allocated in third chunk
784 .  r4 - memory allocated in fourth chunk
785 .  r5 - memory allocated in fifth chunk
786 -  r6 - memory allocated in sixth chunk
787 
788    Level: developer
789 
790 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscCalloc6()`, `PetscFree3()`, `PetscFree4()`, `PetscFree5()`, `PetscFree6()`
791 M*/
792 #define PetscMalloc6(m1, r1, m2, r2, m3, r3, m4, r4, m5, r5, m6, r6) \
793   PetscMallocA(6, PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4), ((size_t)((size_t)m5) * sizeof(**(r5))), (r5), ((size_t)((size_t)m6) * sizeof(**(r6))), (r6))
794 
795 /*MC
796    PetscCalloc6 - Allocates 6 cleared (zeroed) arrays of memory, all aligned to `PETSC_MEMALIGN`
797 
798    Synopsis:
799     #include <petscsys.h>
800    PetscErrorCode PetscCalloc6(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4,size_t m5,type **r5,size_t m6,type **r6)
801 
802    Not Collective
803 
804    Input Parameters:
805 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
806 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
807 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
808 .  m4 - number of elements to allocate in 4th chunk  (may be zero)
809 .  m5 - number of elements to allocate in 5th chunk  (may be zero)
810 -  m6 - number of elements to allocate in 6th chunk  (may be zero)
811 
812    Output Parameters:
813 +  r1 - memory allocated in first chunk
814 .  r2 - memory allocated in second chunk
815 .  r3 - memory allocated in third chunk
816 .  r4 - memory allocated in fourth chunk
817 .  r5 - memory allocated in fifth chunk
818 -  r6 - memory allocated in sixth chunk
819 
820    Level: developer
821 
822 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscMalloc6()`, `PetscFree6()`
823 M*/
824 #define PetscCalloc6(m1, r1, m2, r2, m3, r3, m4, r4, m5, r5, m6, r6) \
825   PetscMallocA(6, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4), ((size_t)((size_t)m5) * sizeof(**(r5))), (r5), ((size_t)((size_t)m6) * sizeof(**(r6))), (r6))
826 
827 /*MC
828    PetscMalloc7 - Allocates 7 arrays of memory, all aligned to `PETSC_MEMALIGN`
829 
830    Synopsis:
831     #include <petscsys.h>
832    PetscErrorCode PetscMalloc7(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4,size_t m5,type **r5,size_t m6,type **r6,size_t m7,type **r7)
833 
834    Not Collective
835 
836    Input Parameters:
837 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
838 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
839 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
840 .  m4 - number of elements to allocate in 4th chunk  (may be zero)
841 .  m5 - number of elements to allocate in 5th chunk  (may be zero)
842 .  m6 - number of elements to allocate in 6th chunk  (may be zero)
843 -  m7 - number of elements to allocate in 7th chunk  (may be zero)
844 
845    Output Parameters:
846 +  r1 - memory allocated in first chunk
847 .  r2 - memory allocated in second chunk
848 .  r3 - memory allocated in third chunk
849 .  r4 - memory allocated in fourth chunk
850 .  r5 - memory allocated in fifth chunk
851 .  r6 - memory allocated in sixth chunk
852 -  r7 - memory allocated in seventh chunk
853 
854    Level: developer
855 
856 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscCalloc7()`, `PetscFree7()`
857 M*/
858 #define PetscMalloc7(m1, r1, m2, r2, m3, r3, m4, r4, m5, r5, m6, r6, m7, r7) \
859   PetscMallocA(7, PETSC_FALSE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4), ((size_t)((size_t)m5) * sizeof(**(r5))), (r5), ((size_t)((size_t)m6) * sizeof(**(r6))), (r6), ((size_t)((size_t)m7) * sizeof(**(r7))), (r7))
860 
861 /*MC
862    PetscCalloc7 - Allocates 7 cleared (zeroed) arrays of memory, all aligned to `PETSC_MEMALIGN`
863 
864    Synopsis:
865     #include <petscsys.h>
866    PetscErrorCode PetscCalloc7(size_t m1,type **r1,size_t m2,type **r2,size_t m3,type **r3,size_t m4,type **r4,size_t m5,type **r5,size_t m6,type **r6,size_t m7,type **r7)
867 
868    Not Collective
869 
870    Input Parameters:
871 +  m1 - number of elements to allocate in 1st chunk  (may be zero)
872 .  m2 - number of elements to allocate in 2nd chunk  (may be zero)
873 .  m3 - number of elements to allocate in 3rd chunk  (may be zero)
874 .  m4 - number of elements to allocate in 4th chunk  (may be zero)
875 .  m5 - number of elements to allocate in 5th chunk  (may be zero)
876 .  m6 - number of elements to allocate in 6th chunk  (may be zero)
877 -  m7 - number of elements to allocate in 7th chunk  (may be zero)
878 
879    Output Parameters:
880 +  r1 - memory allocated in first chunk
881 .  r2 - memory allocated in second chunk
882 .  r3 - memory allocated in third chunk
883 .  r4 - memory allocated in fourth chunk
884 .  r5 - memory allocated in fifth chunk
885 .  r6 - memory allocated in sixth chunk
886 -  r7 - memory allocated in seventh chunk
887 
888    Level: developer
889 
890 .seealso: `PetscFree()`, `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscMalloc7()`, `PetscFree7()`
891 M*/
892 #define PetscCalloc7(m1, r1, m2, r2, m3, r3, m4, r4, m5, r5, m6, r6, m7, r7) \
893   PetscMallocA(7, PETSC_TRUE, __LINE__, PETSC_FUNCTION_NAME, __FILE__, ((size_t)((size_t)m1) * sizeof(**(r1))), (r1), ((size_t)((size_t)m2) * sizeof(**(r2))), (r2), ((size_t)((size_t)m3) * sizeof(**(r3))), (r3), ((size_t)((size_t)m4) * sizeof(**(r4))), (r4), ((size_t)((size_t)m5) * sizeof(**(r5))), (r5), ((size_t)((size_t)m6) * sizeof(**(r6))), (r6), ((size_t)((size_t)m7) * sizeof(**(r7))), (r7))
894 
895 /*MC
896    PetscNew - Allocates memory of a particular type, zeros the memory! Aligned to `PETSC_MEMALIGN`
897 
898    Synopsis:
899     #include <petscsys.h>
900    PetscErrorCode PetscNew(type **result)
901 
902    Not Collective
903 
904    Output Parameter:
905 .  result - memory allocated, sized to match pointer type
906 
907    Level: beginner
908 
909 .seealso: `PetscFree()`, `PetscMalloc()`, `PetscCalloc1()`, `PetscMalloc1()`
910 M*/
911 #define PetscNew(b) PetscCalloc1(1, (b))
912 
913 #define PetscNewLog(o, b) PETSC_DEPRECATED_MACRO(3, 18, 0, "PetscNew()", ) PetscNew(b)
914 
915 /*MC
916    PetscFree - Frees memory
917 
918    Synopsis:
919     #include <petscsys.h>
920    PetscErrorCode PetscFree(void *memory)
921 
922    Not Collective
923 
924    Input Parameter:
925 .   memory - memory to free (the pointer is ALWAYS set to `NULL` upon success)
926 
927    Level: beginner
928 
929    Notes:
930    Do not free memory obtained with `PetscMalloc2()`, `PetscCalloc2()` etc, they must be freed with `PetscFree2()` etc.
931 
932    It is safe to call `PetscFree()` on a `NULL` pointer.
933 
934 .seealso: `PetscNew()`, `PetscMalloc()`, `PetscMalloc1()`, `PetscCalloc1()`
935 M*/
936 #define PetscFree(a) ((PetscErrorCode)((*PetscTrFree)((void *)(a), __LINE__, PETSC_FUNCTION_NAME, __FILE__) || ((a) = PETSC_NULLPTR, PETSC_SUCCESS)))
937 
938 /*MC
939    PetscFree2 - Frees 2 chunks of memory obtained with `PetscMalloc2()`
940 
941    Synopsis:
942     #include <petscsys.h>
943    PetscErrorCode PetscFree2(void *memory1,void *memory2)
944 
945    Not Collective
946 
947    Input Parameters:
948 +   memory1 - memory to free
949 -   memory2 - 2nd memory to free
950 
951    Level: developer
952 
953    Notes:
954     Memory must have been obtained with `PetscMalloc2()`
955 
956     The arguments need to be in the same order as they were in the call to `PetscMalloc2()`
957 
958 .seealso: `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscFree()`
959 M*/
960 #define PetscFree2(m1, m2) PetscFreeA(2, __LINE__, PETSC_FUNCTION_NAME, __FILE__, &(m1), &(m2))
961 
962 /*MC
963    PetscFree3 - Frees 3 chunks of memory obtained with `PetscMalloc3()`
964 
965    Synopsis:
966     #include <petscsys.h>
967    PetscErrorCode PetscFree3(void *memory1,void *memory2,void *memory3)
968 
969    Not Collective
970 
971    Input Parameters:
972 +   memory1 - memory to free
973 .   memory2 - 2nd memory to free
974 -   memory3 - 3rd memory to free
975 
976    Level: developer
977 
978    Notes:
979     Memory must have been obtained with `PetscMalloc3()`
980 
981     The arguments need to be in the same order as they were in the call to `PetscMalloc3()`
982 
983 .seealso: `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscFree()`, `PetscMalloc3()`
984 M*/
985 #define PetscFree3(m1, m2, m3) PetscFreeA(3, __LINE__, PETSC_FUNCTION_NAME, __FILE__, &(m1), &(m2), &(m3))
986 
987 /*MC
988    PetscFree4 - Frees 4 chunks of memory obtained with `PetscMalloc4()`
989 
990    Synopsis:
991     #include <petscsys.h>
992    PetscErrorCode PetscFree4(void *m1,void *m2,void *m3,void *m4)
993 
994    Not Collective
995 
996    Input Parameters:
997 +   m1 - memory to free
998 .   m2 - 2nd memory to free
999 .   m3 - 3rd memory to free
1000 -   m4 - 4th memory to free
1001 
1002    Level: developer
1003 
1004    Notes:
1005     Memory must have been obtained with `PetscMalloc4()`
1006 
1007     The arguments need to be in the same order as they were in the call to `PetscMalloc4()`
1008 
1009 .seealso: `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscFree()`, `PetscMalloc3()`, `PetscMalloc4()`
1010 M*/
1011 #define PetscFree4(m1, m2, m3, m4) PetscFreeA(4, __LINE__, PETSC_FUNCTION_NAME, __FILE__, &(m1), &(m2), &(m3), &(m4))
1012 
1013 /*MC
1014    PetscFree5 - Frees 5 chunks of memory obtained with `PetscMalloc5()`
1015 
1016    Synopsis:
1017     #include <petscsys.h>
1018    PetscErrorCode PetscFree5(void *m1,void *m2,void *m3,void *m4,void *m5)
1019 
1020    Not Collective
1021 
1022    Input Parameters:
1023 +   m1 - memory to free
1024 .   m2 - 2nd memory to free
1025 .   m3 - 3rd memory to free
1026 .   m4 - 4th memory to free
1027 -   m5 - 5th memory to free
1028 
1029    Level: developer
1030 
1031    Notes:
1032     Memory must have been obtained with `PetscMalloc5()`
1033 
1034     The arguments need to be in the same order as they were in the call to `PetscMalloc5()`
1035 
1036 .seealso: `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscFree()`, `PetscMalloc3()`, `PetscMalloc4()`, `PetscMalloc5()`
1037 M*/
1038 #define PetscFree5(m1, m2, m3, m4, m5) PetscFreeA(5, __LINE__, PETSC_FUNCTION_NAME, __FILE__, &(m1), &(m2), &(m3), &(m4), &(m5))
1039 
1040 /*MC
1041    PetscFree6 - Frees 6 chunks of memory obtained with `PetscMalloc6()`
1042 
1043    Synopsis:
1044     #include <petscsys.h>
1045    PetscErrorCode PetscFree6(void *m1,void *m2,void *m3,void *m4,void *m5,void *m6)
1046 
1047    Not Collective
1048 
1049    Input Parameters:
1050 +   m1 - memory to free
1051 .   m2 - 2nd memory to free
1052 .   m3 - 3rd memory to free
1053 .   m4 - 4th memory to free
1054 .   m5 - 5th memory to free
1055 -   m6 - 6th memory to free
1056 
1057    Level: developer
1058 
1059    Notes:
1060     Memory must have been obtained with `PetscMalloc6()`
1061 
1062     The arguments need to be in the same order as they were in the call to `PetscMalloc6()`
1063 
1064 .seealso: `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscFree()`, `PetscMalloc3()`, `PetscMalloc4()`, `PetscMalloc5()`, `PetscMalloc6()`
1065 M*/
1066 #define PetscFree6(m1, m2, m3, m4, m5, m6) PetscFreeA(6, __LINE__, PETSC_FUNCTION_NAME, __FILE__, &(m1), &(m2), &(m3), &(m4), &(m5), &(m6))
1067 
1068 /*MC
1069    PetscFree7 - Frees 7 chunks of memory obtained with `PetscMalloc7()`
1070 
1071    Synopsis:
1072     #include <petscsys.h>
1073    PetscErrorCode PetscFree7(void *m1,void *m2,void *m3,void *m4,void *m5,void *m6,void *m7)
1074 
1075    Not Collective
1076 
1077    Input Parameters:
1078 +   m1 - memory to free
1079 .   m2 - 2nd memory to free
1080 .   m3 - 3rd memory to free
1081 .   m4 - 4th memory to free
1082 .   m5 - 5th memory to free
1083 .   m6 - 6th memory to free
1084 -   m7 - 7th memory to free
1085 
1086    Level: developer
1087 
1088    Notes:
1089     Memory must have been obtained with `PetscMalloc7()`
1090 
1091     The arguments need to be in the same order as they were in the call to `PetscMalloc7()`
1092 
1093 .seealso: `PetscNew()`, `PetscMalloc()`, `PetscMalloc2()`, `PetscFree()`, `PetscMalloc3()`, `PetscMalloc4()`, `PetscMalloc5()`, `PetscMalloc6()`,
1094           `PetscMalloc7()`
1095 M*/
1096 #define PetscFree7(m1, m2, m3, m4, m5, m6, m7) PetscFreeA(7, __LINE__, PETSC_FUNCTION_NAME, __FILE__, &(m1), &(m2), &(m3), &(m4), &(m5), &(m6), &(m7))
1097 
1098 PETSC_EXTERN PetscErrorCode PetscMallocA(int, PetscBool, int, const char *, const char *, size_t, void *, ...);
1099 PETSC_EXTERN PetscErrorCode PetscFreeA(int, int, const char *, const char *, void *, ...);
1100 PETSC_EXTERN                PetscErrorCode (*PetscTrMalloc)(size_t, PetscBool, int, const char[], const char[], void **);
1101 PETSC_EXTERN                PetscErrorCode (*PetscTrFree)(void *, int, const char[], const char[]);
1102 PETSC_EXTERN                PetscErrorCode (*PetscTrRealloc)(size_t, int, const char[], const char[], void **);
1103 PETSC_EXTERN PetscErrorCode PetscMallocSetCoalesce(PetscBool);
1104 PETSC_EXTERN PetscErrorCode PetscMallocSet(PetscErrorCode (*)(size_t, PetscBool, int, const char[], const char[], void **), PetscErrorCode (*)(void *, int, const char[], const char[]), PetscErrorCode (*)(size_t, int, const char[], const char[], void **));
1105 PETSC_EXTERN PetscErrorCode PetscMallocClear(void);
1106 
1107 /*
1108   Unlike PetscMallocSet and PetscMallocClear which overwrite the existing settings, these two functions save the previous choice of allocator, and should be used in pair.
1109 */
1110 PETSC_EXTERN PetscErrorCode PetscMallocSetDRAM(void);
1111 PETSC_EXTERN PetscErrorCode PetscMallocResetDRAM(void);
1112 #if defined(PETSC_HAVE_CUDA)
1113 PETSC_EXTERN PetscErrorCode PetscMallocSetCUDAHost(void);
1114 PETSC_EXTERN PetscErrorCode PetscMallocResetCUDAHost(void);
1115 #endif
1116 #if defined(PETSC_HAVE_HIP)
1117 PETSC_EXTERN PetscErrorCode PetscMallocSetHIPHost(void);
1118 PETSC_EXTERN PetscErrorCode PetscMallocResetHIPHost(void);
1119 #endif
1120 
1121 #define MPIU_PETSCLOGDOUBLE  MPI_DOUBLE
1122 #define MPIU_2PETSCLOGDOUBLE MPI_2DOUBLE_PRECISION
1123 
1124 /*
1125    Routines for tracing memory corruption/bleeding with default PETSc memory allocation
1126 */
1127 PETSC_EXTERN PetscErrorCode PetscMallocDump(FILE *);
1128 PETSC_EXTERN PetscErrorCode PetscMallocView(FILE *);
1129 PETSC_EXTERN PetscErrorCode PetscMallocGetCurrentUsage(PetscLogDouble *);
1130 PETSC_EXTERN PetscErrorCode PetscMallocGetMaximumUsage(PetscLogDouble *);
1131 PETSC_EXTERN PetscErrorCode PetscMallocPushMaximumUsage(int);
1132 PETSC_EXTERN PetscErrorCode PetscMallocPopMaximumUsage(int, PetscLogDouble *);
1133 PETSC_EXTERN PetscErrorCode PetscMallocSetDebug(PetscBool, PetscBool);
1134 PETSC_EXTERN PetscErrorCode PetscMallocGetDebug(PetscBool *, PetscBool *, PetscBool *);
1135 PETSC_EXTERN PetscErrorCode PetscMallocValidate(int, const char[], const char[]);
1136 PETSC_EXTERN PetscErrorCode PetscMallocViewSet(PetscLogDouble);
1137 PETSC_EXTERN PetscErrorCode PetscMallocViewGet(PetscBool *);
1138 PETSC_EXTERN PetscErrorCode PetscMallocLogRequestedSizeSet(PetscBool);
1139 PETSC_EXTERN PetscErrorCode PetscMallocLogRequestedSizeGet(PetscBool *);
1140 
1141 PETSC_EXTERN PetscErrorCode PetscDataTypeToMPIDataType(PetscDataType, MPI_Datatype *);
1142 PETSC_EXTERN PetscErrorCode PetscMPIDataTypeToPetscDataType(MPI_Datatype, PetscDataType *);
1143 PETSC_EXTERN PetscErrorCode PetscDataTypeGetSize(PetscDataType, size_t *);
1144 PETSC_EXTERN PetscErrorCode PetscDataTypeFromString(const char *, PetscDataType *, PetscBool *);
1145 
1146 /*
1147    These are MPI operations for MPI_Allreduce() etc
1148 */
1149 PETSC_EXTERN MPI_Op MPIU_MAXSUM_OP;
1150 #if defined(PETSC_USE_REAL___FLOAT128) || defined(PETSC_USE_REAL___FP16)
1151 PETSC_EXTERN MPI_Op MPIU_SUM;
1152 PETSC_EXTERN MPI_Op MPIU_MAX;
1153 PETSC_EXTERN MPI_Op MPIU_MIN;
1154 #else
1155   #define MPIU_SUM MPI_SUM
1156   #define MPIU_MAX MPI_MAX
1157   #define MPIU_MIN MPI_MIN
1158 #endif
1159 PETSC_EXTERN MPI_Op         Petsc_Garbage_SetIntersectOp;
1160 PETSC_EXTERN PetscErrorCode PetscMaxSum(MPI_Comm, const PetscInt[], PetscInt *, PetscInt *);
1161 
1162 #if (defined(PETSC_HAVE_REAL___FLOAT128) && !defined(PETSC_SKIP_REAL___FLOAT128)) || (defined(PETSC_HAVE_REAL___FP16) && !defined(PETSC_SKIP_REAL___FP16))
1163 /*MC
1164    MPIU_SUM___FP16___FLOAT128 - MPI_Op that acts as a replacement for `MPI_SUM` with
1165    custom `MPI_Datatype` `MPIU___FLOAT128`, `MPIU___COMPLEX128`, and `MPIU___FP16`.
1166 
1167    Level: advanced
1168 
1169    Developer Note:
1170    This should be unified with `MPIU_SUM`
1171 
1172 .seealso: `MPIU_REAL`, `MPIU_SCALAR`, `MPIU_COMPLEX`
1173 M*/
1174 PETSC_EXTERN MPI_Op MPIU_SUM___FP16___FLOAT128;
1175 #endif
1176 PETSC_EXTERN PetscErrorCode PetscMaxSum(MPI_Comm, const PetscInt[], PetscInt *, PetscInt *);
1177 
1178 PETSC_EXTERN PetscErrorCode MPIULong_Send(void *, PetscInt, MPI_Datatype, PetscMPIInt, PetscMPIInt, MPI_Comm) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(1, 3);
1179 PETSC_EXTERN PetscErrorCode MPIULong_Recv(void *, PetscInt, MPI_Datatype, PetscMPIInt, PetscMPIInt, MPI_Comm) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(1, 3);
1180 
1181 /*
1182     Defines PETSc error handling.
1183 */
1184 #include <petscerror.h>
1185 
1186 PETSC_EXTERN PetscBool   PetscCIEnabled;                    /* code is running in the PETSc test harness CI */
1187 PETSC_EXTERN PetscBool   PetscCIEnabledPortableErrorOutput; /* error output is stripped to ensure portability of error messages across systems */
1188 PETSC_EXTERN const char *PetscCIFilename(const char *);
1189 PETSC_EXTERN int         PetscCILinenumber(int);
1190 
1191 #define PETSC_SMALLEST_CLASSID ((PetscClassId)1211211)
1192 PETSC_EXTERN PetscClassId   PETSC_LARGEST_CLASSID;
1193 PETSC_EXTERN PetscClassId   PETSC_OBJECT_CLASSID;
1194 PETSC_EXTERN PetscErrorCode PetscClassIdRegister(const char[], PetscClassId *);
1195 PETSC_EXTERN PetscErrorCode PetscObjectGetId(PetscObject, PetscObjectId *);
1196 PETSC_EXTERN PetscErrorCode PetscObjectCompareId(PetscObject, PetscObjectId, PetscBool *);
1197 
1198 /*
1199    Routines that get memory usage information from the OS
1200 */
1201 PETSC_EXTERN PetscErrorCode PetscMemoryGetCurrentUsage(PetscLogDouble *);
1202 PETSC_EXTERN PetscErrorCode PetscMemoryGetMaximumUsage(PetscLogDouble *);
1203 PETSC_EXTERN PetscErrorCode PetscMemorySetGetMaximumUsage(void);
1204 PETSC_EXTERN PetscErrorCode PetscMemoryTrace(const char[]);
1205 
1206 PETSC_EXTERN PetscErrorCode PetscSleep(PetscReal);
1207 
1208 /*
1209    Initialization of PETSc
1210 */
1211 PETSC_EXTERN PetscErrorCode PetscInitialize(int *, char ***, const char[], const char[]);
1212 PETSC_EXTERN PetscErrorCode PetscInitializeNoPointers(int, char **, const char[], const char[]);
1213 PETSC_EXTERN PetscErrorCode PetscInitializeNoArguments(void);
1214 PETSC_EXTERN PetscErrorCode PetscInitialized(PetscBool *);
1215 PETSC_EXTERN PetscErrorCode PetscFinalized(PetscBool *);
1216 PETSC_EXTERN PetscErrorCode PetscFinalize(void);
1217 PETSC_EXTERN PetscErrorCode PetscInitializeFortran(void);
1218 PETSC_EXTERN PetscErrorCode PetscGetArgs(int *, char ***);
1219 PETSC_EXTERN PetscErrorCode PetscGetArguments(char ***);
1220 PETSC_EXTERN PetscErrorCode PetscFreeArguments(char **);
1221 
1222 PETSC_EXTERN PetscErrorCode PetscEnd(void);
1223 PETSC_EXTERN PetscErrorCode PetscSysInitializePackage(void);
1224 PETSC_EXTERN PetscErrorCode PetscSysFinalizePackage(void);
1225 
1226 PETSC_EXTERN PetscErrorCode PetscPythonInitialize(const char[], const char[]);
1227 PETSC_EXTERN PetscErrorCode PetscPythonFinalize(void);
1228 PETSC_EXTERN PetscErrorCode PetscPythonPrintError(void);
1229 PETSC_EXTERN PetscErrorCode PetscPythonMonitorSet(PetscObject, const char[]);
1230 
1231 PETSC_EXTERN PetscErrorCode PetscMonitorCompare(PetscErrorCode (*)(void), void *, PetscErrorCode (*)(void **), PetscErrorCode (*)(void), void *, PetscErrorCode (*)(void **), PetscBool *);
1232 
1233 /*
1234      These are so that in extern C code we can caste function pointers to non-extern C
1235    function pointers. Since the regular C++ code expects its function pointers to be C++
1236 */
1237 
1238 /*S
1239   PetscVoidFn - A prototype of a void (fn)(void) function
1240 
1241   Level: developer
1242 
1243   Notes:
1244   The deprecated `PetscVoidFunction` works as a replacement for `PetscVoidFn` *.
1245 
1246   The deprecated `PetscVoidStarFunction` works as a replacement for `PetscVoidFn` **.
1247 
1248 .seealso: `PetscObject`, `PetscObjectDestroy()`
1249 S*/
1250 PETSC_EXTERN_TYPEDEF typedef void(PetscVoidFn)(void);
1251 
1252 PETSC_EXTERN_TYPEDEF typedef PetscVoidFn  *PetscVoidFunction;
1253 PETSC_EXTERN_TYPEDEF typedef PetscVoidFn **PetscVoidStarFunction;
1254 
1255 /*S
1256   PetscErrorCodeFn - A prototype of a PetscErrorCode (fn)(void) function
1257 
1258   Level: developer
1259 
1260   Notes:
1261   The deprecated `PetscErrorCodeFunction` works as a replacement for `PetscErrorCodeFn` *.
1262 
1263 .seealso: `PetscObject`, `PetscObjectDestroy()`
1264 S*/
1265 PETSC_EXTERN_TYPEDEF typedef PetscErrorCode(PetscErrorCodeFn)(void);
1266 
1267 PETSC_EXTERN_TYPEDEF typedef PetscErrorCodeFn *PetscErrorCodeFunction;
1268 
1269 /*
1270     Functions that can act on any PETSc object.
1271 */
1272 PETSC_EXTERN PetscErrorCode PetscObjectDestroy(PetscObject *);
1273 PETSC_EXTERN PetscErrorCode PetscObjectGetComm(PetscObject, MPI_Comm *);
1274 PETSC_EXTERN PetscErrorCode PetscObjectGetClassId(PetscObject, PetscClassId *);
1275 PETSC_EXTERN PetscErrorCode PetscObjectGetClassName(PetscObject, const char *[]);
1276 PETSC_EXTERN PetscErrorCode PetscObjectGetType(PetscObject, const char *[]);
1277 PETSC_EXTERN PetscErrorCode PetscObjectSetName(PetscObject, const char[]);
1278 PETSC_EXTERN PetscErrorCode PetscObjectGetName(PetscObject, const char *[]);
1279 PETSC_EXTERN PetscErrorCode PetscObjectSetTabLevel(PetscObject, PetscInt);
1280 PETSC_EXTERN PetscErrorCode PetscObjectGetTabLevel(PetscObject, PetscInt *);
1281 PETSC_EXTERN PetscErrorCode PetscObjectIncrementTabLevel(PetscObject, PetscObject, PetscInt);
1282 PETSC_EXTERN PetscErrorCode PetscObjectReference(PetscObject);
1283 PETSC_EXTERN PetscErrorCode PetscObjectGetReference(PetscObject, PetscInt *);
1284 PETSC_EXTERN PetscErrorCode PetscObjectDereference(PetscObject);
1285 PETSC_EXTERN PetscErrorCode PetscObjectGetNewTag(PetscObject, PetscMPIInt *);
1286 PETSC_EXTERN PetscErrorCode PetscObjectCompose(PetscObject, const char[], PetscObject);
1287 PETSC_EXTERN PetscErrorCode PetscObjectRemoveReference(PetscObject, const char[]);
1288 PETSC_EXTERN PetscErrorCode PetscObjectQuery(PetscObject, const char[], PetscObject *);
1289 PETSC_EXTERN PetscErrorCode PetscObjectComposeFunction_Private(PetscObject, const char[], void (*)(void));
1290 #define PetscObjectComposeFunction(a, b, ...) PetscObjectComposeFunction_Private((a), (b), (PetscVoidFn *)(__VA_ARGS__))
1291 PETSC_EXTERN PetscErrorCode PetscObjectSetFromOptions(PetscObject);
1292 PETSC_EXTERN PetscErrorCode PetscObjectSetUp(PetscObject);
1293 PETSC_EXTERN PetscErrorCode PetscObjectSetPrintedOptions(PetscObject);
1294 PETSC_EXTERN PetscErrorCode PetscObjectInheritPrintedOptions(PetscObject, PetscObject);
1295 PETSC_EXTERN PetscErrorCode PetscCommGetNewTag(MPI_Comm, PetscMPIInt *);
1296 
1297 /*MC
1298    PetscObjectParameterSetDefault - sets a parameter default value in a `PetscObject` to a new default value.
1299    If the current value matches the old default value, then the current value is also set to the new value.
1300 
1301    No Fortran Support
1302 
1303    Synopsis:
1304    #include <petscsys.h>
1305    PetscBool PetscObjectParameterSetDefault(PetscObject obj, char* NAME, PetscReal value);
1306 
1307    Input Parameters:
1308 +  obj - the `PetscObject`
1309 .  NAME - the name of the parameter, unquoted
1310 -  value - the new value
1311 
1312    Level: developer
1313 
1314    Notes:
1315    The defaults for an object are the values set when the object's type is set.
1316 
1317    This should only be used in object constructors, such as, `SNESCreate_NGS()`.
1318 
1319    This only works for parameters that are declared in the struct with `PetscObjectParameterDeclare()`
1320 
1321 .seealso: `PetscObjectParameterDeclare()`, `PetscInitialize()`, `PetscFinalize()`, `PetscObject`, `SNESParametersInitialize()`
1322 M*/
1323 #define PetscObjectParameterSetDefault(obj, NAME, value) \
1324   do { \
1325     if (obj->NAME == obj->default_##NAME) obj->NAME = value; \
1326     obj->default_##NAME = value; \
1327   } while (0)
1328 
1329 /*MC
1330    PetscObjectParameterDeclare - declares a parameter in a `PetscObject` and a location to store its default
1331 
1332    No Fortran Support
1333 
1334    Synopsis:
1335    #include <petscsys.h>
1336    PetscBool PetscObjectParameterDeclare(type, char* NAME)
1337 
1338    Input Parameters:
1339 +  type - the type of the parameter, for example `PetscInt`
1340 -  NAME - the name of the parameter, unquoted
1341 
1342    Level: developer.
1343 
1344 .seealso: `PetscObjectParameterSetDefault()`, `PetscInitialize()`, `PetscFinalize()`, `PetscObject`, `SNESParametersInitialize()`
1345 M*/
1346 #define PetscObjectParameterDeclare(type, NAME) type NAME, default_##NAME
1347 
1348 #include <petscviewertypes.h>
1349 #include <petscoptions.h>
1350 
1351 PETSC_EXTERN PetscErrorCode PetscMallocTraceSet(PetscViewer, PetscBool, PetscLogDouble);
1352 PETSC_EXTERN PetscErrorCode PetscMallocTraceGet(PetscBool *);
1353 
1354 PETSC_EXTERN PetscErrorCode PetscObjectsListGetGlobalNumbering(MPI_Comm, PetscInt, PetscObject *, PetscInt *, PetscInt *);
1355 
1356 PETSC_EXTERN PetscErrorCode PetscMemoryView(PetscViewer, const char[]);
1357 PETSC_EXTERN PetscErrorCode PetscObjectPrintClassNamePrefixType(PetscObject, PetscViewer);
1358 PETSC_EXTERN PetscErrorCode PetscObjectView(PetscObject, PetscViewer);
1359 #define PetscObjectQueryFunction(obj, name, fptr) PetscObjectQueryFunction_Private((obj), (name), (PetscVoidFn **)(fptr))
1360 PETSC_EXTERN PetscErrorCode PetscObjectQueryFunction_Private(PetscObject, const char[], void (**)(void));
1361 PETSC_EXTERN PetscErrorCode PetscObjectSetOptionsPrefix(PetscObject, const char[]);
1362 PETSC_EXTERN PetscErrorCode PetscObjectAppendOptionsPrefix(PetscObject, const char[]);
1363 PETSC_EXTERN PetscErrorCode PetscObjectPrependOptionsPrefix(PetscObject, const char[]);
1364 PETSC_EXTERN PetscErrorCode PetscObjectGetOptionsPrefix(PetscObject, const char *[]);
1365 PETSC_EXTERN PetscErrorCode PetscObjectChangeTypeName(PetscObject, const char[]);
1366 PETSC_EXTERN PetscErrorCode PetscObjectRegisterDestroy(PetscObject);
1367 PETSC_EXTERN PetscErrorCode PetscObjectRegisterDestroyAll(void);
1368 PETSC_EXTERN PetscErrorCode PetscObjectViewFromOptions(PetscObject, PetscObject, const char[]);
1369 PETSC_EXTERN PetscErrorCode PetscObjectName(PetscObject);
1370 PETSC_EXTERN PetscErrorCode PetscObjectTypeCompare(PetscObject, const char[], PetscBool *);
1371 PETSC_EXTERN PetscErrorCode PetscObjectObjectTypeCompare(PetscObject, PetscObject, PetscBool *);
1372 PETSC_EXTERN PetscErrorCode PetscObjectBaseTypeCompare(PetscObject, const char[], PetscBool *);
1373 PETSC_EXTERN PetscErrorCode PetscObjectTypeCompareAny(PetscObject, PetscBool *, const char[], ...);
1374 PETSC_EXTERN PetscErrorCode PetscObjectBaseTypeCompareAny(PetscObject, PetscBool *, const char[], ...);
1375 PETSC_EXTERN PetscErrorCode PetscRegisterFinalize(PetscErrorCode (*)(void));
1376 PETSC_EXTERN PetscErrorCode PetscRegisterFinalizeAll(void);
1377 
1378 #if defined(PETSC_HAVE_SAWS)
1379 PETSC_EXTERN PetscErrorCode PetscSAWsBlock(void);
1380 PETSC_EXTERN PetscErrorCode PetscObjectSAWsViewOff(PetscObject);
1381 PETSC_EXTERN PetscErrorCode PetscObjectSAWsSetBlock(PetscObject, PetscBool);
1382 PETSC_EXTERN PetscErrorCode PetscObjectSAWsBlock(PetscObject);
1383 PETSC_EXTERN PetscErrorCode PetscObjectSAWsGrantAccess(PetscObject);
1384 PETSC_EXTERN PetscErrorCode PetscObjectSAWsTakeAccess(PetscObject);
1385 PETSC_EXTERN void           PetscStackSAWsGrantAccess(void);
1386 PETSC_EXTERN void           PetscStackSAWsTakeAccess(void);
1387 PETSC_EXTERN PetscErrorCode PetscStackViewSAWs(void);
1388 PETSC_EXTERN PetscErrorCode PetscStackSAWsViewOff(void);
1389 
1390 #else
1391   #define PetscSAWsBlock()                  PETSC_SUCCESS
1392   #define PetscObjectSAWsViewOff(obj)       PETSC_SUCCESS
1393   #define PetscObjectSAWsSetBlock(obj, flg) PETSC_SUCCESS
1394   #define PetscObjectSAWsBlock(obj)         PETSC_SUCCESS
1395   #define PetscObjectSAWsGrantAccess(obj)   PETSC_SUCCESS
1396   #define PetscObjectSAWsTakeAccess(obj)    PETSC_SUCCESS
1397   #define PetscStackViewSAWs()              PETSC_SUCCESS
1398   #define PetscStackSAWsViewOff()           PETSC_SUCCESS
1399   #define PetscStackSAWsTakeAccess()
1400   #define PetscStackSAWsGrantAccess()
1401 
1402 #endif
1403 
1404 PETSC_EXTERN PetscErrorCode PetscDLOpen(const char[], PetscDLMode, PetscDLHandle *);
1405 PETSC_EXTERN PetscErrorCode PetscDLClose(PetscDLHandle *);
1406 PETSC_EXTERN PetscErrorCode PetscDLSym(PetscDLHandle, const char[], void **);
1407 PETSC_EXTERN PetscErrorCode PetscDLAddr(void (*)(void), char **);
1408 #ifdef PETSC_HAVE_CXX
1409 PETSC_EXTERN PetscErrorCode PetscDemangleSymbol(const char *, char **);
1410 #endif
1411 
1412 PETSC_EXTERN PetscErrorCode PetscMallocGetStack(void *, PetscStack **);
1413 
1414 PETSC_EXTERN PetscErrorCode PetscObjectsDump(FILE *, PetscBool);
1415 PETSC_EXTERN PetscErrorCode PetscObjectsView(PetscViewer);
1416 PETSC_EXTERN PetscErrorCode PetscObjectsGetObject(const char *, PetscObject *, const char **);
1417 PETSC_EXTERN PetscErrorCode PetscObjectListDestroy(PetscObjectList *);
1418 PETSC_EXTERN PetscErrorCode PetscObjectListFind(PetscObjectList, const char[], PetscObject *);
1419 PETSC_EXTERN PetscErrorCode PetscObjectListReverseFind(PetscObjectList, PetscObject, char **, PetscBool *);
1420 PETSC_EXTERN PetscErrorCode PetscObjectListAdd(PetscObjectList *, const char[], PetscObject);
1421 PETSC_EXTERN PetscErrorCode PetscObjectListRemoveReference(PetscObjectList *, const char[]);
1422 PETSC_EXTERN PetscErrorCode PetscObjectListDuplicate(PetscObjectList, PetscObjectList *);
1423 
1424 /*
1425     Dynamic library lists. Lists of names of routines in objects or in dynamic
1426   link libraries that will be loaded as needed.
1427 */
1428 
1429 #define PetscFunctionListAdd(list, name, fptr) PetscFunctionListAdd_Private((list), (name), (PetscVoidFn *)(fptr))
1430 PETSC_EXTERN PetscErrorCode PetscFunctionListAdd_Private(PetscFunctionList *, const char[], PetscVoidFn *);
1431 PETSC_EXTERN PetscErrorCode PetscFunctionListDestroy(PetscFunctionList *);
1432 PETSC_EXTERN PetscErrorCode PetscFunctionListClear(PetscFunctionList);
1433 #define PetscFunctionListFind(list, name, fptr) PetscFunctionListFind_Private((list), (name), (PetscVoidFn **)(fptr))
1434 PETSC_EXTERN PetscErrorCode PetscFunctionListFind_Private(PetscFunctionList, const char[], PetscVoidFn **);
1435 PETSC_EXTERN PetscErrorCode PetscFunctionListPrintTypes(MPI_Comm, FILE *, const char[], const char[], const char[], const char[], PetscFunctionList, const char[], const char[]);
1436 PETSC_EXTERN PetscErrorCode PetscFunctionListDuplicate(PetscFunctionList, PetscFunctionList *);
1437 PETSC_EXTERN PetscErrorCode PetscFunctionListView(PetscFunctionList, PetscViewer);
1438 PETSC_EXTERN PetscErrorCode PetscFunctionListGet(PetscFunctionList, const char ***, int *);
1439 PETSC_EXTERN PetscErrorCode PetscFunctionListPrintNonEmpty(PetscFunctionList);
1440 PETSC_EXTERN PetscErrorCode PetscFunctionListPrintAll(void);
1441 
1442 PETSC_EXTERN PetscDLLibrary PetscDLLibrariesLoaded;
1443 PETSC_EXTERN PetscErrorCode PetscDLLibraryAppend(MPI_Comm, PetscDLLibrary *, const char[]);
1444 PETSC_EXTERN PetscErrorCode PetscDLLibraryPrepend(MPI_Comm, PetscDLLibrary *, const char[]);
1445 PETSC_EXTERN PetscErrorCode PetscDLLibrarySym(MPI_Comm, PetscDLLibrary *, const char[], const char[], void **);
1446 PETSC_EXTERN PetscErrorCode PetscDLLibraryPrintPath(PetscDLLibrary);
1447 PETSC_EXTERN PetscErrorCode PetscDLLibraryRetrieve(MPI_Comm, const char[], char *, size_t, PetscBool *);
1448 PETSC_EXTERN PetscErrorCode PetscDLLibraryOpen(MPI_Comm, const char[], PetscDLLibrary *);
1449 PETSC_EXTERN PetscErrorCode PetscDLLibraryClose(PetscDLLibrary);
1450 
1451 /*
1452      Useful utility routines
1453 */
1454 PETSC_EXTERN PetscErrorCode PetscSplitOwnership(MPI_Comm, PetscInt *, PetscInt *);
1455 PETSC_EXTERN PetscErrorCode PetscSplitOwnershipBlock(MPI_Comm, PetscInt, PetscInt *, PetscInt *);
1456 PETSC_EXTERN PetscErrorCode PetscSplitOwnershipEqual(MPI_Comm, PetscInt *, PetscInt *);
1457 PETSC_EXTERN PetscErrorCode PetscSequentialPhaseBegin(MPI_Comm, PetscMPIInt);
1458 PETSC_EXTERN PetscErrorCode PetscSequentialPhaseEnd(MPI_Comm, PetscMPIInt);
1459 PETSC_EXTERN PetscErrorCode PetscBarrier(PetscObject);
1460 PETSC_EXTERN PetscErrorCode PetscMPIDump(FILE *);
1461 PETSC_EXTERN PetscErrorCode PetscGlobalMinMaxInt(MPI_Comm, const PetscInt[2], PetscInt[2]);
1462 PETSC_EXTERN PetscErrorCode PetscGlobalMinMaxReal(MPI_Comm, const PetscReal[2], PetscReal[2]);
1463 
1464 /*MC
1465     PetscNot - negates a logical type value and returns result as a `PetscBool`
1466 
1467     Level: beginner
1468 
1469     Note:
1470     This is useful in cases like
1471 .vb
1472      int        *a;
1473      PetscBool  flag = PetscNot(a)
1474 .ve
1475      where !a would not return a `PetscBool` because we cannot provide a cast from int to `PetscBool` in C.
1476 
1477 .seealso: `PetscBool`, `PETSC_TRUE`, `PETSC_FALSE`
1478 M*/
1479 #define PetscNot(a) ((a) ? PETSC_FALSE : PETSC_TRUE)
1480 
1481 /*MC
1482    PetscHelpPrintf - Prints help messages.
1483 
1484    Synopsis:
1485     #include <petscsys.h>
1486      PetscErrorCode (*PetscHelpPrintf)(MPI_Comm comm, const char format[],args);
1487 
1488    Not Collective, only applies on MPI rank 0; No Fortran Support
1489 
1490    Input Parameters:
1491 +  comm - the MPI communicator over which the help message is printed
1492 .  format - the usual printf() format string
1493 -  args - arguments to be printed
1494 
1495    Level: developer
1496 
1497    Notes:
1498    You can change how help messages are printed by replacing the function pointer with a function that does not simply write to stdout.
1499 
1500    To use, write your own function, for example,
1501 .vb
1502    PetscErrorCode mypetschelpprintf(MPI_Comm comm,const char format[],....)
1503    {
1504      PetscFunctionReturn(PETSC_SUCCESS);
1505    }
1506 .ve
1507 then do the assignment
1508 .vb
1509   PetscHelpPrintf = mypetschelpprintf;
1510 .ve
1511 
1512   You can do the assignment before `PetscInitialize()`.
1513 
1514   The default routine used is called `PetscHelpPrintfDefault()`.
1515 
1516 .seealso: `PetscFPrintf()`, `PetscSynchronizedPrintf()`, `PetscErrorPrintf()`, `PetscHelpPrintfDefault()`
1517 M*/
1518 PETSC_EXTERN PetscErrorCode (*PetscHelpPrintf)(MPI_Comm, const char[], ...) PETSC_ATTRIBUTE_FORMAT(2, 3);
1519 
1520 /*
1521      Defines PETSc profiling.
1522 */
1523 #include <petsclog.h>
1524 
1525 /*
1526       Simple PETSc parallel IO for ASCII printing
1527 */
1528 PETSC_EXTERN PetscErrorCode PetscFixFilename(const char[], char[]);
1529 PETSC_EXTERN PetscErrorCode PetscFOpen(MPI_Comm, const char[], const char[], FILE **);
1530 PETSC_EXTERN PetscErrorCode PetscFClose(MPI_Comm, FILE *);
1531 PETSC_EXTERN PetscErrorCode PetscFPrintf(MPI_Comm, FILE *, const char[], ...) PETSC_ATTRIBUTE_FORMAT(3, 4);
1532 PETSC_EXTERN PetscErrorCode PetscFFlush(FILE *);
1533 PETSC_EXTERN PetscErrorCode PetscPrintf(MPI_Comm, const char[], ...) PETSC_ATTRIBUTE_FORMAT(2, 3);
1534 PETSC_EXTERN PetscErrorCode PetscSNPrintf(char *, size_t, const char[], ...) PETSC_ATTRIBUTE_FORMAT(3, 4);
1535 PETSC_EXTERN PetscErrorCode PetscSNPrintfCount(char *, size_t, const char[], size_t *, ...) PETSC_ATTRIBUTE_FORMAT(3, 5);
1536 PETSC_EXTERN PetscErrorCode PetscFormatRealArray(char[], size_t, const char *, PetscInt, const PetscReal[]);
1537 
1538 PETSC_EXTERN PetscErrorCode PetscErrorPrintfDefault(const char[], ...) PETSC_ATTRIBUTE_FORMAT(1, 2);
1539 PETSC_EXTERN PetscErrorCode PetscErrorPrintfNone(const char[], ...) PETSC_ATTRIBUTE_FORMAT(1, 2);
1540 PETSC_EXTERN PetscErrorCode PetscHelpPrintfDefault(MPI_Comm, const char[], ...) PETSC_ATTRIBUTE_FORMAT(2, 3);
1541 
1542 PETSC_EXTERN PetscErrorCode PetscFormatConvertGetSize(const char *, size_t *);
1543 PETSC_EXTERN PetscErrorCode PetscFormatConvert(const char *, char *);
1544 
1545 PETSC_EXTERN PetscErrorCode PetscPOpen(MPI_Comm, const char[], const char[], const char[], FILE **);
1546 PETSC_EXTERN PetscErrorCode PetscPClose(MPI_Comm, FILE *);
1547 PETSC_EXTERN PetscErrorCode PetscPOpenSetMachine(const char[]);
1548 
1549 PETSC_EXTERN PetscErrorCode PetscSynchronizedPrintf(MPI_Comm, const char[], ...) PETSC_ATTRIBUTE_FORMAT(2, 3);
1550 PETSC_EXTERN PetscErrorCode PetscSynchronizedFPrintf(MPI_Comm, FILE *, const char[], ...) PETSC_ATTRIBUTE_FORMAT(3, 4);
1551 PETSC_EXTERN PetscErrorCode PetscSynchronizedFlush(MPI_Comm, FILE *);
1552 PETSC_EXTERN PetscErrorCode PetscSynchronizedFGets(MPI_Comm, FILE *, size_t, char[]);
1553 PETSC_EXTERN PetscErrorCode PetscStartMatlab(MPI_Comm, const char[], const char[], FILE **);
1554 PETSC_EXTERN PetscErrorCode PetscGetPetscDir(const char *[]);
1555 
1556 PETSC_EXTERN PetscClassId   PETSC_CONTAINER_CLASSID;
1557 PETSC_EXTERN PetscErrorCode PetscContainerGetPointer(PetscContainer, void **);
1558 PETSC_EXTERN PetscErrorCode PetscContainerSetPointer(PetscContainer, void *);
1559 PETSC_EXTERN PetscErrorCode PetscContainerDestroy(PetscContainer *);
1560 PETSC_EXTERN PetscErrorCode PetscContainerCreate(MPI_Comm, PetscContainer *);
1561 PETSC_EXTERN PetscErrorCode PetscContainerSetUserDestroy(PetscContainer, PetscErrorCode (*)(void *));
1562 PETSC_EXTERN PetscErrorCode PetscContainerUserDestroyDefault(void *);
1563 PETSC_EXTERN PetscErrorCode PetscObjectContainerCompose(PetscObject, const char *name, void *, PetscErrorCode (*)(void *));
1564 PETSC_EXTERN PetscErrorCode PetscObjectContainerQuery(PetscObject, const char *, void **);
1565 
1566 /*
1567    For use in debuggers
1568 */
1569 PETSC_EXTERN PetscMPIInt    PetscGlobalRank;
1570 PETSC_EXTERN PetscMPIInt    PetscGlobalSize;
1571 PETSC_EXTERN PetscErrorCode PetscIntView(PetscInt, const PetscInt[], PetscViewer);
1572 PETSC_EXTERN PetscErrorCode PetscRealView(PetscInt, const PetscReal[], PetscViewer);
1573 PETSC_EXTERN PetscErrorCode PetscScalarView(PetscInt, const PetscScalar[], PetscViewer);
1574 
1575 /*
1576     Basic memory and string operations. These are usually simple wrappers
1577    around the basic Unix system calls, but a few of them have additional
1578    functionality and/or error checking.
1579 */
1580 #include <petscstring.h>
1581 
1582 #include <stddef.h>
1583 #include <stdlib.h>
1584 
1585 #if defined(PETSC_CLANG_STATIC_ANALYZER)
1586   #define PetscPrefetchBlock(a, b, c, d)
1587 #else
1588   /*MC
1589    PetscPrefetchBlock - Prefetches a block of memory
1590 
1591    Synopsis:
1592     #include <petscsys.h>
1593     void PetscPrefetchBlock(const anytype *a,size_t n,int rw,int t)
1594 
1595    Not Collective
1596 
1597    Input Parameters:
1598 +  a  - pointer to first element to fetch (any type but usually `PetscInt` or `PetscScalar`)
1599 .  n  - number of elements to fetch
1600 .  rw - 1 if the memory will be written to, otherwise 0 (ignored by many processors)
1601 -  t  - temporal locality (PETSC_PREFETCH_HINT_{NTA,T0,T1,T2}), see note
1602 
1603    Level: developer
1604 
1605    Notes:
1606    The last two arguments (`rw` and `t`) must be compile-time constants.
1607 
1608    Adopting Intel's x86/x86-64 conventions, there are four levels of temporal locality.  Not all architectures offer
1609    equivalent locality hints, but the following macros are always defined to their closest analogue.
1610 +  `PETSC_PREFETCH_HINT_NTA` - Non-temporal.  Prefetches directly to L1, evicts to memory (skips higher level cache unless it was already there when prefetched).
1611 .  `PETSC_PREFETCH_HINT_T0`  - Fetch to all levels of cache and evict to the closest level.  Use this when the memory will be reused regularly despite necessary eviction from L1.
1612 .  `PETSC_PREFETCH_HINT_T1`  - Fetch to level 2 and higher (not L1).
1613 -  `PETSC_PREFETCH_HINT_T2`  - Fetch to high-level cache only.  (On many systems, T0 and T1 are equivalent.)
1614 
1615    This function does nothing on architectures that do not support prefetch and never errors (even if passed an invalid
1616    address).
1617 
1618 M*/
1619   #define PetscPrefetchBlock(a, n, rw, t) \
1620     do { \
1621       const char *_p = (const char *)(a), *_end = (const char *)((a) + (n)); \
1622       for (; _p < _end; _p += PETSC_LEVEL1_DCACHE_LINESIZE) PETSC_Prefetch(_p, (rw), (t)); \
1623     } while (0)
1624 #endif
1625 /*
1626       Determine if some of the kernel computation routines use
1627    Fortran (rather than C) for the numerical calculations. On some machines
1628    and compilers (like complex numbers) the Fortran version of the routines
1629    is faster than the C/C++ versions. The flag --with-fortran-kernels
1630    should be used with ./configure to turn these on.
1631 */
1632 #if defined(PETSC_USE_FORTRAN_KERNELS)
1633 
1634   #if !defined(PETSC_USE_FORTRAN_KERNEL_MULTCRL)
1635     #define PETSC_USE_FORTRAN_KERNEL_MULTCRL
1636   #endif
1637 
1638   #if !defined(PETSC_USE_FORTRAN_KERNEL_MULTAIJ)
1639     #define PETSC_USE_FORTRAN_KERNEL_MULTAIJ
1640   #endif
1641 
1642   #if !defined(PETSC_USE_FORTRAN_KERNEL_MULTTRANSPOSEAIJ)
1643     #define PETSC_USE_FORTRAN_KERNEL_MULTTRANSPOSEAIJ
1644   #endif
1645 
1646   #if !defined(PETSC_USE_FORTRAN_KERNEL_MAXPY)
1647     #define PETSC_USE_FORTRAN_KERNEL_MAXPY
1648   #endif
1649 
1650   #if !defined(PETSC_USE_FORTRAN_KERNEL_SOLVEAIJ)
1651     #define PETSC_USE_FORTRAN_KERNEL_SOLVEAIJ
1652   #endif
1653 
1654   #if !defined(PETSC_USE_FORTRAN_KERNEL_SOLVEBAIJ)
1655     #define PETSC_USE_FORTRAN_KERNEL_SOLVEBAIJ
1656   #endif
1657 
1658   #if !defined(PETSC_USE_FORTRAN_KERNEL_MULTADDAIJ)
1659     #define PETSC_USE_FORTRAN_KERNEL_MULTADDAIJ
1660   #endif
1661 
1662   #if !defined(PETSC_USE_FORTRAN_KERNEL_MDOT)
1663     #define PETSC_USE_FORTRAN_KERNEL_MDOT
1664   #endif
1665 
1666   #if !defined(PETSC_USE_FORTRAN_KERNEL_XTIMESY)
1667     #define PETSC_USE_FORTRAN_KERNEL_XTIMESY
1668   #endif
1669 
1670   #if !defined(PETSC_USE_FORTRAN_KERNEL_AYPX)
1671     #define PETSC_USE_FORTRAN_KERNEL_AYPX
1672   #endif
1673 
1674   #if !defined(PETSC_USE_FORTRAN_KERNEL_WAXPY)
1675     #define PETSC_USE_FORTRAN_KERNEL_WAXPY
1676   #endif
1677 
1678 #endif
1679 
1680 /*
1681     Macros for indicating code that should be compiled with a C interface,
1682    rather than a C++ interface. Any routines that are dynamically loaded
1683    (such as the PCCreate_XXX() routines) must be wrapped so that the name
1684    mangler does not change the functions symbol name. This just hides the
1685    ugly extern "C" {} wrappers.
1686 */
1687 #if defined(__cplusplus)
1688   #define EXTERN_C_BEGIN extern "C" {
1689   #define EXTERN_C_END   }
1690 #else
1691   #define EXTERN_C_BEGIN
1692   #define EXTERN_C_END
1693 #endif
1694 
1695 /*MC
1696    MPI_Comm - the basic object used by MPI to determine which processes are involved in a
1697    communication
1698 
1699    Level: beginner
1700 
1701    Note:
1702    This manual page is a place-holder because MPICH does not have a manual page for `MPI_Comm`
1703 
1704 .seealso: `PETSC_COMM_WORLD`, `PETSC_COMM_SELF`
1705 M*/
1706 
1707 #if defined(PETSC_HAVE_MPIIO)
1708 PETSC_EXTERN PetscErrorCode MPIU_File_write_all(MPI_File, void *, PetscMPIInt, MPI_Datatype, MPI_Status *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(2, 4);
1709 PETSC_EXTERN PetscErrorCode MPIU_File_read_all(MPI_File, void *, PetscMPIInt, MPI_Datatype, MPI_Status *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(2, 4);
1710 PETSC_EXTERN PetscErrorCode MPIU_File_write_at(MPI_File, MPI_Offset, void *, PetscMPIInt, MPI_Datatype, MPI_Status *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 5);
1711 PETSC_EXTERN PetscErrorCode MPIU_File_read_at(MPI_File, MPI_Offset, void *, PetscMPIInt, MPI_Datatype, MPI_Status *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 5);
1712 PETSC_EXTERN PetscErrorCode MPIU_File_write_at_all(MPI_File, MPI_Offset, void *, PetscMPIInt, MPI_Datatype, MPI_Status *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 5);
1713 PETSC_EXTERN PetscErrorCode MPIU_File_read_at_all(MPI_File, MPI_Offset, void *, PetscMPIInt, MPI_Datatype, MPI_Status *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(3, 5);
1714 #endif
1715 
1716 /*@C
1717    PetscIntCast - casts a `PetscInt64` (which is 64 bits in size) to a `PetscInt` (which may be 32-bits in size), generates an
1718    error if the `PetscInt` is not large enough to hold the number.
1719 
1720    Not Collective; No Fortran Support
1721 
1722    Input Parameter:
1723 .  a - the `PetscInt64` value
1724 
1725    Output Parameter:
1726 .  b - the resulting `PetscInt` value
1727 
1728    Level: advanced
1729 
1730    Note:
1731    If integers needed for the applications are too large to fit in 32-bit ints you can ./configure using `--with-64-bit-indices` to make `PetscInt` use 64-bit integers
1732 
1733 .seealso: `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscMPIIntCast()`, `PetscBLASIntCast()`, `PetscIntMultError()`, `PetscIntSumError()`
1734 @*/
1735 static inline PetscErrorCode PetscIntCast(PetscInt64 a, PetscInt *b)
1736 {
1737   PetscFunctionBegin;
1738   // if using 64-bit indices already then this comparison is tautologically true
1739   PetscCheck(a < PETSC_MAX_INT, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "%" PetscInt64_FMT " is too big for PetscInt, you may need to ./configure using --with-64-bit-indices", a);
1740   if (b) *b = (PetscInt)a;
1741   PetscFunctionReturn(PETSC_SUCCESS);
1742 }
1743 
1744 /*@C
1745    PetscCountCast - casts a `PetscCount` to a `PetscInt` (which may be 32-bits in size), generates an
1746    error if the `PetscInt` is not large enough to hold the number.
1747 
1748    Not Collective; No Fortran Support
1749 
1750    Input Parameter:
1751 .  a - the `PetscCount` value
1752 
1753    Output Parameter:
1754 .  b - the resulting `PetscInt` value
1755 
1756    Level: advanced
1757 
1758    Note:
1759    If integers needed for the applications are too large to fit in 32-bit integers you can ./configure using `--with-64-bit-indices` to make `PetscInt` use 64-bit integers
1760 
1761 .seealso: `PetscCount`, `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscMPIIntCast()`, `PetscBLASIntCast()`, `PetscIntMultError()`, `PetscIntSumError()`, `PetscIntCast()`
1762 @*/
1763 static inline PetscErrorCode PetscCountCast(PetscCount a, PetscInt *b)
1764 {
1765   PetscFunctionBegin;
1766   *b = 0;
1767   PetscCheck(sizeof(PetscCount) <= sizeof(PetscInt) || a <= PETSC_MAX_INT, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "%" PetscCount_FMT " is too big for PetscInt, you may need to ./configure using --with-64-bit-indices", a);
1768   *b = (PetscInt)a;
1769   PetscFunctionReturn(PETSC_SUCCESS);
1770 }
1771 
1772 /*@C
1773    PetscBLASIntCast - casts a `PetscInt` (which may be 64-bits in size) to a `PetscBLASInt` (which may be 32-bits in size), generates an
1774    error if the `PetscBLASInt` is not large enough to hold the number.
1775 
1776    Not Collective; No Fortran Support
1777 
1778    Input Parameter:
1779 .  a - the `PetscInt` value
1780 
1781    Output Parameter:
1782 .  b - the resulting `PetscBLASInt` value
1783 
1784    Level: advanced
1785 
1786    Note:
1787    Errors if the integer is negative since PETSc calls to BLAS/LAPACK never need to cast negative integer inputs
1788 
1789 .seealso: `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscMPIIntCast()`, `PetscIntCast()`, `PetscCountCast()`
1790 @*/
1791 static inline PetscErrorCode PetscBLASIntCast(PetscInt a, PetscBLASInt *b)
1792 {
1793   PetscFunctionBegin;
1794   *b = 0;
1795   if (PetscDefined(USE_64BIT_INDICES) && !PetscDefined(HAVE_64BIT_BLAS_INDICES)) {
1796     PetscCheck(a <= PETSC_BLAS_INT_MAX, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "%" PetscInt_FMT " is too big for BLAS/LAPACK, which is restricted to 32-bit integers. Either you have an invalidly large integer error in your code or you must ./configure PETSc with --with-64-bit-blas-indices for the case you are running", a);
1797   }
1798   PetscCheck(a >= 0, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "Passing negative integer to BLAS/LAPACK routine");
1799   *b = (PetscBLASInt)a;
1800   PetscFunctionReturn(PETSC_SUCCESS);
1801 }
1802 
1803 /*@C
1804    PetscCuBLASIntCast - like `PetscBLASIntCast()`, but for `PetscCuBLASInt`.
1805 
1806    Not Collective; No Fortran Support
1807 
1808    Input Parameter:
1809 .  a - the `PetscInt` value
1810 
1811    Output Parameter:
1812 .  b - the resulting `PetscCuBLASInt` value
1813 
1814    Level: advanced
1815 
1816    Note:
1817    Errors if the integer is negative since PETSc calls to cuBLAS and friends never need to cast negative integer inputs
1818 
1819 .seealso: `PetscCuBLASInt`, `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscBLASIntCast()`, `PetscMPIIntCast()`, `PetscIntCast()`
1820 @*/
1821 static inline PetscErrorCode PetscCuBLASIntCast(PetscInt a, PetscCuBLASInt *b)
1822 {
1823   PetscFunctionBegin;
1824   *b = 0;
1825   PetscCheck(a <= PETSC_CUBLAS_INT_MAX, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "%" PetscInt_FMT " is too big for cuBLAS, which is restricted to 32-bit integers.", a);
1826   PetscCheck(a >= 0, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "Passing negative integer %" PetscInt_FMT "to cuBLAS routine", a);
1827   *b = (PetscCuBLASInt)a;
1828   PetscFunctionReturn(PETSC_SUCCESS);
1829 }
1830 
1831 /*@C
1832    PetscHipBLASIntCast - like `PetscBLASIntCast()`, but for `PetscHipBLASInt`.
1833 
1834    Not Collective; No Fortran Support
1835 
1836    Input Parameter:
1837 .  a - the `PetscInt` value
1838 
1839    Output Parameter:
1840 .  b - the resulting `PetscHipBLASInt` value
1841 
1842    Level: advanced
1843 
1844    Note:
1845    Errors if the integer is negative since PETSc calls to hipBLAS and friends never need to cast negative integer inputs
1846 
1847 .seealso: `PetscHipBLASInt`, `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscBLASIntCast()`, `PetscMPIIntCast()`, `PetscIntCast()`
1848 @*/
1849 static inline PetscErrorCode PetscHipBLASIntCast(PetscInt a, PetscHipBLASInt *b)
1850 {
1851   PetscFunctionBegin;
1852   *b = 0;
1853   PetscCheck(a <= PETSC_HIPBLAS_INT_MAX, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "%" PetscInt_FMT " is too big for hipBLAS, which is restricted to 32-bit integers.", a);
1854   PetscCheck(a >= 0, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "Passing negative integer %" PetscInt_FMT "to hipBLAS routine", a);
1855   *b = (PetscHipBLASInt)a;
1856   PetscFunctionReturn(PETSC_SUCCESS);
1857 }
1858 
1859 /*@C
1860    PetscMPIIntCast - casts a `PetscInt` (which may be 64-bits in size) to a `PetscMPIInt` (which may be 32-bits in size), generates an
1861    error if the `PetscMPIInt` is not large enough to hold the number.
1862 
1863    Not Collective; No Fortran Support
1864 
1865    Input Parameter:
1866 .  a - the `PetscInt` value
1867 
1868    Output Parameter:
1869 .  b - the resulting `PetscMPIInt` value
1870 
1871    Level: advanced
1872 
1873 .seealso: `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscBLASIntCast()`, `PetscIntCast()`
1874 @*/
1875 static inline PetscErrorCode PetscMPIIntCast(PetscInt a, PetscMPIInt *b)
1876 {
1877   PetscFunctionBegin;
1878   *b = 0;
1879   PetscCheck(a <= PETSC_MPI_INT_MAX, PETSC_COMM_SELF, PETSC_ERR_ARG_OUTOFRANGE, "%" PetscInt_FMT " is too big for MPI buffer length. Maximum supported value is %d", a, PETSC_MPI_INT_MAX);
1880   *b = (PetscMPIInt)a;
1881   PetscFunctionReturn(PETSC_SUCCESS);
1882 }
1883 
1884 #define PetscInt64Mult(a, b) (((PetscInt64)(a)) * ((PetscInt64)(b)))
1885 
1886 /*@C
1887   PetscRealIntMultTruncate - Computes the product of a positive `PetscReal` and a positive
1888   `PetscInt` and truncates the value to slightly less than the maximal possible value.
1889 
1890   Not Collective; No Fortran Support
1891 
1892   Input Parameters:
1893 + a - The `PetscReal` value
1894 - b - The `PetscInt` value
1895 
1896   Level: advanced
1897 
1898   Notes:
1899   Returns the result as a `PetscInt` value.
1900 
1901   Use `PetscInt64Mult()` to compute the product of two `PetscInt` as a `PetscInt64`.
1902 
1903   Use `PetscIntMultTruncate()` to compute the product of two positive `PetscInt` and truncate
1904   to fit a `PetscInt`.
1905 
1906   Use `PetscIntMultError()` to compute the product of two `PetscInt` if you wish to generate an
1907   error if the result will not fit in a `PetscInt`.
1908 
1909   Developer Notes:
1910   We currently assume that `PetscInt` addition can never overflow, this is obviously wrong but
1911   requires many more checks.
1912 
1913   This is used where we compute approximate sizes for workspace and need to insure the
1914   workspace is index-able.
1915 
1916 .seealso: `PetscReal`, `PetscInt`, `PetscInt64Mult()`, `PetscIntMultError()`, `PetscIntSumError()`
1917 @*/
1918 static inline PetscInt PetscRealIntMultTruncate(PetscReal a, PetscInt b)
1919 {
1920   PetscInt64 r = (PetscInt64)(a * (PetscReal)b);
1921   if (r > PETSC_MAX_INT - 100) r = PETSC_MAX_INT - 100;
1922   return (PetscInt)r;
1923 }
1924 
1925 /*@C
1926    PetscIntMultTruncate - Computes the product of two positive `PetscInt` and truncates the value to slightly less than the maximal possible value
1927 
1928    Not Collective; No Fortran Support
1929 
1930    Input Parameters:
1931 +  a - the `PetscInt` value
1932 -  b - the second value
1933 
1934    Returns:
1935    The result as a `PetscInt` value
1936 
1937    Level: advanced
1938 
1939    Notes:
1940    Use `PetscInt64Mult()` to compute the product of two `PetscInt` as a `PetscInt64`
1941 
1942    Use `PetscRealIntMultTruncate()` to compute the product of a `PetscReal` and a `PetscInt` and truncate to fit a `PetscInt`
1943 
1944    Use `PetscIntMultError()` to compute the product of two `PetscInt` if you wish to generate an error if the result will not fit in a `PetscInt`
1945 
1946    Developer Notes:
1947    We currently assume that `PetscInt` addition can never overflow, this is obviously wrong but requires many more checks.
1948 
1949    This is used where we compute approximate sizes for workspace and need to insure the workspace is index-able.
1950 
1951 .seealso: `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscBLASIntCast()`, `PetscInt64Mult()`, `PetscIntMultError()`, `PetscIntSumError()`,
1952           `PetscIntSumTruncate()`
1953 @*/
1954 static inline PetscInt PetscIntMultTruncate(PetscInt a, PetscInt b)
1955 {
1956   PetscInt64 r = PetscInt64Mult(a, b);
1957   if (r > PETSC_MAX_INT - 100) r = PETSC_MAX_INT - 100;
1958   return (PetscInt)r;
1959 }
1960 
1961 /*@C
1962    PetscIntSumTruncate - Computes the sum of two positive `PetscInt` and truncates the value to slightly less than the maximal possible value
1963 
1964    Not Collective; No Fortran Support
1965 
1966    Input Parameters:
1967 +  a - the `PetscInt` value
1968 -  b - the second value
1969 
1970    Returns:
1971    The result as a `PetscInt` value
1972 
1973    Level: advanced
1974 
1975    Notes:
1976    Use `PetscInt64Mult()` to compute the product of two `PetscInt` as a `PetscInt64`
1977 
1978    Use `PetscRealIntMultTruncate()` to compute the product of a `PetscReal` and a `PetscInt` and truncate to fit a `PetscInt`
1979 
1980    Use `PetscIntMultError()` to compute the product of two `PetscInt` if you wish to generate an error if the result will not fit in a `PetscInt`
1981 
1982    Developer Note:
1983    This is used where we compute approximate sizes for workspace and need to insure the workspace is index-able.
1984 
1985 .seealso: `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscBLASIntCast()`, `PetscInt64Mult()`, `PetscIntMultError()`
1986 @*/
1987 static inline PetscInt PetscIntSumTruncate(PetscInt a, PetscInt b)
1988 {
1989   PetscInt64 r = ((PetscInt64)a) + ((PetscInt64)b);
1990   if (r > PETSC_MAX_INT - 100) r = PETSC_MAX_INT - 100;
1991   return (PetscInt)r;
1992 }
1993 
1994 /*@C
1995    PetscIntMultError - Computes the product of two positive `PetscInt` and generates an error with overflow.
1996 
1997    Not Collective; No Fortran Support
1998 
1999    Input Parameters:
2000 +  a - the `PetscInt` value
2001 -  b - the second value
2002 
2003    Output Parameter:
2004 .  result - the result as a `PetscInt` value, or `NULL` if you do not want the result, you just want to check if it overflows
2005 
2006    Level: advanced
2007 
2008    Notes:
2009    Use `PetscInt64Mult()` to compute the product of two `PetscInt` and store in a `PetscInt64`
2010 
2011    Use `PetscIntMultTruncate()` to compute the product of two `PetscInt` and truncate it to fit in a `PetscInt`
2012 
2013    Developer Note:
2014    In most places in the source code we currently assume that `PetscInt` addition does not overflow, this is obviously wrong but requires many more checks.
2015    `PetscIntSumError()` can be used to check for this situation.
2016 
2017 .seealso: `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscBLASIntCast()`, `PetscIntMult64()`, `PetscIntSumError()`
2018 @*/
2019 static inline PetscErrorCode PetscIntMultError(PetscInt a, PetscInt b, PetscInt *result)
2020 {
2021   PetscInt64 r = PetscInt64Mult(a, b);
2022 
2023   PetscFunctionBegin;
2024   if (result) *result = (PetscInt)r;
2025   if (!PetscDefined(USE_64BIT_INDICES)) {
2026     PetscCheck(r <= PETSC_MAX_INT, PETSC_COMM_SELF, PETSC_ERR_SUP, "Product of two integers %" PetscInt_FMT " %" PetscInt_FMT " overflow, either you have an invalidly large integer error in your code or you must ./configure PETSc with --with-64-bit-indices for the case you are running", a, b);
2027   }
2028   PetscFunctionReturn(PETSC_SUCCESS);
2029 }
2030 
2031 /*@C
2032 
2033    PetscIntSumError - Computes the sum of two positive `PetscInt` and generates an error with overflow.
2034 
2035    Not Collective; No Fortran Support
2036 
2037    Input Parameters:
2038 +  a - the `PetscInt` value
2039 -  b - the second value
2040 
2041    Output Parameter:
2042 .  c - the result as a `PetscInt` value,  or `NULL` if you do not want the result, you just want to check if it overflows
2043 
2044    Level: advanced
2045 
2046    Notes:
2047    Use `PetscInt64Mult()` to compute the product of two 32-bit `PetscInt` and store in a `PetscInt64`
2048 
2049    Use `PetscIntMultTruncate()` to compute the product of two `PetscInt` and truncate it to fit in a `PetscInt`
2050 
2051 .seealso: `PetscBLASInt`, `PetscMPIInt`, `PetscInt`, `PetscBLASIntCast()`, `PetscInt64Mult()`, `PetscIntMultError()`
2052 @*/
2053 static inline PetscErrorCode PetscIntSumError(PetscInt a, PetscInt b, PetscInt *result)
2054 {
2055   PetscInt64 r = ((PetscInt64)a) + ((PetscInt64)b);
2056 
2057   PetscFunctionBegin;
2058   if (result) *result = (PetscInt)r;
2059   if (!PetscDefined(USE_64BIT_INDICES)) {
2060     PetscCheck(r <= PETSC_MAX_INT, PETSC_COMM_SELF, PETSC_ERR_SUP, "Sum of two integers %" PetscInt_FMT " %" PetscInt_FMT " overflow, either you have an invalidly large integer error in your code or you must ./configure PETSc with --with-64-bit-indices for the case you are running", a, b);
2061   }
2062   PetscFunctionReturn(PETSC_SUCCESS);
2063 }
2064 
2065 /*
2066      The IBM include files define hz, here we hide it so that it may be used as a regular user variable.
2067 */
2068 #if defined(hz)
2069   #undef hz
2070 #endif
2071 
2072 #if defined(PETSC_HAVE_SYS_TYPES_H)
2073   #include <sys/types.h>
2074 #endif
2075 
2076 /*MC
2077 
2078     PETSC_VERSION - This manual page provides information about how PETSc documents and uses its version information. This information is available to both C/C++
2079                     and Fortran compilers when `petscsys.h` is included.
2080 
2081     The current PETSc version and the API for accessing it are defined in <A HREF="PETSC_DOC_OUT_ROOT_PLACEHOLDER/include/petscversion.h.html">include/petscversion.html</A>
2082 
2083     The complete version number is given as the triple  PETSC_VERSION_MAJOR.PETSC_VERSION_MINOR.PETSC_VERSION_SUBMINOR (in short hand x.y.z)
2084 
2085     A change in the minor version number (y) indicates possible/likely changes in the PETSc API. Note this is different than with the semantic versioning convention
2086     where only a change in the major version number (x) indicates a change in the API.
2087 
2088     A subminor greater than zero indicates a patch release. Version x.y.z maintains source and binary compatibility with version x.y.w for all z and w
2089 
2090     Use the macros PETSC_VERSION_EQ(x,y,z), PETSC_VERSION_LT(x,y,z), PETSC_VERSION_LE(x,y,z), PETSC_VERSION_GT(x,y,z),
2091     PETSC_VERSION_GE(x,y,z) to determine if the current version is equal to, less than, less than or equal to, greater than or greater than or equal to a given
2092     version number (x.y.z).
2093 
2094     `PETSC_RELEASE_DATE` is the date the x.y version was released (i.e. the version before any patch releases)
2095 
2096     `PETSC_VERSION_DATE` is the date the x.y.z version was released
2097 
2098     `PETSC_VERSION_GIT` is the last git commit to the repository given in the form vx.y.z-wwwww
2099 
2100     `PETSC_VERSION_DATE_GIT` is the date of the last git commit to the repository
2101 
2102     `PETSC_VERSION_()` is deprecated and will eventually be removed.
2103 
2104     Level: intermediate
2105 M*/
2106 
2107 PETSC_EXTERN PetscErrorCode PetscGetArchType(char[], size_t);
2108 PETSC_EXTERN PetscErrorCode PetscGetHostName(char[], size_t);
2109 PETSC_EXTERN PetscErrorCode PetscGetUserName(char[], size_t);
2110 PETSC_EXTERN PetscErrorCode PetscGetProgramName(char[], size_t);
2111 PETSC_EXTERN PetscErrorCode PetscSetProgramName(const char[]);
2112 PETSC_EXTERN PetscErrorCode PetscGetDate(char[], size_t);
2113 PETSC_EXTERN PetscErrorCode PetscGetVersion(char[], size_t);
2114 PETSC_EXTERN PetscErrorCode PetscGetVersionNumber(PetscInt *, PetscInt *, PetscInt *, PetscInt *);
2115 
2116 PETSC_EXTERN PetscErrorCode PetscSortedInt(PetscInt, const PetscInt[], PetscBool *);
2117 PETSC_EXTERN PetscErrorCode PetscSortedInt64(PetscInt, const PetscInt64[], PetscBool *);
2118 PETSC_EXTERN PetscErrorCode PetscSortedMPIInt(PetscInt, const PetscMPIInt[], PetscBool *);
2119 PETSC_EXTERN PetscErrorCode PetscSortedReal(PetscInt, const PetscReal[], PetscBool *);
2120 PETSC_EXTERN PetscErrorCode PetscSortInt(PetscInt, PetscInt[]);
2121 PETSC_EXTERN PetscErrorCode PetscSortInt64(PetscInt, PetscInt64[]);
2122 PETSC_EXTERN PetscErrorCode PetscSortCount(PetscInt, PetscCount[]);
2123 PETSC_EXTERN PetscErrorCode PetscSortReverseInt(PetscInt, PetscInt[]);
2124 PETSC_EXTERN PetscErrorCode PetscSortedRemoveDupsInt(PetscInt *, PetscInt[]);
2125 PETSC_EXTERN PetscErrorCode PetscSortedCheckDupsInt(PetscInt, const PetscInt[], PetscBool *);
2126 PETSC_EXTERN PetscErrorCode PetscSortRemoveDupsInt(PetscInt *, PetscInt[]);
2127 PETSC_EXTERN PetscErrorCode PetscCheckDupsInt(PetscInt, const PetscInt[], PetscBool *);
2128 PETSC_EXTERN PetscErrorCode PetscFindInt(PetscInt, PetscInt, const PetscInt[], PetscInt *);
2129 PETSC_EXTERN PetscErrorCode PetscFindMPIInt(PetscMPIInt, PetscInt, const PetscMPIInt[], PetscInt *);
2130 PETSC_EXTERN PetscErrorCode PetscSortIntWithPermutation(PetscInt, const PetscInt[], PetscInt[]);
2131 PETSC_EXTERN PetscErrorCode PetscSortStrWithPermutation(PetscInt, const char *[], PetscInt[]);
2132 PETSC_EXTERN PetscErrorCode PetscSortIntWithArray(PetscInt, PetscInt[], PetscInt[]);
2133 PETSC_EXTERN PetscErrorCode PetscSortIntWithCountArray(PetscCount, PetscInt[], PetscCount[]);
2134 PETSC_EXTERN PetscErrorCode PetscSortIntWithArrayPair(PetscInt, PetscInt[], PetscInt[], PetscInt[]);
2135 PETSC_EXTERN PetscErrorCode PetscSortIntWithIntCountArrayPair(PetscCount, PetscInt[], PetscInt[], PetscCount[]);
2136 PETSC_EXTERN PetscErrorCode PetscSortMPIInt(PetscInt, PetscMPIInt[]);
2137 PETSC_EXTERN PetscErrorCode PetscSortRemoveDupsMPIInt(PetscInt *, PetscMPIInt[]);
2138 PETSC_EXTERN PetscErrorCode PetscSortMPIIntWithArray(PetscMPIInt, PetscMPIInt[], PetscMPIInt[]);
2139 PETSC_EXTERN PetscErrorCode PetscSortMPIIntWithIntArray(PetscMPIInt, PetscMPIInt[], PetscInt[]);
2140 PETSC_EXTERN PetscErrorCode PetscSortIntWithScalarArray(PetscInt, PetscInt[], PetscScalar[]);
2141 PETSC_EXTERN PetscErrorCode PetscSortIntWithDataArray(PetscInt, PetscInt[], void *, size_t, void *);
2142 PETSC_EXTERN PetscErrorCode PetscSortReal(PetscInt, PetscReal[]);
2143 PETSC_EXTERN PetscErrorCode PetscSortRealWithArrayInt(PetscInt, PetscReal[], PetscInt[]);
2144 PETSC_EXTERN PetscErrorCode PetscSortRealWithPermutation(PetscInt, const PetscReal[], PetscInt[]);
2145 PETSC_EXTERN PetscErrorCode PetscSortRemoveDupsReal(PetscInt *, PetscReal[]);
2146 PETSC_EXTERN PetscErrorCode PetscFindReal(PetscReal, PetscInt, const PetscReal[], PetscReal, PetscInt *);
2147 PETSC_EXTERN PetscErrorCode PetscSortSplit(PetscInt, PetscInt, PetscScalar[], PetscInt[]);
2148 PETSC_EXTERN PetscErrorCode PetscSortSplitReal(PetscInt, PetscInt, PetscReal[], PetscInt[]);
2149 PETSC_EXTERN PetscErrorCode PetscProcessTree(PetscInt, const PetscBool[], const PetscInt[], PetscInt *, PetscInt **, PetscInt **, PetscInt **, PetscInt **);
2150 PETSC_EXTERN PetscErrorCode PetscMergeIntArrayPair(PetscInt, const PetscInt[], const PetscInt[], PetscInt, const PetscInt[], const PetscInt[], PetscInt *, PetscInt **, PetscInt **);
2151 PETSC_EXTERN PetscErrorCode PetscMergeIntArray(PetscInt, const PetscInt[], PetscInt, const PetscInt[], PetscInt *, PetscInt **);
2152 PETSC_EXTERN PetscErrorCode PetscMergeMPIIntArray(PetscInt, const PetscMPIInt[], PetscInt, const PetscMPIInt[], PetscInt *, PetscMPIInt **);
2153 PETSC_EXTERN PetscErrorCode PetscParallelSortedInt(MPI_Comm, PetscInt, const PetscInt[], PetscBool *);
2154 
2155 PETSC_EXTERN PetscErrorCode PetscTimSort(PetscInt, void *, size_t, int (*)(const void *, const void *, void *), void *);
2156 PETSC_EXTERN PetscErrorCode PetscIntSortSemiOrdered(PetscInt, PetscInt[]);
2157 PETSC_EXTERN PetscErrorCode PetscMPIIntSortSemiOrdered(PetscInt, PetscMPIInt[]);
2158 PETSC_EXTERN PetscErrorCode PetscRealSortSemiOrdered(PetscInt, PetscReal[]);
2159 PETSC_EXTERN PetscErrorCode PetscTimSortWithArray(PetscInt, void *, size_t, void *, size_t, int (*)(const void *, const void *, void *), void *);
2160 PETSC_EXTERN PetscErrorCode PetscIntSortSemiOrderedWithArray(PetscInt, PetscInt[], PetscInt[]);
2161 PETSC_EXTERN PetscErrorCode PetscMPIIntSortSemiOrderedWithArray(PetscInt, PetscMPIInt[], PetscMPIInt[]);
2162 PETSC_EXTERN PetscErrorCode PetscRealSortSemiOrderedWithArrayInt(PetscInt, PetscReal[], PetscInt[]);
2163 
2164 PETSC_EXTERN PetscErrorCode PetscSetDisplay(void);
2165 PETSC_EXTERN PetscErrorCode PetscGetDisplay(char[], size_t);
2166 
2167 /*J
2168     PetscRandomType - String with the name of a PETSc randomizer
2169 
2170    Level: beginner
2171 
2172    Note:
2173    To use `PETSCSPRNG` or `PETSCRANDOM123` you must have ./configure PETSc
2174    with the option `--download-sprng` or `--download-random123`. We recommend the default provided with PETSc.
2175 
2176 .seealso: `PetscRandomSetType()`, `PetscRandom`, `PetscRandomCreate()`
2177 J*/
2178 typedef const char *PetscRandomType;
2179 #define PETSCRAND      "rand"
2180 #define PETSCRAND48    "rand48"
2181 #define PETSCSPRNG     "sprng"
2182 #define PETSCRANDER48  "rander48"
2183 #define PETSCRANDOM123 "random123"
2184 #define PETSCCURAND    "curand"
2185 
2186 /* Logging support */
2187 PETSC_EXTERN PetscClassId PETSC_RANDOM_CLASSID;
2188 
2189 PETSC_EXTERN PetscErrorCode PetscRandomInitializePackage(void);
2190 PETSC_EXTERN PetscErrorCode PetscRandomFinalizePackage(void);
2191 
2192 /* Dynamic creation and loading functions */
2193 PETSC_EXTERN PetscFunctionList PetscRandomList;
2194 
2195 PETSC_EXTERN PetscErrorCode PetscRandomRegister(const char[], PetscErrorCode (*)(PetscRandom));
2196 PETSC_EXTERN PetscErrorCode PetscRandomSetType(PetscRandom, PetscRandomType);
2197 PETSC_EXTERN PetscErrorCode PetscRandomSetFromOptions(PetscRandom);
2198 PETSC_EXTERN PetscErrorCode PetscRandomGetType(PetscRandom, PetscRandomType *);
2199 PETSC_EXTERN PetscErrorCode PetscRandomViewFromOptions(PetscRandom, PetscObject, const char[]);
2200 PETSC_EXTERN PetscErrorCode PetscRandomView(PetscRandom, PetscViewer);
2201 
2202 PETSC_EXTERN PetscErrorCode PetscRandomCreate(MPI_Comm, PetscRandom *);
2203 PETSC_EXTERN PetscErrorCode PetscRandomGetValue(PetscRandom, PetscScalar *);
2204 PETSC_EXTERN PetscErrorCode PetscRandomGetValueReal(PetscRandom, PetscReal *);
2205 PETSC_EXTERN PetscErrorCode PetscRandomGetValues(PetscRandom, PetscInt, PetscScalar *);
2206 PETSC_EXTERN PetscErrorCode PetscRandomGetValuesReal(PetscRandom, PetscInt, PetscReal *);
2207 PETSC_EXTERN PetscErrorCode PetscRandomGetInterval(PetscRandom, PetscScalar *, PetscScalar *);
2208 PETSC_EXTERN PetscErrorCode PetscRandomSetInterval(PetscRandom, PetscScalar, PetscScalar);
2209 PETSC_EXTERN PetscErrorCode PetscRandomSetSeed(PetscRandom, unsigned long);
2210 PETSC_EXTERN PetscErrorCode PetscRandomGetSeed(PetscRandom, unsigned long *);
2211 PETSC_EXTERN PetscErrorCode PetscRandomSeed(PetscRandom);
2212 PETSC_EXTERN PetscErrorCode PetscRandomDestroy(PetscRandom *);
2213 
2214 PETSC_EXTERN PetscErrorCode PetscGetFullPath(const char[], char[], size_t);
2215 PETSC_EXTERN PetscErrorCode PetscGetRelativePath(const char[], char[], size_t);
2216 PETSC_EXTERN PetscErrorCode PetscGetWorkingDirectory(char[], size_t);
2217 PETSC_EXTERN PetscErrorCode PetscGetRealPath(const char[], char[]);
2218 PETSC_EXTERN PetscErrorCode PetscGetHomeDirectory(char[], size_t);
2219 PETSC_EXTERN PetscErrorCode PetscTestFile(const char[], char, PetscBool *);
2220 PETSC_EXTERN PetscErrorCode PetscTestDirectory(const char[], char, PetscBool *);
2221 PETSC_EXTERN PetscErrorCode PetscMkdir(const char[]);
2222 PETSC_EXTERN PetscErrorCode PetscMkdtemp(char[]);
2223 PETSC_EXTERN PetscErrorCode PetscRMTree(const char[]);
2224 
2225 /*MC
2226    PetscBinaryBigEndian - indicates if values in memory are stored with big endian format
2227 
2228    Synopsis:
2229    #include <petscsys.h>
2230    PetscBool PetscBinaryBigEndian(void);
2231 
2232    No Fortran Support
2233 
2234    Level: developer
2235 
2236 .seealso: `PetscInitialize()`, `PetscFinalize()`, `PetscInitializeCalled`
2237 M*/
2238 static inline PetscBool PetscBinaryBigEndian(void)
2239 {
2240   long _petsc_v = 1;
2241   return ((char *)&_petsc_v)[0] ? PETSC_FALSE : PETSC_TRUE;
2242 }
2243 
2244 PETSC_EXTERN PetscErrorCode PetscBinaryRead(int, void *, PetscInt, PetscInt *, PetscDataType);
2245 PETSC_EXTERN PetscErrorCode PetscBinarySynchronizedRead(MPI_Comm, int, void *, PetscInt, PetscInt *, PetscDataType);
2246 PETSC_EXTERN PetscErrorCode PetscBinaryWrite(int, const void *, PetscInt, PetscDataType);
2247 PETSC_EXTERN PetscErrorCode PetscBinarySynchronizedWrite(MPI_Comm, int, const void *, PetscInt, PetscDataType);
2248 PETSC_EXTERN PetscErrorCode PetscBinaryOpen(const char[], PetscFileMode, int *);
2249 PETSC_EXTERN PetscErrorCode PetscBinaryClose(int);
2250 PETSC_EXTERN PetscErrorCode PetscSharedTmp(MPI_Comm, PetscBool *);
2251 PETSC_EXTERN PetscErrorCode PetscSharedWorkingDirectory(MPI_Comm, PetscBool *);
2252 PETSC_EXTERN PetscErrorCode PetscGetTmp(MPI_Comm, char[], size_t);
2253 PETSC_EXTERN PetscErrorCode PetscFileRetrieve(MPI_Comm, const char[], char[], size_t, PetscBool *);
2254 PETSC_EXTERN PetscErrorCode PetscLs(MPI_Comm, const char[], char[], size_t, PetscBool *);
2255 #if defined(PETSC_USE_SOCKET_VIEWER)
2256 PETSC_EXTERN PetscErrorCode PetscOpenSocket(const char[], int, int *);
2257 #endif
2258 
2259 PETSC_EXTERN PetscErrorCode PetscBinarySeek(int, off_t, PetscBinarySeekType, off_t *);
2260 PETSC_EXTERN PetscErrorCode PetscBinarySynchronizedSeek(MPI_Comm, int, off_t, PetscBinarySeekType, off_t *);
2261 PETSC_EXTERN PetscErrorCode PetscByteSwap(void *, PetscDataType, PetscInt);
2262 
2263 PETSC_EXTERN PetscErrorCode PetscSetDebugTerminal(const char[]);
2264 PETSC_EXTERN PetscErrorCode PetscSetDebugger(const char[], PetscBool);
2265 PETSC_EXTERN PetscErrorCode PetscSetDefaultDebugger(void);
2266 PETSC_EXTERN PetscErrorCode PetscSetDebuggerFromString(const char *);
2267 PETSC_EXTERN PetscErrorCode PetscAttachDebugger(void);
2268 PETSC_EXTERN PetscErrorCode PetscStopForDebugger(void);
2269 PETSC_EXTERN PetscErrorCode PetscWaitOnError(void);
2270 
2271 PETSC_EXTERN PetscErrorCode PetscGatherNumberOfMessages(MPI_Comm, const PetscMPIInt[], const PetscMPIInt[], PetscMPIInt *);
2272 PETSC_EXTERN PetscErrorCode PetscGatherMessageLengths(MPI_Comm, PetscMPIInt, PetscMPIInt, const PetscMPIInt[], PetscMPIInt **, PetscMPIInt **);
2273 PETSC_EXTERN PetscErrorCode PetscGatherMessageLengths2(MPI_Comm, PetscMPIInt, PetscMPIInt, const PetscMPIInt[], const PetscMPIInt[], PetscMPIInt **, PetscMPIInt **, PetscMPIInt **);
2274 PETSC_EXTERN PetscErrorCode PetscPostIrecvInt(MPI_Comm, PetscMPIInt, PetscMPIInt, const PetscMPIInt[], const PetscMPIInt[], PetscInt ***, MPI_Request **);
2275 PETSC_EXTERN PetscErrorCode PetscPostIrecvScalar(MPI_Comm, PetscMPIInt, PetscMPIInt, const PetscMPIInt[], const PetscMPIInt[], PetscScalar ***, MPI_Request **);
2276 PETSC_EXTERN PetscErrorCode PetscCommBuildTwoSided(MPI_Comm, PetscMPIInt, MPI_Datatype, PetscMPIInt, const PetscMPIInt *, const void *, PetscMPIInt *, PetscMPIInt **, void *) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(6, 3);
2277 PETSC_EXTERN PetscErrorCode PetscCommBuildTwoSidedF(MPI_Comm, PetscMPIInt, MPI_Datatype, PetscMPIInt, const PetscMPIInt[], const void *, PetscMPIInt *, PetscMPIInt **, void *, PetscMPIInt, PetscErrorCode (*send)(MPI_Comm, const PetscMPIInt[], PetscMPIInt, PetscMPIInt, void *, MPI_Request[], void *), PetscErrorCode (*recv)(MPI_Comm, const PetscMPIInt[], PetscMPIInt, void *, MPI_Request[], void *), void *ctx) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(6, 3);
2278 PETSC_EXTERN PetscErrorCode PetscCommBuildTwoSidedFReq(MPI_Comm, PetscMPIInt, MPI_Datatype, PetscMPIInt, const PetscMPIInt[], const void *, PetscMPIInt *, PetscMPIInt **, void *, PetscMPIInt, MPI_Request **, MPI_Request **, PetscErrorCode (*send)(MPI_Comm, const PetscMPIInt[], PetscMPIInt, PetscMPIInt, void *, MPI_Request[], void *), PetscErrorCode (*recv)(MPI_Comm, const PetscMPIInt[], PetscMPIInt, void *, MPI_Request[], void *), void *ctx) PETSC_ATTRIBUTE_MPI_POINTER_WITH_TYPE(6, 3);
2279 
2280 PETSC_EXTERN PetscErrorCode PetscCommBuildTwoSidedSetType(MPI_Comm, PetscBuildTwoSidedType);
2281 PETSC_EXTERN PetscErrorCode PetscCommBuildTwoSidedGetType(MPI_Comm, PetscBuildTwoSidedType *);
2282 
2283 PETSC_EXTERN PetscErrorCode PetscSSEIsEnabled(MPI_Comm, PetscBool *, PetscBool *);
2284 
2285 PETSC_EXTERN MPI_Comm PetscObjectComm(PetscObject);
2286 
2287 struct _n_PetscSubcomm {
2288   MPI_Comm         parent;    /* parent communicator */
2289   MPI_Comm         dupparent; /* duplicate parent communicator, under which the processors of this subcomm have contiguous rank */
2290   MPI_Comm         child;     /* the sub-communicator */
2291   PetscMPIInt      n;         /* num of subcommunicators under the parent communicator */
2292   PetscMPIInt      color;     /* color of processors belong to this communicator */
2293   PetscMPIInt     *subsize;   /* size of subcommunicator[color] */
2294   PetscSubcommType type;
2295   char            *subcommprefix;
2296 };
2297 
2298 static inline MPI_Comm PetscSubcommParent(PetscSubcomm scomm)
2299 {
2300   return scomm->parent;
2301 }
2302 static inline MPI_Comm PetscSubcommChild(PetscSubcomm scomm)
2303 {
2304   return scomm->child;
2305 }
2306 static inline MPI_Comm PetscSubcommContiguousParent(PetscSubcomm scomm)
2307 {
2308   return scomm->dupparent;
2309 }
2310 PETSC_EXTERN PetscErrorCode PetscSubcommCreate(MPI_Comm, PetscSubcomm *);
2311 PETSC_EXTERN PetscErrorCode PetscSubcommDestroy(PetscSubcomm *);
2312 PETSC_EXTERN PetscErrorCode PetscSubcommSetNumber(PetscSubcomm, PetscInt);
2313 PETSC_EXTERN PetscErrorCode PetscSubcommSetType(PetscSubcomm, PetscSubcommType);
2314 PETSC_EXTERN PetscErrorCode PetscSubcommSetTypeGeneral(PetscSubcomm, PetscMPIInt, PetscMPIInt);
2315 PETSC_EXTERN PetscErrorCode PetscSubcommView(PetscSubcomm, PetscViewer);
2316 PETSC_EXTERN PetscErrorCode PetscSubcommSetFromOptions(PetscSubcomm);
2317 PETSC_EXTERN PetscErrorCode PetscSubcommSetOptionsPrefix(PetscSubcomm, const char[]);
2318 PETSC_EXTERN PetscErrorCode PetscSubcommGetParent(PetscSubcomm, MPI_Comm *);
2319 PETSC_EXTERN PetscErrorCode PetscSubcommGetContiguousParent(PetscSubcomm, MPI_Comm *);
2320 PETSC_EXTERN PetscErrorCode PetscSubcommGetChild(PetscSubcomm, MPI_Comm *);
2321 
2322 PETSC_EXTERN PetscErrorCode PetscHeapCreate(PetscInt, PetscHeap *);
2323 PETSC_EXTERN PetscErrorCode PetscHeapAdd(PetscHeap, PetscInt, PetscInt);
2324 PETSC_EXTERN PetscErrorCode PetscHeapPop(PetscHeap, PetscInt *, PetscInt *);
2325 PETSC_EXTERN PetscErrorCode PetscHeapPeek(PetscHeap, PetscInt *, PetscInt *);
2326 PETSC_EXTERN PetscErrorCode PetscHeapStash(PetscHeap, PetscInt, PetscInt);
2327 PETSC_EXTERN PetscErrorCode PetscHeapUnstash(PetscHeap);
2328 PETSC_EXTERN PetscErrorCode PetscHeapDestroy(PetscHeap *);
2329 PETSC_EXTERN PetscErrorCode PetscHeapView(PetscHeap, PetscViewer);
2330 
2331 PETSC_EXTERN PetscErrorCode PetscProcessPlacementView(PetscViewer);
2332 PETSC_EXTERN PetscErrorCode PetscShmCommGet(MPI_Comm, PetscShmComm *);
2333 PETSC_EXTERN PetscErrorCode PetscShmCommGlobalToLocal(PetscShmComm, PetscMPIInt, PetscMPIInt *);
2334 PETSC_EXTERN PetscErrorCode PetscShmCommLocalToGlobal(PetscShmComm, PetscMPIInt, PetscMPIInt *);
2335 PETSC_EXTERN PetscErrorCode PetscShmCommGetMpiShmComm(PetscShmComm, MPI_Comm *);
2336 
2337 /* routines to better support OpenMP multithreading needs of some PETSc third party libraries */
2338 PETSC_EXTERN PetscErrorCode PetscOmpCtrlCreate(MPI_Comm, PetscInt, PetscOmpCtrl *);
2339 PETSC_EXTERN PetscErrorCode PetscOmpCtrlGetOmpComms(PetscOmpCtrl, MPI_Comm *, MPI_Comm *, PetscBool *);
2340 PETSC_EXTERN PetscErrorCode PetscOmpCtrlDestroy(PetscOmpCtrl *);
2341 PETSC_EXTERN PetscErrorCode PetscOmpCtrlBarrier(PetscOmpCtrl);
2342 PETSC_EXTERN PetscErrorCode PetscOmpCtrlOmpRegionOnMasterBegin(PetscOmpCtrl);
2343 PETSC_EXTERN PetscErrorCode PetscOmpCtrlOmpRegionOnMasterEnd(PetscOmpCtrl);
2344 
2345 PETSC_EXTERN PetscErrorCode PetscSegBufferCreate(size_t, size_t, PetscSegBuffer *);
2346 PETSC_EXTERN PetscErrorCode PetscSegBufferDestroy(PetscSegBuffer *);
2347 PETSC_EXTERN PetscErrorCode PetscSegBufferGet(PetscSegBuffer, size_t, void *);
2348 PETSC_EXTERN PetscErrorCode PetscSegBufferExtractAlloc(PetscSegBuffer, void *);
2349 PETSC_EXTERN PetscErrorCode PetscSegBufferExtractTo(PetscSegBuffer, void *);
2350 PETSC_EXTERN PetscErrorCode PetscSegBufferExtractInPlace(PetscSegBuffer, void *);
2351 PETSC_EXTERN PetscErrorCode PetscSegBufferGetSize(PetscSegBuffer, size_t *);
2352 PETSC_EXTERN PetscErrorCode PetscSegBufferUnuse(PetscSegBuffer, size_t);
2353 
2354 /*MC
2355   PetscSegBufferGetInts - access an array of `PetscInt` from a `PetscSegBuffer`
2356 
2357   Synopsis:
2358   #include <petscsys.h>
2359   PetscErrorCode PetscSegBufferGetInts(PetscSegBuffer seg, size_t count, PetscInt *PETSC_RESTRICT *slot);
2360 
2361   No Fortran Support
2362 
2363   Input Parameters:
2364 + seg   - `PetscSegBuffer` buffer
2365 - count - number of entries needed
2366 
2367   Output Parameter:
2368 . buf - address of new buffer for contiguous data
2369 
2370   Level: intermediate
2371 
2372   Developer Note:
2373   Type-safe wrapper to encourage use of PETSC_RESTRICT. Does not use PetscFunctionBegin because the error handling
2374   prevents the compiler from completely erasing the stub. This is called in inner loops so it has to be as fast as
2375   possible.
2376 
2377 .seealso: `PetscSegBuffer`, `PetscSegBufferGet()`, `PetscInitialize()`, `PetscFinalize()`, `PetscInitializeCalled`
2378 M*/
2379 /* */
2380 static inline PetscErrorCode PetscSegBufferGetInts(PetscSegBuffer seg, size_t count, PetscInt *PETSC_RESTRICT *slot)
2381 {
2382   return PetscSegBufferGet(seg, count, (void **)slot);
2383 }
2384 
2385 extern PetscOptionsHelpPrinted PetscOptionsHelpPrintedSingleton;
2386 PETSC_EXTERN PetscErrorCode    PetscOptionsHelpPrintedDestroy(PetscOptionsHelpPrinted *);
2387 PETSC_EXTERN PetscErrorCode    PetscOptionsHelpPrintedCreate(PetscOptionsHelpPrinted *);
2388 PETSC_EXTERN PetscErrorCode    PetscOptionsHelpPrintedCheck(PetscOptionsHelpPrinted, const char *, const char *, PetscBool *);
2389 
2390 #include <stdarg.h>
2391 PETSC_EXTERN PetscErrorCode PetscVSNPrintf(char *, size_t, const char[], size_t *, va_list);
2392 PETSC_EXTERN                PetscErrorCode (*PetscVFPrintf)(FILE *, const char[], va_list);
2393 
2394 PETSC_EXTERN PetscSegBuffer PetscCitationsList;
2395 
2396 /*@
2397      PetscCitationsRegister - Register a bibtex item to obtain credit for an implemented algorithm used in the code.
2398 
2399      Not Collective; No Fortran Support
2400 
2401      Input Parameters:
2402 +    cite - the bibtex item, formatted to displayed on multiple lines nicely
2403 -    set - a boolean variable initially set to `PETSC_FALSE`; this is used to insure only a single registration of the citation
2404 
2405      Options Database Key:
2406 .     -citations [filename]   - print out the bibtex entries for the given computation
2407 
2408      Level: intermediate
2409 @*/
2410 static inline PetscErrorCode PetscCitationsRegister(const char cit[], PetscBool *set)
2411 {
2412   size_t len;
2413   char  *vstring;
2414 
2415   PetscFunctionBegin;
2416   if (set && *set) PetscFunctionReturn(PETSC_SUCCESS);
2417   PetscCall(PetscStrlen(cit, &len));
2418   PetscCall(PetscSegBufferGet(PetscCitationsList, len, &vstring));
2419   PetscCall(PetscArraycpy(vstring, cit, len));
2420   if (set) *set = PETSC_TRUE;
2421   PetscFunctionReturn(PETSC_SUCCESS);
2422 }
2423 
2424 PETSC_EXTERN PetscErrorCode PetscGoogleDriveAuthorize(MPI_Comm, char[], char[], size_t);
2425 PETSC_EXTERN PetscErrorCode PetscGoogleDriveRefresh(MPI_Comm, const char[], char[], size_t);
2426 PETSC_EXTERN PetscErrorCode PetscGoogleDriveUpload(MPI_Comm, const char[], const char[]);
2427 
2428 PETSC_EXTERN PetscErrorCode PetscBoxAuthorize(MPI_Comm, char[], char[], size_t);
2429 PETSC_EXTERN PetscErrorCode PetscBoxRefresh(MPI_Comm, const char[], char[], char[], size_t);
2430 PETSC_EXTERN PetscErrorCode PetscBoxUpload(MPI_Comm, const char[], const char[]);
2431 
2432 PETSC_EXTERN PetscErrorCode PetscGlobusGetTransfers(MPI_Comm, const char[], char[], size_t);
2433 PETSC_EXTERN PetscErrorCode PetscGlobusAuthorize(MPI_Comm, char[], size_t);
2434 PETSC_EXTERN PetscErrorCode PetscGlobusUpload(MPI_Comm, const char[], const char[]);
2435 
2436 PETSC_EXTERN PetscErrorCode PetscPullJSONValue(const char[], const char[], char[], size_t, PetscBool *);
2437 PETSC_EXTERN PetscErrorCode PetscPushJSONValue(char[], const char[], const char[], size_t);
2438 
2439 #if defined(PETSC_USE_DEBUG)
2440 static inline unsigned int PetscStrHash(const char *str)
2441 {
2442   unsigned int c, hash = 5381;
2443 
2444   while ((c = (unsigned int)*str++)) hash = ((hash << 5) + hash) + c; /* hash * 33 + c */
2445   return hash;
2446 }
2447 
2448   /*MC
2449    MPIU_Allreduce - a PETSc replacement for `MPI_Allreduce()` that tries to determine if the call from all the MPI ranks occur from the
2450                     same place in the PETSc code. This helps to detect bugs where different MPI ranks follow different code paths
2451                     resulting in inconsistent and incorrect calls to `MPI_Allreduce()`.
2452 
2453    Synopsis:
2454      #include <petscsys.h>
2455      PetscErrorCode MPIU_Allreduce(void *indata,void *outdata,PetscMPIInt count,MPI_Datatype datatype, MPI_Op op, MPI_Comm comm);
2456 
2457    Collective
2458 
2459    Input Parameters:
2460 +  a - pointer to the input data to be reduced
2461 .  c - the number of MPI data items in a and b
2462 .  d - the MPI datatype, for example `MPI_INT`
2463 .  e - the MPI operation, for example `MPI_SUM`
2464 -  fcomm - the MPI communicator on which the operation occurs
2465 
2466    Output Parameter:
2467 .  b - the reduced values
2468 
2469    Level: developer
2470 
2471    Notes:
2472    In optimized mode this directly calls `MPI_Allreduce()`
2473 
2474    This is defined as a macro that can return error codes internally so it cannot be used in a subroutine that returns void.
2475 
2476    The error code this returns should be checked with `PetscCall()` even though it looks like an MPI function because it always returns PETSc error codes
2477 
2478 .seealso: `MPI_Allreduce()`
2479 M*/
2480   #define MPIU_Allreduce(a, b, c, d, e, fcomm) \
2481     PetscMacroReturnStandard( \
2482     PetscMPIInt a_b1[6], a_b2[6]; \
2483     int _mpiu_allreduce_c_int = (int)(c); \
2484     a_b1[0] = -(PetscMPIInt)__LINE__; \
2485     a_b1[1] = -a_b1[0]; \
2486     a_b1[2] = -(PetscMPIInt)PetscStrHash(PETSC_FUNCTION_NAME); \
2487     a_b1[3] = -a_b1[2]; \
2488     a_b1[4] = -(PetscMPIInt)(c); \
2489     a_b1[5] = -a_b1[4]; \
2490     \
2491     PetscCallMPI(MPI_Allreduce(a_b1, a_b2, 6, MPI_INT, MPI_MAX, fcomm)); \
2492     PetscCheck(-a_b2[0] == a_b2[1], PETSC_COMM_SELF, PETSC_ERR_PLIB, "MPI_Allreduce() called in different locations (code lines) on different processors"); \
2493     PetscCheck(-a_b2[2] == a_b2[3], PETSC_COMM_SELF, PETSC_ERR_PLIB, "MPI_Allreduce() called in different locations (functions) on different processors"); \
2494     PetscCheck(-a_b2[4] == a_b2[5], PETSC_COMM_SELF, PETSC_ERR_PLIB, "MPI_Allreduce() called with different counts %d on different processors", _mpiu_allreduce_c_int); \
2495     PetscCallMPI(MPI_Allreduce((a), (b), (c), (d), (e), (fcomm)));)
2496 #else
2497   #define MPIU_Allreduce(a, b, c, d, e, fcomm) PetscMacroReturnStandard(PetscCallMPI(MPI_Allreduce((a), (b), (c), (d), (e), (fcomm))))
2498 #endif
2499 
2500 #if defined(PETSC_HAVE_MPI_PROCESS_SHARED_MEMORY)
2501 PETSC_EXTERN PetscErrorCode MPIU_Win_allocate_shared(MPI_Aint, PetscMPIInt, MPI_Info, MPI_Comm, void *, MPI_Win *);
2502 PETSC_EXTERN PetscErrorCode MPIU_Win_shared_query(MPI_Win, PetscMPIInt, MPI_Aint *, PetscMPIInt *, void *);
2503 #endif
2504 
2505 /* this is a vile hack */
2506 #if defined(PETSC_HAVE_NECMPI)
2507   #if !defined(PETSC_NECMPI_VERSION_MAJOR) || !defined(PETSC_NECMPI_VERSION_MINOR) || PETSC_NECMPI_VERSION_MAJOR < 2 || (PETSC_NECMPI_VERSION_MAJOR == 2 && PETSC_NECMPI_VERSION_MINOR < 18)
2508     #define MPI_Type_free(a) (*(a) = MPI_DATATYPE_NULL, 0);
2509   #endif
2510 #endif
2511 
2512 /*
2513     List of external packages and queries on it
2514 */
2515 PETSC_EXTERN PetscErrorCode PetscHasExternalPackage(const char[], PetscBool *);
2516 
2517 /* this cannot go here because it may be in a different shared library */
2518 PETSC_EXTERN PetscErrorCode PCMPIServerBegin(void);
2519 PETSC_EXTERN PetscErrorCode PCMPIServerEnd(void);
2520 PETSC_EXTERN PetscBool      PCMPIServerActive;
2521 PETSC_EXTERN PetscBool      PCMPIServerInSolve;
2522 PETSC_EXTERN PetscBool      PCMPIServerUseShmget;
2523 PETSC_EXTERN PetscErrorCode PetscShmgetAllocateArray(size_t, size_t, void **);
2524 PETSC_EXTERN PetscErrorCode PetscShmgetDeallocateArray(void **);
2525 PETSC_EXTERN PetscErrorCode PetscShmgetMapAddresses(MPI_Comm, PetscInt, const void **, void **);
2526 PETSC_EXTERN PetscErrorCode PetscShmgetUnmapAddresses(PetscInt, void **);
2527 PETSC_EXTERN PetscErrorCode PetscShmgetAddressesFinalize(void);
2528 
2529 typedef struct {
2530   PetscInt n;
2531   void    *addr[3];
2532 } PCMPIServerAddresses;
2533 PETSC_EXTERN PetscErrorCode PCMPIServerAddressesDestroy(void *);
2534 
2535 #define PETSC_HAVE_FORTRAN PETSC_DEPRECATED_MACRO(3, 20, 0, "PETSC_USE_FORTRAN_BINDINGS", ) PETSC_USE_FORTRAN_BINDINGS
2536 
2537 PETSC_EXTERN PetscErrorCode PetscBLASSetNumThreads(PetscInt);
2538 PETSC_EXTERN PetscErrorCode PetscBLASGetNumThreads(PetscInt *);
2539 
2540 /*MC
2541    PetscSafePointerPlusOffset - Checks that a pointer is not `NULL` before applying an offset
2542 
2543    Level: beginner
2544 
2545    Note:
2546    This is needed to avoid errors with undefined-behavior sanitizers such as
2547    UBSan, assuming PETSc has been configured with `-fsanitize=undefined` as part of the compiler flags
2548 M*/
2549 #define PetscSafePointerPlusOffset(ptr, offset) ((ptr) ? (ptr) + (offset) : NULL)
2550