Home
last modified time | relevance | path

Searched refs:PetscCallHIP (Results 1 – 14 of 14) sorted by relevance

/petsc/src/mat/impls/aij/mpi/mpihipsparse/
H A Dmpiaijhipsparse.hip.cxx27 PetscCallHIP(hipFree(coo->Ajmap1)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
28 PetscCallHIP(hipFree(coo->Aperm1)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
29 PetscCallHIP(hipFree(coo->Bjmap1)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
30 PetscCallHIP(hipFree(coo->Bperm1)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
31 PetscCallHIP(hipFree(coo->Aimap2)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
32 PetscCallHIP(hipFree(coo->Ajmap2)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
33 PetscCallHIP(hipFree(coo->Aperm2)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
34 PetscCallHIP(hipFree(coo->Bimap2)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
35 PetscCallHIP(hipFree(coo->Bjmap2)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
36 PetscCallHIP(hipFree(coo->Bperm2)); in MatCOOStructDestroy_MPIAIJHIPSPARSE()
[all …]
/petsc/src/sys/objects/device/tests/
H A Dex2hip.hip.cxx22 …PetscCallHIP(hipStreamSynchronize(NULL)); /* Initialize HIP runtime to get more accurate timing be… in main()
27 else PetscCallHIP(hipMalloc((void **)&ptrs[i], (i + 16) * sizeof(PetscScalar))); in main()
42 else PetscCallHIP(hipFree(ptrs[i])); in main()
/petsc/src/mat/impls/aij/seq/seqhipsparse/
H A Daijhipsparse.hip.cxx280 PetscCallHIP(hipHostMalloc((void **)&AALo, nzLower * sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
283 PetscCallHIP(hipHostMalloc((void **)&AiLo, (n + 1) * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
284 PetscCallHIP(hipHostMalloc((void **)&AjLo, nzLower * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
342 PetscCallHIP(hipMalloc(&loTriFactor->solveBuffer, loTriFactor->solveBufferSize)); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
348 PetscCallHIP(WaitForHIP()); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
354 PetscCallHIP(hipHostFree(AiLo)); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
355 PetscCallHIP(hipHostFree(AjLo)); in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
358 …if (!loTriFactor->AA_h) PetscCallHIP(hipHostMalloc((void **)&loTriFactor->AA_h, nzLower * sizeof(P… in MatSeqAIJHIPSPARSEBuildILULowerTriMatrix()
402 PetscCallHIP(hipHostMalloc((void **)&AAUp, nzUpper * sizeof(PetscScalar))); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
405 PetscCallHIP(hipHostMalloc((void **)&AiUp, (n + 1) * sizeof(PetscInt))); in MatSeqAIJHIPSPARSEBuildILUUpperTriMatrix()
[all …]
/petsc/include/
H A Dpetscdevice_hip.h61 #define PetscCallHIP(...) \ macro
70 #define CHKERRHIP(...) PetscCallHIP(__VA_ARGS__)
75 PetscCallHIP(hipGetLastError()); \
77 PetscCallHIP(hipDeviceSynchronize()); \
/petsc/src/sys/memory/hip/
H A Dmhiphost.hip.cxx6 PetscCallHIP(hipHostMalloc(result, a)); in PetscHIPHostMalloc()
12 PetscCallHIP(hipHostFree(aa)); in PetscHIPHostFree()
/petsc/src/mat/impls/sell/seq/seqhip/
H A Dsellhip.hip.cxx29 if ((*hipstruct)->colidx) PetscCallHIP(hipFree((*hipstruct)->colidx)); in MatSeqSELLHIP_Destroy()
30 if ((*hipstruct)->val) PetscCallHIP(hipFree((*hipstruct)->val)); in MatSeqSELLHIP_Destroy()
31 if ((*hipstruct)->sliidx) PetscCallHIP(hipFree((*hipstruct)->sliidx)); in MatSeqSELLHIP_Destroy()
32 if ((*hipstruct)->chunk_slice_map) PetscCallHIP(hipFree((*hipstruct)->chunk_slice_map)); in MatSeqSELLHIP_Destroy()
48 …PetscCallHIP(hipMemcpy(hipstruct->val, a->val, a->sliidx[a->totalslices] * sizeof(MatScalar), hipM… in MatSeqSELLHIPCopyToGPU()
51 if (hipstruct->colidx) PetscCallHIP(hipFree(hipstruct->colidx)); in MatSeqSELLHIPCopyToGPU()
52 if (hipstruct->val) PetscCallHIP(hipFree(hipstruct->val)); in MatSeqSELLHIPCopyToGPU()
53 if (hipstruct->sliidx) PetscCallHIP(hipFree(hipstruct->sliidx)); in MatSeqSELLHIPCopyToGPU()
54 if (hipstruct->chunk_slice_map) PetscCallHIP(hipFree(hipstruct->chunk_slice_map)); in MatSeqSELLHIPCopyToGPU()
59 … PetscCallHIP(hipMalloc((void **)&hipstruct->colidx, a->maxallocmat * sizeof(*hipstruct->colidx))); in MatSeqSELLHIPCopyToGPU()
[all …]
/petsc/src/mat/impls/hypre/hip/
H A Dhypre2.hip.cxx15 PetscCallHIP(hipGetLastError()); in MatZeroRows_HIP()
/petsc/src/vec/vec/tests/
H A Dex15k.kokkos.cxx23 #define SyncDevice() PetscCallHIP(hipDeviceSynchronize())
/petsc/src/sys/logging/handler/impls/roctx/
H A Dlogroctx.c58 PetscCallHIP(hipDeviceSynchronize()); in PetscLogHandlerEventEnd_ROCTX()
/petsc/src/mat/tests/
H A Dex5k.kokkos.cxx38 #define SyncDevice() PetscCallHIP(hipDeviceSynchronize())
H A Dex6k.kokkos.cxx40 #define SyncDevice() PetscCallHIP(hipDeviceSynchronize())
/petsc/src/tao/unconstrained/tutorials/
H A Drosenbrock4.h317 PetscCallHIP(hipGetLastError()); \
/petsc/doc/changes/
H A D317.md72 - Add `PetscCallHIP()`, `PetscCallHIPBLAS()`, and `PetscCallHIPSOLVER()`. These supersede `CHKERRHI…
/petsc/src/ksp/pc/impls/fieldsplit/
H A Dfieldsplit.c1152 …else if (PetscMemTypeHIP(mtype)) PetscCallHIP(hipMalloc((void **)&array, sizeof(PetscScalar) * m *… in PCSetUpOnBlocks_FieldSplit_Schur()
1493 PetscCallHIP(hipFree(array)); in PCMatApply_FieldSplit_Schur()
1494 PetscCallHIP(hipMalloc((void **)&array, sizeof(PetscScalar) * m * (P + Q))); in PCMatApply_FieldSplit_Schur()