1 // Copyright (c) 2017-2026, Lawrence Livermore National Security, LLC and other CEED contributors.
6 // This file is part of CEED:  http://github.com/ceed
8 #include "ceed-hip-ref.h"
10 #include <ceed.h>
11 #include <ceed/backend.h>
15 #include "../hip/ceed-hip-common.h"
28 int CeedGetHipblasHandle_Hip(Ceed ceed, hipblasHandle_t *handle) {  in CeedGetHipblasHandle_Hip()  argument
31   CeedCallBackend(CeedGetData(ceed, &data));  in CeedGetHipblasHandle_Hip()
33     CeedCallHipblas(ceed, hipblasCreate(&data->hipblas_handle));  in CeedGetHipblasHandle_Hip()
34     CeedCallHipblas(ceed, hipblasSetPointerMode(data->hipblas_handle, HIPBLAS_POINTER_MODE_HOST));  in CeedGetHipblasHandle_Hip()
43 static int CeedInit_Hip_ref(const char *resource, Ceed ceed) {  in CeedInit_Hip_ref()  argument
47   CeedCallBackend(CeedGetResourceRoot(ceed, resource, ":", &resource_root));  in CeedInit_Hip_ref()
48 …CeedCheck(!strcmp(resource_root, "/gpu/hip/ref"), ceed, CEED_ERROR_BACKEND, "Hip backend cannot us…  in CeedInit_Hip_ref()
50   CeedCallBackend(CeedSetDeterministic(ceed, true));  in CeedInit_Hip_ref()
53   CeedCallBackend(CeedSetData(ceed, data));  in CeedInit_Hip_ref()
54   CeedCallBackend(CeedInit_Hip(ceed, resource));  in CeedInit_Hip_ref()
56 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "GetPreferredMemType", CeedGetPreferred…  in CeedInit_Hip_ref()
57   CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "VectorCreate", CeedVectorCreate_Hip));  in CeedInit_Hip_ref()
58 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateTensorH1", CeedBasisCreateT…  in CeedInit_Hip_ref()
59 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateH1", CeedBasisCreateH1_Hip)…  in CeedInit_Hip_ref()
60 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHdiv", CeedBasisCreateHdiv_…  in CeedInit_Hip_ref()
61 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHcurl", CeedBasisCreateHcur…  in CeedInit_Hip_ref()
62 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreate", CeedElemRestri…  in CeedInit_Hip_ref()
63 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreateAtPoints", CeedEl…  in CeedInit_Hip_ref()
64 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionCreate", CeedQFunctionCreate_…  in CeedInit_Hip_ref()
65 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionContextCreate", CeedQFunction…  in CeedInit_Hip_ref()
66 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "OperatorCreate", CeedOperatorCreate_Hi…  in CeedInit_Hip_ref()
67 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "OperatorCreateAtPoints", CeedOperatorC…  in CeedInit_Hip_ref()
68   CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "Destroy", CeedDestroy_Hip));  in CeedInit_Hip_ref()