← Back to branch summary

~ubuntu-branches/ubuntu/saucy/darktable/saucy

« back to all changes in this revision

Viewing changes to src/external/CL/cl_platform.h

  • Committer: Bazaar Package Importer
  • Author(s): David Bremner
  • Date: 2011-07-12 09:36:46 UTC
  • mfrom: (1.1.1 upstream)
  • Revision ID: james.westby@ubuntu.com-20110712093646-yp9dbxan44dmw15h
Tags: 0.9-1
* New upstream release.
* Remove all patches now upstream; only patch for
  -Wno-error=unused-but-set-variable remains.
* Bump Standards-Version to 3.9.2 (no changes)

Show diffs side-by-side

added added

removed removed

Lines of Context:
src/external/CL/cl_platform.h
 
1
/**********************************************************************************
 
2
 * Copyright (c) 2008-2010 The Khronos Group Inc.
 
3
 *
 
4
 * Permission is hereby granted, free of charge, to any person obtaining a
 
5
 * copy of this software and/or associated documentation files (the
 
6
 * "Materials"), to deal in the Materials without restriction, including
 
7
 * without limitation the rights to use, copy, modify, merge, publish,
 
8
 * distribute, sublicense, and/or sell copies of the Materials, and to
 
9
 * permit persons to whom the Materials are furnished to do so, subject to
 
10
 * the following conditions:
 
11
 *
 
12
 * The above copyright notice and this permission notice shall be included
 
13
 * in all copies or substantial portions of the Materials.
 
14
 *
 
15
 * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
 
16
 * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
 
17
 * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
 
18
 * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY
 
19
 * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT,
 
20
 * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE
 
21
 * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS.
 
22
 **********************************************************************************/
 
23
 
 
24
/* $Revision: 11803 $ on $Date: 2010-06-25 10:02:12 -0700 (Fri, 25 Jun 2010) $ */
 
25
 
 
26
#ifndef __CL_PLATFORM_H
 
27
#define __CL_PLATFORM_H
 
28
 
 
29
#ifdef __APPLE__
 
30
    /* Contains #defines for AVAILABLE_MAC_OS_X_VERSION_10_6_AND_LATER below */
 
31
    #include <AvailabilityMacros.h>
 
32
#endif
 
33
 
 
34
#ifdef __cplusplus
 
35
extern "C" {
 
36
#endif
 
37
 
 
38
#if defined(_WIN32)
 
39
    #define CL_API_ENTRY
 
40
    #define CL_API_CALL     __stdcall
 
41
    #define CL_CALLBACK     __stdcall
 
42
#else
 
43
    #define CL_API_ENTRY
 
44
    #define CL_API_CALL
 
45
    #define CL_CALLBACK
 
46
#endif
 
47
 
 
48
#ifdef __APPLE__
 
49
    #define CL_EXTENSION_WEAK_LINK                  __attribute__((weak_import))       
 
50
    #define CL_API_SUFFIX__VERSION_1_0              AVAILABLE_MAC_OS_X_VERSION_10_6_AND_LATER
 
51
    #define CL_EXT_SUFFIX__VERSION_1_0              CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_6_AND_LATER
 
52
    #define CL_API_SUFFIX__VERSION_1_1              CL_EXTENSION_WEAK_LINK
 
53
    #define CL_EXT_SUFFIX__VERSION_1_1              CL_EXTENSION_WEAK_LINK
 
54
    #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED   CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_6_AND_LATER
 
55
#else
 
56
    #define CL_EXTENSION_WEAK_LINK                         
 
57
    #define CL_API_SUFFIX__VERSION_1_0
 
58
    #define CL_EXT_SUFFIX__VERSION_1_0
 
59
    #define CL_API_SUFFIX__VERSION_1_1
 
60
    #define CL_EXT_SUFFIX__VERSION_1_1
 
61
    #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
 
62
#endif
 
63
 
 
64
#if (defined (_WIN32) && defined(_MSC_VER))
 
65
 
 
66
/* scalar types  */
 
67
typedef signed   __int8         cl_char;
 
68
typedef unsigned __int8         cl_uchar;
 
69
typedef signed   __int16        cl_short;
 
70
typedef unsigned __int16        cl_ushort;
 
71
typedef signed   __int32        cl_int;
 
72
typedef unsigned __int32        cl_uint;
 
73
typedef signed   __int64        cl_long;
 
74
typedef unsigned __int64        cl_ulong;
 
75
 
 
76
typedef unsigned __int16        cl_half;
 
77
typedef float                   cl_float;
 
78
typedef double                  cl_double;
 
79
 
 
80
/* Macro names and corresponding values defined by OpenCL */
 
81
#define CL_CHAR_BIT         8
 
82
#define CL_SCHAR_MAX        127
 
83
#define CL_SCHAR_MIN        (-127-1)
 
84
#define CL_CHAR_MAX         CL_SCHAR_MAX
 
85
#define CL_CHAR_MIN         CL_SCHAR_MIN
 
86
#define CL_UCHAR_MAX        255
 
87
#define CL_SHRT_MAX         32767
 
88
#define CL_SHRT_MIN         (-32767-1)
 
89
#define CL_USHRT_MAX        65535
 
90
#define CL_INT_MAX          2147483647
 
91
#define CL_INT_MIN          (-2147483647-1)
 
92
#define CL_UINT_MAX         0xffffffffU
 
93
#define CL_LONG_MAX         ((cl_long) 0x7FFFFFFFFFFFFFFFLL)
 
94
#define CL_LONG_MIN         ((cl_long) -0x7FFFFFFFFFFFFFFFLL - 1LL)
 
95
#define CL_ULONG_MAX        ((cl_ulong) 0xFFFFFFFFFFFFFFFFULL)
 
96
 
 
97
#define CL_FLT_DIG          6
 
98
#define CL_FLT_MANT_DIG     24
 
99
#define CL_FLT_MAX_10_EXP   +38
 
100
#define CL_FLT_MAX_EXP      +128
 
101
#define CL_FLT_MIN_10_EXP   -37
 
102
#define CL_FLT_MIN_EXP      -125
 
103
#define CL_FLT_RADIX        2
 
104
#define CL_FLT_MAX          340282346638528859811704183484516925440.0f
 
105
#define CL_FLT_MIN          1.175494350822287507969e-38f
 
106
#define CL_FLT_EPSILON      0x1.0p-23f
 
107
 
 
108
#define CL_DBL_DIG          15
 
109
#define CL_DBL_MANT_DIG     53
 
110
#define CL_DBL_MAX_10_EXP   +308
 
111
#define CL_DBL_MAX_EXP      +1024
 
112
#define CL_DBL_MIN_10_EXP   -307
 
113
#define CL_DBL_MIN_EXP      -1021
 
114
#define CL_DBL_RADIX        2
 
115
#define CL_DBL_MAX          179769313486231570814527423731704356798070567525844996598917476803157260780028538760589558632766878171540458953514382464234321326889464182768467546703537516986049910576551282076245490090389328944075868508455133942304583236903222948165808559332123348274797826204144723168738177180919299881250404026184124858368.0
 
116
#define CL_DBL_MIN          2.225073858507201383090e-308
 
117
#define CL_DBL_EPSILON      2.220446049250313080847e-16
 
118
 
 
119
#define  CL_M_E             2.718281828459045090796
 
120
#define  CL_M_LOG2E         1.442695040888963387005
 
121
#define  CL_M_LOG10E        0.434294481903251816668
 
122
#define  CL_M_LN2           0.693147180559945286227
 
123
#define  CL_M_LN10          2.302585092994045901094
 
124
#define  CL_M_PI            3.141592653589793115998
 
125
#define  CL_M_PI_2          1.570796326794896557999
 
126
#define  CL_M_PI_4          0.785398163397448278999
 
127
#define  CL_M_1_PI          0.318309886183790691216
 
128
#define  CL_M_2_PI          0.636619772367581382433
 
129
#define  CL_M_2_SQRTPI      1.128379167095512558561
 
130
#define  CL_M_SQRT2         1.414213562373095145475
 
131
#define  CL_M_SQRT1_2       0.707106781186547572737
 
132
 
 
133
#define  CL_M_E_F           2.71828174591064f
 
134
#define  CL_M_LOG2E_F       1.44269502162933f
 
135
#define  CL_M_LOG10E_F      0.43429449200630f
 
136
#define  CL_M_LN2_F         0.69314718246460f
 
137
#define  CL_M_LN10_F        2.30258512496948f
 
138
#define  CL_M_PI_F          3.14159274101257f
 
139
#define  CL_M_PI_2_F        1.57079637050629f
 
140
#define  CL_M_PI_4_F        0.78539818525314f
 
141
#define  CL_M_1_PI_F        0.31830987334251f
 
142
#define  CL_M_2_PI_F        0.63661974668503f
 
143
#define  CL_M_2_SQRTPI_F    1.12837922573090f
 
144
#define  CL_M_SQRT2_F       1.41421353816986f
 
145
#define  CL_M_SQRT1_2_F     0.70710676908493f
 
146
 
 
147
#define CL_NAN              (CL_INFINITY - CL_INFINITY)
 
148
#define CL_HUGE_VALF        ((cl_float) 1e50)
 
149
#define CL_HUGE_VAL         ((cl_double) 1e500)
 
150
#define CL_MAXFLOAT         CL_FLT_MAX
 
151
#define CL_INFINITY         CL_HUGE_VALF
 
152
 
 
153
#else
 
154
 
 
155
#include <stdint.h>
 
156
 
 
157
/* scalar types  */
 
158
typedef int8_t          cl_char;
 
159
typedef uint8_t         cl_uchar;
 
160
typedef int16_t         cl_short    __attribute__((aligned(2)));
 
161
typedef uint16_t        cl_ushort   __attribute__((aligned(2)));
 
162
typedef int32_t         cl_int      __attribute__((aligned(4)));
 
163
typedef uint32_t        cl_uint     __attribute__((aligned(4)));
 
164
typedef int64_t         cl_long     __attribute__((aligned(8)));
 
165
typedef uint64_t        cl_ulong    __attribute__((aligned(8)));
 
166
 
 
167
typedef uint16_t        cl_half     __attribute__((aligned(2)));
 
168
typedef float           cl_float    __attribute__((aligned(4)));
 
169
typedef double          cl_double   __attribute__((aligned(8)));
 
170
 
 
171
/* Macro names and corresponding values defined by OpenCL */
 
172
#define CL_CHAR_BIT         8
 
173
#define CL_SCHAR_MAX        127
 
174
#define CL_SCHAR_MIN        (-127-1)
 
175
#define CL_CHAR_MAX         CL_SCHAR_MAX
 
176
#define CL_CHAR_MIN         CL_SCHAR_MIN
 
177
#define CL_UCHAR_MAX        255
 
178
#define CL_SHRT_MAX         32767
 
179
#define CL_SHRT_MIN         (-32767-1)
 
180
#define CL_USHRT_MAX        65535
 
181
#define CL_INT_MAX          2147483647
 
182
#define CL_INT_MIN          (-2147483647-1)
 
183
#define CL_UINT_MAX         0xffffffffU
 
184
#define CL_LONG_MAX         ((cl_long) 0x7FFFFFFFFFFFFFFFLL)
 
185
#define CL_LONG_MIN         ((cl_long) -0x7FFFFFFFFFFFFFFFLL - 1LL)
 
186
#define CL_ULONG_MAX        ((cl_ulong) 0xFFFFFFFFFFFFFFFFULL)
 
187
 
 
188
#define CL_FLT_DIG          6
 
189
#define CL_FLT_MANT_DIG     24
 
190
#define CL_FLT_MAX_10_EXP   +38
 
191
#define CL_FLT_MAX_EXP      +128
 
192
#define CL_FLT_MIN_10_EXP   -37
 
193
#define CL_FLT_MIN_EXP      -125
 
194
#define CL_FLT_RADIX        2
 
195
#define CL_FLT_MAX          0x1.fffffep127f
 
196
#define CL_FLT_MIN          0x1.0p-126f
 
197
#define CL_FLT_EPSILON      0x1.0p-23f
 
198
 
 
199
#define CL_DBL_DIG          15
 
200
#define CL_DBL_MANT_DIG     53
 
201
#define CL_DBL_MAX_10_EXP   +308
 
202
#define CL_DBL_MAX_EXP      +1024
 
203
#define CL_DBL_MIN_10_EXP   -307
 
204
#define CL_DBL_MIN_EXP      -1021
 
205
#define CL_DBL_RADIX        2
 
206
#define CL_DBL_MAX          0x1.fffffffffffffp1023
 
207
#define CL_DBL_MIN          0x1.0p-1022
 
208
#define CL_DBL_EPSILON      0x1.0p-52
 
209
 
 
210
#define  CL_M_E             2.718281828459045090796
 
211
#define  CL_M_LOG2E         1.442695040888963387005
 
212
#define  CL_M_LOG10E        0.434294481903251816668
 
213
#define  CL_M_LN2           0.693147180559945286227
 
214
#define  CL_M_LN10          2.302585092994045901094
 
215
#define  CL_M_PI            3.141592653589793115998
 
216
#define  CL_M_PI_2          1.570796326794896557999
 
217
#define  CL_M_PI_4          0.785398163397448278999
 
218
#define  CL_M_1_PI          0.318309886183790691216
 
219
#define  CL_M_2_PI          0.636619772367581382433
 
220
#define  CL_M_2_SQRTPI      1.128379167095512558561
 
221
#define  CL_M_SQRT2         1.414213562373095145475
 
222
#define  CL_M_SQRT1_2       0.707106781186547572737
 
223
 
 
224
#define  CL_M_E_F           2.71828174591064f
 
225
#define  CL_M_LOG2E_F       1.44269502162933f
 
226
#define  CL_M_LOG10E_F      0.43429449200630f
 
227
#define  CL_M_LN2_F         0.69314718246460f
 
228
#define  CL_M_LN10_F        2.30258512496948f
 
229
#define  CL_M_PI_F          3.14159274101257f
 
230
#define  CL_M_PI_2_F        1.57079637050629f
 
231
#define  CL_M_PI_4_F        0.78539818525314f
 
232
#define  CL_M_1_PI_F        0.31830987334251f
 
233
#define  CL_M_2_PI_F        0.63661974668503f
 
234
#define  CL_M_2_SQRTPI_F    1.12837922573090f
 
235
#define  CL_M_SQRT2_F       1.41421353816986f
 
236
#define  CL_M_SQRT1_2_F     0.70710676908493f
 
237
 
 
238
#if defined( __GNUC__ )
 
239
   #define CL_HUGE_VALF     __builtin_huge_valf()
 
240
   #define CL_HUGE_VAL      __builtin_huge_val()
 
241
   #define CL_NAN           __builtin_nanf( "" )
 
242
#else
 
243
   #define CL_HUGE_VALF     ((cl_float) 1e50)
 
244
   #define CL_HUGE_VAL      ((cl_double) 1e500)
 
245
   float nanf( const char * );
 
246
   #define CL_NAN           nanf( "" )  
 
247
#endif
 
248
#define CL_MAXFLOAT         CL_FLT_MAX
 
249
#define CL_INFINITY         CL_HUGE_VALF
 
250
 
 
251
#endif
 
252
 
 
253
#include <stddef.h>
 
254
 
 
255
/* Mirror types to GL types. Mirror types allow us to avoid deciding which headers to load based on whether we are using GL or GLES here. */
 
256
typedef unsigned int cl_GLuint;
 
257
typedef int          cl_GLint;
 
258
typedef unsigned int cl_GLenum;
 
259
 
 
260
/*
 
261
 * Vector types 
 
262
 *
 
263
 *  Note:   OpenCL requires that all types be naturally aligned. 
 
264
 *          This means that vector types must be naturally aligned.
 
265
 *          For example, a vector of four floats must be aligned to
 
266
 *          a 16 byte boundary (calculated as 4 * the natural 4-byte 
 
267
 *          alignment of the float).  The alignment qualifiers here
 
268
 *          will only function properly if your compiler supports them
 
269
 *          and if you don't actively work to defeat them.  For example,
 
270
 *          in order for a cl_float4 to be 16 byte aligned in a struct,
 
271
 *          the start of the struct must itself be 16-byte aligned. 
 
272
 *
 
273
 *          Maintaining proper alignment is the user's responsibility.
 
274
 */
 
275
 
 
276
/* Define basic vector types */
 
277
#if defined( __VEC__ )
 
278
   #include <altivec.h>   /* may be omitted depending on compiler. AltiVec spec provides no way to detect whether the header is required. */
 
279
   typedef vector unsigned char     __cl_uchar16;
 
280
   typedef vector signed char       __cl_char16;
 
281
   typedef vector unsigned short    __cl_ushort8;
 
282
   typedef vector signed short      __cl_short8;
 
283
   typedef vector unsigned int      __cl_uint4;
 
284
   typedef vector signed int        __cl_int4;
 
285
   typedef vector float             __cl_float4;
 
286
   #define  __CL_UCHAR16__  1
 
287
   #define  __CL_CHAR16__   1
 
288
   #define  __CL_USHORT8__  1
 
289
   #define  __CL_SHORT8__   1
 
290
   #define  __CL_UINT4__    1
 
291
   #define  __CL_INT4__     1
 
292
   #define  __CL_FLOAT4__   1
 
293
#endif
 
294
 
 
295
#if defined( __SSE__ )
 
296
    #if defined( __MINGW64__ )
 
297
        #include <intrin.h>
 
298
    #else
 
299
        #include <xmmintrin.h>
 
300
    #endif
 
301
    #if defined( __GNUC__ )
 
302
        typedef float __cl_float4   __attribute__((vector_size(16)));
 
303
    #else
 
304
        typedef __m128 __cl_float4;
 
305
    #endif
 
306
    #define __CL_FLOAT4__   1
 
307
#endif
 
308
 
 
309
#if defined( __SSE2__ )
 
310
    #if defined( __MINGW64__ )
 
311
        #include <intrin.h>
 
312
    #else
 
313
        #include <emmintrin.h>
 
314
    #endif
 
315
    #if defined( __GNUC__ )
 
316
        typedef cl_uchar    __cl_uchar16    __attribute__((vector_size(16)));
 
317
        typedef cl_char     __cl_char16     __attribute__((vector_size(16)));
 
318
        typedef cl_ushort   __cl_ushort8    __attribute__((vector_size(16)));
 
319
        typedef cl_short    __cl_short8     __attribute__((vector_size(16)));
 
320
        typedef cl_uint     __cl_uint4      __attribute__((vector_size(16)));
 
321
        typedef cl_int      __cl_int4       __attribute__((vector_size(16)));
 
322
        typedef cl_ulong    __cl_ulong2     __attribute__((vector_size(16)));
 
323
        typedef cl_long     __cl_long2      __attribute__((vector_size(16)));
 
324
        typedef cl_double   __cl_double2    __attribute__((vector_size(16)));
 
325
    #else
 
326
        typedef __m128i __cl_uchar16;
 
327
        typedef __m128i __cl_char16;
 
328
        typedef __m128i __cl_ushort8;
 
329
        typedef __m128i __cl_short8;
 
330
        typedef __m128i __cl_uint4;
 
331
        typedef __m128i __cl_int4;
 
332
        typedef __m128i __cl_ulong2;
 
333
        typedef __m128i __cl_long2;
 
334
        typedef __m128d __cl_double2;
 
335
    #endif
 
336
    #define __CL_UCHAR16__  1
 
337
    #define __CL_CHAR16__   1
 
338
    #define __CL_USHORT8__  1
 
339
    #define __CL_SHORT8__   1
 
340
    #define __CL_INT4__     1
 
341
    #define __CL_UINT4__    1
 
342
    #define __CL_ULONG2__   1
 
343
    #define __CL_LONG2__    1
 
344
    #define __CL_DOUBLE2__  1
 
345
#endif
 
346
 
 
347
#if defined( __MMX__ )
 
348
    #include <mmintrin.h>
 
349
    #if defined( __GNUC__ )
 
350
        typedef cl_uchar    __cl_uchar8     __attribute__((vector_size(8)));
 
351
        typedef cl_char     __cl_char8      __attribute__((vector_size(8)));
 
352
        typedef cl_ushort   __cl_ushort4    __attribute__((vector_size(8)));
 
353
        typedef cl_short    __cl_short4     __attribute__((vector_size(8)));
 
354
        typedef cl_uint     __cl_uint2      __attribute__((vector_size(8)));
 
355
        typedef cl_int      __cl_int2       __attribute__((vector_size(8)));
 
356
        typedef cl_ulong    __cl_ulong1     __attribute__((vector_size(8)));
 
357
        typedef cl_long     __cl_long1      __attribute__((vector_size(8)));
 
358
        typedef cl_float    __cl_float2     __attribute__((vector_size(8)));
 
359
    #else
 
360
        typedef __m64       __cl_uchar8;
 
361
        typedef __m64       __cl_char8;
 
362
        typedef __m64       __cl_ushort4;
 
363
        typedef __m64       __cl_short4;
 
364
        typedef __m64       __cl_uint2;
 
365
        typedef __m64       __cl_int2;
 
366
        typedef __m64       __cl_ulong1;
 
367
        typedef __m64       __cl_long1;
 
368
        typedef __m64       __cl_float2;
 
369
    #endif
 
370
    #define __CL_UCHAR8__   1
 
371
    #define __CL_CHAR8__    1
 
372
    #define __CL_USHORT4__  1
 
373
    #define __CL_SHORT4__   1
 
374
    #define __CL_INT2__     1
 
375
    #define __CL_UINT2__    1
 
376
    #define __CL_ULONG1__   1
 
377
    #define __CL_LONG1__    1
 
378
    #define __CL_FLOAT2__   1
 
379
#endif
 
380
 
 
381
#if defined( __AVX__ )
 
382
    #if defined( __MINGW64__ )
 
383
        #include <intrin.h>
 
384
    #else
 
385
        #include <immintrin.h> 
 
386
    #endif
 
387
    #if defined( __GNUC__ )
 
388
        typedef cl_float    __cl_float8     __attribute__((vector_size(32)));
 
389
        typedef cl_double   __cl_double4    __attribute__((vector_size(32)));
 
390
    #else
 
391
        typedef __m256      __cl_float8;
 
392
        typedef __m256d     __cl_double4;
 
393
    #endif
 
394
    #define __CL_FLOAT8__   1
 
395
    #define __CL_DOUBLE4__  1
 
396
#endif
 
397
 
 
398
/* Define alignment keys */
 
399
#if defined( __GNUC__ )
 
400
    #define CL_ALIGNED(_x)          __attribute__ ((aligned(_x)))
 
401
#elif defined( _WIN32) && (_MSC_VER)
 
402
    /* Alignment keys neutered on windows because MSVC can't swallow function arguments with alignment requirements     */
 
403
    /* http://msdn.microsoft.com/en-us/library/373ak2y1%28VS.71%29.aspx                                                 */
 
404
    /* #include <crtdefs.h>                                                                                             */
 
405
    /* #define CL_ALIGNED(_x)          _CRT_ALIGN(_x)                                                                   */
 
406
    #define CL_ALIGNED(_x)
 
407
#else
 
408
   #warning  Need to implement some method to align data here
 
409
   #define  CL_ALIGNED(_x)
 
410
#endif
 
411
 
 
412
/* Indicate whether .xyzw, .s0123 and .hi.lo are supported */
 
413
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
414
    /* .xyzw and .s0123...{f|F} are supported */
 
415
    #define CL_HAS_NAMED_VECTOR_FIELDS 1
 
416
    /* .hi and .lo are supported */
 
417
    #define CL_HAS_HI_LO_VECTOR_FIELDS 1
 
418
#endif
 
419
 
 
420
/* Define cl_vector types */
 
421
 
 
422
/* ---- cl_charn ---- */
 
423
typedef union
 
424
{
 
425
    cl_char  CL_ALIGNED(2) s[2];
 
426
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
427
   __extension__ struct{ cl_char  x, y; };
 
428
   __extension__ struct{ cl_char  s0, s1; };
 
429
   __extension__ struct{ cl_char  lo, hi; };
 
430
#endif
 
431
#if defined( __CL_CHAR2__) 
 
432
    __cl_char2     v2;
 
433
#endif
 
434
}cl_char2;
 
435
 
 
436
typedef union
 
437
{
 
438
    cl_char  CL_ALIGNED(4) s[4];
 
439
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
440
   __extension__ struct{ cl_char  x, y, z, w; };
 
441
   __extension__ struct{ cl_char  s0, s1, s2, s3; };
 
442
   __extension__ struct{ cl_char2 lo, hi; };
 
443
#endif
 
444
#if defined( __CL_CHAR2__) 
 
445
    __cl_char2     v2[2];
 
446
#endif
 
447
#if defined( __CL_CHAR4__) 
 
448
    __cl_char4     v4;
 
449
#endif
 
450
}cl_char4;
 
451
 
 
452
/* cl_char3 is identical in size, alignment and behavior to cl_char4. See section 6.1.5. */
 
453
typedef  cl_char4  cl_char3;
 
454
 
 
455
typedef union
 
456
{
 
457
    cl_char   CL_ALIGNED(8) s[8];
 
458
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
459
   __extension__ struct{ cl_char  x, y, z, w; };
 
460
   __extension__ struct{ cl_char  s0, s1, s2, s3, s4, s5, s6, s7; };
 
461
   __extension__ struct{ cl_char4 lo, hi; };
 
462
#endif
 
463
#if defined( __CL_CHAR2__) 
 
464
    __cl_char2     v2[4];
 
465
#endif
 
466
#if defined( __CL_CHAR4__) 
 
467
    __cl_char4     v4[2];
 
468
#endif
 
469
#if defined( __CL_CHAR8__ )
 
470
    __cl_char8     v8;
 
471
#endif
 
472
}cl_char8;
 
473
 
 
474
typedef union
 
475
{
 
476
    cl_char  CL_ALIGNED(16) s[16];
 
477
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
478
   __extension__ struct{ cl_char  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
479
   __extension__ struct{ cl_char  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
480
   __extension__ struct{ cl_char8 lo, hi; };
 
481
#endif
 
482
#if defined( __CL_CHAR2__) 
 
483
    __cl_char2     v2[8];
 
484
#endif
 
485
#if defined( __CL_CHAR4__) 
 
486
    __cl_char4     v4[4];
 
487
#endif
 
488
#if defined( __CL_CHAR8__ )
 
489
    __cl_char8     v8[2];
 
490
#endif
 
491
#if defined( __CL_CHAR16__ )
 
492
    __cl_char16    v16;
 
493
#endif
 
494
}cl_char16;
 
495
 
 
496
 
 
497
/* ---- cl_ucharn ---- */
 
498
typedef union
 
499
{
 
500
    cl_uchar  CL_ALIGNED(2) s[2];
 
501
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
502
   __extension__ struct{ cl_uchar  x, y; };
 
503
   __extension__ struct{ cl_uchar  s0, s1; };
 
504
   __extension__ struct{ cl_uchar  lo, hi; };
 
505
#endif
 
506
#if defined( __cl_uchar2__) 
 
507
    __cl_uchar2     v2;
 
508
#endif
 
509
}cl_uchar2;
 
510
 
 
511
typedef union
 
512
{
 
513
    cl_uchar  CL_ALIGNED(4) s[4];
 
514
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
515
   __extension__ struct{ cl_uchar  x, y, z, w; };
 
516
   __extension__ struct{ cl_uchar  s0, s1, s2, s3; };
 
517
   __extension__ struct{ cl_uchar2 lo, hi; };
 
518
#endif
 
519
#if defined( __CL_UCHAR2__) 
 
520
    __cl_uchar2     v2[2];
 
521
#endif
 
522
#if defined( __CL_UCHAR4__) 
 
523
    __cl_uchar4     v4;
 
524
#endif
 
525
}cl_uchar4;
 
526
 
 
527
/* cl_uchar3 is identical in size, alignment and behavior to cl_uchar4. See section 6.1.5. */
 
528
typedef  cl_uchar4  cl_uchar3;
 
529
 
 
530
typedef union
 
531
{
 
532
    cl_uchar   CL_ALIGNED(8) s[8];
 
533
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
534
   __extension__ struct{ cl_uchar  x, y, z, w; };
 
535
   __extension__ struct{ cl_uchar  s0, s1, s2, s3, s4, s5, s6, s7; };
 
536
   __extension__ struct{ cl_uchar4 lo, hi; };
 
537
#endif
 
538
#if defined( __CL_UCHAR2__) 
 
539
    __cl_uchar2     v2[4];
 
540
#endif
 
541
#if defined( __CL_UCHAR4__) 
 
542
    __cl_uchar4     v4[2];
 
543
#endif
 
544
#if defined( __CL_UCHAR8__ )
 
545
    __cl_uchar8     v8;
 
546
#endif
 
547
}cl_uchar8;
 
548
 
 
549
typedef union
 
550
{
 
551
    cl_uchar  CL_ALIGNED(16) s[16];
 
552
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
553
   __extension__ struct{ cl_uchar  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
554
   __extension__ struct{ cl_uchar  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
555
   __extension__ struct{ cl_uchar8 lo, hi; };
 
556
#endif
 
557
#if defined( __CL_UCHAR2__) 
 
558
    __cl_uchar2     v2[8];
 
559
#endif
 
560
#if defined( __CL_UCHAR4__) 
 
561
    __cl_uchar4     v4[4];
 
562
#endif
 
563
#if defined( __CL_UCHAR8__ )
 
564
    __cl_uchar8     v8[2];
 
565
#endif
 
566
#if defined( __CL_UCHAR16__ )
 
567
    __cl_uchar16    v16;
 
568
#endif
 
569
}cl_uchar16;
 
570
 
 
571
 
 
572
/* ---- cl_shortn ---- */
 
573
typedef union
 
574
{
 
575
    cl_short  CL_ALIGNED(4) s[2];
 
576
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
577
   __extension__ struct{ cl_short  x, y; };
 
578
   __extension__ struct{ cl_short  s0, s1; };
 
579
   __extension__ struct{ cl_short  lo, hi; };
 
580
#endif
 
581
#if defined( __CL_SHORT2__) 
 
582
    __cl_short2     v2;
 
583
#endif
 
584
}cl_short2;
 
585
 
 
586
typedef union
 
587
{
 
588
    cl_short  CL_ALIGNED(8) s[4];
 
589
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
590
   __extension__ struct{ cl_short  x, y, z, w; };
 
591
   __extension__ struct{ cl_short  s0, s1, s2, s3; };
 
592
   __extension__ struct{ cl_short2 lo, hi; };
 
593
#endif
 
594
#if defined( __CL_SHORT2__) 
 
595
    __cl_short2     v2[2];
 
596
#endif
 
597
#if defined( __CL_SHORT4__) 
 
598
    __cl_short4     v4;
 
599
#endif
 
600
}cl_short4;
 
601
 
 
602
/* cl_short3 is identical in size, alignment and behavior to cl_short4. See section 6.1.5. */
 
603
typedef  cl_short4  cl_short3;
 
604
 
 
605
typedef union
 
606
{
 
607
    cl_short   CL_ALIGNED(16) s[8];
 
608
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
609
   __extension__ struct{ cl_short  x, y, z, w; };
 
610
   __extension__ struct{ cl_short  s0, s1, s2, s3, s4, s5, s6, s7; };
 
611
   __extension__ struct{ cl_short4 lo, hi; };
 
612
#endif
 
613
#if defined( __CL_SHORT2__) 
 
614
    __cl_short2     v2[4];
 
615
#endif
 
616
#if defined( __CL_SHORT4__) 
 
617
    __cl_short4     v4[2];
 
618
#endif
 
619
#if defined( __CL_SHORT8__ )
 
620
    __cl_short8     v8;
 
621
#endif
 
622
}cl_short8;
 
623
 
 
624
typedef union
 
625
{
 
626
    cl_short  CL_ALIGNED(32) s[16];
 
627
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
628
   __extension__ struct{ cl_short  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
629
   __extension__ struct{ cl_short  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
630
   __extension__ struct{ cl_short8 lo, hi; };
 
631
#endif
 
632
#if defined( __CL_SHORT2__) 
 
633
    __cl_short2     v2[8];
 
634
#endif
 
635
#if defined( __CL_SHORT4__) 
 
636
    __cl_short4     v4[4];
 
637
#endif
 
638
#if defined( __CL_SHORT8__ )
 
639
    __cl_short8     v8[2];
 
640
#endif
 
641
#if defined( __CL_SHORT16__ )
 
642
    __cl_short16    v16;
 
643
#endif
 
644
}cl_short16;
 
645
 
 
646
 
 
647
/* ---- cl_ushortn ---- */
 
648
typedef union
 
649
{
 
650
    cl_ushort  CL_ALIGNED(4) s[2];
 
651
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
652
   __extension__ struct{ cl_ushort  x, y; };
 
653
   __extension__ struct{ cl_ushort  s0, s1; };
 
654
   __extension__ struct{ cl_ushort  lo, hi; };
 
655
#endif
 
656
#if defined( __CL_USHORT2__) 
 
657
    __cl_ushort2     v2;
 
658
#endif
 
659
}cl_ushort2;
 
660
 
 
661
typedef union
 
662
{
 
663
    cl_ushort  CL_ALIGNED(8) s[4];
 
664
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
665
   __extension__ struct{ cl_ushort  x, y, z, w; };
 
666
   __extension__ struct{ cl_ushort  s0, s1, s2, s3; };
 
667
   __extension__ struct{ cl_ushort2 lo, hi; };
 
668
#endif
 
669
#if defined( __CL_USHORT2__) 
 
670
    __cl_ushort2     v2[2];
 
671
#endif
 
672
#if defined( __CL_USHORT4__) 
 
673
    __cl_ushort4     v4;
 
674
#endif
 
675
}cl_ushort4;
 
676
 
 
677
/* cl_ushort3 is identical in size, alignment and behavior to cl_ushort4. See section 6.1.5. */
 
678
typedef  cl_ushort4  cl_ushort3;
 
679
 
 
680
typedef union
 
681
{
 
682
    cl_ushort   CL_ALIGNED(16) s[8];
 
683
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
684
   __extension__ struct{ cl_ushort  x, y, z, w; };
 
685
   __extension__ struct{ cl_ushort  s0, s1, s2, s3, s4, s5, s6, s7; };
 
686
   __extension__ struct{ cl_ushort4 lo, hi; };
 
687
#endif
 
688
#if defined( __CL_USHORT2__) 
 
689
    __cl_ushort2     v2[4];
 
690
#endif
 
691
#if defined( __CL_USHORT4__) 
 
692
    __cl_ushort4     v4[2];
 
693
#endif
 
694
#if defined( __CL_USHORT8__ )
 
695
    __cl_ushort8     v8;
 
696
#endif
 
697
}cl_ushort8;
 
698
 
 
699
typedef union
 
700
{
 
701
    cl_ushort  CL_ALIGNED(32) s[16];
 
702
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
703
   __extension__ struct{ cl_ushort  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
704
   __extension__ struct{ cl_ushort  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
705
   __extension__ struct{ cl_ushort8 lo, hi; };
 
706
#endif
 
707
#if defined( __CL_USHORT2__) 
 
708
    __cl_ushort2     v2[8];
 
709
#endif
 
710
#if defined( __CL_USHORT4__) 
 
711
    __cl_ushort4     v4[4];
 
712
#endif
 
713
#if defined( __CL_USHORT8__ )
 
714
    __cl_ushort8     v8[2];
 
715
#endif
 
716
#if defined( __CL_USHORT16__ )
 
717
    __cl_ushort16    v16;
 
718
#endif
 
719
}cl_ushort16;
 
720
 
 
721
/* ---- cl_intn ---- */
 
722
typedef union
 
723
{
 
724
    cl_int  CL_ALIGNED(8) s[2];
 
725
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
726
   __extension__ struct{ cl_int  x, y; };
 
727
   __extension__ struct{ cl_int  s0, s1; };
 
728
   __extension__ struct{ cl_int  lo, hi; };
 
729
#endif
 
730
#if defined( __CL_INT2__) 
 
731
    __cl_int2     v2;
 
732
#endif
 
733
}cl_int2;
 
734
 
 
735
typedef union
 
736
{
 
737
    cl_int  CL_ALIGNED(16) s[4];
 
738
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
739
   __extension__ struct{ cl_int  x, y, z, w; };
 
740
   __extension__ struct{ cl_int  s0, s1, s2, s3; };
 
741
   __extension__ struct{ cl_int2 lo, hi; };
 
742
#endif
 
743
#if defined( __CL_INT2__) 
 
744
    __cl_int2     v2[2];
 
745
#endif
 
746
#if defined( __CL_INT4__) 
 
747
    __cl_int4     v4;
 
748
#endif
 
749
}cl_int4;
 
750
 
 
751
/* cl_int3 is identical in size, alignment and behavior to cl_int4. See section 6.1.5. */
 
752
typedef  cl_int4  cl_int3;
 
753
 
 
754
typedef union
 
755
{
 
756
    cl_int   CL_ALIGNED(32) s[8];
 
757
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
758
   __extension__ struct{ cl_int  x, y, z, w; };
 
759
   __extension__ struct{ cl_int  s0, s1, s2, s3, s4, s5, s6, s7; };
 
760
   __extension__ struct{ cl_int4 lo, hi; };
 
761
#endif
 
762
#if defined( __CL_INT2__) 
 
763
    __cl_int2     v2[4];
 
764
#endif
 
765
#if defined( __CL_INT4__) 
 
766
    __cl_int4     v4[2];
 
767
#endif
 
768
#if defined( __CL_INT8__ )
 
769
    __cl_int8     v8;
 
770
#endif
 
771
}cl_int8;
 
772
 
 
773
typedef union
 
774
{
 
775
    cl_int  CL_ALIGNED(64) s[16];
 
776
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
777
   __extension__ struct{ cl_int  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
778
   __extension__ struct{ cl_int  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
779
   __extension__ struct{ cl_int8 lo, hi; };
 
780
#endif
 
781
#if defined( __CL_INT2__) 
 
782
    __cl_int2     v2[8];
 
783
#endif
 
784
#if defined( __CL_INT4__) 
 
785
    __cl_int4     v4[4];
 
786
#endif
 
787
#if defined( __CL_INT8__ )
 
788
    __cl_int8     v8[2];
 
789
#endif
 
790
#if defined( __CL_INT16__ )
 
791
    __cl_int16    v16;
 
792
#endif
 
793
}cl_int16;
 
794
 
 
795
 
 
796
/* ---- cl_uintn ---- */
 
797
typedef union
 
798
{
 
799
    cl_uint  CL_ALIGNED(8) s[2];
 
800
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
801
   __extension__ struct{ cl_uint  x, y; };
 
802
   __extension__ struct{ cl_uint  s0, s1; };
 
803
   __extension__ struct{ cl_uint  lo, hi; };
 
804
#endif
 
805
#if defined( __CL_UINT2__) 
 
806
    __cl_uint2     v2;
 
807
#endif
 
808
}cl_uint2;
 
809
 
 
810
typedef union
 
811
{
 
812
    cl_uint  CL_ALIGNED(16) s[4];
 
813
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
814
   __extension__ struct{ cl_uint  x, y, z, w; };
 
815
   __extension__ struct{ cl_uint  s0, s1, s2, s3; };
 
816
   __extension__ struct{ cl_uint2 lo, hi; };
 
817
#endif
 
818
#if defined( __CL_UINT2__) 
 
819
    __cl_uint2     v2[2];
 
820
#endif
 
821
#if defined( __CL_UINT4__) 
 
822
    __cl_uint4     v4;
 
823
#endif
 
824
}cl_uint4;
 
825
 
 
826
/* cl_uint3 is identical in size, alignment and behavior to cl_uint4. See section 6.1.5. */
 
827
typedef  cl_uint4  cl_uint3;
 
828
 
 
829
typedef union
 
830
{
 
831
    cl_uint   CL_ALIGNED(32) s[8];
 
832
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
833
   __extension__ struct{ cl_uint  x, y, z, w; };
 
834
   __extension__ struct{ cl_uint  s0, s1, s2, s3, s4, s5, s6, s7; };
 
835
   __extension__ struct{ cl_uint4 lo, hi; };
 
836
#endif
 
837
#if defined( __CL_UINT2__) 
 
838
    __cl_uint2     v2[4];
 
839
#endif
 
840
#if defined( __CL_UINT4__) 
 
841
    __cl_uint4     v4[2];
 
842
#endif
 
843
#if defined( __CL_UINT8__ )
 
844
    __cl_uint8     v8;
 
845
#endif
 
846
}cl_uint8;
 
847
 
 
848
typedef union
 
849
{
 
850
    cl_uint  CL_ALIGNED(64) s[16];
 
851
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
852
   __extension__ struct{ cl_uint  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
853
   __extension__ struct{ cl_uint  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
854
   __extension__ struct{ cl_uint8 lo, hi; };
 
855
#endif
 
856
#if defined( __CL_UINT2__) 
 
857
    __cl_uint2     v2[8];
 
858
#endif
 
859
#if defined( __CL_UINT4__) 
 
860
    __cl_uint4     v4[4];
 
861
#endif
 
862
#if defined( __CL_UINT8__ )
 
863
    __cl_uint8     v8[2];
 
864
#endif
 
865
#if defined( __CL_UINT16__ )
 
866
    __cl_uint16    v16;
 
867
#endif
 
868
}cl_uint16;
 
869
 
 
870
/* ---- cl_longn ---- */
 
871
typedef union
 
872
{
 
873
    cl_long  CL_ALIGNED(16) s[2];
 
874
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
875
   __extension__ struct{ cl_long  x, y; };
 
876
   __extension__ struct{ cl_long  s0, s1; };
 
877
   __extension__ struct{ cl_long  lo, hi; };
 
878
#endif
 
879
#if defined( __CL_LONG2__) 
 
880
    __cl_long2     v2;
 
881
#endif
 
882
}cl_long2;
 
883
 
 
884
typedef union
 
885
{
 
886
    cl_long  CL_ALIGNED(32) s[4];
 
887
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
888
   __extension__ struct{ cl_long  x, y, z, w; };
 
889
   __extension__ struct{ cl_long  s0, s1, s2, s3; };
 
890
   __extension__ struct{ cl_long2 lo, hi; };
 
891
#endif
 
892
#if defined( __CL_LONG2__) 
 
893
    __cl_long2     v2[2];
 
894
#endif
 
895
#if defined( __CL_LONG4__) 
 
896
    __cl_long4     v4;
 
897
#endif
 
898
}cl_long4;
 
899
 
 
900
/* cl_long3 is identical in size, alignment and behavior to cl_long4. See section 6.1.5. */
 
901
typedef  cl_long4  cl_long3;
 
902
 
 
903
typedef union
 
904
{
 
905
    cl_long   CL_ALIGNED(64) s[8];
 
906
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
907
   __extension__ struct{ cl_long  x, y, z, w; };
 
908
   __extension__ struct{ cl_long  s0, s1, s2, s3, s4, s5, s6, s7; };
 
909
   __extension__ struct{ cl_long4 lo, hi; };
 
910
#endif
 
911
#if defined( __CL_LONG2__) 
 
912
    __cl_long2     v2[4];
 
913
#endif
 
914
#if defined( __CL_LONG4__) 
 
915
    __cl_long4     v4[2];
 
916
#endif
 
917
#if defined( __CL_LONG8__ )
 
918
    __cl_long8     v8;
 
919
#endif
 
920
}cl_long8;
 
921
 
 
922
typedef union
 
923
{
 
924
    cl_long  CL_ALIGNED(128) s[16];
 
925
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
926
   __extension__ struct{ cl_long  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
927
   __extension__ struct{ cl_long  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
928
   __extension__ struct{ cl_long8 lo, hi; };
 
929
#endif
 
930
#if defined( __CL_LONG2__) 
 
931
    __cl_long2     v2[8];
 
932
#endif
 
933
#if defined( __CL_LONG4__) 
 
934
    __cl_long4     v4[4];
 
935
#endif
 
936
#if defined( __CL_LONG8__ )
 
937
    __cl_long8     v8[2];
 
938
#endif
 
939
#if defined( __CL_LONG16__ )
 
940
    __cl_long16    v16;
 
941
#endif
 
942
}cl_long16;
 
943
 
 
944
 
 
945
/* ---- cl_ulongn ---- */
 
946
typedef union
 
947
{
 
948
    cl_ulong  CL_ALIGNED(16) s[2];
 
949
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
950
   __extension__ struct{ cl_ulong  x, y; };
 
951
   __extension__ struct{ cl_ulong  s0, s1; };
 
952
   __extension__ struct{ cl_ulong  lo, hi; };
 
953
#endif
 
954
#if defined( __CL_ULONG2__) 
 
955
    __cl_ulong2     v2;
 
956
#endif
 
957
}cl_ulong2;
 
958
 
 
959
typedef union
 
960
{
 
961
    cl_ulong  CL_ALIGNED(32) s[4];
 
962
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
963
   __extension__ struct{ cl_ulong  x, y, z, w; };
 
964
   __extension__ struct{ cl_ulong  s0, s1, s2, s3; };
 
965
   __extension__ struct{ cl_ulong2 lo, hi; };
 
966
#endif
 
967
#if defined( __CL_ULONG2__) 
 
968
    __cl_ulong2     v2[2];
 
969
#endif
 
970
#if defined( __CL_ULONG4__) 
 
971
    __cl_ulong4     v4;
 
972
#endif
 
973
}cl_ulong4;
 
974
 
 
975
/* cl_ulong3 is identical in size, alignment and behavior to cl_ulong4. See section 6.1.5. */
 
976
typedef  cl_ulong4  cl_ulong3;
 
977
 
 
978
typedef union
 
979
{
 
980
    cl_ulong   CL_ALIGNED(64) s[8];
 
981
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
982
   __extension__ struct{ cl_ulong  x, y, z, w; };
 
983
   __extension__ struct{ cl_ulong  s0, s1, s2, s3, s4, s5, s6, s7; };
 
984
   __extension__ struct{ cl_ulong4 lo, hi; };
 
985
#endif
 
986
#if defined( __CL_ULONG2__) 
 
987
    __cl_ulong2     v2[4];
 
988
#endif
 
989
#if defined( __CL_ULONG4__) 
 
990
    __cl_ulong4     v4[2];
 
991
#endif
 
992
#if defined( __CL_ULONG8__ )
 
993
    __cl_ulong8     v8;
 
994
#endif
 
995
}cl_ulong8;
 
996
 
 
997
typedef union
 
998
{
 
999
    cl_ulong  CL_ALIGNED(128) s[16];
 
1000
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1001
   __extension__ struct{ cl_ulong  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
1002
   __extension__ struct{ cl_ulong  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
1003
   __extension__ struct{ cl_ulong8 lo, hi; };
 
1004
#endif
 
1005
#if defined( __CL_ULONG2__) 
 
1006
    __cl_ulong2     v2[8];
 
1007
#endif
 
1008
#if defined( __CL_ULONG4__) 
 
1009
    __cl_ulong4     v4[4];
 
1010
#endif
 
1011
#if defined( __CL_ULONG8__ )
 
1012
    __cl_ulong8     v8[2];
 
1013
#endif
 
1014
#if defined( __CL_ULONG16__ )
 
1015
    __cl_ulong16    v16;
 
1016
#endif
 
1017
}cl_ulong16;
 
1018
 
 
1019
 
 
1020
/* --- cl_floatn ---- */
 
1021
 
 
1022
typedef union
 
1023
{
 
1024
    cl_float  CL_ALIGNED(8) s[2];
 
1025
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1026
   __extension__ struct{ cl_float  x, y; };
 
1027
   __extension__ struct{ cl_float  s0, s1; };
 
1028
   __extension__ struct{ cl_float  lo, hi; };
 
1029
#endif
 
1030
#if defined( __CL_FLOAT2__) 
 
1031
    __cl_float2     v2;
 
1032
#endif
 
1033
}cl_float2;
 
1034
 
 
1035
typedef union
 
1036
{
 
1037
    cl_float  CL_ALIGNED(16) s[4];
 
1038
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1039
   __extension__ struct{ cl_float   x, y, z, w; };
 
1040
   __extension__ struct{ cl_float   s0, s1, s2, s3; };
 
1041
   __extension__ struct{ cl_float2  lo, hi; };
 
1042
#endif
 
1043
#if defined( __CL_FLOAT2__) 
 
1044
    __cl_float2     v2[2];
 
1045
#endif
 
1046
#if defined( __CL_FLOAT4__) 
 
1047
    __cl_float4     v4;
 
1048
#endif
 
1049
}cl_float4;
 
1050
 
 
1051
/* cl_float3 is identical in size, alignment and behavior to cl_float4. See section 6.1.5. */
 
1052
typedef  cl_float4  cl_float3;
 
1053
 
 
1054
typedef union
 
1055
{
 
1056
    cl_float   CL_ALIGNED(32) s[8];
 
1057
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1058
   __extension__ struct{ cl_float   x, y, z, w; };
 
1059
   __extension__ struct{ cl_float   s0, s1, s2, s3, s4, s5, s6, s7; };
 
1060
   __extension__ struct{ cl_float4  lo, hi; };
 
1061
#endif
 
1062
#if defined( __CL_FLOAT2__) 
 
1063
    __cl_float2     v2[4];
 
1064
#endif
 
1065
#if defined( __CL_FLOAT4__) 
 
1066
    __cl_float4     v4[2];
 
1067
#endif
 
1068
#if defined( __CL_FLOAT8__ )
 
1069
    __cl_float8     v8;
 
1070
#endif
 
1071
}cl_float8;
 
1072
 
 
1073
typedef union
 
1074
{
 
1075
    cl_float  CL_ALIGNED(64) s[16];
 
1076
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1077
   __extension__ struct{ cl_float  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
1078
   __extension__ struct{ cl_float  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
1079
   __extension__ struct{ cl_float8 lo, hi; };
 
1080
#endif
 
1081
#if defined( __CL_FLOAT2__) 
 
1082
    __cl_float2     v2[8];
 
1083
#endif
 
1084
#if defined( __CL_FLOAT4__) 
 
1085
    __cl_float4     v4[4];
 
1086
#endif
 
1087
#if defined( __CL_FLOAT8__ )
 
1088
    __cl_float8     v8[2];
 
1089
#endif
 
1090
#if defined( __CL_FLOAT16__ )
 
1091
    __cl_float16    v16;
 
1092
#endif
 
1093
}cl_float16;
 
1094
 
 
1095
/* --- cl_doublen ---- */
 
1096
 
 
1097
typedef union
 
1098
{
 
1099
    cl_double  CL_ALIGNED(16) s[2];
 
1100
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1101
   __extension__ struct{ cl_double  x, y; };
 
1102
   __extension__ struct{ cl_double s0, s1; };
 
1103
   __extension__ struct{ cl_double lo, hi; };
 
1104
#endif
 
1105
#if defined( __CL_DOUBLE2__) 
 
1106
    __cl_double2     v2;
 
1107
#endif
 
1108
}cl_double2;
 
1109
 
 
1110
typedef union
 
1111
{
 
1112
    cl_double  CL_ALIGNED(32) s[4];
 
1113
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1114
   __extension__ struct{ cl_double  x, y, z, w; };
 
1115
   __extension__ struct{ cl_double  s0, s1, s2, s3; };
 
1116
   __extension__ struct{ cl_double2 lo, hi; };
 
1117
#endif
 
1118
#if defined( __CL_DOUBLE2__) 
 
1119
    __cl_double2     v2[2];
 
1120
#endif
 
1121
#if defined( __CL_DOUBLE4__) 
 
1122
    __cl_double4     v4;
 
1123
#endif
 
1124
}cl_double4;
 
1125
 
 
1126
/* cl_double3 is identical in size, alignment and behavior to cl_double4. See section 6.1.5. */
 
1127
typedef  cl_double4  cl_double3;
 
1128
 
 
1129
typedef union
 
1130
{
 
1131
    cl_double   CL_ALIGNED(64) s[8];
 
1132
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1133
   __extension__ struct{ cl_double  x, y, z, w; };
 
1134
   __extension__ struct{ cl_double  s0, s1, s2, s3, s4, s5, s6, s7; };
 
1135
   __extension__ struct{ cl_double4 lo, hi; };
 
1136
#endif
 
1137
#if defined( __CL_DOUBLE2__) 
 
1138
    __cl_double2     v2[4];
 
1139
#endif
 
1140
#if defined( __CL_DOUBLE4__) 
 
1141
    __cl_double4     v4[2];
 
1142
#endif
 
1143
#if defined( __CL_DOUBLE8__ )
 
1144
    __cl_double8     v8;
 
1145
#endif
 
1146
}cl_double8;
 
1147
 
 
1148
typedef union
 
1149
{
 
1150
    cl_double  CL_ALIGNED(128) s[16];
 
1151
#if defined( __GNUC__) && ! defined( __STRICT_ANSI__ )
 
1152
   __extension__ struct{ cl_double  x, y, z, w, __spacer4, __spacer5, __spacer6, __spacer7, __spacer8, __spacer9, sa, sb, sc, sd, se, sf; };
 
1153
   __extension__ struct{ cl_double  s0, s1, s2, s3, s4, s5, s6, s7, s8, s9, sA, sB, sC, sD, sE, sF; };
 
1154
   __extension__ struct{ cl_double8 lo, hi; };
 
1155
#endif
 
1156
#if defined( __CL_DOUBLE2__) 
 
1157
    __cl_double2     v2[8];
 
1158
#endif
 
1159
#if defined( __CL_DOUBLE4__) 
 
1160
    __cl_double4     v4[4];
 
1161
#endif
 
1162
#if defined( __CL_DOUBLE8__ )
 
1163
    __cl_double8     v8[2];
 
1164
#endif
 
1165
#if defined( __CL_DOUBLE16__ )
 
1166
    __cl_double16    v16;
 
1167
#endif
 
1168
}cl_double16;
 
1169
 
 
1170
/* Macro to facilitate debugging 
 
1171
 * Usage:
 
1172
 *   Place CL_PROGRAM_STRING_DEBUG_INFO on the line before the first line of your source. 
 
1173
 *   The first line ends with:   CL_PROGRAM_STRING_BEGIN \"
 
1174
 *   Each line thereafter of OpenCL C source must end with: \n\
 
1175
 *   The last line ends in ";
 
1176
 *
 
1177
 *   Example:
 
1178
 *
 
1179
 *   const char *my_program = CL_PROGRAM_STRING_BEGIN "\
 
1180
 *   kernel void foo( int a, float * b )             \n\
 
1181
 *   {                                               \n\
 
1182
 *      // my comment                                \n\
 
1183
 *      *b[ get_global_id(0)] = a;                   \n\
 
1184
 *   }                                               \n\
 
1185
 *   ";
 
1186
 *
 
1187
 * This should correctly set up the line, (column) and file information for your source 
 
1188
 * string so you can do source level debugging.
 
1189
 */
 
1190
#define  __CL_STRINGIFY( _x )               # _x
 
1191
#define  _CL_STRINGIFY( _x )                __CL_STRINGIFY( _x )
 
1192
#define  CL_PROGRAM_STRING_DEBUG_INFO       "#line "  _CL_STRINGIFY(__LINE__) " \"" __FILE__ "\" \n\n" 
 
1193
  
 
1194
#ifdef __cplusplus
 
1195
}
 
1196
#endif
 
1197
 
 
1198
#endif  /* __CL_PLATFORM_H  */