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