| /libCEED/backends/magma/ |
| H A D | ceed-magma-basis.c | 318 CeedInt q_comp_interp, q_comp_deriv; in CeedBasisApplyNonTensorCore_Magma() local 328 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisApplyNonTensorCore_Magma() 340 impl->NB_interp[iN] = nontensor_rtc_get_nb(arch, 'n', q_comp_interp, P, Q, n_array[iN]); in CeedBasisApplyNonTensorCore_Magma() 341 impl->NB_interp_t[iN] = nontensor_rtc_get_nb(arch, 't', q_comp_interp, P, Q, n_array[iN]); in CeedBasisApplyNonTensorCore_Magma() 357 …gma(ceed_delegate, basis_kernel_source, &impl->module[iN], 8, "BASIS_Q_COMP_INTERP", q_comp_interp, in CeedBasisApplyNonTensorCore_Magma() 658 CeedInt q_comp_interp; in CeedBasisCreateH1_Magma() local 660 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateH1_Magma() 661 …CeedCallBackend(magma_malloc((void **)&impl->d_interp, num_qpts * num_nodes * q_comp_interp * size… in CeedBasisCreateH1_Magma() 662 …magma_setvector(num_qpts * num_nodes * q_comp_interp, sizeof(interp[0]), interp, 1, impl->d_interp… in CeedBasisCreateH1_Magma() 722 CeedInt q_comp_interp; in CeedBasisCreateHdiv_Magma() local [all …]
|
| /libCEED/backends/hip-ref/ |
| H A D | ceed-hip-ref-basis.c | 448 CeedInt num_comp, q_comp_interp, q_comp_grad; in CeedBasisCreateH1_Hip() local 456 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateH1_Hip() 463 const CeedInt interp_bytes = q_bytes * num_nodes * q_comp_interp; in CeedBasisCreateH1_Hip() 480 … q_comp_interp, "BASIS_Q_COMP_DERIV", q_comp_grad, "BASIS_NUM_COMP", num_comp)); in CeedBasisCreateH1_Hip() 503 CeedInt num_comp, q_comp_interp, q_comp_div; in CeedBasisCreateHdiv_Hip() local 511 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateHdiv_Hip() 518 const CeedInt interp_bytes = q_bytes * num_nodes * q_comp_interp; in CeedBasisCreateHdiv_Hip() 535 … q_comp_interp, "BASIS_Q_COMP_DERIV", q_comp_div, "BASIS_NUM_COMP", num_comp)); in CeedBasisCreateHdiv_Hip() 558 CeedInt num_comp, q_comp_interp, q_comp_curl; in CeedBasisCreateHcurl_Hip() local 566 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateHcurl_Hip() [all …]
|
| H A D | ceed-hip-ref-operator.c | 1231 CeedInt q_comp_interp, q_comp_grad; in CeedOperatorAssembleDiagonalSetup_Hip() local 1235 … CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Hip() 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() 1253 CeedInt q_comp_interp, q_comp_div; in CeedOperatorAssembleDiagonalSetup_Hip() local 1257 … CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Hip() 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() 1275 CeedInt q_comp_interp, q_comp_curl; in CeedOperatorAssembleDiagonalSetup_Hip() local 1279 … CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Hip() [all …]
|
| /libCEED/backends/cuda-ref/ |
| H A D | ceed-cuda-ref-basis.c | 449 CeedInt num_comp, q_comp_interp, q_comp_grad; in CeedBasisCreateH1_Cuda() local 457 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateH1_Cuda() 464 const CeedInt interp_bytes = q_bytes * num_nodes * q_comp_interp; in CeedBasisCreateH1_Cuda() 481 … q_comp_interp, "BASIS_Q_COMP_DERIV", q_comp_grad, "BASIS_NUM_COMP", num_comp)); in CeedBasisCreateH1_Cuda() 504 CeedInt num_comp, q_comp_interp, q_comp_div; in CeedBasisCreateHdiv_Cuda() local 512 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateHdiv_Cuda() 519 const CeedInt interp_bytes = q_bytes * num_nodes * q_comp_interp; in CeedBasisCreateHdiv_Cuda() 536 … q_comp_interp, "BASIS_Q_COMP_DERIV", q_comp_div, "BASIS_NUM_COMP", num_comp)); in CeedBasisCreateHdiv_Cuda() 559 CeedInt num_comp, q_comp_interp, q_comp_curl; in CeedBasisCreateHcurl_Cuda() local 567 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateHcurl_Cuda() [all …]
|
| H A D | ceed-cuda-ref-operator.c | 1234 CeedInt q_comp_interp, q_comp_grad; in CeedOperatorAssembleDiagonalSetup_Cuda() local 1238 … CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda() 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() 1256 CeedInt q_comp_interp, q_comp_div; in CeedOperatorAssembleDiagonalSetup_Cuda() local 1260 … CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda() 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() 1278 CeedInt q_comp_interp, q_comp_curl; in CeedOperatorAssembleDiagonalSetup_Cuda() local 1282 … CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda() [all …]
|
| /libCEED/backends/hip-shared/ |
| H A D | ceed-hip-shared-basis.c | 731 CeedInt num_comp, q_comp_interp, q_comp_grad; in CeedBasisCreateH1_Hip_shared() local 753 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateH1_Hip_shared() 760 const CeedInt interp_bytes = q_bytes * num_nodes * q_comp_interp; in CeedBasisCreateH1_Hip_shared()
|
| /libCEED/backends/cuda-shared/ |
| H A D | ceed-cuda-shared-basis.c | 665 CeedInt num_comp, q_comp_interp, q_comp_grad; in CeedBasisCreateH1_Cuda_shared() local 687 CeedCallBackend(CeedBasisGetNumQuadratureComponents(basis, CEED_EVAL_INTERP, &q_comp_interp)); in CeedBasisCreateH1_Cuda_shared() 694 const CeedInt interp_bytes = q_bytes * num_nodes * q_comp_interp; in CeedBasisCreateH1_Cuda_shared()
|