| /libCEED/backends/hip/ |
| H A D | ceed-hip-compile.h | 22 …Ceed ceed, hipFunction_t kernel, int grid_size, int block_size_x, int block_size_y, int block_size… 25 … ceed, hipFunction_t kernel, hipStream_t stream, int grid_size, int block_size_x, int block_size_y, 27 … ceed, hipFunction_t kernel, hipStream_t stream, int grid_size, int block_size_x, int block_size_y,
|
| H A D | ceed-hip-compile.cpp | 220 …tion_t kernel, const int grid_size, const int block_size_x, const int block_size_y, const int bloc… in CeedRunKernelDim_Hip() argument 222 …CeedCallHip(ceed, hipModuleLaunchKernel(kernel, grid_size, 1, 1, block_size_x, block_size_y, block… in CeedRunKernelDim_Hip() 230 … const int block_size_y, const int block_size_z, const int shared_mem_size, const bool throw_error, in CeedRunKernelDimSharedCore_Hip() argument 232 …hipError_t result = hipModuleLaunchKernel(kernel, grid_size, 1, 1, block_size_x, block_size_y, blo… in CeedRunKernelDimSharedCore_Hip() 254 … const int block_size_y, const int block_size_z, const int shared_mem_size, void **args) { in CeedRunKernelDimShared_Hip() argument 257 …ernelDimSharedCore_Hip(ceed, kernel, stream, grid_size, block_size_x, block_size_y, block_size_z, … in CeedRunKernelDimShared_Hip() 263 …const int block_size_y, const int block_size_z, const int shared_mem_size, bool *is_good_run, void… in CeedTryRunKernelDimShared_Hip() argument 264 …ernelDimSharedCore_Hip(ceed, kernel, stream, grid_size, block_size_x, block_size_y, block_size_z, … in CeedTryRunKernelDimShared_Hip()
|
| /libCEED/backends/cuda/ |
| H A D | ceed-cuda-compile.h | 24 …da(Ceed ceed, CUfunction kernel, int grid_size, int block_size_x, int block_size_y, int block_size… 26 …a(Ceed ceed, CUfunction kernel, CUstream stream, int grid_size, int block_size_x, int block_size_y, 28 …a(Ceed ceed, CUfunction kernel, CUstream stream, int grid_size, int block_size_x, int block_size_y,
|
| H A D | ceed-cuda-compile.cpp | 462 …nction kernel, const int grid_size, const int block_size_x, const int block_size_y, const int bloc… in CeedRunKernelDim_Cuda() argument 464 …dRunKernelDimShared_Cuda(ceed, kernel, NULL, grid_size, block_size_x, block_size_y, block_size_z, … in CeedRunKernelDim_Cuda() 472 … const int block_size_y, const int block_size_z, const int shared_mem_size, const bool throw_error, in CeedRunKernelDimSharedCore_Cuda() argument 477 …CUresult result = cuLaunchKernel(kernel, grid_size, 1, 1, block_size_x, block_size_y, block_size_z… in CeedRunKernelDimSharedCore_Cuda() 488 … max_threads_per_block, block_size_x, block_size_y, block_size_z, shared_size_bytes, num_regs); in CeedRunKernelDimSharedCore_Cuda() 493 … max_threads_per_block, block_size_x, block_size_y, block_size_z, shared_size_bytes, num_regs); in CeedRunKernelDimSharedCore_Cuda() 502 …ction kernel, CUstream stream, const int grid_size, const int block_size_x, const int block_size_y, in CeedRunKernelDimShared_Cuda() argument 506 …rnelDimSharedCore_Cuda(ceed, kernel, stream, grid_size, block_size_x, block_size_y, block_size_z, … in CeedRunKernelDimShared_Cuda() 511 …ction kernel, CUstream stream, const int grid_size, const int block_size_x, const int block_size_y, in CeedTryRunKernelDimShared_Cuda() argument 513 …rnelDimSharedCore_Cuda(ceed, kernel, stream, grid_size, block_size_x, block_size_y, block_size_z, … in CeedTryRunKernelDimShared_Cuda()
|
| /libCEED/backends/sycl/ |
| H A D | ceed-sycl-compile.sycl.cpp | 169 …ed ceed, sycl::kernel *kernel, const int grid_size, const int block_size_x, const int block_size_y, in CeedRunKernelDimSharedSycl() argument 171 sycl::range<3> local_range(block_size_z, block_size_y, block_size_x); in CeedRunKernelDimSharedSycl() 172 sycl::range<3> global_range(grid_size * block_size_z, block_size_y, block_size_x); in CeedRunKernelDimSharedSycl()
|
| H A D | ceed-sycl-compile.hpp | 21 …ed ceed, sycl::kernel *kernel, const int grid_size, const int block_size_x, const int block_size_y,
|
| /libCEED/backends/sycl-ref/ |
| H A D | ceed-sycl-ref.hpp | 97 CeedInt num_elem, block_size_x, block_size_y, elems_per_block; member
|
| H A D | ceed-sycl-ref-operator.sycl.cpp | 1114 asmb->block_size_y = elem_size; in CeedOperatorAssembleSingleSetup_Sycl() 1217 const CeedInt block_size_y = asmb->block_size_y; in CeedOperatorLinearAssemble_Sycl() local 1219 sycl::range<3> kernel_range(num_elem, block_size_y, block_size_x); in CeedOperatorLinearAssemble_Sycl()
|
| /libCEED/backends/cuda-ref/ |
| H A D | ceed-cuda-ref.h | 130 CeedInt block_size_x, block_size_y, elems_per_block; member
|
| H A D | ceed-cuda-ref-operator.c | 1608 asmb->block_size_y = elem_size_out; in CeedOperatorAssembleSingleSetup_Cuda() 1611 …bool fallback = asmb->block_size_x * asmb->block_size_y * asmb->elems_per_block > cuda_data->devic… in CeedOperatorAssembleSingleSetup_Cuda() 1615 asmb->block_size_y = 1; in CeedOperatorAssembleSingleSetup_Cuda() 1626 …asmb->block_size_x * asmb->block_size_y * asmb->elems_per_block, "BLOCK_SIZE_Y", asmb->block_size_… in CeedOperatorAssembleSingleSetup_Cuda() 1782 … ? elem_size_in * elem_size_out : 0) + (curl_orients_in ? elem_size_in * asmb->block_size_y : 0)) * in CeedOperatorAssembleSingle_Cuda() 1788 …uda(ceed, asmb->LinearAssemble, NULL, grid, asmb->block_size_x, asmb->block_size_y, asmb->elems_pe… in CeedOperatorAssembleSingle_Cuda()
|
| H A D | ceed-cuda-ref-basis.c | 66 const int block_size_y = dim >= 2 ? Q_1d : 1; in CeedBasisApplyCore_Cuda() local 68 …end(CeedRunKernelDim_Cuda(ceed, data->Weight, num_elem, block_size_x, block_size_y, 1, weight_args… in CeedBasisApplyCore_Cuda()
|
| /libCEED/backends/hip-ref/ |
| H A D | ceed-hip-ref.h | 135 CeedInt block_size_x, block_size_y, elems_per_block; member
|
| H A D | ceed-hip-ref-operator.c | 1605 asmb->block_size_y = elem_size_out; in CeedOperatorAssembleSingleSetup_Hip() 1608 …bool fallback = asmb->block_size_x * asmb->block_size_y * asmb->elems_per_block > hip_data->device… in CeedOperatorAssembleSingleSetup_Hip() 1612 asmb->block_size_y = 1; in CeedOperatorAssembleSingleSetup_Hip() 1623 …asmb->block_size_x * asmb->block_size_y * asmb->elems_per_block, "BLOCK_SIZE_Y", asmb->block_size_… in CeedOperatorAssembleSingleSetup_Hip() 1779 … ? elem_size_in * elem_size_out : 0) + (curl_orients_in ? elem_size_in * asmb->block_size_y : 0)) * in CeedOperatorAssembleSingle_Hip() 1785 …Hip(ceed, asmb->LinearAssemble, NULL, grid, asmb->block_size_x, asmb->block_size_y, asmb->elems_pe… in CeedOperatorAssembleSingle_Hip()
|
| H A D | ceed-hip-ref-basis.c | 66 const int block_size_y = dim >= 2 ? Q_1d : 1; in CeedBasisApplyCore_Hip() local 68 …CeedCallBackend(CeedRunKernelDim_Hip(ceed, data->Weight, num_elem, block_size_x, block_size_y, 1, … in CeedBasisApplyCore_Hip()
|