Lines Matching refs:CeedCallHip
64 CeedCallHip(ceed, hipModuleUnload(impl->diag->module)); in CeedOperatorDestroy_Hip()
67 CeedCallHip(ceed, hipModuleUnload(impl->diag->module_point_block)); in CeedOperatorDestroy_Hip()
69 CeedCallHip(ceed, hipFree(impl->diag->d_eval_modes_in)); in CeedOperatorDestroy_Hip()
70 CeedCallHip(ceed, hipFree(impl->diag->d_eval_modes_out)); in CeedOperatorDestroy_Hip()
71 CeedCallHip(ceed, hipFree(impl->diag->d_identity)); in CeedOperatorDestroy_Hip()
72 CeedCallHip(ceed, hipFree(impl->diag->d_interp_in)); in CeedOperatorDestroy_Hip()
73 CeedCallHip(ceed, hipFree(impl->diag->d_interp_out)); in CeedOperatorDestroy_Hip()
74 CeedCallHip(ceed, hipFree(impl->diag->d_grad_in)); in CeedOperatorDestroy_Hip()
75 CeedCallHip(ceed, hipFree(impl->diag->d_grad_out)); in CeedOperatorDestroy_Hip()
76 CeedCallHip(ceed, hipFree(impl->diag->d_div_in)); in CeedOperatorDestroy_Hip()
77 CeedCallHip(ceed, hipFree(impl->diag->d_div_out)); in CeedOperatorDestroy_Hip()
78 CeedCallHip(ceed, hipFree(impl->diag->d_curl_in)); in CeedOperatorDestroy_Hip()
79 CeedCallHip(ceed, hipFree(impl->diag->d_curl_out)); in CeedOperatorDestroy_Hip()
92 CeedCallHip(ceed, hipModuleUnload(impl->asmb->module)); in CeedOperatorDestroy_Hip()
93 CeedCallHip(ceed, hipFree(impl->asmb->d_B_in)); in CeedOperatorDestroy_Hip()
94 CeedCallHip(ceed, hipFree(impl->asmb->d_B_out)); in CeedOperatorDestroy_Hip()
1218 CeedCallHip(ceed, hipMalloc((void **)&diag->d_identity, interp_bytes)); in CeedOperatorAssembleDiagonalSetup_Hip()
1219 CeedCallHip(ceed, hipMemcpy(diag->d_identity, identity, interp_bytes, hipMemcpyHostToDevice)); 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()
1242 CeedCallHip(ceed, hipMalloc((void **)&d_grad, interp_bytes * q_comp_grad)); in CeedOperatorAssembleDiagonalSetup_Hip()
1243 … CeedCallHip(ceed, hipMemcpy(d_grad, grad, interp_bytes * q_comp_grad, hipMemcpyHostToDevice)); 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()
1264 CeedCallHip(ceed, hipMalloc((void **)&d_div, interp_bytes * q_comp_div)); in CeedOperatorAssembleDiagonalSetup_Hip()
1265 CeedCallHip(ceed, hipMemcpy(d_div, div, interp_bytes * q_comp_div, hipMemcpyHostToDevice)); in CeedOperatorAssembleDiagonalSetup_Hip()
1283 CeedCallHip(ceed, hipMalloc((void **)&d_interp, interp_bytes * q_comp_interp)); in CeedOperatorAssembleDiagonalSetup_Hip()
1284 …CeedCallHip(ceed, hipMemcpy(d_interp, interp, interp_bytes * q_comp_interp, hipMemcpyHostToDevice)… in CeedOperatorAssembleDiagonalSetup_Hip()
1286 CeedCallHip(ceed, hipMalloc((void **)&d_curl, interp_bytes * q_comp_curl)); in CeedOperatorAssembleDiagonalSetup_Hip()
1287 … CeedCallHip(ceed, hipMemcpy(d_curl, curl, interp_bytes * q_comp_curl, hipMemcpyHostToDevice)); in CeedOperatorAssembleDiagonalSetup_Hip()
1300 …CeedCallHip(ceed, hipMalloc((void **)&diag->d_eval_modes_in, num_eval_modes_in * eval_modes_bytes)… in CeedOperatorAssembleDiagonalSetup_Hip()
1301 …CeedCallHip(ceed, hipMemcpy(diag->d_eval_modes_in, eval_modes_in, num_eval_modes_in * eval_modes_b… in CeedOperatorAssembleDiagonalSetup_Hip()
1302 …CeedCallHip(ceed, hipMalloc((void **)&diag->d_eval_modes_out, num_eval_modes_out * eval_modes_byte… in CeedOperatorAssembleDiagonalSetup_Hip()
1303 …CeedCallHip(ceed, hipMemcpy(diag->d_eval_modes_out, eval_modes_out, num_eval_modes_out * eval_mode… in CeedOperatorAssembleDiagonalSetup_Hip()
1389 …CeedCallHip(ceed, CeedCompile_Hip(ceed, diagonal_kernel_source, module, 8, "NUM_EVAL_MODES_IN", nu… in CeedOperatorAssembleDiagonalSetupCompile_Hip()
1392 …CeedCallHip(ceed, CeedGetKernel_Hip(ceed, *module, "LinearDiagonal", is_point_block ? &diag->Linea… in CeedOperatorAssembleDiagonalSetupCompile_Hip()
1643 CeedCallHip(ceed, hipMalloc((void **)&asmb->d_B_in, in_bytes)); in CeedOperatorAssembleSingleSetup_Hip()
1655 …CeedCallHip(ceed, hipMemcpy(&asmb->d_B_in[i * elem_size_in * num_qpts_in], h_B_in, elem_size_in * … in CeedOperatorAssembleSingleSetup_Hip()
1678 CeedCallHip(ceed, hipMalloc((void **)&asmb->d_B_out, out_bytes)); in CeedOperatorAssembleSingleSetup_Hip()
1690 …CeedCallHip(ceed, hipMemcpy(&asmb->d_B_out[i * elem_size_out * num_qpts_out], h_B_out, elem_size_o… in CeedOperatorAssembleSingleSetup_Hip()