1 // Copyright (c) 2017-2026, Lawrence Livermore National Security, LLC and other CEED contributors.
2 // All Rights Reserved. See the top-level LICENSE and NOTICE files for details.
4 // SPDX-License-Identifier: BSD-2-Clause
6 // This file is part of CEED:  http://github.com/ceed
8 #include "ceed-cuda-ref.h"
10 #include <ceed.h>
11 #include <ceed/backend.h>
15 #include "../cuda/ceed-cuda-common.h"
17 //------------------------------------------------------------------------------
19 //------------------------------------------------------------------------------
25 //------------------------------------------------------------------------------
27 //------------------------------------------------------------------------------
28 int CeedGetCublasHandle_Cuda(Ceed ceed, cublasHandle_t *handle) {  in CeedGetCublasHandle_Cuda()  argument
31   CeedCallBackend(CeedGetData(ceed, &data));  in CeedGetCublasHandle_Cuda()
32   if (!data->cublas_handle) CeedCallCublas(ceed, cublasCreate(&data->cublas_handle));  in CeedGetCublasHandle_Cuda()
33   *handle = data->cublas_handle;  in CeedGetCublasHandle_Cuda()
37 //------------------------------------------------------------------------------
39 //------------------------------------------------------------------------------
40 static int CeedInit_Cuda_ref(const char *resource, Ceed ceed) {  in CeedInit_Cuda_ref()  argument
44   CeedCallBackend(CeedGetResourceRoot(ceed, resource, ":", &resource_root));  in CeedInit_Cuda_ref()
45 …CeedCheck(!strcmp(resource_root, "/gpu/cuda/ref"), ceed, CEED_ERROR_BACKEND, "Cuda backend cannot …  in CeedInit_Cuda_ref()
47   CeedCallBackend(CeedSetDeterministic(ceed, true));  in CeedInit_Cuda_ref()
50   CeedCallBackend(CeedSetData(ceed, data));  in CeedInit_Cuda_ref()
51   CeedCallBackend(CeedInit_Cuda(ceed, resource));  in CeedInit_Cuda_ref()
53 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "GetPreferredMemType", CeedGetPreferred…  in CeedInit_Cuda_ref()
54 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "VectorCreate", CeedVectorCreate_Cuda));  in CeedInit_Cuda_ref()
55 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateTensorH1", CeedBasisCreateT…  in CeedInit_Cuda_ref()
56 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateH1", CeedBasisCreateH1_Cuda…  in CeedInit_Cuda_ref()
57 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHdiv", CeedBasisCreateHdiv_…  in CeedInit_Cuda_ref()
58 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHcurl", CeedBasisCreateHcur…  in CeedInit_Cuda_ref()
59 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreate", CeedElemRestri…  in CeedInit_Cuda_ref()
60 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreateAtPoints", CeedEl…  in CeedInit_Cuda_ref()
61 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionCreate", CeedQFunctionCreate_…  in CeedInit_Cuda_ref()
62 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionContextCreate", CeedQFunction…  in CeedInit_Cuda_ref()
63 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "OperatorCreate", CeedOperatorCreate_Cu…  in CeedInit_Cuda_ref()
64 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "OperatorCreateAtPoints", CeedOperatorC…  in CeedInit_Cuda_ref()
65   CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "Destroy", CeedDestroy_Cuda));  in CeedInit_Cuda_ref()
69 //------------------------------------------------------------------------------
71 //------------------------------------------------------------------------------
74 //------------------------------------------------------------------------------