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