[Piglit] [PATCH] CL: Add get_num_groups tests

[Aaron Watry]

Signed-off-by: Aaron Watry <awatry at gmail.com>
---
 tests/cl/program/execute/get-num-groups.cl | 144 +++++++++++++++++++++++++++++
 1 file changed, 144 insertions(+)
 create mode 100644 tests/cl/program/execute/get-num-groups.cl

diff --git a/tests/cl/program/execute/get-num-groups.cl b/tests/cl/program/execute/get-num-groups.cl
new file mode 100644
index 0000000..7e0cd0b
--- /dev/null
+++ b/tests/cl/program/execute/get-num-groups.cl
@@ -0,0 +1,144 @@
+/*!
+[config]
+name: get_num_groups
+clc_version_min: 10
+
+[test]
+name: 1D, global_size 1 0 0, local_size 1 0 0
+kernel_name: fill1d
+dimensions: 1
+global_size: 1 0 0
+local_size: 1 0 0
+arg_out: 0 buffer int[1] 1
+
+[test]
+name: 1D, global_size 2 0 0, local_size 1 0 0
+kernel_name: fill1d
+dimensions: 1
+global_size: 2 0 0
+local_size: 1 0 0
+arg_out: 0 buffer int[2] 2 2
+
+[test]
+name: 1D, global_size 4 0 0, local_size 1 0 0
+kernel_name: fill1d
+dimensions: 1
+global_size: 4 0 0
+local_size: 1 0 0
+arg_out: 0 buffer int[4] 4 4 4 4
+
+[test]
+name: 1D, global_size 4 0 0, local_size 2 0 0
+kernel_name: fill1d
+dimensions: 1
+global_size: 4 0 0
+local_size: 2 0 0
+arg_out: 0 buffer int[4] 2 2 2 2
+
+[test]
+name: 1D, global_size 4 0 0, local_size 4 0 0
+kernel_name: fill1d
+dimensions: 1
+global_size: 4 0 0
+local_size: 4 0 0
+arg_out: 0 buffer int[4] 1 1 1 1
+
+[test]
+name: 2D, global_size 4 4 0, local_size 1 1 0
+kernel_name: fill2d
+dimensions: 2
+global_size: 4 4 0
+local_size: 1 1 0
+arg_out: 0 buffer int[32] 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 \
+                          4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4
+
+[test]
+name: 2D, global_size 4 4 0, local_size 2 2 0
+kernel_name: fill2d
+dimensions: 2
+global_size: 4 4 0
+local_size: 2 2 0
+arg_out: 0 buffer int[32] 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 \
+                          2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2
+
+[test]
+name: 2D, global_size 4 4 0, local_size 4 4 0
+kernel_name: fill2d
+dimensions: 2
+global_size: 4 4 0
+local_size: 4 4 0
+arg_out: 0 buffer int[32] 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 \
+                          1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1
+
+[test]
+name: 3D, global_size 4 4 4, local_size 1 1 1
+kernel_name: fill3d
+dimensions: 3
+global_size: 4 4 4
+local_size: 1 1 1
+arg_out: 0 buffer int[144] 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 \
+                           4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 \
+                           4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 \
+                           4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 \
+                           4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 \
+                           4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4 4
+
+[test]
+name: 3D, global_size 4 4 4, local_size 2 2 2
+kernel_name: fill3d
+dimensions: 3
+global_size: 4 4 4
+local_size: 2 2 2
+arg_out: 0 buffer int[144] 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 \
+                           2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 \
+                           2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 \
+                           2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 \
+                           2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 \
+                           2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2 2
+
+[test]
+name: 3D, global_size 4 4 4, local_size 4 4 4
+kernel_name: fill3d
+dimensions: 3
+global_size: 4 4 4
+local_size: 4 4 4
+arg_out: 0 buffer int[144] 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 \
+                           1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 \
+                           1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 \
+                           1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 \
+                           1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 \
+                           1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1 1
+
+[test]
+name: 3D, global_size 4 4 4, local_size 4 2 1
+kernel_name: fill3d
+dimensions: 3
+global_size: 4 4 4
+local_size: 4 2 1
+arg_out: 0 buffer int[144] 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 \
+                           1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 \
+                           1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 \
+                           1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 \
+                           1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 \
+                           1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4 1 2 4
+
+!*/
+
+kernel void fill1d(global int* out) {
+	unsigned int id = get_global_id(0);
+	out[id] = get_num_groups(0);
+}
+
+kernel void fill2d(global int* out) {
+	unsigned int id = get_global_id(0) + get_global_size(0)*get_global_id(1);
+	out[2*id] = get_num_groups(0);
+	out[2*id+1] = get_num_groups(1);
+}
+
+kernel void fill3d(global int* out) {
+	
+	unsigned int id =  get_global_id(0) + get_global_size(0)*get_global_id(1) + get_global_size(0)*get_global_size(1)*get_global_id(2);
+	out[3*id] = get_num_groups(0);
+	out[3*id+1] = get_num_groups(1);
+	out[3*id+2] = get_num_groups(2);
+}
-- 
1.8.1.2