147       if (data->d_points_per_elem) CeedCallCuda(ceed, cudaFree(data->d_points_per_elem));  in CeedBasisApplyAtPointsCore_Cuda()
148       CeedCallCuda(ceed, cudaMalloc((void **)&data->d_points_per_elem, num_bytes));  in CeedBasisApplyAtPointsCore_Cuda()
154 …CeedCallCuda(ceed, cudaMemcpy(data->d_points_per_elem, num_points, num_bytes, cudaMemcpyHostToDevi…  in CeedBasisApplyAtPointsCore_Cuda()
173       CeedCallCuda(ceed, cudaMalloc((void **)&data->d_chebyshev_interp_1d, interp_bytes));  in CeedBasisApplyAtPointsCore_Cuda()
174 …CeedCallCuda(ceed, cudaMemcpy(data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, cuda…  in CeedBasisApplyAtPointsCore_Cuda()
182     if (data->moduleAtPoints) CeedCallCuda(ceed, cuModuleUnload(data->moduleAtPoints));  in CeedBasisApplyAtPointsCore_Cuda()
363   CeedCallCuda(ceed, cuModuleUnload(data->module));  in CeedBasisDestroy_Cuda()
364   if (data->moduleAtPoints) CeedCallCuda(ceed, cuModuleUnload(data->moduleAtPoints));  in CeedBasisDestroy_Cuda()
365   if (data->d_q_weight_1d) CeedCallCuda(ceed, cudaFree(data->d_q_weight_1d));  in CeedBasisDestroy_Cuda()
367   if (data->d_points_per_elem) CeedCallCuda(ceed, cudaFree(data->d_points_per_elem));  in CeedBasisDestroy_Cuda()
368   CeedCallCuda(ceed, cudaFree(data->d_interp_1d));  in CeedBasisDestroy_Cuda()
369   CeedCallCuda(ceed, cudaFree(data->d_grad_1d));  in CeedBasisDestroy_Cuda()
370   CeedCallCuda(ceed, cudaFree(data->d_chebyshev_interp_1d));  in CeedBasisDestroy_Cuda()
385   CeedCallCuda(ceed, cuModuleUnload(data->module));  in CeedBasisDestroyNonTensor_Cuda()
386   if (data->d_q_weight) CeedCallCuda(ceed, cudaFree(data->d_q_weight));  in CeedBasisDestroyNonTensor_Cuda()
387   CeedCallCuda(ceed, cudaFree(data->d_interp));  in CeedBasisDestroyNonTensor_Cuda()
388   CeedCallCuda(ceed, cudaFree(data->d_grad));  in CeedBasisDestroyNonTensor_Cuda()
389   CeedCallCuda(ceed, cudaFree(data->d_div));  in CeedBasisDestroyNonTensor_Cuda()
390   CeedCallCuda(ceed, cudaFree(data->d_curl));  in CeedBasisDestroyNonTensor_Cuda()
412     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_q_weight_1d, q_bytes));  in CeedBasisCreateTensorH1_Cuda()
413 … CeedCallCuda(ceed, cudaMemcpy(data->d_q_weight_1d, q_weight_1d, q_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateTensorH1_Cuda()
415   CeedCallCuda(ceed, cudaMalloc((void **)&data->d_interp_1d, interp_bytes));  in CeedBasisCreateTensorH1_Cuda()
416 …CeedCallCuda(ceed, cudaMemcpy(data->d_interp_1d, interp_1d, interp_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateTensorH1_Cuda()
417   CeedCallCuda(ceed, cudaMalloc((void **)&data->d_grad_1d, interp_bytes));  in CeedBasisCreateTensorH1_Cuda()
418   CeedCallCuda(ceed, cudaMemcpy(data->d_grad_1d, grad_1d, interp_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateTensorH1_Cuda()
460     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_q_weight, q_bytes));  in CeedBasisCreateH1_Cuda()
461     CeedCallCuda(ceed, cudaMemcpy(data->d_q_weight, q_weight, q_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateH1_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()
472     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_grad, grad_bytes));  in CeedBasisCreateH1_Cuda()
473     CeedCallCuda(ceed, cudaMemcpy(data->d_grad, grad, grad_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateH1_Cuda()
515     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_q_weight, q_bytes));  in CeedBasisCreateHdiv_Cuda()
516     CeedCallCuda(ceed, cudaMemcpy(data->d_q_weight, q_weight, q_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateHdiv_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()
527     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_div, div_bytes));  in CeedBasisCreateHdiv_Cuda()
528     CeedCallCuda(ceed, cudaMemcpy(data->d_div, div, div_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateHdiv_Cuda()
570     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_q_weight, q_bytes));  in CeedBasisCreateHcurl_Cuda()
571     CeedCallCuda(ceed, cudaMemcpy(data->d_q_weight, q_weight, q_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateHcurl_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()
582     CeedCallCuda(ceed, cudaMalloc((void **)&data->d_curl, curl_bytes));  in CeedBasisCreateHcurl_Cuda()
583     CeedCallCuda(ceed, cudaMemcpy(data->d_curl, curl, curl_bytes, cudaMemcpyHostToDevice));  in CeedBasisCreateHcurl_Cuda()