| [cc87898] | 1 | /**********************************************************************************
|
|---|
| 2 | * Copyright (c) 2008-2012 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 AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER
|
|---|
| 53 | #define GCL_API_SUFFIX__VERSION_1_1 AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER
|
|---|
| 54 | #define CL_EXT_SUFFIX__VERSION_1_1 CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER
|
|---|
| 55 | #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
|
|---|
| 56 | #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_6_AND_LATER_BUT_DEPRECATED_IN_MAC_OS_X_VERSION_10_7
|
|---|
| 57 |
|
|---|
| 58 | #ifdef AVAILABLE_MAC_OS_X_VERSION_10_8_AND_LATER
|
|---|
| 59 | #define CL_API_SUFFIX__VERSION_1_2 AVAILABLE_MAC_OS_X_VERSION_10_8_AND_LATER
|
|---|
| 60 | #define GCL_API_SUFFIX__VERSION_1_2 AVAILABLE_MAC_OS_X_VERSION_10_8_AND_LATER
|
|---|
| 61 | #define CL_EXT_SUFFIX__VERSION_1_2 CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_8_AND_LATER
|
|---|
| 62 | #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
|
|---|
| 63 | #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER_BUT_DEPRECATED_IN_MAC_OS_X_VERSION_10_8
|
|---|
| 64 | #else
|
|---|
| 65 | #warning This path should never happen outside of internal operating system development. AvailabilityMacros do not function correctly here!
|
|---|
| 66 | #define CL_API_SUFFIX__VERSION_1_2 AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER
|
|---|
| 67 | #define GCL_API_SUFFIX__VERSION_1_2 AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER
|
|---|
| 68 | #define CL_EXT_SUFFIX__VERSION_1_2 CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER
|
|---|
| 69 | #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
|
|---|
| 70 | #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED CL_EXTENSION_WEAK_LINK AVAILABLE_MAC_OS_X_VERSION_10_7_AND_LATER
|
|---|
| 71 | #endif
|
|---|
| 72 | #else
|
|---|
| 73 | #ifdef __GNUC__
|
|---|
| 74 | #ifdef CL_USE_DEPRECATED_OPENCL_1_0_APIS
|
|---|
| 75 | #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
|
|---|
| 76 | #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
|
|---|
| 77 | #else
|
|---|
| 78 | #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED __attribute__((deprecated))
|
|---|
| 79 | #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
|
|---|
| 80 | #endif
|
|---|
| 81 |
|
|---|
| 82 | #ifdef CL_USE_DEPRECATED_OPENCL_1_1_APIS
|
|---|
| 83 | #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED
|
|---|
| 84 | #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
|
|---|
| 85 | #else
|
|---|
| 86 | #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED __attribute__((deprecated))
|
|---|
| 87 | #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
|
|---|
| 88 | #endif
|
|---|
| 89 | #elif _WIN32
|
|---|
| 90 | #ifdef CL_USE_DEPRECATED_OPENCL_1_0_APIS
|
|---|
| 91 | #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
|
|---|
| 92 | #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
|
|---|
| 93 | #else
|
|---|
| 94 | #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
|
|---|
| 95 | #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED __declspec(deprecated)
|
|---|
| 96 | #endif
|
|---|
| 97 |
|
|---|
| 98 | #ifdef CL_USE_DEPRECATED_OPENCL_1_1_APIS
|
|---|
| 99 | #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED
|
|---|
| 100 | #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
|
|---|
| 101 | #else
|
|---|
| 102 | #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED
|
|---|
| 103 | #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED ___declspec(deprecated)
|
|---|
| 104 | #endif
|
|---|
| 105 | #else
|
|---|
| 106 | #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
|
|---|
| 107 | #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
|
|---|
| 108 |
|
|---|
| 109 | #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED
|
|---|
| 110 | #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
|
|---|
| 111 | #endif
|
|---|
| 112 | #endif
|
|---|
| 113 |
|
|---|
| 114 | #if (defined (_WIN32) && defined(_MSC_VER))
|
|---|
| 115 |
|
|---|
| 116 | /*
|
|---|
| 117 | typedef signed __int8 cl_char;
|
|---|
| 118 | typedef unsigned __int8 cl_uchar;
|
|---|
| 119 | typedef signed __int16 cl_short;
|
|---|
| 120 | typedef unsigned __int16 cl_ushort;
|
|---|
| 121 | typedef signed __int32 cl_int;
|
|---|
| 122 | typedef unsigned __int32 cl_uint;
|
|---|
| 123 | typedef signed __int64 cl_long;
|
|---|
| 124 | typedef unsigned __int64 cl_ulong;
|
|---|
| 125 |
|
|---|
| 126 | typedef unsigned __int16 cl_half;
|
|---|
| 127 | typedef float cl_float;
|
|---|
| 128 | typedef double cl_double;
|
|---|
| 129 | */
|
|---|
| 130 | /* Macro names and corresponding values defined by OpenCL */
|
|---|
| 131 | #define CL_CHAR_BIT 8
|
|---|
| 132 | #define CL_SCHAR_MAX 127
|
|---|
| 133 | #define CL_SCHAR_MIN (-127-1)
|
|---|
| 134 | #define CL_CHAR_MAX CL_SCHAR_MAX
|
|---|
| 135 | #define CL_CHAR_MIN CL_SCHAR_MIN
|
|---|
| 136 | #define CL_UCHAR_MAX 255
|
|---|
| 137 | #define CL_SHRT_MAX 32767
|
|---|
| 138 | #define CL_SHRT_MIN (-32767-1)
|
|---|
| 139 | #define CL_USHRT_MAX 65535
|
|---|
| 140 | #define CL_INT_MAX 2147483647
|
|---|
| 141 | #define CL_INT_MIN (-2147483647-1)
|
|---|
| 142 | #define CL_UINT_MAX 0xffffffffU
|
|---|
| 143 | #define CL_LONG_MAX ((cl_long) 0x7FFFFFFFFFFFFFFFLL)
|
|---|
| 144 | #define CL_LONG_MIN ((cl_long) -0x7FFFFFFFFFFFFFFFLL - 1LL)
|
|---|
| 145 | #define CL_ULONG_MAX ((cl_ulong) 0xFFFFFFFFFFFFFFFFULL)
|
|---|
| 146 |
|
|---|
| 147 | #define CL_FLT_DIG 6
|
|---|
| 148 | #define CL_FLT_MANT_DIG 24
|
|---|
| 149 | #define CL_FLT_MAX_10_EXP +38
|
|---|
| 150 | #define CL_FLT_MAX_EXP +128
|
|---|
| 151 | #define CL_FLT_MIN_10_EXP -37
|
|---|
| 152 | #define CL_FLT_MIN_EXP -125
|
|---|
| 153 | #define CL_FLT_RADIX 2
|
|---|
| 154 | #define CL_FLT_MAX 340282346638528859811704183484516925440.0f
|
|---|
| 155 | #define CL_FLT_MIN 1.175494350822287507969e-38f
|
|---|
| 156 | #define CL_FLT_EPSILON 0x1.0p-23f
|
|---|
| 157 |
|
|---|
| 158 | #define CL_DBL_DIG 15
|
|---|
| 159 | #define CL_DBL_MANT_DIG 53
|
|---|
| 160 | #define CL_DBL_MAX_10_EXP +308
|
|---|
| 161 | #define CL_DBL_MAX_EXP +1024
|
|---|
| 162 | #define CL_DBL_MIN_10_EXP -307
|
|---|
| 163 | #define CL_DBL_MIN_EXP -1021
|
|---|
| 164 | #define CL_DBL_RADIX 2
|
|---|
| 165 | #define CL_DBL_MAX 179769313486231570814527423731704356798070567525844996598917476803157260780028538760589558632766878171540458953514382464234321326889464182768467546703537516986049910576551282076245490090389328944075868508455133942304583236903222948165808559332123348274797826204144723168738177180919299881250404026184124858368.0
|
|---|
| 166 | #define CL_DBL_MIN 2.225073858507201383090e-308
|
|---|
| 167 | #define CL_DBL_EPSILON 2.220446049250313080847e-16
|
|---|
| 168 |
|
|---|
| 169 | #define CL_M_E 2.718281828459045090796
|
|---|
| 170 | #define CL_M_LOG2E 1.442695040888963387005
|
|---|
| 171 | #define CL_M_LOG10E 0.434294481903251816668
|
|---|
| 172 | #define CL_M_LN2 0.693147180559945286227
|
|---|
| 173 | #define CL_M_LN10 2.302585092994045901094
|
|---|
| 174 | #define CL_M_PI 3.141592653589793115998
|
|---|
| 175 | #define CL_M_PI_2 1.570796326794896557999
|
|---|
| 176 | #define CL_M_PI_4 0.785398163397448278999
|
|---|
| 177 | #define CL_M_1_PI 0.318309886183790691216
|
|---|
| 178 | #define CL_M_2_PI 0.636619772367581382433
|
|---|
| 179 | #define CL_M_2_SQRTPI 1.128379167095512558561
|
|---|
| 180 | #define CL_M_SQRT2 1.414213562373095145475
|
|---|
| 181 | #define CL_M_SQRT1_2 0.707106781186547572737
|
|---|
| 182 |
|
|---|
| 183 | #define CL_M_E_F 2.71828174591064f
|
|---|
| 184 | #define CL_M_LOG2E_F 1.44269502162933f
|
|---|
| 185 | #define CL_M_LOG10E_F 0.43429449200630f
|
|---|
| 186 | #define CL_M_LN2_F 0.69314718246460f
|
|---|
| 187 | #define CL_M_LN10_F 2.30258512496948f
|
|---|
| 188 | #define CL_M_PI_F 3.14159274101257f
|
|---|
| 189 | #define CL_M_PI_2_F 1.57079637050629f
|
|---|
| 190 | #define CL_M_PI_4_F 0.78539818525314f
|
|---|
| 191 | #define CL_M_1_PI_F 0.31830987334251f
|
|---|
| 192 | #define CL_M_2_PI_F 0.63661974668503f
|
|---|
| 193 | #define CL_M_2_SQRTPI_F 1.12837922573090f
|
|---|
| 194 | #define CL_M_SQRT2_F 1.41421353816986f
|
|---|
| 195 | #define CL_M_SQRT1_2_F 0.70710676908493f
|
|---|
| 196 |
|
|---|
| 197 | #define CL_NAN (CL_INFINITY - CL_INFINITY)
|
|---|
| 198 | #define CL_HUGE_VALF ((cl_float) 1e50)
|
|---|
| 199 | #define CL_HUGE_VAL ((cl_double) 1e500)
|
|---|
| 200 | #define CL_MAXFLOAT CL_FLT_MAX
|
|---|
| 201 | #define CL_INFINITY CL_HUGE_VALF
|
|---|
| 202 |
|
|---|
| 203 | #else
|
|---|
| 204 | /*
|
|---|
| 205 | #include <stdint.h>
|
|---|
| 206 |
|
|---|
| 207 | // scalar types
|
|---|
| 208 | typedef int8_t cl_char;
|
|---|
| 209 | typedef uint8_t cl_uchar;
|
|---|
| 210 | typedef int16_t cl_short __attribute__((aligned(2)));
|
|---|
| 211 | typedef uint16_t cl_ushort __attribute__((aligned(2)));
|
|---|
| 212 | typedef int32_t cl_int __attribute__((aligned(4)));
|
|---|
| 213 | typedef uint32_t cl_uint __attribute__((aligned(4)));
|
|---|
| 214 | typedef int64_t cl_long __attribute__((aligned(8)));
|
|---|
| 215 | typedef uint64_t cl_ulong __attribute__((aligned(8)));
|
|---|
| 216 |
|
|---|
| 217 | typedef uint16_t cl_half __attribute__((aligned(2)));
|
|---|
| 218 | typedef float cl_float __attribute__((aligned(4)));
|
|---|
| 219 | typedef double cl_double __attribute__((aligned(8)));
|
|---|
| 220 | */
|
|---|
| 221 | /* Macro names and corresponding values defined by OpenCL */
|
|---|
| 222 | #define CL_CHAR_BIT 8
|
|---|
| 223 | #define CL_SCHAR_MAX 127
|
|---|
| 224 | #define CL_SCHAR_MIN (-127-1)
|
|---|
| 225 | #define CL_CHAR_MAX CL_SCHAR_MAX
|
|---|
| 226 | #define CL_CHAR_MIN CL_SCHAR_MIN
|
|---|
| 227 | #define CL_UCHAR_MAX 255
|
|---|
| 228 | #define CL_SHRT_MAX 32767
|
|---|
| 229 | #define CL_SHRT_MIN (-32767-1)
|
|---|
| 230 | #define CL_USHRT_MAX 65535
|
|---|
| 231 | #define CL_INT_MAX 2147483647
|
|---|
| 232 | #define CL_INT_MIN (-2147483647-1)
|
|---|
| 233 | #define CL_UINT_MAX 0xffffffffU
|
|---|
| 234 | #define CL_LONG_MAX ((cl_long) 0x7FFFFFFFFFFFFFFFLL)
|
|---|
| 235 | #define CL_LONG_MIN ((cl_long) -0x7FFFFFFFFFFFFFFFLL - 1LL)
|
|---|
| 236 | #define CL_ULONG_MAX ((cl_ulong) 0xFFFFFFFFFFFFFFFFULL)
|
|---|
| 237 |
|
|---|
| 238 | #define CL_FLT_DIG 6
|
|---|
| 239 | #define CL_FLT_MANT_DIG 24
|
|---|
| 240 | #define CL_FLT_MAX_10_EXP +38
|
|---|
| 241 | #define CL_FLT_MAX_EXP +128
|
|---|
| 242 | #define CL_FLT_MIN_10_EXP -37
|
|---|
| 243 | #define CL_FLT_MIN_EXP -125
|
|---|
| 244 | #define CL_FLT_RADIX 2
|
|---|
| 245 | #define CL_FLT_MAX 0x1.fffffep127f
|
|---|
| 246 | #define CL_FLT_MIN 0x1.0p-126f
|
|---|
| 247 | #define CL_FLT_EPSILON 0x1.0p-23f
|
|---|
| 248 |
|
|---|
| 249 | #define CL_DBL_DIG 15
|
|---|
| 250 | #define CL_DBL_MANT_DIG 53
|
|---|
| 251 | #define CL_DBL_MAX_10_EXP +308
|
|---|
| 252 | #define CL_DBL_MAX_EXP +1024
|
|---|
| 253 | #define CL_DBL_MIN_10_EXP -307
|
|---|
| 254 | #define CL_DBL_MIN_EXP -1021
|
|---|
| 255 | #define CL_DBL_RADIX 2
|
|---|
| 256 | #define CL_DBL_MAX 0x1.fffffffffffffp1023
|
|---|
| 257 | #define CL_DBL_MIN 0x1.0p-1022
|
|---|
| 258 | #define CL_DBL_EPSILON 0x1.0p-52
|
|---|
| 259 |
|
|---|
| 260 | #define CL_M_E 2.718281828459045090796
|
|---|
| 261 | #define CL_M_LOG2E 1.442695040888963387005
|
|---|
| 262 | #define CL_M_LOG10E 0.434294481903251816668
|
|---|
| 263 | #define CL_M_LN2 0.693147180559945286227
|
|---|
| 264 | #define CL_M_LN10 2.302585092994045901094
|
|---|
| 265 | #define CL_M_PI 3.141592653589793115998
|
|---|
| 266 | #define CL_M_PI_2 1.570796326794896557999
|
|---|
| 267 | #define CL_M_PI_4 0.785398163397448278999
|
|---|
| 268 | #define CL_M_1_PI 0.318309886183790691216
|
|---|
| 269 | #define CL_M_2_PI 0.636619772367581382433
|
|---|
| 270 | #define CL_M_2_SQRTPI 1.128379167095512558561
|
|---|
| 271 | #define CL_M_SQRT2 1.414213562373095145475
|
|---|
| 272 | #define CL_M_SQRT1_2 0.707106781186547572737
|
|---|
| 273 |
|
|---|
| 274 | #define CL_M_E_F 2.71828174591064f
|
|---|
| 275 | #define CL_M_LOG2E_F 1.44269502162933f
|
|---|
| 276 | #define CL_M_LOG10E_F 0.43429449200630f
|
|---|
| 277 | #define CL_M_LN2_F 0.69314718246460f
|
|---|
| 278 | #define CL_M_LN10_F 2.30258512496948f
|
|---|
| 279 | #define CL_M_PI_F 3.14159274101257f
|
|---|
| 280 | #define CL_M_PI_2_F 1.57079637050629f
|
|---|
| 281 | #define CL_M_PI_4_F 0.78539818525314f
|
|---|
| 282 | #define CL_M_1_PI_F 0.31830987334251f
|
|---|
| 283 | #define CL_M_2_PI_F 0.63661974668503f
|
|---|
| 284 | #define CL_M_2_SQRTPI_F 1.12837922573090f
|
|---|
| 285 | #define CL_M_SQRT2_F 1.41421353816986f
|
|---|
| 286 | #define CL_M_SQRT1_2_F 0.70710676908493f
|
|---|
| 287 |
|
|---|
| 288 | #if defined( __GNUC__ )
|
|---|
| 289 | #define CL_HUGE_VALF __builtin_huge_valf()
|
|---|
| 290 | #define CL_HUGE_VAL __builtin_huge_val()
|
|---|
| 291 | #define CL_NAN __builtin_nanf( "" )
|
|---|
| 292 | #else
|
|---|
| 293 | #define CL_HUGE_VALF ((cl_float) 1e50)
|
|---|
| 294 | #define CL_HUGE_VAL ((cl_double) 1e500)
|
|---|
| 295 | float nanf( const char * );
|
|---|
| 296 | #define CL_NAN nanf( "" )
|
|---|
| 297 | #endif
|
|---|
| 298 | #define CL_MAXFLOAT CL_FLT_MAX
|
|---|
| 299 | #define CL_INFINITY CL_HUGE_VALF
|
|---|
| 300 |
|
|---|
| 301 | #endif
|
|---|
| 302 |
|
|---|
| 303 | #include <stddef.h>
|
|---|
| 304 |
|
|---|
| 305 | /* 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. */
|
|---|
| 306 | typedef unsigned int cl_GLuint;
|
|---|
| 307 | typedef int cl_GLint;
|
|---|
| 308 | typedef unsigned int cl_GLenum;
|
|---|
| 309 | //There were vector types, not anymore
|
|---|
| 310 | /* Macro to facilitate debugging
|
|---|
| 311 | * Usage:
|
|---|
| 312 | * Place CL_PROGRAM_STRING_DEBUG_INFO on the line before the first line of your source.
|
|---|
| 313 | * The first line ends with: CL_PROGRAM_STRING_DEBUG_INFO \"
|
|---|
| 314 | * Each line thereafter of OpenCL C source must end with: \n\
|
|---|
| 315 | * The last line ends in ";
|
|---|
| 316 | *
|
|---|
| 317 | * Example:
|
|---|
| 318 | *
|
|---|
| 319 | * const char *my_program = CL_PROGRAM_STRING_DEBUG_INFO "\
|
|---|
| 320 | * kernel void foo( int a, float * b ) \n\
|
|---|
| 321 | * { \n\
|
|---|
| 322 | * // my comment \n\
|
|---|
| 323 | * *b[ get_global_id(0)] = a; \n\
|
|---|
| 324 | * } \n\
|
|---|
| 325 | * ";
|
|---|
| 326 | *
|
|---|
| 327 | * This should correctly set up the line, (column) and file information for your source
|
|---|
| 328 | * string so you can do source level debugging.
|
|---|
| 329 | */
|
|---|
| 330 | #define __CL_STRINGIFY( _x ) # _x
|
|---|
| 331 | #define _CL_STRINGIFY( _x ) __CL_STRINGIFY( _x )
|
|---|
| 332 | #define CL_PROGRAM_STRING_DEBUG_INFO "#line " _CL_STRINGIFY(__LINE__) " \"" __FILE__ "\" \n\n"
|
|---|
| 333 |
|
|---|
| 334 | #ifdef __cplusplus
|
|---|
| 335 | }
|
|---|
| 336 | #endif
|
|---|
| 337 |
|
|---|
| 338 | #endif /* __CL_PLATFORM_H */
|
|---|
