Lines Matching refs:CeedCallCuda

30   if (impl->module) CeedCallCuda(ceed, cuModuleUnload(impl->module));  in CeedOperatorDestroy_Cuda_gen()
31 if (impl->module_assemble_full) CeedCallCuda(ceed, cuModuleUnload(impl->module_assemble_full)); in CeedOperatorDestroy_Cuda_gen()
32 …if (impl->module_assemble_diagonal) CeedCallCuda(ceed, cuModuleUnload(impl->module_assemble_diagon… in CeedOperatorDestroy_Cuda_gen()
33 …if (impl->module_assemble_qfunction) CeedCallCuda(ceed, cuModuleUnload(impl->module_assemble_qfunc… in CeedOperatorDestroy_Cuda_gen()
34 if (impl->points.num_per_elem) CeedCallCuda(ceed, cudaFree((void **)impl->points.num_per_elem)); in CeedOperatorDestroy_Cuda_gen()
192 … if (data->points.num_per_elem) CeedCallCuda(ceed, cudaFree((void **)data->points.num_per_elem)); in CeedOperatorApplyAddCore_Cuda_gen()
193 CeedCallCuda(ceed, cudaMalloc((void **)&data->points.num_per_elem, num_bytes)); in CeedOperatorApplyAddCore_Cuda_gen()
194CeedCallCuda(ceed, cudaMemcpy((void *)data->points.num_per_elem, points_per_elem, num_bytes, cudaM… in CeedOperatorApplyAddCore_Cuda_gen()
208CeedCallCuda(ceed, cuOccupancyMaxPotentialBlockSize(&min_grid_size, &max_threads_per_block, data->… in CeedOperatorApplyAddCore_Cuda_gen()
311 if (is_sequential) CeedCallCuda(ceed, cudaStreamCreate(&stream)); in CeedOperatorApplyAddComposite_Cuda_gen()
317 if (!is_sequential) CeedCallCuda(ceed, cudaStreamCreate(&stream)); in CeedOperatorApplyAddComposite_Cuda_gen()
319 if (!is_sequential) CeedCallCuda(ceed, cudaStreamDestroy(stream)); in CeedOperatorApplyAddComposite_Cuda_gen()
322 if (is_sequential) CeedCallCuda(ceed, cudaStreamDestroy(stream)); in CeedOperatorApplyAddComposite_Cuda_gen()
325 CeedCallCuda(ceed, cudaDeviceSynchronize()); in CeedOperatorApplyAddComposite_Cuda_gen()
463CeedCallCuda(ceed, cuOccupancyMaxPotentialBlockSize(&min_grid_size, &max_threads_per_block, data->… in CeedOperatorLinearAssembleQFunctionCore_Cuda_gen()
479 CeedCallCuda(ceed, cudaDeviceSynchronize()); in CeedOperatorLinearAssembleQFunctionCore_Cuda_gen()
620 … if (data->points.num_per_elem) CeedCallCuda(ceed, cudaFree((void **)data->points.num_per_elem)); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda_gen()
621 CeedCallCuda(ceed, cudaMalloc((void **)&data->points.num_per_elem, num_bytes)); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda_gen()
622CeedCallCuda(ceed, cudaMemcpy((void *)data->points.num_per_elem, points_per_elem, num_bytes, cudaM… in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda_gen()
638CeedCallCuda(ceed, cuOccupancyMaxPotentialBlockSize(&min_grid_size, &max_threads_per_block, data->… in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda_gen()
647 CeedCallCuda(ceed, cudaDeviceSynchronize()); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda_gen()
783 … if (data->points.num_per_elem) CeedCallCuda(ceed, cudaFree((void **)data->points.num_per_elem)); in CeedOperatorAssembleSingleAtPoints_Cuda_gen()
784 CeedCallCuda(ceed, cudaMalloc((void **)&data->points.num_per_elem, num_bytes)); in CeedOperatorAssembleSingleAtPoints_Cuda_gen()
785CeedCallCuda(ceed, cudaMemcpy((void *)data->points.num_per_elem, points_per_elem, num_bytes, cudaM… in CeedOperatorAssembleSingleAtPoints_Cuda_gen()
803CeedCallCuda(ceed, cuOccupancyMaxPotentialBlockSize(&min_grid_size, &max_threads_per_block, data->… in CeedOperatorAssembleSingleAtPoints_Cuda_gen()
812 CeedCallCuda(ceed, cudaDeviceSynchronize()); in CeedOperatorAssembleSingleAtPoints_Cuda_gen()