Lines Matching refs:CeedCallCuda

65       CeedCallCuda(ceed, cuModuleUnload(impl->diag->module));  in CeedOperatorDestroy_Cuda()
68 CeedCallCuda(ceed, cuModuleUnload(impl->diag->module_point_block)); in CeedOperatorDestroy_Cuda()
70 CeedCallCuda(ceed, cudaFree(impl->diag->d_eval_modes_in)); in CeedOperatorDestroy_Cuda()
71 CeedCallCuda(ceed, cudaFree(impl->diag->d_eval_modes_out)); in CeedOperatorDestroy_Cuda()
72 CeedCallCuda(ceed, cudaFree(impl->diag->d_identity)); in CeedOperatorDestroy_Cuda()
73 CeedCallCuda(ceed, cudaFree(impl->diag->d_interp_in)); in CeedOperatorDestroy_Cuda()
74 CeedCallCuda(ceed, cudaFree(impl->diag->d_interp_out)); in CeedOperatorDestroy_Cuda()
75 CeedCallCuda(ceed, cudaFree(impl->diag->d_grad_in)); in CeedOperatorDestroy_Cuda()
76 CeedCallCuda(ceed, cudaFree(impl->diag->d_grad_out)); in CeedOperatorDestroy_Cuda()
77 CeedCallCuda(ceed, cudaFree(impl->diag->d_div_in)); in CeedOperatorDestroy_Cuda()
78 CeedCallCuda(ceed, cudaFree(impl->diag->d_div_out)); in CeedOperatorDestroy_Cuda()
79 CeedCallCuda(ceed, cudaFree(impl->diag->d_curl_in)); in CeedOperatorDestroy_Cuda()
80 CeedCallCuda(ceed, cudaFree(impl->diag->d_curl_out)); in CeedOperatorDestroy_Cuda()
93 CeedCallCuda(ceed, cuModuleUnload(impl->asmb->module)); in CeedOperatorDestroy_Cuda()
94 CeedCallCuda(ceed, cudaFree(impl->asmb->d_B_in)); in CeedOperatorDestroy_Cuda()
95 CeedCallCuda(ceed, cudaFree(impl->asmb->d_B_out)); in CeedOperatorDestroy_Cuda()
1221 CeedCallCuda(ceed, cudaMalloc((void **)&diag->d_identity, interp_bytes)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1222CeedCallCuda(ceed, cudaMemcpy(diag->d_identity, identity, interp_bytes, cudaMemcpyHostToDevice)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1242 CeedCallCuda(ceed, cudaMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1243CeedCallCuda(ceed, cudaMemcpy(d_interp, interp, interp_bytes * q_comp_interp, cudaMemcpyHostToDevi… in CeedOperatorAssembleDiagonalSetup_Cuda()
1245 CeedCallCuda(ceed, cudaMalloc((void **)&d_grad, interp_bytes * q_comp_grad)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1246CeedCallCuda(ceed, cudaMemcpy(d_grad, grad, interp_bytes * q_comp_grad, cudaMemcpyHostToDevice)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1264 CeedCallCuda(ceed, cudaMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1265CeedCallCuda(ceed, cudaMemcpy(d_interp, interp, interp_bytes * q_comp_interp, cudaMemcpyHostToDevi… in CeedOperatorAssembleDiagonalSetup_Cuda()
1267 CeedCallCuda(ceed, cudaMalloc((void **)&d_div, interp_bytes * q_comp_div)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1268CeedCallCuda(ceed, cudaMemcpy(d_div, div, interp_bytes * q_comp_div, cudaMemcpyHostToDevice)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1286 CeedCallCuda(ceed, cudaMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1287CeedCallCuda(ceed, cudaMemcpy(d_interp, interp, interp_bytes * q_comp_interp, cudaMemcpyHostToDevi… in CeedOperatorAssembleDiagonalSetup_Cuda()
1289 CeedCallCuda(ceed, cudaMalloc((void **)&d_curl, interp_bytes * q_comp_curl)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1290CeedCallCuda(ceed, cudaMemcpy(d_curl, curl, interp_bytes * q_comp_curl, cudaMemcpyHostToDevice)); in CeedOperatorAssembleDiagonalSetup_Cuda()
1303CeedCallCuda(ceed, cudaMalloc((void **)&diag->d_eval_modes_in, num_eval_modes_in * eval_modes_byte… in CeedOperatorAssembleDiagonalSetup_Cuda()
1304CeedCallCuda(ceed, cudaMemcpy(diag->d_eval_modes_in, eval_modes_in, num_eval_modes_in * eval_modes… in CeedOperatorAssembleDiagonalSetup_Cuda()
1305CeedCallCuda(ceed, cudaMalloc((void **)&diag->d_eval_modes_out, num_eval_modes_out * eval_modes_by… in CeedOperatorAssembleDiagonalSetup_Cuda()
1306CeedCallCuda(ceed, cudaMemcpy(diag->d_eval_modes_out, eval_modes_out, num_eval_modes_out * eval_mo… in CeedOperatorAssembleDiagonalSetup_Cuda()
1392CeedCallCuda(ceed, CeedCompile_Cuda(ceed, diagonal_kernel_source, module, 8, "NUM_EVAL_MODES_IN", … in CeedOperatorAssembleDiagonalSetupCompile_Cuda()
1395CeedCallCuda(ceed, CeedGetKernel_Cuda(ceed, *module, "LinearDiagonal", is_point_block ? &diag->Lin… in CeedOperatorAssembleDiagonalSetupCompile_Cuda()
1646 CeedCallCuda(ceed, cudaMalloc((void **)&asmb->d_B_in, in_bytes)); in CeedOperatorAssembleSingleSetup_Cuda()
1658CeedCallCuda(ceed, cudaMemcpy(&asmb->d_B_in[i * elem_size_in * num_qpts_in], h_B_in, elem_size_in … in CeedOperatorAssembleSingleSetup_Cuda()
1681 CeedCallCuda(ceed, cudaMalloc((void **)&asmb->d_B_out, out_bytes)); in CeedOperatorAssembleSingleSetup_Cuda()
1693CeedCallCuda(ceed, cudaMemcpy(&asmb->d_B_out[i * elem_size_out * num_qpts_out], h_B_out, elem_size… in CeedOperatorAssembleSingleSetup_Cuda()