Home
last modified time | relevance | path

Searched refs:dim3 (Results 1 – 25 of 25) sorted by relevance

/llvm-project-15.0.7/clang/test/CodeGenCUDA/Inputs/
H A Dcuda.h25 struct dim3 { struct
33 int hipConfigureCall(dim3 gridSize, dim3 blockSize, size_t sharedSize = 0,
35 extern "C" hipError_t __hipPushCallConfiguration(dim3 gridSize, dim3 blockSize,
39 extern "C" hipError_t hipLaunchKernel(const void *func, dim3 gridDim,
40 dim3 blockDim, void **args,
44 extern "C" hipError_t hipLaunchKernel_spt(const void *func, dim3 gridDim,
45 dim3 blockDim, void **args,
52 extern "C" int cudaConfigureCall(dim3 gridSize, dim3 blockSize,
55 extern "C" int __cudaPushCallConfiguration(dim3 gridSize, dim3 blockSize,
58 extern "C" cudaError_t cudaLaunchKernel(const void *func, dim3 gridDim,
[all …]
/llvm-project-15.0.7/clang/test/SemaCUDA/Inputs/
H A Dcuda.h16 struct dim3 { struct
18 __host__ __device__ dim3(unsigned x, unsigned y = 1, unsigned z = 1) : x(x), y(y), z(z) {} in x() argument
24 int hipConfigureCall(dim3 gridSize, dim3 blockSize, size_t sharedSize = 0,
26 extern "C" hipError_t __hipPushCallConfiguration(dim3 gridSize, dim3 blockSize,
29 extern "C" hipError_t hipLaunchKernel(const void *func, dim3 gridDim,
30 dim3 blockDim, void **args,
37 extern "C" int cudaConfigureCall(dim3 gridSize, dim3 blockSize,
40 extern "C" int __cudaPushCallConfiguration(dim3 gridSize, dim3 blockSize,
43 extern "C" cudaError_t cudaLaunchKernel(const void *func, dim3 gridDim,
44 dim3 blockDim, void **args,
/llvm-project-15.0.7/clang/test/AST/Inputs/
H A Dcuda.h16 struct dim3 { struct
18 __host__ __device__ dim3(unsigned x, unsigned y = 1, unsigned z = 1) : x(x), y(y), z(z) {} in x() argument
24 int hipConfigureCall(dim3 gridSize, dim3 blockSize, size_t sharedSize = 0,
26 extern "C" hipError_t __hipPushCallConfiguration(dim3 gridSize, dim3 blockSize,
29 extern "C" hipError_t hipLaunchKernel(const void *func, dim3 gridDim,
30 dim3 blockDim, void **args,
37 extern "C" int cudaConfigureCall(dim3 gridSize, dim3 blockSize,
40 extern "C" int __cudaPushCallConfiguration(dim3 gridSize, dim3 blockSize,
43 extern "C" cudaError_t cudaLaunchKernel(const void *func, dim3 gridDim,
44 dim3 blockDim, void **args,
/llvm-project-15.0.7/clang/lib/Headers/
H A D__clang_cuda_runtime_wrapper.h440 __device__ inline __cuda_builtin_threadIdx_t::operator dim3() const { in dim3() function
441 return dim3(x, y, z); in dim3()
448 __device__ inline __cuda_builtin_blockIdx_t::operator dim3() const { in dim3() function
449 return dim3(x, y, z); in dim3()
456 __device__ inline __cuda_builtin_blockDim_t::operator dim3() const { in dim3() function
457 return dim3(x, y, z); in dim3()
464 __device__ inline __cuda_builtin_gridDim_t::operator dim3() const { in dim3() function
465 return dim3(x, y, z); in dim3()
484 #define dim3 __cuda_builtin_blockDim_t macro
497 extern "C" unsigned __cudaPushCallConfiguration(dim3 gridDim, dim3 blockDim,
H A D__clang_cuda_builtin_vars.h15 struct dim3;
58 __attribute__((device)) operator dim3() const;
71 __attribute__((device)) operator dim3() const;
84 __attribute__((device)) operator dim3() const;
97 __attribute__((device)) operator dim3() const;
/llvm-project-15.0.7/clang/test/PCH/Inputs/
H A Dcuda.h12 struct dim3 { struct
14 __host__ __device__ dim3(unsigned x, unsigned y = 1, unsigned z = 1) : x(x), y(y), z(z) {} in x() argument
19 int cudaConfigureCall(dim3 gridSize, dim3 blockSize, size_t sharedSize = 0,
/llvm-project-15.0.7/polly/test/GPGPU/
H A Dscalar-parameter.ll25 ; CODE-NEXT: dim3 k0_dimBlock(32);
26 ; CODE-NEXT: dim3 k0_dimGrid(32);
79 ; CODE-NEXT: dim3 k0_dimBlock(32);
80 ; CODE-NEXT: dim3 k0_dimGrid(32);
128 ; CODE-NEXT: dim3 k0_dimBlock(32);
129 ; CODE-NEXT: dim3 k0_dimGrid(32);
177 ; CODE-NEXT: dim3 k0_dimBlock(32);
178 ; CODE-NEXT: dim3 k0_dimGrid(32);
227 ; CODE-NEXT: dim3 k0_dimGrid(32);
287 ; CODE-NEXT: dim3 k0_dimGrid(32);
[all …]
H A Dnon-read-only-scalars.ll34 ; CODE: dim3 k0_dimBlock(32);
35 ; CODE-NEXT: dim3 k0_dimGrid(1);
41 ; CODE-NEXT: dim3 k1_dimBlock;
42 ; CODE-NEXT: dim3 k1_dimGrid;
48 ; CODE-NEXT: dim3 k2_dimBlock;
49 ; CODE-NEXT: dim3 k2_dimGrid;
H A Dmostly-sequential.ll18 ; CODE-NEXT: dim3 k0_dimBlock(32);
19 ; CODE-NEXT: dim3 k0_dimGrid(4);
25 ; CODE-NEXT: dim3 k1_dimBlock;
26 ; CODE-NEXT: dim3 k1_dimGrid;
H A Dmanaged-pointers-preparation.ll22 ; CODE-NEXT: dim3 k0_dimBlock;
23 ; CODE-NEXT: dim3 k0_dimGrid;
30 ; CODE-NEXT: dim3 k1_dimBlock;
31 ; CODE-NEXT: dim3 k1_dimGrid;
H A Dnon-zero-array-offset.ll13 ; CODE: dim3 k0_dimBlock(8);
14 ; CODE-NEXT: dim3 k0_dimGrid(1);
20 ; CODE-NEXT: dim3 k1_dimBlock(8);
21 ; CODE-NEXT: dim3 k1_dimGrid(1);
H A Dhost-statement.ll25 ; CODE-NEXT: dim3 k0_dimBlock(32);
26 ; CODE-NEXT: dim3 k0_dimGrid(16);
33 ; CODE-NEXT: dim3 k1_dimBlock(32);
34 ; CODE-NEXT: dim3 k1_dimGrid(p_1 <= -1048034 ? 32768 : -p_1 + floord(31 * p_1 + 30, 32) + 16);
40 ; CODE-NEXT: dim3 k2_dimBlock(16, 32);
41 ; CODE-NEXT: dim3 k2_dimGrid(16, p_1 <= -7650 ? 256 : -p_1 + floord(31 * p_1 + 30, 32) + 16);
H A Dparametric-loop-bound.ll19 ; CODE-NEXT: dim3 k0_dimBlock(32);
20 ; CODE-NEXT: dim3 k0_dimGrid(n >= 1048545 ? 32768 : (n + 31) / 32);
H A Dsize-cast.ll15 ; CODE-NEXT: dim3 k0_dimBlock(32);
16 ; CODE-NEXT: dim3 k0_dimGrid(arg >= 1048545 ? 32768 : (arg + 31) / 32);
H A Dinvalid-kernel.ll26 ; CODE-NEXT: dim3 k0_dimBlock(32);
27 ; CODE-NEXT: dim3 k0_dimGrid(32);
H A Dregion-stmt.ll11 ; CODE-NEXT: dim3 k0_dimBlock(32);
12 ; CODE-NEXT: dim3 k0_dimGrid(4);
H A Dscheduler-timeout.ll35 ; CODE-NEXT: dim3 k0_dimBlock(16, 32);
36 ; CODE-NEXT: dim3 k0_dimGrid(128, 128);
42 ; CODE-NEXT: dim3 k1_dimBlock(16, 32);
43 ; CODE-NEXT: dim3 k1_dimGrid(128, 128);
H A Dphi-nodes-in-kernel.ll38 ; CODE-NEXT: dim3 k0_dimBlock(32);
39 ; CODE-NEXT: dim3 k0_dimGrid(2);
H A Duntouched-arrays.ll9 ; CODE-NEXT: dim3 k0_dimBlock(10);
10 ; CODE-NEXT: dim3 k0_dimGrid(1);
H A Dhost-control-flow.ll20 ; CODE-NEXT: dim3 k0_dimBlock(32);
21 ; CODE-NEXT: dim3 k0_dimGrid(4);
H A Ddouble-parallel-loop.ll78 ; CODE-NEXT: dim3 k0_dimBlock(16, 32);
79 ; CODE-NEXT: dim3 k0_dimGrid(32, 32);
/llvm-project-15.0.7/mlir/lib/Conversion/SCFToGPU/
H A DSCFToGPU.cpp58 static Value getDim3Value(const gpu::KernelDim3 &dim3, unsigned pos) { in getDim3Value() argument
61 return dim3.x; in getDim3Value()
63 return dim3.y; in getDim3Value()
65 return dim3.z; in getDim3Value()
/llvm-project-15.0.7/clang/test/Headers/Inputs/include/
H A Dcuda.h15 struct dim3 { struct
17 __host__ __device__ dim3(unsigned x, unsigned y = 1, unsigned z = 1) : x(x), y(y), z(z) {} in x() argument
/llvm-project-15.0.7/mlir/test/Dialect/Linalg/
H A Dloops.mlir749 // CHECK: %[[dim3:.*]] = memref.dim %[[arg2]], %[[c1]] : memref<?x?xf32>
751 // CHECK: scf.for %[[arg4:.*]] = %[[c0]] to %[[dim3]] step %[[c1]] {
774 // CHECKPARALLEL: %[[dim3:.*]] = memref.dim %[[arg2]], %[[c1]] : memref<?x?xf32>
775 …allel (%[[arg3:.*]], %[[arg4:.*]]) = (%[[c0]], %[[c0]]) to (%[[dim2]], %[[dim3]]) step (%[[c1]], %…
804 // CHECK: %[[dim3:.*]] = memref.dim %[[arg2]], %[[c0]] : memref<?x?x?xf32>
807 // CHECK: scf.for %[[arg3:.*]] = %[[c0]] to %[[dim3]] step %[[c1]] {
835 // CHECKPARALLEL: %[[dim3:.*]] = memref.dim %[[arg2]], %[[c0]] : memref<?x?x?xf32>
838 …g3:.*]], %[[arg4:.*]], %[[arg5:.*]]) = (%[[c0]], %[[c0]], %[[c0]]) to (%[[dim3]], %[[dim4]], %[[di…
/llvm-project-15.0.7/llvm/test/DebugInfo/NVPTX/
H A Ddebug-info.ll9054 !624 = !DISubprogram(name: "operator dim3", linkageName: "_ZNK25__cuda_builtin_blockDim_tcv4dim3Ev"…
9057 !627 = distinct !DICompositeType(tag: DW_TAG_structure_type, name: "dim3", file: !593, line: 417, s…
9062 !632 = !DISubprogram(name: "dim3", scope: !627, file: !593, line: 421, type: !633, isLocal: false, …
9066 !636 = !DISubprogram(name: "dim3", scope: !627, file: !593, line: 422, type: !637, isLocal: false, …