| /libCEED/backends/cuda-ref/ |
| H A D | ceed-cuda-ref.c | 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()
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()
[all …]
|
| H A D | ceed-cuda-ref-basis.c | 24 Ceed ceed; in CeedBasisApplyCore_Cuda() local
32 CeedCallBackend(CeedBasisGetCeed(basis, &ceed)); in CeedBasisApplyCore_Cuda()
37 …else CeedCheck(eval_mode == CEED_EVAL_WEIGHT, ceed, CEED_ERROR_BACKEND, "An input vector is requir… in CeedBasisApplyCore_Cuda()
54 CeedCallBackend(CeedRunKernel_Cuda(ceed, data->Interp, num_elem, block_size, interp_args)); in CeedBasisApplyCore_Cuda()
60 CeedCallBackend(CeedRunKernel_Cuda(ceed, data->Grad, num_elem, block_size, grad_args)); in CeedBasisApplyCore_Cuda()
63 …CeedCheck(data->d_q_weight_1d, ceed, CEED_ERROR_BACKEND, "%s not supported; q_weights_1d not set",… in CeedBasisApplyCore_Cuda()
68 …CeedCallBackend(CeedRunKernelDim_Cuda(ceed, data->Weight, num_elem, block_size_x, block_size_y, 1,… in CeedBasisApplyCore_Cuda()
75 return CeedError(ceed, CEED_ERROR_BACKEND, "%s not supported", CeedEvalModes[eval_mode]); in CeedBasisApplyCore_Cuda()
83 CeedCallBackend(CeedDestroy(&ceed)); in CeedBasisApplyCore_Cuda()
104 Ceed ceed; in CeedBasisApplyAtPointsCore_Cuda() local
[all …]
|
| /libCEED/backends/hip-ref/ |
| H A D | ceed-hip-ref.c | 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()
[all …]
|
| H A D | ceed-hip-ref-basis.c | 23 Ceed ceed; in CeedBasisApplyCore_Hip() local
31 CeedCallBackend(CeedBasisGetCeed(basis, &ceed)); in CeedBasisApplyCore_Hip()
36 …else CeedCheck(eval_mode == CEED_EVAL_WEIGHT, ceed, CEED_ERROR_BACKEND, "An input vector is requir… in CeedBasisApplyCore_Hip()
54 CeedCallBackend(CeedRunKernel_Hip(ceed, data->Interp, num_elem, block_size, interp_args)); in CeedBasisApplyCore_Hip()
60 CeedCallBackend(CeedRunKernel_Hip(ceed, data->Grad, num_elem, block_size, grad_args)); in CeedBasisApplyCore_Hip()
63 …CeedCheck(data->d_q_weight_1d, ceed, CEED_ERROR_BACKEND, "%s not supported; q_weights_1d not set",… in CeedBasisApplyCore_Hip()
68 …CeedCallBackend(CeedRunKernelDim_Hip(ceed, data->Weight, num_elem, block_size_x, block_size_y, 1, … in CeedBasisApplyCore_Hip()
75 return CeedError(ceed, CEED_ERROR_BACKEND, "%s not supported", CeedEvalModes[eval_mode]); in CeedBasisApplyCore_Hip()
83 CeedCallBackend(CeedDestroy(&ceed)); in CeedBasisApplyCore_Hip()
103 Ceed ceed; in CeedBasisApplyAtPointsCore_Hip() local
[all …]
|
| /libCEED/backends/ref/ |
| H A D | ceed-ref.c | 17 static int CeedInit_Ref(const char *resource, Ceed ceed) { in CeedInit_Ref() argument
18 …pu/self") || !strcmp(resource, "/cpu/self/ref") || !strcmp(resource, "/cpu/self/ref/serial"), ceed, in CeedInit_Ref()
20 CeedCallBackend(CeedSetDeterministic(ceed, true)); in CeedInit_Ref()
22 CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "VectorCreate", CeedVectorCreate_Ref)); in CeedInit_Ref()
23 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateTensorH1", CeedBasisCreateT… in CeedInit_Ref()
24 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateH1", CeedBasisCreateH1_Ref)… in CeedInit_Ref()
25 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHdiv", CeedBasisCreateHdiv_… in CeedInit_Ref()
26 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHcurl", CeedBasisCreateHcur… in CeedInit_Ref()
27 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "TensorContractCreate", CeedTensorContr… in CeedInit_Ref()
28 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreate", CeedElemRestri… in CeedInit_Ref()
[all …]
|
| /libCEED/examples/fluids/src/ |
| H A D | setuplibceed.c | 18 Ceed ceed = user->ceed; in CreateKSPMassOperator_Unstabilized() local
31 PetscCallCeed(ceed, CeedOperatorCompositeGetSubList(user->op_rhs_ctx->op, &sub_ops)); in CreateKSPMassOperator_Unstabilized()
32 PetscCallCeed(ceed, CeedOperatorGetFieldByName(sub_ops[sub_op_index], "q", &field)); in CreateKSPMassOperator_Unstabilized()
33 PetscCallCeed(ceed, CeedOperatorFieldGetData(field, NULL, &elem_restr_q, &basis_q, NULL)); in CreateKSPMassOperator_Unstabilized()
35 PetscCallCeed(ceed, CeedOperatorGetFieldByName(sub_ops[sub_op_index], "qdata", &field)); in CreateKSPMassOperator_Unstabilized()
36 PetscCallCeed(ceed, CeedOperatorFieldGetData(field, NULL, &elem_restr_qd_i, NULL, &q_data)); in CreateKSPMassOperator_Unstabilized()
39 PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(elem_restr_q, &num_comp_q)); in CreateKSPMassOperator_Unstabilized()
40 PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(elem_restr_qd_i, &q_data_size)); in CreateKSPMassOperator_Unstabilized()
42 PetscCall(CreateMassQFunction(ceed, num_comp_q, q_data_size, &qf_mass)); in CreateKSPMassOperator_Unstabilized()
43 PetscCallCeed(ceed, CeedOperatorCreate(ceed, qf_mass, NULL, NULL, op_mass)); in CreateKSPMassOperator_Unstabilized()
[all …]
|
| H A D | strong_boundary_conditions.c | 16 PetscErrorCode SetupStrongSTG_Ceed(Ceed ceed, CeedData ceed_data, DM dm, ProblemData problem, Simpl… in SetupStrongSTG_Ceed() argument
36 PetscCall(CreateBasisFromPlex(ceed, dm, label, label_value, height, dm_field, &basis_q_sur)); in SetupStrongSTG_Ceed()
37 …PetscCall(CreateBasisFromPlex(ceed, dm_coord, label, label_value, height, dm_field, &basis_x_sur)); in SetupStrongSTG_Ceed()
39 PetscCallCeed(ceed, CeedBasisCreateProjection(basis_x_sur, basis_q_sur, &basis_x_to_q_sur)); in SetupStrongSTG_Ceed()
41 PetscCallCeed(ceed, CeedBasisDestroy(&basis_q_sur)); in SetupStrongSTG_Ceed()
42 PetscCallCeed(ceed, CeedBasisDestroy(&basis_x_sur)); in SetupStrongSTG_Ceed()
46 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, SetupStrongBC, SetupStrongBC_loc, &qf_set… in SetupStrongSTG_Ceed()
47 PetscCallCeed(ceed, CeedQFunctionAddInput(qf_setup, "x", num_comp_x, CEED_EVAL_INTERP)); in SetupStrongSTG_Ceed()
48 …PetscCallCeed(ceed, CeedQFunctionAddInput(qf_setup, "dxdX", num_comp_x * dim_boundary, CEED_EVAL_G… in SetupStrongSTG_Ceed()
49 PetscCallCeed(ceed, CeedQFunctionAddInput(qf_setup, "multiplicity", num_comp_q, CEED_EVAL_NONE)); in SetupStrongSTG_Ceed()
[all …]
|
| H A D | qdata.c | 73 PetscErrorCode QDataGet(Ceed ceed, DM dm, DMLabel domain_label, PetscInt label_value, CeedElemRestr… in QDataGet() argument
82 PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(elem_restr_x, &num_comp_x)); in QDataGet()
88 … PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, Setup2d, Setup2d_loc, &qf_setup)); in QDataGet()
91 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, Setup2D_3Dcoords, Setup2D_3Dcoords_loc, &… in QDataGet()
96 PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, Setup, Setup_loc, &qf_setup)); in QDataGet()
101 PetscCallCeed(ceed, CeedQFunctionSetUserFlopsEstimate(qf_setup, 0)); in QDataGet()
102 …PetscCallCeed(ceed, CeedQFunctionAddInput(qf_setup, "dx", num_comp_x * (dim - height), CEED_EVAL_G… in QDataGet()
103 PetscCallCeed(ceed, CeedQFunctionAddInput(qf_setup, "weight", 1, CEED_EVAL_WEIGHT)); in QDataGet()
104 …PetscCallCeed(ceed, CeedQFunctionAddOutput(qf_setup, "surface qdata", *q_data_size, CEED_EVAL_NONE… in QDataGet()
106 …PetscCall(DMPlexCeedElemRestrictionQDataCreate(ceed, dm, domain_label, label_value, height, *q_dat… in QDataGet()
[all …]
|
| H A D | differential_filter.c | 18 PetscErrorCode DifferentialFilterCreateOperators(Ceed ceed, User user, CeedData ceed_data, CeedQFun… in DifferentialFilterCreateOperators() argument
26 PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(ceed_data->elem_restr_x, &num_comp_x)); in DifferentialFilterCreateOperators()
27 PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(ceed_data->elem_restr_q, &num_comp_q)); in DifferentialFilterCreateOperators()
28 …PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(ceed_data->elem_restr_qd_i, &num_comp_qd)); in DifferentialFilterCreateOperators()
35 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, DifferentialFilter_RHS_Prim, Differential… in DifferentialFilterCreateOperators()
38 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, DifferentialFilter_RHS_Conserv, Different… in DifferentialFilterCreateOperators()
41 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, DifferentialFilter_RHS_Entropy, Different… in DifferentialFilterCreateOperators()
45 PetscCallCeed(ceed, CeedQFunctionDestroy(&qf_rhs)); in DifferentialFilterCreateOperators()
46 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, DifferentialFilter_MMS_RHS, DifferentialF… in DifferentialFilterCreateOperators()
49 PetscCallCeed(ceed, CeedQFunctionSetContext(qf_rhs, diff_filter_qfctx)); in DifferentialFilterCreateOperators()
[all …]
|
| H A D | grid_anisotropy_tensor.c | 14 PetscErrorCode GridAnisotropyTensorProjectionSetupApply(Ceed ceed, User user, CeedData ceed_data, C… in GridAnisotropyTensorProjectionSetupApply() argument
52 …PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(ceed_data->elem_restr_qd_i, &q_data_size)); in GridAnisotropyTensorProjectionSetupApply()
54 …PetscCall(DMPlexCeedElemRestrictionCreate(ceed, grid_aniso_proj->dm, domain_label, label_value, he… in GridAnisotropyTensorProjectionSetupApply()
55 …PetscCall(CreateBasisFromPlex(ceed, grid_aniso_proj->dm, domain_label, label_value, height, dm_fie… in GridAnisotropyTensorProjectionSetupApply()
58 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, AnisotropyTensorProjection, AnisotropyTen… in GridAnisotropyTensorProjectionSetupApply()
59 PetscCallCeed(ceed, CeedQFunctionAddInput(qf_rhs_assemble, "qdata", q_data_size, CEED_EVAL_NONE)); in GridAnisotropyTensorProjectionSetupApply()
60 …PetscCallCeed(ceed, CeedQFunctionAddOutput(qf_rhs_assemble, "v", grid_aniso_proj->num_comp, CEED_E… in GridAnisotropyTensorProjectionSetupApply()
62 PetscCallCeed(ceed, CeedOperatorCreate(ceed, qf_rhs_assemble, NULL, NULL, &op_rhs_assemble)); in GridAnisotropyTensorProjectionSetupApply()
63 …PetscCallCeed(ceed, CeedOperatorSetField(op_rhs_assemble, "qdata", ceed_data->elem_restr_qd_i, CEE… in GridAnisotropyTensorProjectionSetupApply()
64 …PetscCallCeed(ceed, CeedOperatorSetField(op_rhs_assemble, "v", *elem_restr_grid_aniso, basis_grid_… in GridAnisotropyTensorProjectionSetupApply()
[all …]
|
| H A D | velocity_gradient_projection.c | 42 PetscErrorCode VelocityGradientProjectionSetup(Ceed ceed, User user, CeedData ceed_data, ProblemDat… in VelocityGradientProjectionSetup() argument
60 PetscCallCeed(ceed, CeedBasisGetNumComponents(ceed_data->basis_x, &num_comp_x)); in VelocityGradientProjectionSetup()
61 PetscCallCeed(ceed, CeedBasisGetNumComponents(ceed_data->basis_q, &num_comp_input)); in VelocityGradientProjectionSetup()
62 …PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(ceed_data->elem_restr_qd_i, &q_data_size)); in VelocityGradientProjectionSetup()
63 …PetscCall(DMPlexCeedElemRestrictionCreate(ceed, grad_velo_proj->dm, domain_label, label_value, hei… in VelocityGradientProjectionSetup()
65 …PetscCall(CreateBasisFromPlex(ceed, grad_velo_proj->dm, domain_label, label_value, height, dm_fiel… in VelocityGradientProjectionSetup()
70 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, VelocityGradientProjectionRHS_Prim, Veloc… in VelocityGradientProjectionSetup()
74 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, VelocityGradientProjectionRHS_Conserv, Ve… in VelocityGradientProjectionSetup()
78 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, VelocityGradientProjectionRHS_Entropy, Ve… in VelocityGradientProjectionSetup()
83 …PetscCallCeed(ceed, CeedQFunctionSetContext(qf_rhs_assemble, problem->apply_vol_ifunction.qfunctio… in VelocityGradientProjectionSetup()
[all …]
|
| H A D | inverse_multiplicity.c | 27 PetscErrorCode GetInverseMultiplicity(Ceed ceed, DM dm, DMLabel domain_label, PetscInt label_value,… in GetInverseMultiplicity() argument
40 …PetscCall(DMPlexCeedElemRestrictionCollocatedCreate(ceed, dm, domain_label, label_value, height, 1… in GetInverseMultiplicity()
41 …PetscCallCeed(ceed, CeedElemRestrictionCreateVector(*elem_restr_inv_multiplicity, inv_multiplicity… in GetInverseMultiplicity()
43 …PetscCall(DMPlexCeedElemRestrictionCreate(ceed, dm, domain_label, label_value, height, dm_field, &… in GetInverseMultiplicity()
44 PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(elem_restr, &num_comp)); in GetInverseMultiplicity()
45 PetscCallCeed(ceed, CeedElemRestrictionCreateVector(elem_restr, &multiplicity, NULL)); in GetInverseMultiplicity()
53 PetscCallCeed(ceed, CeedElemRestrictionGetMultiplicity(elem_restr, multiplicity)); in GetInverseMultiplicity()
60 PetscCallCeed(ceed, CeedElemRestrictionGetMultiplicity(elem_restr, multiplicity)); in GetInverseMultiplicity()
63 …PetscCallCeed(ceed, CeedQFunctionCreateInterior(ceed, 1, InverseMultiplicity, InverseMultiplicity_… in GetInverseMultiplicity()
64 …PetscCallCeed(ceed, CeedQFunctionAddInput(qf_multiplicity, "multiplicity", num_comp, CEED_EVAL_NON… in GetInverseMultiplicity()
[all …]
|
| H A D | turb_spanstats.c | 135 static PetscErrorCode CreateElemRestrColloc_CompMajor(Ceed ceed, CeedInt num_comp, CeedBasis basis,… in CreateElemRestrColloc_CompMajor() argument
140 PetscCallCeed(ceed, CeedBasisGetNumQuadraturePoints(basis, &num_elem_qpts)); in CreateElemRestrColloc_CompMajor()
141 PetscCallCeed(ceed, CeedElemRestrictionGetNumElements(elem_restr_base, &loc_num_elem)); in CreateElemRestrColloc_CompMajor()
144 …PetscCallCeed(ceed, CeedElemRestrictionCreateStrided(ceed, loc_num_elem, num_elem_qpts, num_comp, … in CreateElemRestrColloc_CompMajor()
150 PetscErrorCode GetQuadratureCoords(Ceed ceed, DM dm, CeedElemRestriction elem_restr_x, CeedBasis ba… in GetQuadratureCoords() argument
160 PetscCallCeed(ceed, CeedElemRestrictionGetNumComponents(elem_restr_x, &num_comp_x)); in GetQuadratureCoords()
161 …PetscCall(CreateElemRestrColloc_CompMajor(ceed, num_comp_x, basis_x, elem_restr_x, &elem_restr_qx)… in GetQuadratureCoords()
162 PetscCallCeed(ceed, CeedElemRestrictionGetLVectorSize(elem_restr_qx, &l_vec_size)); in GetQuadratureCoords()
166 …PetscCallCeed(ceed, CeedQFunctionCreateIdentity(ceed, num_comp_x, CEED_EVAL_INTERP, CEED_EVAL_NONE… in GetQuadratureCoords()
169 PetscCallCeed(ceed, CeedOperatorCreate(ceed, qf_quad_coords, NULL, NULL, &op_quad_coords)); in GetQuadratureCoords()
[all …]
|
| /libCEED/interface/ |
| H A D | ceed.c | 150 static int CeedWorkVectorsCreate(Ceed ceed) { in CeedWorkVectorsCreate() argument
151 CeedCall(CeedCalloc(1, &ceed->work_vectors)); in CeedWorkVectorsCreate()
164 static int CeedWorkVectorsDestroy(Ceed ceed) { in CeedWorkVectorsDestroy() argument
165 if (!ceed->work_vectors) return CEED_ERROR_SUCCESS; in CeedWorkVectorsDestroy()
166 for (CeedSize i = 0; i < ceed->work_vectors->num_vecs; i++) { in CeedWorkVectorsDestroy()
167 …CeedCheck(!ceed->work_vectors->is_in_use[i], ceed, CEED_ERROR_ACCESS, "Work vector %" CeedSize_FMT… in CeedWorkVectorsDestroy()
169 CeedCall(CeedObjectReference((CeedObject)ceed)); in CeedWorkVectorsDestroy()
170 CeedCall(CeedObjectReference((CeedObject)ceed)); in CeedWorkVectorsDestroy()
171 CeedCall(CeedVectorDestroy(&ceed->work_vectors->vecs[i])); in CeedWorkVectorsDestroy()
173 CeedObjectDereference((CeedObject)ceed); in CeedWorkVectorsDestroy()
[all …]
|
| /libCEED/backends/sycl-ref/ |
| H A D | ceed-sycl-ref.sycl.cpp | 28 static int CeedInit_Sycl_ref(const char *resource, Ceed ceed) { in CeedInit_Sycl_ref() argument
32 CeedCallBackend(CeedGetResourceRoot(ceed, resource, ":", &resource_root)); in CeedInit_Sycl_ref()
33 …e_root, "/gpu/sycl/ref") || !std::strcmp(resource_root, "/cpu/sycl/ref"), ceed, CEED_ERROR_BACKEND, in CeedInit_Sycl_ref()
36 CeedCallBackend(CeedSetDeterministic(ceed, true)); in CeedInit_Sycl_ref()
39 CeedCallBackend(CeedSetData(ceed, data)); in CeedInit_Sycl_ref()
40 CeedCallBackend(CeedInit_Sycl(ceed, resource)); in CeedInit_Sycl_ref()
42 CeedCallBackend(CeedSetBackendFunctionCpp(ceed, "Ceed", ceed, "SetStream", CeedSetStream_Sycl)); in CeedInit_Sycl_ref()
43 …CeedCallBackend(CeedSetBackendFunctionCpp(ceed, "Ceed", ceed, "GetPreferredMemType", CeedGetPrefer… in CeedInit_Sycl_ref()
44 …CeedCallBackend(CeedSetBackendFunctionCpp(ceed, "Ceed", ceed, "VectorCreate", &CeedVectorCreate_Sy… in CeedInit_Sycl_ref()
45 …CeedCallBackend(CeedSetBackendFunctionCpp(ceed, "Ceed", ceed, "BasisCreateTensorH1", &CeedBasisCre… in CeedInit_Sycl_ref()
[all …]
|
| /libCEED/backends/cuda/ |
| H A D | ceed-cuda-compile.cpp | 30 #define CeedChk_Nvrtc(ceed, x) … argument
33 …if (result != NVRTC_SUCCESS) return CeedError((ceed), CEED_ERROR_BACKEND, nvrtcGetErrorString(resu…
36 #define CeedCallNvrtc(ceed, ...) \ argument
39 CeedChk_Nvrtc(ceed, ierr_q_); \
42 #define CeedCallSystem(ceed, command, message) CeedCallBackend(CeedCallSystem_Core(ceed, command, m… argument
47 static int CeedCallSystem_Core(Ceed ceed, const char *command, const char *message) { in CeedCallSystem_Core() argument
48 CeedDebug(ceed, "Running command:\n$ %s", command); in CeedCallSystem_Core()
51 …CeedCheck(output_stream != nullptr, ceed, CEED_ERROR_BACKEND, "Failed to %s\ncommand:\n$ %s", mess… in CeedCallSystem_Core()
59 CeedDebug(ceed, "output:\n%s\n", output.c_str()); in CeedCallSystem_Core()
60 …CeedCheck(pclose(output_stream) == 0, ceed, CEED_ERROR_BACKEND, "Failed to %s\ncommand:\n$ %s\nerr… in CeedCallSystem_Core()
[all …]
|
| /libCEED/backends/hip/ |
| H A D | ceed-hip-compile.cpp | 21 #define CeedChk_hiprtc(ceed, x) … argument
24 …if (result != HIPRTC_SUCCESS) return CeedError((ceed), CEED_ERROR_BACKEND, hiprtcGetErrorString(re…
27 #define CeedCallHiprtc(ceed, ...) \ argument
30 CeedChk_hiprtc(ceed, ierr_q_); \
36 static int CeedCompileCore_Hip(Ceed ceed, const char *source, const bool throw_error, bool *is_comp… in CeedCompileCore_Hip() argument
53 CeedCallHip(ceed, hipRuntimeGetVersion(&runtime_version)); in CeedCompileCore_Hip()
82 CeedCallBackend(CeedGetData(ceed, (void **)&ceed_data)); in CeedCompileCore_Hip()
83 CeedCallHip(ceed, hipGetDeviceProperties(&prop, ceed_data->device_id)); in CeedCompileCore_Hip()
92 CeedCallBackend(CeedGetJitSourceRoots(ceed, &num_jit_source_dirs, &jit_source_dirs)); in CeedCompileCore_Hip()
100 CeedCallBackend(CeedRestoreJitSourceRoots(ceed, &jit_source_dirs)); in CeedCompileCore_Hip()
[all …]
|
| /libCEED/backends/memcheck/ |
| H A D | ceed-memcheck-serial.c | 17 static int CeedInit_Memcheck(const char *resource, Ceed ceed) { in CeedInit_Memcheck() argument
20 … "/cpu/self/memcheck") || !strcmp(resource, "/cpu/self/memcheck/serial"), ceed, CEED_ERROR_BACKEND, in CeedInit_Memcheck()
25 CeedCallBackend(CeedSetDelegate(ceed, ceed_ref)); in CeedInit_Memcheck()
28 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "VectorCreate", CeedVectorCreate_Memche… in CeedInit_Memcheck()
29 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreate", CeedElemRestri… in CeedInit_Memcheck()
30 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreateBlocked", CeedEle… in CeedInit_Memcheck()
31 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreateAtPoints", CeedEl… in CeedInit_Memcheck()
32 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionCreate", CeedQFunctionCreate_… in CeedInit_Memcheck()
33 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionContextCreate", CeedQFunction… in CeedInit_Memcheck()
|
| H A D | ceed-memcheck-blocked.c | 17 static int CeedInit_Memcheck(const char *resource, Ceed ceed) { in CeedInit_Memcheck() argument
20 …CeedCheck(!strcmp(resource, "/cpu/self/memcheck/blocked"), ceed, CEED_ERROR_BACKEND, "Valgrind Mem… in CeedInit_Memcheck()
24 CeedCallBackend(CeedSetDelegate(ceed, ceed_ref)); in CeedInit_Memcheck()
27 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "VectorCreate", CeedVectorCreate_Memche… in CeedInit_Memcheck()
28 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreate", CeedElemRestri… in CeedInit_Memcheck()
29 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreateBlocked", CeedEle… in CeedInit_Memcheck()
30 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "ElemRestrictionCreateAtPoints", CeedEl… in CeedInit_Memcheck()
31 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionCreate", CeedQFunctionCreate_… in CeedInit_Memcheck()
32 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionContextCreate", CeedQFunction… in CeedInit_Memcheck()
|
| /libCEED/backends/hip-gen/ |
| H A D | ceed-hip-gen.c | 19 static int CeedInit_Hip_gen(const char *resource, Ceed ceed) { in CeedInit_Hip_gen() argument
24 CeedCallBackend(CeedGetResourceRoot(ceed, resource, ":", &resource_root)); in CeedInit_Hip_gen()
25 …CeedCheck(!strcmp(resource_root, "/gpu/hip") || !strcmp(resource_root, "/gpu/hip/gen"), ceed, CEED… in CeedInit_Hip_gen()
30 CeedCallBackend(CeedSetData(ceed, data)); in CeedInit_Hip_gen()
31 CeedCallBackend(CeedInit_Hip(ceed, resource)); in CeedInit_Hip_gen()
34 CeedCallBackend(CeedSetDelegate(ceed, ceed_shared)); in CeedInit_Hip_gen()
38 CeedCallBackend(CeedSetOperatorFallbackCeed(ceed, ceed_ref)); in CeedInit_Hip_gen()
41 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionCreate", CeedQFunctionCreate_… in CeedInit_Hip_gen()
42 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "OperatorCreate", CeedOperatorCreate_Hi… in CeedInit_Hip_gen()
43 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "CompositeOperatorCreate", CeedOperator… in CeedInit_Hip_gen()
[all …]
|
| /libCEED/backends/cuda-gen/ |
| H A D | ceed-cuda-gen.c | 19 static int CeedInit_Cuda_gen(const char *resource, Ceed ceed) { in CeedInit_Cuda_gen() argument
24 CeedCallBackend(CeedGetResourceRoot(ceed, resource, ":", &resource_root)); in CeedInit_Cuda_gen()
25 …CeedCheck(!strcmp(resource_root, "/gpu/cuda") || !strcmp(resource_root, "/gpu/cuda/gen"), ceed, CE… in CeedInit_Cuda_gen()
30 CeedCallBackend(CeedSetData(ceed, data)); in CeedInit_Cuda_gen()
31 CeedCallBackend(CeedInit_Cuda(ceed, resource)); in CeedInit_Cuda_gen()
34 CeedCallBackend(CeedSetDelegate(ceed, ceed_shared)); in CeedInit_Cuda_gen()
38 CeedCallBackend(CeedSetOperatorFallbackCeed(ceed, ceed_ref)); in CeedInit_Cuda_gen()
41 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "QFunctionCreate", CeedQFunctionCreate_… in CeedInit_Cuda_gen()
42 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "OperatorCreate", CeedOperatorCreate_Cu… in CeedInit_Cuda_gen()
43 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "CompositeOperatorCreate", CeedOperator… in CeedInit_Cuda_gen()
[all …]
|
| /libCEED/tests/ |
| H A D | t131-vector.c | 13 Ceed ceed; in main() local
17 CeedInit(argv[1], &ceed); in main()
20 CeedGetWorkVector(ceed, 10, &x); in main()
21 CeedGetWorkVector(ceed, 20, &y); in main()
22 CeedGetWorkVector(ceed, 30, &z); in main()
25 CeedGetWorkVectorMemoryUsage(ceed, &usage_mb); in main()
29 CeedRestoreWorkVector(ceed, &x); in main()
30 CeedRestoreWorkVector(ceed, &z); in main()
36 CeedClearWorkVectors(ceed, 30); in main()
37 CeedGetWorkVectorMemoryUsage(ceed, &usage_mb); in main()
[all …]
|
| /libCEED/backends/magma/ |
| H A D | ceed-magma.c | 20 static int CeedInit_Magma(const char *resource, Ceed ceed) { in CeedInit_Magma() argument
25 …ce, "/gpu/cuda/magma", nrc) || !strncmp(resource, "/gpu/hip/magma", nrc), ceed, CEED_ERROR_BACKEND, in CeedInit_Magma()
29 CeedCallBackend(CeedSetData(ceed, data)); in CeedInit_Magma()
30 CeedCallBackend(CeedInit_Magma_common(ceed, resource)); in CeedInit_Magma()
38 CeedCallBackend(CeedSetDelegate(ceed, ceed_ref)); in CeedInit_Magma()
41 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateTensorH1", CeedBasisCreateT… in CeedInit_Magma()
42 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateH1", CeedBasisCreateH1_Magm… in CeedInit_Magma()
43 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHdiv", CeedBasisCreateHdiv_… in CeedInit_Magma()
44 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateHcurl", CeedBasisCreateHcur… in CeedInit_Magma()
45 CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "Destroy", CeedDestroy_Magma)); in CeedInit_Magma()
|
| /libCEED/python/tests/ |
| H A D | test-1-vector.py | 23 def check_values(ceed, x, value): argument
34 ceed = libceed.Ceed(ceed_resource)
37 x = ceed.Vector(n)
39 a = np.arange(10, 10 + n, dtype=ceed.scalar_type())
52 ceed = libceed.Ceed(ceed_resource)
54 x = ceed.Vector(n)
56 a = np.arange(10, 10 + n, dtype=ceed.scalar_type())
64 check_values(ceed, x, 3.0)
67 x = ceed.Vector(n)
70 check_values(ceed, x, 5.0)
[all …]
|
| /libCEED/backends/cuda-shared/ |
| H A D | ceed-cuda-shared.c | 20 static int CeedInit_Cuda_shared(const char *resource, Ceed ceed) { in CeedInit_Cuda_shared() argument
25 CeedCallBackend(CeedGetResourceRoot(ceed, resource, ":", &resource_root)); in CeedInit_Cuda_shared()
26 …CeedCheck(!strcmp(resource_root, "/gpu/cuda/shared"), ceed, CEED_ERROR_BACKEND, "Cuda backend cann… in CeedInit_Cuda_shared()
28 CeedCallBackend(CeedSetDeterministic(ceed, true)); in CeedInit_Cuda_shared()
31 CeedCallBackend(CeedSetData(ceed, data)); in CeedInit_Cuda_shared()
32 CeedCallBackend(CeedInit_Cuda(ceed, resource)); in CeedInit_Cuda_shared()
35 CeedCallBackend(CeedSetDelegate(ceed, ceed_ref)); in CeedInit_Cuda_shared()
38 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateTensorH1", CeedBasisCreateT… in CeedInit_Cuda_shared()
39 …CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "BasisCreateH1", CeedBasisCreateH1_Cuda… in CeedInit_Cuda_shared()
40 CeedCallBackend(CeedSetBackendFunction(ceed, "Ceed", ceed, "Destroy", CeedDestroy_Cuda)); in CeedInit_Cuda_shared()
|