1/* This testcase is part of GDB, the GNU debugger.
2
3   Copyright 2011 Free Software Foundation, Inc.
4
5   This program is free software; you can redistribute it and/or modify
6   it under the terms of the GNU General Public License as published by
7   the Free Software Foundation; either version 3 of the License, or
8   (at your option) any later version.
9
10   This program is distributed in the hope that it will be useful,
11   but WITHOUT ANY WARRANTY; without even the implied warranty of
12   MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
13   GNU General Public License for more details.
14
15   You should have received a copy of the GNU General Public License
16   along with this program.  If not, see <http://www.gnu.org/licenses/>.
17
18   Contributed by Ulrich Weigand <ulrich.weigand.ibm.com>  */
19
20__constant int opencl_version = __OPENCL_VERSION__;
21
22#ifdef HAVE_cl_khr_fp64
23#pragma OPENCL EXTENSION cl_khr_fp64 : enable
24__constant int have_cl_khr_fp64 = 1;
25#else
26__constant int have_cl_khr_fp64 = 0;
27#endif
28
29#ifdef HAVE_cl_khr_fp16
30#pragma OPENCL EXTENSION cl_khr_fp16 : enable
31__constant int have_cl_khr_fp16 = 1;
32#else
33__constant int have_cl_khr_fp16 = 0;
34#endif
35
36#define def_call_func(type) \
37  type call_##type (type a, type b) { return a + b; }
38
39#ifdef CL_VERSION_1_1
40#define def_call_family(type) \
41  def_call_func(type) \
42  def_call_func(type##2) \
43  def_call_func(type##3) \
44  def_call_func(type##4) \
45  def_call_func(type##8) \
46  def_call_func(type##16)
47#else
48#define def_call_family(type) \
49  def_call_func(type) \
50  def_call_func(type##2) \
51  def_call_func(type##4) \
52  def_call_func(type##8) \
53  def_call_func(type##16)
54#endif
55
56def_call_family(char)
57def_call_family(uchar)
58def_call_family(short)
59def_call_family(ushort)
60def_call_family(int)
61def_call_family(uint)
62def_call_family(long)
63def_call_family(ulong)
64#ifdef cl_khr_fp16
65def_call_family(half)
66#endif
67def_call_family(float)
68#ifdef cl_khr_fp64
69def_call_family(double)
70#endif
71
72#define call_func(type, var) \
73  var = call_##type (var, var);
74
75#ifdef CL_VERSION_1_1
76#define call_family(type, var) \
77  call_func(type, var) \
78  call_func(type##2, var##2) \
79  call_func(type##3, var##3) \
80  call_func(type##4, var##4) \
81  call_func(type##8, var##8) \
82  call_func(type##16, var##16)
83#else
84#define call_family(type, var) \
85  call_func(type, var) \
86  call_func(type##2, var##2) \
87  call_func(type##4, var##4) \
88  call_func(type##8, var##8) \
89  call_func(type##16, var##16)
90#endif
91
92__kernel void testkernel (__global int *data)
93{
94  bool b = 0;
95
96  char   c   = 1;
97  char2  c2  = (char2) (1, 2);
98#ifdef CL_VERSION_1_1
99  char3  c3  = (char3) (1, 2, 3);
100#endif
101  char4  c4  = (char4) (1, 2, 3, 4);
102  char8  c8  = (char8) (1, 2, 3, 4, 5, 6, 7, 8);
103  char16 c16 = (char16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
104
105  uchar   uc   = 1;
106  uchar2  uc2  = (uchar2) (1, 2);
107#ifdef CL_VERSION_1_1
108  uchar3  uc3  = (uchar3) (1, 2, 3);
109#endif
110  uchar4  uc4  = (uchar4) (1, 2, 3, 4);
111  uchar8  uc8  = (uchar8) (1, 2, 3, 4, 5, 6, 7, 8);
112  uchar16 uc16 = (uchar16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
113
114  short   s   = 1;
115  short2  s2  = (short2) (1, 2);
116#ifdef CL_VERSION_1_1
117  short3  s3  = (short3) (1, 2, 3);
118#endif
119  short4  s4  = (short4) (1, 2, 3, 4);
120  short8  s8  = (short8) (1, 2, 3, 4, 5, 6, 7, 8);
121  short16 s16 = (short16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
122
123  ushort   us   = 1;
124  ushort2  us2  = (ushort2) (1, 2);
125#ifdef CL_VERSION_1_1
126  ushort3  us3  = (ushort3) (1, 2, 3);
127#endif
128  ushort4  us4  = (ushort4) (1, 2, 3, 4);
129  ushort8  us8  = (ushort8) (1, 2, 3, 4, 5, 6, 7, 8);
130  ushort16 us16 = (ushort16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
131
132  int   i   = 1;
133  int2  i2  = (int2) (1, 2);
134#ifdef CL_VERSION_1_1
135  int3  i3  = (int3) (1, 2, 3);
136#endif
137  int4  i4  = (int4) (1, 2, 3, 4);
138  int8  i8  = (int8) (1, 2, 3, 4, 5, 6, 7, 8);
139  int16 i16 = (int16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
140
141  uint   ui   = 1;
142  uint2  ui2  = (uint2) (1, 2);
143#ifdef CL_VERSION_1_1
144  uint3  ui3  = (uint3) (1, 2, 3);
145#endif
146  uint4  ui4  = (uint4) (1, 2, 3, 4);
147  uint8  ui8  = (uint8) (1, 2, 3, 4, 5, 6, 7, 8);
148  uint16 ui16 = (uint16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
149
150  long   l   = 1;
151  long2  l2  = (long2) (1, 2);
152#ifdef CL_VERSION_1_1
153  long3  l3  = (long3) (1, 2, 3);
154#endif
155  long4  l4  = (long4) (1, 2, 3, 4);
156  long8  l8  = (long8) (1, 2, 3, 4, 5, 6, 7, 8);
157  long16 l16 = (long16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
158
159  ulong   ul   = 1;
160  ulong2  ul2  = (ulong2) (1, 2);
161#ifdef CL_VERSION_1_1
162  ulong3  ul3  = (ulong3) (1, 2, 3);
163#endif
164  ulong4  ul4  = (ulong4) (1, 2, 3, 4);
165  ulong8  ul8  = (ulong8) (1, 2, 3, 4, 5, 6, 7, 8);
166  ulong16 ul16 = (ulong16)(1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16);
167
168#ifdef cl_khr_fp16
169  half   h   = 1.0;
170  half2  h2  = (half2) (1.0, 2.0);
171#ifdef CL_VERSION_1_1
172  half3  h3  = (half3) (1.0, 2.0, 3.0);
173#endif
174  half4  h4  = (half4) (1.0, 2.0, 3.0, 4.0);
175  half8  h8  = (half8) (1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0);
176  half16 h16 = (half16)(1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0, 9.0, 10.0, 11.0, 12.0, 13.0, 14.0, 15.0, 16.0);
177#endif
178
179  float   f   = 1.0;
180  float2  f2  = (float2) (1.0, 2.0);
181#ifdef CL_VERSION_1_1
182  float3  f3  = (float3) (1.0, 2.0, 3.0);
183#endif
184  float4  f4  = (float4) (1.0, 2.0, 3.0, 4.0);
185  float8  f8  = (float8) (1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0);
186  float16 f16 = (float16)(1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0, 9.0, 10.0, 11.0, 12.0, 13.0, 14.0, 15.0, 16.0);
187
188#ifdef cl_khr_fp64
189  double   d   = 1.0;
190  double2  d2  = (double2) (1.0, 2.0);
191#ifdef CL_VERSION_1_1
192  double3  d3  = (double3) (1.0, 2.0, 3.0);
193#endif
194  double4  d4  = (double4) (1.0, 2.0, 3.0, 4.0);
195  double8  d8  = (double8) (1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0);
196  double16 d16 = (double16)(1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0, 9.0, 10.0, 11.0, 12.0, 13.0, 14.0, 15.0, 16.0);
197#endif
198
199  /* marker! */
200
201  call_family (char, c);
202  call_family (uchar, uc);
203  call_family (short, s);
204  call_family (ushort, us);
205  call_family (int, i);
206  call_family (uint, ui);
207  call_family (long, l);
208  call_family (ulong, ul);
209#ifdef cl_khr_fp16
210  call_family (half, h);
211#endif
212  call_family (float, f);
213#ifdef cl_khr_fp64
214  call_family (double, d);
215#endif
216
217  data[get_global_id(0)] = 1;
218}
219