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