ceed-cuda-shared-basis.c - OpenGrok cross reference for /libCEED/backends/cuda-shared/ceed-cuda-shared-basis.c

Lines Matching refs:CeedCallCuda
255       if (data->d_points_per_elem) CeedCallCuda(ceed, cudaFree(data->d_points_per_elem));  in CeedBasisApplyAtPointsCore_Cuda_shared()
256       CeedCallCuda(ceed, cudaMalloc((void **)&data->d_points_per_elem, num_bytes));  in CeedBasisApplyAtPointsCore_Cuda_shared()
262 …CeedCallCuda(ceed, cudaMemcpy(data->d_points_per_elem, num_points, num_bytes, cudaMemcpyHostToDevi…  in CeedBasisApplyAtPointsCore_Cuda_shared()
281       CeedCallCuda(ceed, cudaMalloc((void **)&data->d_chebyshev_interp_1d, interp_bytes));  in CeedBasisApplyAtPointsCore_Cuda_shared()
282 …CeedCallCuda(ceed, cudaMemcpy(data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, cuda…  in CeedBasisApplyAtPointsCore_Cuda_shared()
290     if (data->moduleAtPoints) CeedCallCuda(ceed, cuModuleUnload(data->moduleAtPoints));  in CeedBasisApplyAtPointsCore_Cuda_shared()
577   CeedCallCuda(ceed, cuModuleUnload(data->module));  in CeedBasisDestroy_Cuda_shared()
578   if (data->moduleAtPoints) CeedCallCuda(ceed, cuModuleUnload(data->moduleAtPoints));  in CeedBasisDestroy_Cuda_shared()
579   if (data->d_q_weight_1d) CeedCallCuda(ceed, cudaFree(data->d_q_weight_1d));  in CeedBasisDestroy_Cuda_shared()
581   if (data->d_points_per_elem) CeedCallCuda(ceed, cudaFree(data->d_points_per_elem));  in CeedBasisDestroy_Cuda_shared()
582   CeedCallCuda(ceed, cudaFree(data->d_interp_1d));  in CeedBasisDestroy_Cuda_shared()
583   CeedCallCuda(ceed, cudaFree(data->d_grad_1d));  in CeedBasisDestroy_Cuda_shared()
584   CeedCallCuda(ceed, cudaFree(data->d_collo_grad_1d));  in CeedBasisDestroy_Cuda_shared()
585   CeedCallCuda(ceed, cudaFree(data->d_chebyshev_interp_1d));  in CeedBasisDestroy_Cuda_shared()
607     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_q_weight_1d, q_bytes));  in CeedBasisCreateTensorH1_Cuda_shared()
608 … CeedCallCuda(ceed, cudaMemcpy(data->d_q_weight_1d, q_weight_1d, q_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateTensorH1_Cuda_shared()
610   CeedCallCuda(ceed, cudaMalloc((void **)&data->d_interp_1d, interp_bytes));  in CeedBasisCreateTensorH1_Cuda_shared()
611 …CeedCallCuda(ceed, cudaMemcpy(data->d_interp_1d, interp_1d, interp_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateTensorH1_Cuda_shared()
612   CeedCallCuda(ceed, cudaMalloc((void **)&data->d_grad_1d, interp_bytes));  in CeedBasisCreateTensorH1_Cuda_shared()
613   CeedCallCuda(ceed, cudaMemcpy(data->d_grad_1d, grad_1d, interp_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateTensorH1_Cuda_shared()
624     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_collo_grad_1d, q_bytes * Q_1d));  in CeedBasisCreateTensorH1_Cuda_shared()
625 …CeedCallCuda(ceed, cudaMemcpy(data->d_collo_grad_1d, collo_grad_1d, q_bytes * Q_1d, cudaMemcpyHost…  in CeedBasisCreateTensorH1_Cuda_shared()
690     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_q_weight_1d, q_bytes));  in CeedBasisCreateH1_Cuda_shared()
691     CeedCallCuda(ceed, cudaMemcpy(data->d_q_weight_1d, q_weight, q_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateH1_Cuda_shared()
696     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_interp_1d, interp_bytes));  in CeedBasisCreateH1_Cuda_shared()
697     CeedCallCuda(ceed, cudaMemcpy(data->d_interp_1d, interp, interp_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateH1_Cuda_shared()
702     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_grad_1d, grad_bytes));  in CeedBasisCreateH1_Cuda_shared()
703     CeedCallCuda(ceed, cudaMemcpy(data->d_grad_1d, grad, grad_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateH1_Cuda_shared()