| /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()
|