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