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