| /petsc/src/sys/objects/device/util/ |
| H A D | memory.c | 36 cudaError_t cerr; in PetscGetMemType() local
39 …cerr = cudaPointerGetAttributes(&attr, ptr); /* Do not check error since before CUDA 11.0, passing… in PetscGetMemType()
40 …if (cerr) cerr = cudaGetLastError(); /* If there was an error, return it and then reset it… in PetscGetMemType()
46 if (cerr == cudaSuccess && mtype == cudaMemoryTypeDevice) *type = PETSC_MEMTYPE_DEVICE; in PetscGetMemType()
53 hipError_t cerr; in PetscGetMemType() local
56 cerr = hipPointerGetAttributes(&attr, ptr); in PetscGetMemType()
57 if (cerr) cerr = hipGetLastError(); in PetscGetMemType()
63 if (cerr == hipSuccess && mtype == hipMemoryTypeDevice) *type = PETSC_MEMTYPE_DEVICE; in PetscGetMemType()
|
| /petsc/src/sys/objects/device/tests/ |
| H A D | ex2cu.cu | 14 cudaError_t cerr; in main() local
32 cerr = cudaPointerGetAttributes(&attr, ptrs[i]); in main()
33 if (cerr) cerr = cudaGetLastError(); in main()
|
| H A D | ex2hip.hip.cxx | 14 hipError_t cerr; in main() local
32 cerr = hipPointerGetAttributes(&attr, ptrs[i]); in main()
33 if (cerr) cerr = hipGetLastError(); in main()
|
| /petsc/src/sys/objects/device/impls/cupm/ |
| H A D | cupmdevice.cxx | 260 } else if (const auto cerr = cupmGetDeviceCount(&ndev)) { in initialize() local
263 …mName(), cupmName(), static_cast<PetscErrorCode>(cerr), cupmGetErrorName(cerr), cupmGetErrorString… in initialize()
267 initId.first = -static_cast<decltype(initId.first)>(cerr); in initialize()
314 const auto cerr = static_cast<cupmError_t>(-defaultDevice_); in init_device_id_() local
318 …) : %s", cupmName(), static_cast<PetscErrorCode>(cerr), cupmGetErrorName(cerr), cupmGetErrorString… in init_device_id_()
|
| H A D | cupmcontext.hpp | 130 const auto cerr = cupmSolverCreate(&handle); in initialize_handle_() local
131 if (PetscLikely(cerr == CUPMSOLVER_STATUS_SUCCESS)) break; in initialize_handle_()
132 …if ((cerr != CUPMSOLVER_STATUS_NOT_INITIALIZED) && (cerr != CUPMSOLVER_STATUS_ALLOC_FAILED)) Petsc… in initialize_handle_()
137 …PetscCheck(cerr == CUPMSOLVER_STATUS_SUCCESS, PETSC_COMM_SELF, PETSC_ERR_GPU_RESOURCE, "Unable to … in initialize_handle_()
328 switch (auto cerr = cupmStreamQuery(impls_cast_(dctx)->stream.get_stream())) { in query() local
335 cerr = cupmGetLastError(); in query()
336 static_cast<void>(cerr); in query()
339 PetscCallCUPM(cerr); in query()
539 const auto cerr = cupmStreamQuery(stream); in memCopy() local
542 if (cerr == cupmSuccess) { in memCopy()
[all …]
|
| /petsc/include/petsc/private/ |
| H A D | cupminterface.hpp | 574 cupmError_t cerr; in PetscCUPMGetMemType() local
588 cerr = cupmPointerGetAttributes(&attr, data); in PetscCUPMGetMemType()
589 cerr = cupmGetLastError(); in PetscCUPMGetMemType()
593 if (managed) *managed = static_cast<PetscBool>((cerr == cupmSuccess) && attr.isManaged); in PetscCUPMGetMemType()
595 if (PETSC_PKG_CUDA_VERSION_GE(11, 0, 0) && (T == DeviceType::CUDA)) PetscCallCUPM(cerr); in PetscCUPMGetMemType()
599 …if (type) *type = ((cerr == cupmSuccess) && (mtype == cupmMemoryTypeDevice)) ? PETSC_MEMTYPE_CUPM(… in PetscCUPMGetMemType()
600 …if (registered && (cerr == cupmSuccess) && (mtype == cupmMemoryTypeHost)) *registered = PETSC_TRUE; in PetscCUPMGetMemType()
695 auto cerr = cupmGetLastError(); in PetscCUPMMemcpyAsync() local
697 if (PetscUnlikely(cerr != cupmErrorNotReady)) PetscCallCUPM(cerr); in PetscCUPMMemcpyAsync()
800 auto cerr = interface_type::cupmFreeAsync(std::forward<M>(ptr), stream); in cupmFreeAsync() local
[all …]
|
| /petsc/src/vec/is/sf/impls/basic/nvshmem/ |
| H A D | sfnvshmem.cu | 76 cudaError_t cerr; in PetscSFSetUp_Basic_NVSHMEM() local
216 cudaError_t cerr; in PetscSFLinkBuildDependenceBegin() local
231 cudaError_t cerr; in PetscSFLinkBuildDependenceEnd() local
341 cudaError_t cerr; in PetscSFLinkGetDataBegin_NVSHMEM() local
437 cudaError_t cerr; in PetscSFLinkGetDataEnd_NVSHMEM() local
516 cudaError_t cerr; in PetscSFLinkPutDataBegin_NVSHMEM() local
608 cudaError_t cerr; in PetscSFLinkPutDataEnd_NVSHMEM() local
670 cudaError_t cerr; in PetscSFLinkDestroy_NVSHMEM() local
689 cudaError_t cerr; in PetscSFLinkCreate_NVSHMEM() local
|
| /petsc/src/ksp/ksp/tests/ |
| H A D | ex63.cxx | 119 …if (cmdp.parse(argc, argv) != Teuchos::CommandLineProcessor::PARSE_SUCCESSFUL) std::cerr << "Optio… in main()
123 std::cerr << solver_name << " not enabled. Exiting..." << std::endl; in main()
|
| /petsc/src/sys/mpiuni/ |
| H A D | mpi.c | 66 cudaError_t cerr = cudaMemcpy(dst, src, n, cudaMemcpyDefault); in MPIUNI_Memcpy() local
67 if (cerr != cudaSuccess) return MPI_FAILURE; in MPIUNI_Memcpy()
71 hipError_t cerr = hipMemcpy(dst, src, n, hipMemcpyDefault); in MPIUNI_Memcpy()
72 if (cerr != hipSuccess) return MPI_FAILURE; in MPIUNI_Memcpy()
|
| /petsc/src/mat/graphops/partition/impls/chaco/ |
| H A D | chaco.c | 53 int cerr; in MatPartitioningApply_Chaco() local
138 …cerr = interface(nvtxs, start, adjacency, vwgts, NULL, NULL, NULL, NULL, NULL, NULL, assignment, a… in MatPartitioningApply_Chaco()
153 PetscCheck(!cerr, PETSC_COMM_SELF, PETSC_ERR_LIB, "Chaco failed"); in MatPartitioningApply_Chaco()
|
| /petsc/src/ksp/pc/impls/gamg/ |
| H A D | gamg.c | 94 cudaError_t cerr; in PCGAMGCreateLevel_GAMG() local
103 cerr = cudaGetDeviceCount(&devCount); in PCGAMGCreateLevel_GAMG()
105 if (cerr == cudaSuccess && devCount >= 1) { /* There are devices, else go to heuristic */ in PCGAMGCreateLevel_GAMG()
|
| /petsc/src/mat/impls/aij/seq/seqcusparse/ |
| H A D | aijcusparse.cu | 2791 cublasStatus_t cerr; in MatProductNumeric_SeqAIJCUSPARSE_SeqDENSECUDA() local
2794 …cerr = cublasXgeam(cublasv2handle, CUBLAS_OP_T, CUBLAS_OP_T, B->cmap->n, B->rmap->n, &PETSC_CUSPAR… in MatProductNumeric_SeqAIJCUSPARSE_SeqDENSECUDA()
2795 PetscCallCUBLAS(cerr); in MatProductNumeric_SeqAIJCUSPARSE_SeqDENSECUDA()
|
| /petsc/lib/petsc/bin/maint/ |
| H A D | toclapack.sh | 4947 { flag cerr;
|