| /petsc/src/sys/ftn-src/ |
| H A D | f90_fwrap.F90 | 10 PetscScalar, pointer :: ptr(:)
12 ptr => array
20 PetscReal, pointer :: ptr(:)
22 ptr => array
30 PetscInt, pointer :: ptr(:)
32 ptr => array
40 PetscMPIInt, pointer :: ptr(:)
42 ptr => array
50 PetscFortranAddr, pointer :: ptr(:)
52 ptr => array
[all …]
|
| /petsc/src/ksp/ksp/tests/raja/ |
| H A D | memoryManager.hpp | 36 T *ptr; in allocate() local
38 cudaErrchk(cudaMallocManaged((void **)&ptr, sizeof(T) * size, cudaMemAttachGlobal)); in allocate()
40 hipErrchk(hipMalloc((void **)&ptr, sizeof(T) * size)); in allocate()
42 ptr = sycl_res->allocate<T>(size); in allocate()
44 ptr = new T[size]; in allocate()
46 return ptr; in allocate()
50 void deallocate(T *&ptr) in deallocate() argument
52 if (ptr) { in deallocate()
54 cudaErrchk(cudaFree(ptr)); in deallocate()
56 hipErrchk(hipFree(ptr)); in deallocate()
[all …]
|
| /petsc/src/ksp/pc/impls/tfs/ |
| H A D | bitmask.c | 18 PetscErrorCode PCTFS_bm_to_proc(char *ptr, PetscInt p_mask, PetscInt *msg_list) in PCTFS_bm_to_proc() argument
25 ptr += (p_mask - 1); in PCTFS_bm_to_proc()
28 if (*ptr & BIT_0) { in PCTFS_bm_to_proc()
32 if (*ptr & BIT_1) { in PCTFS_bm_to_proc()
36 if (*ptr & BIT_2) { in PCTFS_bm_to_proc()
40 if (*ptr & BIT_3) { in PCTFS_bm_to_proc()
44 if (*ptr & BIT_4) { in PCTFS_bm_to_proc()
48 if (*ptr & BIT_5) { in PCTFS_bm_to_proc()
52 if (*ptr & BIT_6) { in PCTFS_bm_to_proc()
56 if (*ptr & BIT_7) { in PCTFS_bm_to_proc()
[all …]
|
| /petsc/src/sys/ftn-custom/ |
| H A D | f90_cwrap.c | 83 PETSC_EXTERN void f90array1ddestroyscalar_(F90Array1d *ptr PETSC_F90_2PTR_PROTO_NOVAR);
86 PETSC_EXTERN void f90array1ddestroyreal_(F90Array1d *ptr PETSC_F90_2PTR_PROTO_NOVAR);
89 PETSC_EXTERN void f90array1ddestroyint_(F90Array1d *ptr PETSC_F90_2PTR_PROTO_NOVAR);
92 PETSC_EXTERN void f90array1ddestroympiint_(F90Array1d *ptr PETSC_F90_2PTR_PROTO_NOVAR);
95 PETSC_EXTERN void f90array1ddestroyfortranaddr_(F90Array1d *ptr PETSC_F90_2PTR_PROTO_NOVAR);
121 …(void *array, MPI_Datatype type, PetscInt start, PetscInt len, F90Array1d *ptr PETSC_F90_2PTR_PROT… in F90Array1dCreate()
126 f90array1dcreatescalar_(array, &start, &len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in F90Array1dCreate()
129 f90array1dcreatereal_(array, &start, &len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in F90Array1dCreate()
132 f90array1dcreateint_(array, &start, &len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in F90Array1dCreate()
138 f90array1dcreatempiint_(array, &start, &len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in F90Array1dCreate()
[all …]
|
| /petsc/src/vec/vec/interface/ftn-custom/ |
| H A D | zvectorf90.c | 24 PETSC_EXTERN void vecgetarraywrite_(Vec *x, F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptrd)) in vecgetarraywrite_() argument
28 if (!ptr) { in vecgetarraywrite_()
36 *ierr = F90Array1dCreate(fa, MPIU_SCALAR, 1, len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in vecgetarraywrite_()
39 PETSC_EXTERN void vecrestorearraywrite_(Vec *x, F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptr… in vecrestorearraywrite_() argument
42 *ierr = F90Array1dAccess(ptr, MPIU_SCALAR, (void **)&fa PETSC_F90_2PTR_PARAM(ptrd)); in vecrestorearraywrite_()
44 *ierr = F90Array1dDestroy(ptr, MPIU_SCALAR PETSC_F90_2PTR_PARAM(ptrd)); in vecrestorearraywrite_()
49 PETSC_EXTERN void vecgetarray_(Vec *x, F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptrd)) in vecgetarray_() argument
53 if (!ptr) { in vecgetarray_()
61 *ierr = F90Array1dCreate(fa, MPIU_SCALAR, 1, len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in vecgetarray_()
64 PETSC_EXTERN void vecrestorearray_(Vec *x, F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptrd)) in vecrestorearray_() argument
[all …]
|
| /petsc/src/sys/objects/device/interface/ |
| H A D | memory.cxx | 35 PETSC_NODISCARD std::size_t operator()(const T *ptr) const noexcept in operator ()()
37 return reinterpret_cast<std::size_t>(ptr); in operator ()()
83 inline bool PointerAttributes::contains(const void *ptr_begin, const void *ptr) const noexcept in contains()
85 return (ptr >= ptr_begin) && (ptr < (static_cast<const char *>(ptr_begin) + size)); in contains()
156 MemoryMap::map_type::const_iterator MemoryMap::search_for(const void *ptr, bool must_find) const no… in search_for() argument
159 auto it = map.find(const_cast<map_type::key_type>(ptr)); in search_for()
166 it = std::find_if(map.begin(), end_it, [ptr](map_type::const_iterator::reference map_it) { in search_for()
167 return map_it.second.contains(map_it.first, ptr); in search_for()
170 …inter %p was not registered with the memory tracker, call PetscDeviceRegisterMemory() on it", ptr); in search_for()
190 static PetscErrorCode PetscDeviceRegisterMemory_Private(const void *PETSC_RESTRICT ptr, PetscMemTyp… in PetscDeviceRegisterMemory_Private() argument
[all …]
|
| /petsc/src/sys/objects/device/tests/ |
| H A D | ex7.c | 22 PetscScalar *ptr, *tmp_ptr; in TestAllocate() local
35 PetscCall(PetscDeviceMalloc(dctx, mtype, n, &ptr)); in TestAllocate()
36 …PetscCheck(ptr, PETSC_COMM_SELF, PETSC_ERR_POINTER, "PetscDeviceMalloc() return NULL pointer for %… in TestAllocate()
39 for (PetscInt i = 0; i < n; ++i) ptr[i] = (PetscScalar)i; in TestAllocate()
41 PetscCall(PetscDeviceFree(dctx, ptr)); in TestAllocate()
67 PetscCall(PetscDeviceCalloc(dctx, mtype, n, &ptr)); in TestAllocate()
68 …PetscCheck(ptr, PETSC_COMM_SELF, PETSC_ERR_POINTER, "PetscDeviceCalloc() returned NULL pointer for… in TestAllocate()
70 tmp_ptr = ptr; in TestAllocate()
73 PetscCall(PetscDeviceArrayCopy(dctx, tmp_ptr, ptr, n)); in TestAllocate()
77 if (tmp_ptr == ptr) { in TestAllocate()
[all …]
|
| /petsc/src/sys/memory/ |
| H A D | mal.c | 57 int *ptr, shift; in PetscMallocAlign() local
62 ptr = (int *)calloc(1 + (mem + 2 * PETSC_MEMALIGN) / sizeof(int), sizeof(int)); in PetscMallocAlign()
64 ptr = (int *)malloc(mem + 2 * PETSC_MEMALIGN); in PetscMallocAlign()
66 PetscCheck(ptr, PETSC_COMM_SELF, PETSC_ERR_MEM, "Memory requested %.0f", (PetscLogDouble)mem); in PetscMallocAlign()
67 shift = (int)(((PETSC_UINTPTR_T)ptr) % PETSC_MEMALIGN); in PetscMallocAlign()
69 ptr[shift - 1] = shift + SHIFT_CLASSID; in PetscMallocAlign()
70 ptr += shift; in PetscMallocAlign()
71 *result = (void *)ptr; in PetscMallocAlign()
79 PETSC_EXTERN PetscErrorCode PetscFreeAlign(void *ptr, int line, const char func[], const char file[… in PetscFreeAlign() argument
81 if (!ptr) return PETSC_SUCCESS; in PetscFreeAlign()
[all …]
|
| /petsc/include/petsc/private/ |
| H A D | mempoison.h | 92 static inline PetscErrorCode PetscPoisonMemoryRegion(const void *ptr, size_t size) in PetscPoisonMemoryRegion() argument
98 ASAN_POISON_MEMORY_REGION(ptr, size); in PetscPoisonMemoryRegion()
100 (void)VALGRIND_MAKE_MEM_NOACCESS(ptr, size); in PetscPoisonMemoryRegion()
101 (void)VALGRIND_MAKE_MEM_UNDEFINED(ptr, size); in PetscPoisonMemoryRegion()
103 (void)ptr; in PetscPoisonMemoryRegion()
126 static inline PetscErrorCode PetscUnpoisonMemoryRegion(const void *ptr, size_t size) in PetscUnpoisonMemoryRegion() argument
132 ASAN_UNPOISON_MEMORY_REGION(ptr, size); in PetscUnpoisonMemoryRegion()
134 (void)VALGRIND_MAKE_MEM_DEFINED(ptr, size); in PetscUnpoisonMemoryRegion()
136 (void)ptr; in PetscUnpoisonMemoryRegion()
165 static inline PetscErrorCode PetscIsRegionPoisoned(const void *ptr, size_t size, PetscBool3 *poison… in PetscIsRegionPoisoned() argument
[all …]
|
| /petsc/src/sys/error/tests/ |
| H A D | ex2.c | 8 PetscInt *ptr; in main() local
13 …PetscCall(PetscMalloc(1024 * 1024 * 8, &ptr)); /* Almost certainly larger than MMAP_THRESHOLD (128… in main()
14 …PetscCheckPointer(ptr, PETSC_INT)) PetscCall(PetscPrintf(PETSC_COMM_SELF, "Mistook valid pointer %… in main()
15 PetscCall(PetscFree(ptr)); in main()
16 …if (PetscCheckPointer(ptr, PETSC_INT)) PetscCall(PetscPrintf(PETSC_COMM_SELF, "Mistook NULL pointe… in main()
17 ptr = (PetscInt *)~(PETSC_UINTPTR_T)0xf; /* Pointer will almost certainly be invalid */ in main()
18 …if (PetscCheckPointer(ptr, PETSC_INT)) PetscCall(PetscPrintf(PETSC_COMM_SELF, "Mistook invalid poi… in main()
|
| /petsc/src/dm/impls/plex/ |
| H A D | plexpoint.c | 62 PetscErrorCode DMPlexPointLocalRead(DM dm, PetscInt point, const PetscScalar *array, void *ptr) in DMPlexPointLocalRead() argument
69 PetscAssertPointer(ptr, 4); in DMPlexPointLocalRead()
71 *(const PetscScalar **)ptr = (start < end) ? array + start : NULL; in DMPlexPointLocalRead()
100 PetscErrorCode DMPlexPointLocalRef(DM dm, PetscInt point, PetscScalar *array, void *ptr) in DMPlexPointLocalRef() argument
107 PetscAssertPointer(ptr, 4); in DMPlexPointLocalRef()
109 *(PetscScalar **)ptr = (start < end) ? array + start : NULL; in DMPlexPointLocalRef()
166 …PlexPointLocalFieldRead(DM dm, PetscInt point, PetscInt field, const PetscScalar *array, void *ptr) in DMPlexPointLocalFieldRead() argument
173 PetscAssertPointer(ptr, 5); in DMPlexPointLocalFieldRead()
175 *(const PetscScalar **)ptr = array + start; in DMPlexPointLocalFieldRead()
197 …Code DMPlexPointLocalFieldRef(DM dm, PetscInt point, PetscInt field, PetscScalar *array, void *ptr) in DMPlexPointLocalFieldRef() argument
[all …]
|
| /petsc/src/sys/error/ |
| H A D | checkptr.c | 75 PetscBool PetscCheckPointer(const void *ptr, PetscDataType dtype) in PetscCheckPointer() argument
78 if (!ptr) return PETSC_FALSE; in PetscCheckPointer()
96 PETSC_UNUSED PetscInt x = *(volatile PetscInt *)ptr; in PetscCheckPointer()
102 … xreal = ((volatile PetscReal *)ptr)[0], ximag = ((volatile PetscReal *)ptr… in PetscCheckPointer()
105 PETSC_UNUSED PetscScalar x = *(volatile PetscScalar *)ptr; in PetscCheckPointer()
111 PETSC_UNUSED PetscReal x = *(volatile PetscReal *)ptr; in PetscCheckPointer()
115 PETSC_UNUSED PetscBool x = *(volatile PetscBool *)ptr; in PetscCheckPointer()
119 PETSC_UNUSED PetscEnum x = *(volatile PetscEnum *)ptr; in PetscCheckPointer()
123 PETSC_UNUSED char x = *(volatile char *)ptr; in PetscCheckPointer()
127 PETSC_UNUSED volatile PetscClassId classid = ((PetscObject)ptr)->classid; in PetscCheckPointer()
|
| /petsc/src/sys/objects/cxx/memory/ |
| H A D | object_pool.cxx | 128 if (const auto ptr = util::exchange(*in_ptr, nullptr)) { in delete_ptr_() local
131 PetscCall(extract_header_(ptr, &header, false)); in delete_ptr_()
182 this->for_each([&](void *&ptr) in clear_()
186 PetscCall(delete_ptr_(&ptr)); in clear_()
386 PetscErrorCode PoolAllocator::get_attributes(const void *ptr, size_type *size, align_type *align) n… in get_attributes() argument
396 PetscCall(extract_header_(const_cast<void *>(ptr), &header, /* check ptr = */ false)); in get_attributes()
426 void *ptr{}; in try_allocate() local
446 ptr = ptr_list.back(); in try_allocate()
448 PetscCall(PetscUnpoisonMemoryRegion(ptr, size)); in try_allocate()
453 *out_ptr = ptr; in try_allocate()
[all …]
|
| /petsc/src/mat/interface/ftn-custom/ |
| H A D | zmatrixf90.c | 104 PETSC_EXTERN void matgetghosts_(Mat *mat, F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptrd)) in matgetghosts_() argument
111 *ierr = F90Array1dCreate((PetscInt *)ghosts, MPIU_INT, 1, N, ptr PETSC_F90_2PTR_PARAM(ptrd)); in matgetghosts_()
113 PETSC_EXTERN void matdensegetarray2d_(Mat *mat, F90Array2d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptr… in matdensegetarray2d_() argument
129 *ierr = F90Array2dCreate(fa, MPIU_SCALAR, 1, m, 1, N, ptr PETSC_F90_2PTR_PARAM(ptrd)); in matdensegetarray2d_()
131 PETSC_EXTERN void matdenserestorearray2d_(Mat *mat, F90Array2d *ptr, int *ierr PETSC_F90_2PTR_PROTO… in matdenserestorearray2d_() argument
134 *ierr = F90Array2dAccess(ptr, MPIU_SCALAR, (void **)&fa PETSC_F90_2PTR_PARAM(ptrd)); in matdenserestorearray2d_()
136 *ierr = F90Array2dDestroy(ptr, MPIU_SCALAR PETSC_F90_2PTR_PARAM(ptrd)); in matdenserestorearray2d_()
140 PETSC_EXTERN void matdensegetarrayread2d_(Mat *mat, F90Array2d *ptr, int *ierr PETSC_F90_2PTR_PROTO… in matdensegetarrayread2d_() argument
156 *ierr = F90Array2dCreate((void **)fa, MPIU_SCALAR, 1, m, 1, N, ptr PETSC_F90_2PTR_PARAM(ptrd)); in matdensegetarrayread2d_()
158 PETSC_EXTERN void matdenserestorearrayread2d_(Mat *mat, F90Array2d *ptr, int *ierr PETSC_F90_2PTR_P… in matdenserestorearrayread2d_() argument
[all …]
|
| H A D | zmatrixf.c | 35 …(Mat *mat, PetscInt *n, IS *isrow, IS *iscol, MatReuse *scall, F90Array1d *ptr, PetscErrorCode *ie… in matcreatesubmatrices_() argument
41 *ierr = F90Array1dCreate(lsmat, MPIU_FORTRANADDR, 1, *n + 1, ptr PETSC_F90_2PTR_PARAM(ptrd)); in matcreatesubmatrices_()
43 *ierr = F90Array1dAccess(ptr, MPIU_FORTRANADDR, (void **)&lsmat PETSC_F90_2PTR_PARAM(ptrd)); in matcreatesubmatrices_()
48 …(Mat *mat, PetscInt *n, IS *isrow, IS *iscol, MatReuse *scall, F90Array1d *ptr, PetscErrorCode *ie… in matcreatesubmatricesmpi_() argument
55 *ierr = F90Array1dCreate(lsmat, MPIU_FORTRANADDR, 1, *n + 1, ptr PETSC_F90_2PTR_PARAM(ptrd)); in matcreatesubmatricesmpi_()
57 *ierr = F90Array1dAccess(ptr, MPIU_FORTRANADDR, (void **)&lsmat PETSC_F90_2PTR_PARAM(ptrd)); in matcreatesubmatricesmpi_()
63 PETSC_EXTERN void matdestroymatrices_(PetscInt *n, F90Array1d *ptr, PetscErrorCode *ierr PETSC_F90_… in matdestroymatrices_() argument
68 *ierr = F90Array1dAccess(ptr, MPIU_FORTRANADDR, (void **)&lsmat PETSC_F90_2PTR_PARAM(ptrd)); in matdestroymatrices_()
75 *ierr = F90Array1dDestroy(ptr, MPIU_FORTRANADDR PETSC_F90_2PTR_PARAM(ptrd)); in matdestroymatrices_()
80 PETSC_EXTERN void matdestroysubmatrices_(PetscInt *n, F90Array1d *ptr, PetscErrorCode *ierr PETSC_F… in matdestroysubmatrices_() argument
[all …]
|
| /petsc/include/ |
| H A D | petscdevice.h | 144 …pe, n, ptr) PetscDeviceAllocate_Private((dctx), PETSC_FALSE, (mtype), (size_t)(n) * sizeof(**(ptr)… argument
178 …ype, n, ptr) PetscDeviceAllocate_Private((dctx), PETSC_TRUE, (mtype), (size_t)(n) * sizeof(**(ptr)… argument
215 #define PetscDeviceFree(dctx, ptr) ((PetscErrorCode)(PetscDeviceDeallocate_Private((dctx), (ptr)) |… argument
300 #define PetscDeviceArrayZero(dctx, ptr, n) PetscDeviceMemset((dctx), (ptr), 0, (size_t)(n) * sizeof… argument
|
| /petsc/src/vec/is/is/interface/ftn-custom/ |
| H A D | zindexf90.c | 16 PETSC_EXTERN void petsclayoutgetranges_(PetscLayout *map, F90Array1d *ptr, int *ierr PETSC_F90_2PTR… in petsclayoutgetranges_() argument
25 …*ierr = F90Array1dCreate((void *)fa, MPIU_INT, 1, (PetscInt)size + 1, ptr PETSC_F90_2PTR_PARAM(ptr… in petsclayoutgetranges_()
28 PETSC_EXTERN void petsclayoutrestoreranges_(PetscLayout *map, F90Array1d *ptr, int *ierr PETSC_F90_… in petsclayoutrestoreranges_() argument
30 *ierr = F90Array1dDestroy(ptr, MPIU_INT PETSC_F90_2PTR_PARAM(ptrd)); in petsclayoutrestoreranges_()
33 PETSC_EXTERN void isgetindices_(IS *x, F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptrd)) in isgetindices_() argument
42 *ierr = F90Array1dCreate((void *)fa, MPIU_INT, 1, len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in isgetindices_()
44 PETSC_EXTERN void isrestoreindices_(IS *x, F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptrd)) in isrestoreindices_() argument
48 *ierr = F90Array1dAccess(ptr, MPIU_INT, (void **)&fa PETSC_F90_2PTR_PARAM(ptrd)); in isrestoreindices_()
50 *ierr = F90Array1dDestroy(ptr, MPIU_INT PETSC_F90_2PTR_PARAM(ptrd)); in isrestoreindices_()
|
| /petsc/include/petsc/private/cpp/ |
| H A D | object_pool.hpp | 153 auto &&ptr = *it; in for_each()
155 PetscCall(unpoison(ptr, &size)); in for_each()
156 PetscCall(callable(ptr)); in for_each()
157 if (ptr) { in for_each()
158 PetscCall(repoison(ptr, size)); in for_each()
245 PetscErrorCode construct(value_type *ptr, Args &&...args) const noexcept in construct() argument
248 PetscCall(this->underlying().construct_(ptr, std::forward<Args>(args)...)); in construct()
252 PetscErrorCode destroy(value_type *ptr) const noexcept in destroy()
257 PetscCall(underlying.destroy_(ptr)); in destroy()
271 PetscErrorCode invalidate(value_type *ptr) const noexcept in invalidate()
[all …]
|
| /petsc/src/dm/impls/plex/tutorials/ |
| H A D | ex4f90.F90 | 30 print *, tab(1)%ptr%T(1)%ptr
31 print *, tab(1)%ptr%T(2)%ptr
32 print *, tab(2)%ptr%T(1)%ptr
33 print *, tab(2)%ptr%T(2)%ptr
|
| /petsc/src/vec/is/sf/utils/ftn-custom/ |
| H A D | zsfutilsf90.c | 15 PETSC_EXTERN void petscsfdestroyremoteoffsets_(F90Array1d *ptr, int *ierr PETSC_F90_2PTR_PROTO(ptrd… in petscsfdestroyremoteoffsets_() argument
18 *ierr = F90Array1dAccess(ptr, MPIU_INT, (void **)&fa PETSC_F90_2PTR_PARAM(ptrd)); in petscsfdestroyremoteoffsets_()
20 *ierr = F90Array1dDestroy(ptr, MPIU_INT PETSC_F90_2PTR_PARAM(ptrd)); in petscsfdestroyremoteoffsets_()
25 PETSC_EXTERN void petscsfdistributesection_(PetscSF *sf, PetscSection *rootSection, F90Array1d *ptr… in petscsfdistributesection_() argument
27 if (ptr == PETSC_NULL_INTEGER_POINTER_Fortran) { in petscsfdistributesection_()
37 …*ierr = F90Array1dCreate((void *)fa, MPIU_INT, 1, lpEnd - lpStart, ptr PETSC_F90_2PTR_PARAM(ptrd)); in petscsfdistributesection_()
41 …pointSF, PetscSection *rootSection, PetscSection *leafSection, F90Array1d *ptr, int *ierr PETSC_F9… in petscsfcreateremoteoffsets_() argument
50 …*ierr = F90Array1dCreate((void *)fa, MPIU_INT, 1, lpEnd - lpStart, ptr PETSC_F90_2PTR_PARAM(ptrd)); in petscsfcreateremoteoffsets_()
|
| /petsc/src/vec/ftn-mod/ |
| H A D | petscvecmod.F90 | 19 PetscSFNode, pointer :: ptr(:)
20 ptr => array
29 PetscSFNode, pointer :: ptr(:)
30 nullify (ptr)
41 subroutine PetscSFDestroyRemoteOffsets(ptr, ierr)
44 PetscInt, pointer :: ptr(:)
|
| /petsc/src/snes/interface/ftn-custom/ |
| H A D | zsnesf.c | 89 void *ptr; in ourtrprecheckfunction() local
90 …rtranCallback((PetscObject)snes, PETSC_FORTRAN_CALLBACK_CLASS, _cb.trprecheck_pgiptr, NULL, &ptr)); in ourtrprecheckfunction()
92 …e *PETSC_F90_2PTR_PROTO_NOVAR), (&snes, &x, &y, changed_y, _ctx, &ierr PETSC_F90_2PTR_PARAM(ptr))); in ourtrprecheckfunction()
95 …SNES, Vec, Vec, PetscBool *, void *), PetscCtx ctx, PetscErrorCode *ierr PETSC_F90_2PTR_PROTO(ptr)) in snesnewtontrsetprecheck_() argument
100 …rtranCallback((PetscObject)*snes, PETSC_FORTRAN_CALLBACK_CLASS, &_cb.trprecheck_pgiptr, NULL, ptr); in snesnewtontrsetprecheck_()
106 …SNES, Vec, Vec, PetscBool *, void *), PetscCtx ctx, PetscErrorCode *ierr PETSC_F90_2PTR_PROTO(ptr)) in snesnewtontrdcsetprecheck_() argument
111 …rtranCallback((PetscObject)*snes, PETSC_FORTRAN_CALLBACK_CLASS, &_cb.trprecheck_pgiptr, NULL, ptr); in snesnewtontrdcsetprecheck_()
120 void *ptr; in ourtrpostcheckfunction() local
121 …tranCallback((PetscObject)snes, PETSC_FORTRAN_CALLBACK_CLASS, _cb.trpostcheck_pgiptr, NULL, &ptr)); in ourtrpostcheckfunction()
123 …TR_PROTO_NOVAR), (&snes, &x, &y, &w, changed_y, changed_w, _ctx, &ierr PETSC_F90_2PTR_PARAM(ptr))); in ourtrpostcheckfunction()
[all …]
|
| /petsc/src/vec/vec/tutorials/ |
| H A D | ex21.c | 22 PETSC_INTERN void f90array1ddestroymystruct_(F90Array1d *ptr PETSC_F90_2PTR_PROTO_NOVAR);
29 PETSC_INTERN void vecgetarraymystruct_(Vec *x, F90Array1d *ptr, int *__ierr PETSC_F90_2PTR_PROTO(pt… in vecgetarraymystruct_() argument
33 if (!ptr) { in vecgetarraymystruct_()
41 f90array1dcreatemystruct_(fa, &one, &len, ptr PETSC_F90_2PTR_PARAM(ptrd)); in vecgetarraymystruct_()
44 PETSC_INTERN void vecrestorearraymystruct_(Vec *x, F90Array1d *ptr, int *__ierr PETSC_F90_2PTR_PROT… in vecrestorearraymystruct_() argument
47 f90array1daccessmystruct_(ptr, (void **)&fa PETSC_F90_2PTR_PARAM(ptrd)); in vecrestorearraymystruct_()
48 f90array1ddestroymystruct_(ptr PETSC_F90_2PTR_PARAM(ptrd)); in vecrestorearraymystruct_()
|
| /petsc/src/sys/objects/device/impls/ |
| H A D | segmentedmempool.hpp | 409 inline bool MemoryBlock<T, A, S>::owns_pointer(const T *ptr) const noexcept in owns_pointer()
412 return (ptr >= mem_) && (ptr < std::next(mem_, size())); in owns_pointer()
430 inline PetscErrorCode MemoryBlock<T, A, S>::try_allocate_chunk(size_type req_size, T **ptr, const s… in try_allocate_chunk() argument
443 *ptr = mem_ + block_alloced; in try_allocate_chunk()
453 *ptr = mem_ + chunk.start(); in try_allocate_chunk()
514 inline PetscErrorCode MemoryBlock<T, A, S>::try_deallocate_chunk(T **ptr, const stream_type *stream… in try_deallocate_chunk() argument
519 PetscCall(try_find_chunk(*ptr, &chunk)); in try_deallocate_chunk()
522 *ptr = nullptr; in try_deallocate_chunk()
540 inline PetscErrorCode MemoryBlock<T, A, S>::try_find_chunk(const T *ptr, chunk_type **ret_chunk) no… in try_find_chunk() argument
544 if (owns_pointer(ptr)) { in try_find_chunk()
[all …]
|
| /petsc/src/sys/objects/device/impls/cupm/ |
| H A D | cupmallocator.hpp | 49 inline PetscErrorCode HostAllocator<T, P>::allocate(value_type **ptr, size_type n, const StreamBase… in allocate() argument
52 PetscCall(PetscCUPMMallocHost(ptr, n)); in allocate()
58 inline PetscErrorCode HostAllocator<T, P>::deallocate(value_type *ptr, const StreamBase<U> *) noexc… in deallocate() argument
61 PetscCallCUPM(cupmFreeHost(ptr)); in deallocate()
104 inline PetscErrorCode DeviceAllocator<T, P>::allocate(value_type **ptr, size_type n, const StreamBa… in allocate() argument
107 PetscCall(PetscCUPMMallocAsync(ptr, n, stream->get_stream())); in allocate()
113 inline PetscErrorCode DeviceAllocator<T, P>::deallocate(value_type *ptr, const StreamBase<U> *strea… in deallocate() argument
116 PetscCallCUPM(cupmFreeAsync(ptr, stream->get_stream())); in deallocate()
122 inline PetscErrorCode DeviceAllocator<T, P>::zero(value_type *ptr, size_type n, const StreamBase<U>… in zero() argument
125 PetscCall(PetscCUPMMemsetAsync(ptr, 0, n, stream->get_stream(), true)); in zero()
[all …]
|