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