Home
last modified time | relevance | path

Searched refs:d_interp (Results 1 – 10 of 10) sorted by relevance

/libCEED/backends/hip-ref/
H A Dceed-hip-ref-basis.c284 void *interp_args[] = {(void *)&num_elem, &data->d_interp, &d_u, &d_v}; in CeedBasisApplyNonTensorCore_Hip()
386 CeedCallHip(ceed, hipFree(data->d_interp)); in CeedBasisDestroyNonTensor_Hip()
465 CeedCallHip(ceed, hipMalloc((void **)&data->d_interp, interp_bytes)); in CeedBasisCreateH1_Hip()
466 CeedCallHip(ceed, hipMemcpy(data->d_interp, interp, interp_bytes, hipMemcpyHostToDevice)); in CeedBasisCreateH1_Hip()
520 CeedCallHip(ceed, hipMalloc((void **)&data->d_interp, interp_bytes)); in CeedBasisCreateHdiv_Hip()
521 CeedCallHip(ceed, hipMemcpy(data->d_interp, interp, interp_bytes, hipMemcpyHostToDevice)); in CeedBasisCreateHdiv_Hip()
575 CeedCallHip(ceed, hipMalloc((void **)&data->d_interp, interp_bytes)); in CeedBasisCreateHcurl_Hip()
576 CeedCallHip(ceed, hipMemcpy(data->d_interp, interp, interp_bytes, hipMemcpyHostToDevice)); in CeedBasisCreateHcurl_Hip()
H A Dceed-hip-ref-operator.c1233 CeedScalar *d_interp, *d_grad; in CeedOperatorAssembleDiagonalSetup_Hip() local
1239 CeedCallHip(ceed, hipMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Hip()
1240 …CeedCallHip(ceed, hipMemcpy(d_interp, interp, interp_bytes * q_comp_interp, hipMemcpyHostToDevice)… in CeedOperatorAssembleDiagonalSetup_Hip()
1245 diag->d_interp_in = d_interp; in CeedOperatorAssembleDiagonalSetup_Hip()
1248 diag->d_interp_out = d_interp; in CeedOperatorAssembleDiagonalSetup_Hip()
1255 CeedScalar *d_interp, *d_div; in CeedOperatorAssembleDiagonalSetup_Hip() local
1261 CeedCallHip(ceed, hipMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Hip()
1262 …CeedCallHip(ceed, hipMemcpy(d_interp, interp, interp_bytes * q_comp_interp, hipMemcpyHostToDevice)… in CeedOperatorAssembleDiagonalSetup_Hip()
1267 diag->d_interp_in = d_interp; in CeedOperatorAssembleDiagonalSetup_Hip()
1270 diag->d_interp_out = d_interp; in CeedOperatorAssembleDiagonalSetup_Hip()
[all …]
H A Dceed-hip-ref.h97 CeedScalar *d_interp; member
/libCEED/backends/cuda-ref/
H A Dceed-cuda-ref-basis.c285 void *interp_args[] = {(void *)&num_elem, &data->d_interp, &d_u, &d_v}; in CeedBasisApplyNonTensorCore_Cuda()
387 CeedCallCuda(ceed, cudaFree(data->d_interp)); in CeedBasisDestroyNonTensor_Cuda()
466 CeedCallCuda(ceed, cudaMalloc((void **)&data->d_interp, interp_bytes)); in CeedBasisCreateH1_Cuda()
467 CeedCallCuda(ceed, cudaMemcpy(data->d_interp, interp, interp_bytes, cudaMemcpyHostToDevice)); in CeedBasisCreateH1_Cuda()
521 CeedCallCuda(ceed, cudaMalloc((void **)&data->d_interp, interp_bytes)); in CeedBasisCreateHdiv_Cuda()
522 CeedCallCuda(ceed, cudaMemcpy(data->d_interp, interp, interp_bytes, cudaMemcpyHostToDevice)); in CeedBasisCreateHdiv_Cuda()
576 CeedCallCuda(ceed, cudaMalloc((void **)&data->d_interp, interp_bytes)); in CeedBasisCreateHcurl_Cuda()
577 CeedCallCuda(ceed, cudaMemcpy(data->d_interp, interp, interp_bytes, cudaMemcpyHostToDevice)); in CeedBasisCreateHcurl_Cuda()
H A Dceed-cuda-ref-operator.c1236 CeedScalar *d_interp, *d_grad; in CeedOperatorAssembleDiagonalSetup_Cuda() local
1242 CeedCallCuda(ceed, cudaMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1243 …CeedCallCuda(ceed, cudaMemcpy(d_interp, interp, interp_bytes * q_comp_interp, cudaMemcpyHostToDevi… in CeedOperatorAssembleDiagonalSetup_Cuda()
1248 diag->d_interp_in = d_interp; in CeedOperatorAssembleDiagonalSetup_Cuda()
1251 diag->d_interp_out = d_interp; in CeedOperatorAssembleDiagonalSetup_Cuda()
1258 CeedScalar *d_interp, *d_div; in CeedOperatorAssembleDiagonalSetup_Cuda() local
1264 CeedCallCuda(ceed, cudaMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1265 …CeedCallCuda(ceed, cudaMemcpy(d_interp, interp, interp_bytes * q_comp_interp, cudaMemcpyHostToDevi… in CeedOperatorAssembleDiagonalSetup_Cuda()
1270 diag->d_interp_in = d_interp; in CeedOperatorAssembleDiagonalSetup_Cuda()
1273 diag->d_interp_out = d_interp; in CeedOperatorAssembleDiagonalSetup_Cuda()
[all …]
H A Dceed-cuda-ref.h92 CeedScalar *d_interp; member
/libCEED/backends/magma/
H A Dceed-magma-basis.c387 d_b = impl->d_interp; in CeedBasisApplyNonTensorCore_Magma()
518 CeedCallBackend(magma_free(impl->d_interp)); in CeedBasisDestroyNonTensor_Magma()
661 …CeedCallBackend(magma_malloc((void **)&impl->d_interp, num_qpts * num_nodes * q_comp_interp * size… in CeedBasisCreateH1_Magma()
662 …um_qpts * num_nodes * q_comp_interp, sizeof(interp[0]), interp, 1, impl->d_interp, 1, data->queue); in CeedBasisCreateH1_Magma()
725 …CeedCallBackend(magma_malloc((void **)&impl->d_interp, num_qpts * num_nodes * q_comp_interp * size… in CeedBasisCreateHdiv_Magma()
726 …um_qpts * num_nodes * q_comp_interp, sizeof(interp[0]), interp, 1, impl->d_interp, 1, data->queue); in CeedBasisCreateHdiv_Magma()
789 …CeedCallBackend(magma_malloc((void **)&impl->d_interp, num_qpts * num_nodes * q_comp_interp * size… in CeedBasisCreateHcurl_Magma()
790 …um_qpts * num_nodes * q_comp_interp, sizeof(interp[0]), interp, 1, impl->d_interp, 1, data->queue); in CeedBasisCreateHcurl_Magma()
H A Dceed-magma.h71 CeedScalar *d_interp; member
/libCEED/backends/sycl-ref/
H A Dceed-sycl-ref.hpp66 CeedScalar *d_interp; member
H A Dceed-sycl-ref-basis.sycl.cpp351 const CeedScalar *d_B = impl->d_interp; in CeedBasisApplyNonTensorInterp_Sycl()
550 CeedCallSycl(ceed, sycl::free(impl->d_interp, data->sycl_context)); in CeedBasisDestroyNonTensor_Sycl()
661 …CeedCallSycl(ceed, impl->d_interp = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_devi… in CeedBasisCreateH1_Sycl()
662 …sycl::event copy_interp = data->sycl_queue.copy<CeedScalar>(interp, impl->d_interp, interp_length,… in CeedBasisCreateH1_Sycl()