blob: ea09856bbeb8ec305a5253a6304b5783e58a420e (
plain)
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
|
/*!
[config]
[test]
name: 1D 4 (2)
dimensions: 1
global_size: 4 0 0
local_size: 2 0 0
kernel_name: local_size_1d
arg_out: 0 buffer int[4] repeat 2
[test]
name: 2D 4 x 4 (2 x 1)
dimensions: 2
global_size: 4 4 0
local_size: 2 1 0
kernel_name: local_size_2d
arg_out: 0 buffer int[16] repeat 0x21
[test]
name: 3D 8 x 4 x 2 (4 x 2 x 1)
dimensions: 3
global_size: 8 4 2
local_size: 4 2 1
kernel_name: local_size_3d
arg_out: 0 buffer int[64] repeat 0x421
!*/
kernel void local_size_1d(global int *out) {
out[get_global_id(0)] = get_local_size(0);
}
kernel void local_size_2d(global int *out) {
out[get_global_id(0) + get_global_id(1) * get_global_size(0)] =
(get_local_size(0) << 4) | get_local_size(1);
}
kernel void local_size_3d(global int *out) {
out[get_global_id(0) + (get_global_id(1) * get_global_size(0)) +
(get_global_id(2) * get_global_size(0) * get_global_size(1))] =
(get_local_size(0) << 8) | (get_local_size(1) << 4) | get_local_size(2);
}
|
