summaryrefslogtreecommitdiffstats
path: root/source/l/ocl-icd/0001-Updated-to-support-latest-Khronos-headers.patch
diff options
context:
space:
mode:
Diffstat (limited to 'source/l/ocl-icd/0001-Updated-to-support-latest-Khronos-headers.patch')
-rw-r--r--source/l/ocl-icd/0001-Updated-to-support-latest-Khronos-headers.patch2434
1 files changed, 0 insertions, 2434 deletions
diff --git a/source/l/ocl-icd/0001-Updated-to-support-latest-Khronos-headers.patch b/source/l/ocl-icd/0001-Updated-to-support-latest-Khronos-headers.patch
deleted file mode 100644
index 6912d7d2..00000000
--- a/source/l/ocl-icd/0001-Updated-to-support-latest-Khronos-headers.patch
+++ /dev/null
@@ -1,2434 +0,0 @@
-From aed1832c81c0971ea001e12d41e04df834257f94 Mon Sep 17 00:00:00 2001
-From: Brice Videau <bvideau@anl.gov>
-Date: Wed, 12 May 2021 10:24:44 -0500
-Subject: [PATCH] Updated to support latest Khronos headers.
-
-Signed-off-by: Laurent Carlier <lordheavym@gmail.com>
----
- icd_generator.rb | 4 +-
- khronos-headers/CL/cl.h | 46 +--
- khronos-headers/CL/cl_d3d10.h | 12 +-
- khronos-headers/CL/cl_d3d11.h | 12 +-
- khronos-headers/CL/cl_dx9_media_sharing.h | 32 +-
- khronos-headers/CL/cl_egl.h | 8 +-
- khronos-headers/CL/cl_ext.h | 228 +++++++++----
- khronos-headers/CL/cl_gl.h | 22 +-
- khronos-headers/CL/cl_gl_ext.h | 26 +-
- khronos-headers/CL/cl_icd.h | 316 +++++++++---------
- khronos-headers/CL/cl_layer.h | 4 +-
- khronos-headers/CL/cl_platform.h | 125 ++++---
- .../CL/cl_va_api_media_sharing_intel.h | 24 +-
- khronos-headers/CL/opencl.h | 3 +-
- ocl_interface.yaml | 10 +-
- run_dummy_icd.c | 1 -
- 16 files changed, 484 insertions(+), 389 deletions(-)
-
-diff --git a/icd_generator.rb b/icd_generator.rb
-index bb0f2e9..ed4217f 100644
---- a/icd_generator.rb
-+++ b/icd_generator.rb
-@@ -57,7 +57,7 @@ module IcdGenerator
- "clGetGLContextInfoKHR", "clUnloadCompiler",
- "clCreateContext", "clCreateContextFromType", "clWaitForEvents"]
- $header_files = ["/usr/include/CL/cl.h", "/usr/include/CL/cl_gl.h", "/usr/include/CL/cl_egl.h",
-- "/usr/include/CL/cl_ext.h", "/usr/include/CL/cl_gl_ext.h"]
-+ "/usr/include/CL/cl_ext.h"]
- $windows_header_files = ["/usr/include/CL/cl_dx9_media_sharing.h", "/usr/include/CL/cl_d3d11.h", "/usr/include/CL/cl_d3d10.h"]
- $cl_data_type_error = { "cl_platform_id" => "CL_INVALID_PLATFORM",
- "cl_device_id" => "CL_INVALID_DEVICE",
-@@ -246,7 +246,7 @@ EOF
- run_dummy_icd += "\n\n"
- $api_entries.each_key { |func_name|
- next if $forbidden_funcs.include?(func_name)
-- run_dummy_icd += $api_entries[func_name]+";\n"
-+ run_dummy_icd += $api_entries[func_name]+"\n"
- }
- run_dummy_icd += "\n\n"
- run_dummy_icd += "void call_all_OpenCL_functions(cl_platform_id chosen_platform) {\n"
-diff --git a/khronos-headers/CL/cl.h b/khronos-headers/CL/cl.h
-index 3a5aae4..0018a0f 100644
---- a/khronos-headers/CL/cl.h
-+++ b/khronos-headers/CL/cl.h
-@@ -1311,11 +1311,11 @@ clLinkProgram(cl_context context,
-
- #ifdef CL_VERSION_2_2
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_2_2_DEPRECATED cl_int CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_2_2_DEPRECATED cl_int CL_API_CALL
- clSetProgramReleaseCallback(cl_program program,
- void (CL_CALLBACK * pfn_notify)(cl_program program,
- void * user_data),
-- void * user_data) CL_EXT_SUFFIX__VERSION_2_2_DEPRECATED;
-+ void * user_data) CL_API_SUFFIX__VERSION_2_2_DEPRECATED;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clSetProgramSpecializationConstant(cl_program program,
-@@ -1857,11 +1857,11 @@ clGetExtensionFunctionAddressForPlatform(cl_platform_id platform,
- clSetCommandQueueProperty(cl_command_queue command_queue,
- cl_command_queue_properties properties,
- cl_bool enable,
-- cl_command_queue_properties * old_properties) CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED;
-+ cl_command_queue_properties * old_properties) CL_API_SUFFIX__VERSION_1_0_DEPRECATED;
- #endif /* CL_USE_DEPRECATED_OPENCL_1_0_APIS */
-
- /* Deprecated OpenCL 1.1 APIs */
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
- clCreateImage2D(cl_context context,
- cl_mem_flags flags,
- const cl_image_format * image_format,
-@@ -1869,9 +1869,9 @@ clCreateImage2D(cl_context context,
- size_t image_height,
- size_t image_row_pitch,
- void * host_ptr,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
- clCreateImage3D(cl_context context,
- cl_mem_flags flags,
- const cl_image_format * image_format,
-@@ -1881,46 +1881,46 @@ clCreateImage3D(cl_context context,
- size_t image_row_pitch,
- size_t image_slice_pitch,
- void * host_ptr,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
- clEnqueueMarker(cl_command_queue command_queue,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
- clEnqueueWaitForEvents(cl_command_queue command_queue,
- cl_uint num_events,
-- const cl_event * event_list) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ const cl_event * event_list) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
--clEnqueueBarrier(cl_command_queue command_queue) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
-+clEnqueueBarrier(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
--clUnloadCompiler(void) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_int CL_API_CALL
-+clUnloadCompiler(void) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED void * CL_API_CALL
--clGetExtensionFunctionAddress(const char * func_name) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED void * CL_API_CALL
-+clGetExtensionFunctionAddress(const char * func_name) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
- /* Deprecated OpenCL 2.0 APIs */
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_2_DEPRECATED cl_command_queue CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_2_DEPRECATED cl_command_queue CL_API_CALL
- clCreateCommandQueue(cl_context context,
- cl_device_id device,
- cl_command_queue_properties properties,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_2_DEPRECATED cl_sampler CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_2_DEPRECATED cl_sampler CL_API_CALL
- clCreateSampler(cl_context context,
- cl_bool normalized_coords,
- cl_addressing_mode addressing_mode,
- cl_filter_mode filter_mode,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_2_DEPRECATED cl_int CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_2_DEPRECATED cl_int CL_API_CALL
- clEnqueueTask(cl_command_queue command_queue,
- cl_kernel kernel,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2_DEPRECATED;
-
- #ifdef __cplusplus
- }
-diff --git a/khronos-headers/CL/cl_d3d10.h b/khronos-headers/CL/cl_d3d10.h
-index 2b80d90..6adedb0 100644
---- a/khronos-headers/CL/cl_d3d10.h
-+++ b/khronos-headers/CL/cl_d3d10.h
-@@ -75,7 +75,7 @@ typedef cl_uint cl_d3d10_device_set_khr;
-
- /******************************************************************************/
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceIDsFromD3D10KHR_fn)(
-+typedef cl_int (CL_API_CALL *clGetDeviceIDsFromD3D10KHR_fn)(
- cl_platform_id platform,
- cl_d3d10_device_source_khr d3d_device_source,
- void * d3d_object,
-@@ -84,27 +84,27 @@ typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceIDsFromD3D10KHR_fn)(
- cl_device_id * devices,
- cl_uint * num_devices) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromD3D10BufferKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromD3D10BufferKHR_fn)(
- cl_context context,
- cl_mem_flags flags,
- ID3D10Buffer * resource,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromD3D10Texture2DKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromD3D10Texture2DKHR_fn)(
- cl_context context,
- cl_mem_flags flags,
- ID3D10Texture2D * resource,
- UINT subresource,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromD3D10Texture3DKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromD3D10Texture3DKHR_fn)(
- cl_context context,
- cl_mem_flags flags,
- ID3D10Texture3D * resource,
- UINT subresource,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireD3D10ObjectsKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueAcquireD3D10ObjectsKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-@@ -112,7 +112,7 @@ typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireD3D10ObjectsKHR_fn)(
- const cl_event * event_wait_list,
- cl_event * event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseD3D10ObjectsKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueReleaseD3D10ObjectsKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-diff --git a/khronos-headers/CL/cl_d3d11.h b/khronos-headers/CL/cl_d3d11.h
-index 10023dd..50ed906 100644
---- a/khronos-headers/CL/cl_d3d11.h
-+++ b/khronos-headers/CL/cl_d3d11.h
-@@ -75,7 +75,7 @@ typedef cl_uint cl_d3d11_device_set_khr;
-
- /******************************************************************************/
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceIDsFromD3D11KHR_fn)(
-+typedef cl_int (CL_API_CALL *clGetDeviceIDsFromD3D11KHR_fn)(
- cl_platform_id platform,
- cl_d3d11_device_source_khr d3d_device_source,
- void * d3d_object,
-@@ -84,27 +84,27 @@ typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceIDsFromD3D11KHR_fn)(
- cl_device_id * devices,
- cl_uint * num_devices) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromD3D11BufferKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromD3D11BufferKHR_fn)(
- cl_context context,
- cl_mem_flags flags,
- ID3D11Buffer * resource,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromD3D11Texture2DKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromD3D11Texture2DKHR_fn)(
- cl_context context,
- cl_mem_flags flags,
- ID3D11Texture2D * resource,
- UINT subresource,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromD3D11Texture3DKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromD3D11Texture3DKHR_fn)(
- cl_context context,
- cl_mem_flags flags,
- ID3D11Texture3D * resource,
- UINT subresource,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireD3D11ObjectsKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueAcquireD3D11ObjectsKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-@@ -112,7 +112,7 @@ typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireD3D11ObjectsKHR_fn)(
- const cl_event * event_wait_list,
- cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseD3D11ObjectsKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueReleaseD3D11ObjectsKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-diff --git a/khronos-headers/CL/cl_dx9_media_sharing.h b/khronos-headers/CL/cl_dx9_media_sharing.h
-index 4e64b18..b0d2b23 100644
---- a/khronos-headers/CL/cl_dx9_media_sharing.h
-+++ b/khronos-headers/CL/cl_dx9_media_sharing.h
-@@ -76,7 +76,7 @@ typedef struct _cl_dx9_surface_info_khr
-
- /******************************************************************************/
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceIDsFromDX9MediaAdapterKHR_fn)(
-+typedef cl_int (CL_API_CALL *clGetDeviceIDsFromDX9MediaAdapterKHR_fn)(
- cl_platform_id platform,
- cl_uint num_media_adapters,
- cl_dx9_media_adapter_type_khr * media_adapter_type,
-@@ -86,7 +86,7 @@ typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceIDsFromDX9MediaAdapterKHR_f
- cl_device_id * devices,
- cl_uint * num_devices) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromDX9MediaSurfaceKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromDX9MediaSurfaceKHR_fn)(
- cl_context context,
- cl_mem_flags flags,
- cl_dx9_media_adapter_type_khr adapter_type,
-@@ -94,7 +94,7 @@ typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromDX9MediaSurfaceKHR_fn)(
- cl_uint plane,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireDX9MediaSurfacesKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueAcquireDX9MediaSurfacesKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-@@ -102,7 +102,7 @@ typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireDX9MediaSurfacesKHR_fn
- const cl_event * event_wait_list,
- cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseDX9MediaSurfacesKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueReleaseDX9MediaSurfacesKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-@@ -159,16 +159,16 @@ clGetDeviceIDsFromDX9INTEL(
- cl_dx9_device_set_intel dx9_device_set,
- cl_uint num_entries,
- cl_device_id* devices,
-- cl_uint* num_devices) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_uint* num_devices) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL* clGetDeviceIDsFromDX9INTEL_fn)(
-+typedef cl_int (CL_API_CALL* clGetDeviceIDsFromDX9INTEL_fn)(
- cl_platform_id platform,
- cl_dx9_device_source_intel dx9_device_source,
- void* dx9_object,
- cl_dx9_device_set_intel dx9_device_set,
- cl_uint num_entries,
- cl_device_id* devices,
-- cl_uint* num_devices) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_uint* num_devices) CL_API_SUFFIX__VERSION_1_1;
-
- extern CL_API_ENTRY cl_mem CL_API_CALL
- clCreateFromDX9MediaSurfaceINTEL(
-@@ -177,15 +177,15 @@ clCreateFromDX9MediaSurfaceINTEL(
- IDirect3DSurface9* resource,
- HANDLE sharedHandle,
- UINT plane,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromDX9MediaSurfaceINTEL_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromDX9MediaSurfaceINTEL_fn)(
- cl_context context,
- cl_mem_flags flags,
- IDirect3DSurface9* resource,
- HANDLE sharedHandle,
- UINT plane,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_1;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueAcquireDX9ObjectsINTEL(
-@@ -194,15 +194,15 @@ clEnqueueAcquireDX9ObjectsINTEL(
- const cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireDX9ObjectsINTEL_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueAcquireDX9ObjectsINTEL_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_1;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueReleaseDX9ObjectsINTEL(
-@@ -211,15 +211,15 @@ clEnqueueReleaseDX9ObjectsINTEL(
- cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseDX9ObjectsINTEL_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueReleaseDX9ObjectsINTEL_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_1;
-
- #ifdef __cplusplus
- }
-diff --git a/khronos-headers/CL/cl_egl.h b/khronos-headers/CL/cl_egl.h
-index c8bde80..357a37c 100644
---- a/khronos-headers/CL/cl_egl.h
-+++ b/khronos-headers/CL/cl_egl.h
-@@ -56,7 +56,7 @@ clCreateFromEGLImageKHR(cl_context context,
- const cl_egl_image_properties_khr * properties,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *clCreateFromEGLImageKHR_fn)(
-+typedef cl_mem (CL_API_CALL *clCreateFromEGLImageKHR_fn)(
- cl_context context,
- CLeglDisplayKHR egldisplay,
- CLeglImageKHR eglimage,
-@@ -73,7 +73,7 @@ clEnqueueAcquireEGLObjectsKHR(cl_command_queue command_queue,
- const cl_event * event_wait_list,
- cl_event * event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireEGLObjectsKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueAcquireEGLObjectsKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-@@ -90,7 +90,7 @@ clEnqueueReleaseEGLObjectsKHR(cl_command_queue command_queue,
- const cl_event * event_wait_list,
- cl_event * event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseEGLObjectsKHR_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueReleaseEGLObjectsKHR_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem * mem_objects,
-@@ -107,7 +107,7 @@ clCreateEventFromEGLSyncKHR(cl_context context,
- CLeglDisplayKHR display,
- cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_event (CL_API_CALL *clCreateEventFromEGLSyncKHR_fn)(
-+typedef cl_event (CL_API_CALL *clCreateEventFromEGLSyncKHR_fn)(
- cl_context context,
- CLeglSyncKHR sync,
- CLeglDisplayKHR display,
-diff --git a/khronos-headers/CL/cl_ext.h b/khronos-headers/CL/cl_ext.h
-index 4773061..3015f46 100644
---- a/khronos-headers/CL/cl_ext.h
-+++ b/khronos-headers/CL/cl_ext.h
-@@ -54,9 +54,9 @@ extern "C" {
- * before using.
- */
- #define cl_APPLE_SetMemObjectDestructor 1
--cl_int CL_API_ENTRY clSetMemObjectDestructorAPPLE( cl_mem memobj,
-+extern CL_API_ENTRY cl_int CL_API_CALL clSetMemObjectDestructorAPPLE( cl_mem memobj,
- void (* pfn_notify)(cl_mem memobj, void * user_data),
-- void * user_data) CL_EXT_SUFFIX__VERSION_1_0;
-+ void * user_data) CL_API_SUFFIX__VERSION_1_0;
-
-
- /* Context Logging Functions
-@@ -68,22 +68,22 @@ cl_int CL_API_ENTRY clSetMemObjectDestructorAPPLE( cl_mem memobj,
- * clLogMessagesToSystemLog forwards on all log messages to the Apple System Logger
- */
- #define cl_APPLE_ContextLoggingFunctions 1
--extern void CL_API_ENTRY clLogMessagesToSystemLogAPPLE( const char * errstr,
-+extern CL_API_ENTRY void CL_API_CALL clLogMessagesToSystemLogAPPLE( const char * errstr,
- const void * private_info,
- size_t cb,
-- void * user_data) CL_EXT_SUFFIX__VERSION_1_0;
-+ void * user_data) CL_API_SUFFIX__VERSION_1_0;
-
- /* clLogMessagesToStdout sends all log messages to the file descriptor stdout */
--extern void CL_API_ENTRY clLogMessagesToStdoutAPPLE( const char * errstr,
-+extern CL_API_ENTRY void CL_API_CALL clLogMessagesToStdoutAPPLE( const char * errstr,
- const void * private_info,
- size_t cb,
-- void * user_data) CL_EXT_SUFFIX__VERSION_1_0;
-+ void * user_data) CL_API_SUFFIX__VERSION_1_0;
-
- /* clLogMessagesToStderr sends all log messages to the file descriptor stderr */
--extern void CL_API_ENTRY clLogMessagesToStderrAPPLE( const char * errstr,
-+extern CL_API_ENTRY void CL_API_CALL clLogMessagesToStderrAPPLE( const char * errstr,
- const void * private_info,
- size_t cb,
-- void * user_data) CL_EXT_SUFFIX__VERSION_1_0;
-+ void * user_data) CL_API_SUFFIX__VERSION_1_0;
-
-
- /************************
-@@ -102,7 +102,7 @@ clIcdGetPlatformIDsKHR(cl_uint num_entries,
- cl_platform_id * platforms,
- cl_uint * num_platforms);
-
--typedef CL_API_ENTRY cl_int
-+typedef cl_int
- (CL_API_CALL *clIcdGetPlatformIDsKHR_fn)(cl_uint num_entries,
- cl_platform_id * platforms,
- cl_uint * num_platforms);
-@@ -129,11 +129,11 @@ clCreateProgramWithILKHR(cl_context context,
- size_t length,
- cl_int * errcode_ret);
-
--typedef CL_API_ENTRY cl_program
-+typedef cl_program
- (CL_API_CALL *clCreateProgramWithILKHR_fn)(cl_context context,
- const void * il,
- size_t length,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
- /* Extension: cl_khr_image2d_from_buffer
- *
-@@ -176,10 +176,10 @@ typedef CL_API_ENTRY cl_program
-
- #define cl_khr_terminate_context 1
- extern CL_API_ENTRY cl_int CL_API_CALL
--clTerminateContextKHR(cl_context context) CL_EXT_SUFFIX__VERSION_1_2;
-+clTerminateContextKHR(cl_context context) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int
--(CL_API_CALL *clTerminateContextKHR_fn)(cl_context context) CL_EXT_SUFFIX__VERSION_1_2;
-+typedef cl_int
-+(CL_API_CALL *clTerminateContextKHR_fn)(cl_context context) CL_API_SUFFIX__VERSION_1_2;
-
-
- /*
-@@ -204,13 +204,13 @@ extern CL_API_ENTRY cl_command_queue CL_API_CALL
- clCreateCommandQueueWithPropertiesKHR(cl_context context,
- cl_device_id device,
- const cl_queue_properties_khr* properties,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_command_queue
-+typedef cl_command_queue
- (CL_API_CALL *clCreateCommandQueueWithPropertiesKHR_fn)(cl_context context,
- cl_device_id device,
- const cl_queue_properties_khr* properties,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
-
- /******************************************
-@@ -268,16 +268,16 @@ typedef CL_API_ENTRY cl_command_queue
- #define cl_ext_device_fission 1
-
- extern CL_API_ENTRY cl_int CL_API_CALL
--clReleaseDeviceEXT(cl_device_id device) CL_EXT_SUFFIX__VERSION_1_1;
-+clReleaseDeviceEXT(cl_device_id device) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_int
--(CL_API_CALL *clReleaseDeviceEXT_fn)(cl_device_id device) CL_EXT_SUFFIX__VERSION_1_1;
-+typedef cl_int
-+(CL_API_CALL *clReleaseDeviceEXT_fn)(cl_device_id device) CL_API_SUFFIX__VERSION_1_1;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
--clRetainDeviceEXT(cl_device_id device) CL_EXT_SUFFIX__VERSION_1_1;
-+clRetainDeviceEXT(cl_device_id device) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_int
--(CL_API_CALL *clRetainDeviceEXT_fn)(cl_device_id device) CL_EXT_SUFFIX__VERSION_1_1;
-+typedef cl_int
-+(CL_API_CALL *clRetainDeviceEXT_fn)(cl_device_id device) CL_API_SUFFIX__VERSION_1_1;
-
- typedef cl_ulong cl_device_partition_property_ext;
- extern CL_API_ENTRY cl_int CL_API_CALL
-@@ -285,14 +285,14 @@ clCreateSubDevicesEXT(cl_device_id in_device,
- const cl_device_partition_property_ext * properties,
- cl_uint num_entries,
- cl_device_id * out_devices,
-- cl_uint * num_devices) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_uint * num_devices) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_int
-+typedef cl_int
- (CL_API_CALL * clCreateSubDevicesEXT_fn)(cl_device_id in_device,
- const cl_device_partition_property_ext * properties,
- cl_uint num_entries,
- cl_device_id * out_devices,
-- cl_uint * num_devices) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_uint * num_devices) CL_API_SUFFIX__VERSION_1_1;
-
- /* cl_device_partition_property_ext */
- #define CL_DEVICE_PARTITION_EQUALLY_EXT 0x4050
-@@ -346,7 +346,7 @@ clEnqueueMigrateMemObjectEXT(cl_command_queue command_queue,
- const cl_event * event_wait_list,
- cl_event * event);
-
--typedef CL_API_ENTRY cl_int
-+typedef cl_int
- (CL_API_CALL *clEnqueueMigrateMemObjectEXT_fn)(cl_command_queue command_queue,
- cl_uint num_mem_objects,
- const cl_mem * mem_objects,
-@@ -490,7 +490,7 @@ clEnqueueAcquireGrallocObjectsIMG(cl_command_queue command_queue,
- const cl_mem * mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueReleaseGrallocObjectsIMG(cl_command_queue command_queue,
-@@ -498,7 +498,7 @@ clEnqueueReleaseGrallocObjectsIMG(cl_command_queue command_queue,
- const cl_mem * mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
- /******************************************
- * cl_img_generate_mipmap extension *
-@@ -523,7 +523,7 @@ clEnqueueGenerateMipmapIMG(cl_command_queue command_queue,
- const size_t *mip_region,
- cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
-- cl_event *event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event *event) CL_API_SUFFIX__VERSION_1_2;
-
- /******************************************
- * cl_img_mem_properties extension *
-@@ -564,9 +564,9 @@ clGetKernelSubGroupInfoKHR(cl_kernel in_kernel,
- const void * input_value,
- size_t param_value_size,
- void * param_value,
-- size_t * param_value_size_ret) CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED;
-+ size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_2_0_DEPRECATED;
-
--typedef CL_API_ENTRY cl_int
-+typedef cl_int
- (CL_API_CALL * clGetKernelSubGroupInfoKHR_fn)(cl_kernel in_kernel,
- cl_device_id in_device,
- cl_kernel_sub_group_info param_name,
-@@ -574,7 +574,7 @@ typedef CL_API_ENTRY cl_int
- const void * input_value,
- size_t param_value_size,
- void * param_value,
-- size_t * param_value_size_ret) CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED;
-+ size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_2_0_DEPRECATED;
-
-
- /*********************************
-@@ -694,6 +694,46 @@ typedef struct _cl_name_version_khr
- #define CL_DEVICE_NODE_MASK_KHR 0x106E
-
-
-+/***************************************************************
-+* cl_khr_pci_bus_info
-+***************************************************************/
-+#define cl_khr_pci_bus_info 1
-+
-+typedef struct _cl_device_pci_bus_info_khr {
-+ cl_uint pci_domain;
-+ cl_uint pci_bus;
-+ cl_uint pci_device;
-+ cl_uint pci_function;
-+} cl_device_pci_bus_info_khr;
-+
-+/* cl_device_info */
-+#define CL_DEVICE_PCI_BUS_INFO_KHR 0x410F
-+
-+
-+/***************************************************************
-+* cl_khr_suggested_local_work_size
-+***************************************************************/
-+#define cl_khr_suggested_local_work_size 1
-+
-+extern CL_API_ENTRY cl_int CL_API_CALL
-+clGetKernelSuggestedLocalWorkSizeKHR(
-+ cl_command_queue command_queue,
-+ cl_kernel kernel,
-+ cl_uint work_dim,
-+ const size_t* global_work_offset,
-+ const size_t* global_work_size,
-+ size_t* suggested_local_work_size) CL_API_SUFFIX__VERSION_3_0;
-+
-+typedef cl_int (CL_API_CALL *
-+clGetKernelSuggestedLocalWorkSizeKHR_fn)(
-+ cl_command_queue command_queue,
-+ cl_kernel kernel,
-+ cl_uint work_dim,
-+ const size_t* global_work_offset,
-+ const size_t* global_work_size,
-+ size_t* suggested_local_work_size) CL_API_SUFFIX__VERSION_3_0;
-+
-+
- /**********************************
- * cl_arm_import_memory extension *
- **********************************/
-@@ -719,6 +759,12 @@ typedef intptr_t cl_import_properties_arm;
- /* Data consistency with host property */
- #define CL_IMPORT_DMA_BUF_DATA_CONSISTENCY_WITH_HOST_ARM 0x41E3
-
-+/* Index of plane in a multiplanar hardware buffer */
-+#define CL_IMPORT_ANDROID_HARDWARE_BUFFER_PLANE_INDEX_ARM 0x41EF
-+
-+/* Index of layer in a multilayer hardware buffer */
-+#define CL_IMPORT_ANDROID_HARDWARE_BUFFER_LAYER_INDEX_ARM 0x41F0
-+
- /* Import memory size value to indicate a size for the whole buffer */
- #define CL_IMPORT_MEMORY_WHOLE_ALLOCATION_ARM SIZE_MAX
-
-@@ -744,7 +790,7 @@ clImportMemoryARM( cl_context context,
- const cl_import_properties_arm *properties,
- void *memory,
- size_t size,
-- cl_int *errcode_ret) CL_EXT_SUFFIX__VERSION_1_0;
-+ cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
-
- /******************************************
-@@ -787,11 +833,11 @@ extern CL_API_ENTRY void * CL_API_CALL
- clSVMAllocARM(cl_context context,
- cl_svm_mem_flags_arm flags,
- size_t size,
-- cl_uint alignment) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_uint alignment) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY void CL_API_CALL
- clSVMFreeARM(cl_context context,
-- void * svm_pointer) CL_EXT_SUFFIX__VERSION_1_2;
-+ void * svm_pointer) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueSVMFreeARM(cl_command_queue command_queue,
-@@ -804,7 +850,7 @@ clEnqueueSVMFreeARM(cl_command_queue command_queue,
- void * user_data,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueSVMMemcpyARM(cl_command_queue command_queue,
-@@ -814,7 +860,7 @@ clEnqueueSVMMemcpyARM(cl_command_queue command_queue,
- size_t size,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueSVMMemFillARM(cl_command_queue command_queue,
-@@ -824,7 +870,7 @@ clEnqueueSVMMemFillARM(cl_command_queue command_queue,
- size_t size,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueSVMMapARM(cl_command_queue command_queue,
-@@ -834,25 +880,25 @@ clEnqueueSVMMapARM(cl_command_queue command_queue,
- size_t size,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueSVMUnmapARM(cl_command_queue command_queue,
- void * svm_ptr,
- cl_uint num_events_in_wait_list,
- const cl_event * event_wait_list,
-- cl_event * event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event * event) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clSetKernelArgSVMPointerARM(cl_kernel kernel,
- cl_uint arg_index,
-- const void * arg_value) CL_EXT_SUFFIX__VERSION_1_2;
-+ const void * arg_value) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clSetKernelExecInfoARM(cl_kernel kernel,
- cl_kernel_exec_info_arm param_name,
- size_t param_value_size,
-- const void * param_value) CL_EXT_SUFFIX__VERSION_1_2;
-+ const void * param_value) CL_API_SUFFIX__VERSION_1_2;
-
- /********************************
- * cl_arm_get_core_id extension *
-@@ -1060,14 +1106,14 @@ clCreateAcceleratorINTEL(
- cl_accelerator_type_intel accelerator_type,
- size_t descriptor_size,
- const void* descriptor,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_accelerator_intel (CL_API_CALL *clCreateAcceleratorINTEL_fn)(
-+typedef cl_accelerator_intel (CL_API_CALL *clCreateAcceleratorINTEL_fn)(
- cl_context context,
- cl_accelerator_type_intel accelerator_type,
- size_t descriptor_size,
- const void* descriptor,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clGetAcceleratorInfoINTEL(
-@@ -1075,28 +1121,28 @@ clGetAcceleratorInfoINTEL(
- cl_accelerator_info_intel param_name,
- size_t param_value_size,
- void* param_value,
-- size_t* param_value_size_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ size_t* param_value_size_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetAcceleratorInfoINTEL_fn)(
-+typedef cl_int (CL_API_CALL *clGetAcceleratorInfoINTEL_fn)(
- cl_accelerator_intel accelerator,
- cl_accelerator_info_intel param_name,
- size_t param_value_size,
- void* param_value,
-- size_t* param_value_size_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ size_t* param_value_size_ret) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clRetainAcceleratorINTEL(
-- cl_accelerator_intel accelerator) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_accelerator_intel accelerator) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clRetainAcceleratorINTEL_fn)(
-- cl_accelerator_intel accelerator) CL_EXT_SUFFIX__VERSION_1_2;
-+typedef cl_int (CL_API_CALL *clRetainAcceleratorINTEL_fn)(
-+ cl_accelerator_intel accelerator) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clReleaseAcceleratorINTEL(
-- cl_accelerator_intel accelerator) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_accelerator_intel accelerator) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clReleaseAcceleratorINTEL_fn)(
-- cl_accelerator_intel accelerator) CL_EXT_SUFFIX__VERSION_1_2;
-+typedef cl_int (CL_API_CALL *clReleaseAcceleratorINTEL_fn)(
-+ cl_accelerator_intel accelerator) CL_API_SUFFIX__VERSION_1_2;
-
- /******************************************
- * cl_intel_simultaneous_sharing extension *
-@@ -1368,7 +1414,7 @@ clHostMemAllocINTEL(
- cl_uint alignment,
- cl_int* errcode_ret);
-
--typedef CL_API_ENTRY void* (CL_API_CALL *
-+typedef void* (CL_API_CALL *
- clHostMemAllocINTEL_fn)(
- cl_context context,
- const cl_mem_properties_intel* properties,
-@@ -1385,7 +1431,7 @@ clDeviceMemAllocINTEL(
- cl_uint alignment,
- cl_int* errcode_ret);
-
--typedef CL_API_ENTRY void* (CL_API_CALL *
-+typedef void* (CL_API_CALL *
- clDeviceMemAllocINTEL_fn)(
- cl_context context,
- cl_device_id device,
-@@ -1403,7 +1449,7 @@ clSharedMemAllocINTEL(
- cl_uint alignment,
- cl_int* errcode_ret);
-
--typedef CL_API_ENTRY void* (CL_API_CALL *
-+typedef void* (CL_API_CALL *
- clSharedMemAllocINTEL_fn)(
- cl_context context,
- cl_device_id device,
-@@ -1417,7 +1463,7 @@ clMemFreeINTEL(
- cl_context context,
- void* ptr);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clMemFreeINTEL_fn)(
- cl_context context,
- void* ptr);
-@@ -1427,7 +1473,7 @@ clMemBlockingFreeINTEL(
- cl_context context,
- void* ptr);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clMemBlockingFreeINTEL_fn)(
- cl_context context,
- void* ptr);
-@@ -1441,7 +1487,7 @@ clGetMemAllocInfoINTEL(
- void* param_value,
- size_t* param_value_size_ret);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clGetMemAllocInfoINTEL_fn)(
- cl_context context,
- const void* ptr,
-@@ -1456,7 +1502,7 @@ clSetKernelArgMemPointerINTEL(
- cl_uint arg_index,
- const void* arg_value);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clSetKernelArgMemPointerINTEL_fn)(
- cl_kernel kernel,
- cl_uint arg_index,
-@@ -1472,7 +1518,7 @@ clEnqueueMemsetINTEL( /* Deprecated */
- const cl_event* event_wait_list,
- cl_event* event);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clEnqueueMemsetINTEL_fn)( /* Deprecated */
- cl_command_queue command_queue,
- void* dst_ptr,
-@@ -1493,7 +1539,7 @@ clEnqueueMemFillINTEL(
- const cl_event* event_wait_list,
- cl_event* event);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clEnqueueMemFillINTEL_fn)(
- cl_command_queue command_queue,
- void* dst_ptr,
-@@ -1515,7 +1561,7 @@ clEnqueueMemcpyINTEL(
- const cl_event* event_wait_list,
- cl_event* event);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clEnqueueMemcpyINTEL_fn)(
- cl_command_queue command_queue,
- cl_bool blocking,
-@@ -1541,7 +1587,7 @@ clEnqueueMigrateMemINTEL(
- const cl_event* event_wait_list,
- cl_event* event);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clEnqueueMigrateMemINTEL_fn)(
- cl_command_queue command_queue,
- const void* ptr,
-@@ -1563,7 +1609,7 @@ clEnqueueMemAdviseINTEL(
- const cl_event* event_wait_list,
- cl_event* event);
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *
-+typedef cl_int (CL_API_CALL *
- clEnqueueMemAdviseINTEL_fn)(
- cl_command_queue command_queue,
- const void* ptr,
-@@ -1586,16 +1632,16 @@ clCreateBufferWithPropertiesINTEL(
- cl_mem_flags flags,
- size_t size,
- void * host_ptr,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_0;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL *
-+typedef cl_mem (CL_API_CALL *
- clCreateBufferWithPropertiesINTEL_fn)(
- cl_context context,
- const cl_mem_properties_intel* properties,
- cl_mem_flags flags,
- size_t size,
- void * host_ptr,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_0;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
- /******************************************
- * cl_intel_mem_channel_property extension *
-@@ -1612,6 +1658,48 @@ clCreateBufferWithPropertiesINTEL_fn)(
- /* cl_mem_flags */
- #define CL_MEM_FORCE_HOST_MEMORY_INTEL (1 << 20)
-
-+/***************************************************************
-+* cl_intel_command_queue_families
-+***************************************************************/
-+#define cl_intel_command_queue_families 1
-+
-+typedef cl_bitfield cl_command_queue_capabilities_intel;
-+
-+#define CL_QUEUE_FAMILY_MAX_NAME_SIZE_INTEL 64
-+
-+typedef struct _cl_queue_family_properties_intel {
-+ cl_command_queue_properties properties;
-+ cl_command_queue_capabilities_intel capabilities;
-+ cl_uint count;
-+ char name[CL_QUEUE_FAMILY_MAX_NAME_SIZE_INTEL];
-+} cl_queue_family_properties_intel;
-+
-+/* cl_device_info */
-+#define CL_DEVICE_QUEUE_FAMILY_PROPERTIES_INTEL 0x418B
-+
-+/* cl_queue_properties */
-+#define CL_QUEUE_FAMILY_INTEL 0x418C
-+#define CL_QUEUE_INDEX_INTEL 0x418D
-+
-+/* cl_command_queue_capabilities_intel */
-+#define CL_QUEUE_DEFAULT_CAPABILITIES_INTEL 0
-+#define CL_QUEUE_CAPABILITY_CREATE_SINGLE_QUEUE_EVENTS_INTEL (1 << 0)
-+#define CL_QUEUE_CAPABILITY_CREATE_CROSS_QUEUE_EVENTS_INTEL (1 << 1)
-+#define CL_QUEUE_CAPABILITY_SINGLE_QUEUE_EVENT_WAIT_LIST_INTEL (1 << 2)
-+#define CL_QUEUE_CAPABILITY_CROSS_QUEUE_EVENT_WAIT_LIST_INTEL (1 << 3)
-+#define CL_QUEUE_CAPABILITY_TRANSFER_BUFFER_INTEL (1 << 8)
-+#define CL_QUEUE_CAPABILITY_TRANSFER_BUFFER_RECT_INTEL (1 << 9)
-+#define CL_QUEUE_CAPABILITY_MAP_BUFFER_INTEL (1 << 10)
-+#define CL_QUEUE_CAPABILITY_FILL_BUFFER_INTEL (1 << 11)
-+#define CL_QUEUE_CAPABILITY_TRANSFER_IMAGE_INTEL (1 << 12)
-+#define CL_QUEUE_CAPABILITY_MAP_IMAGE_INTEL (1 << 13)
-+#define CL_QUEUE_CAPABILITY_FILL_IMAGE_INTEL (1 << 14)
-+#define CL_QUEUE_CAPABILITY_TRANSFER_BUFFER_IMAGE_INTEL (1 << 15)
-+#define CL_QUEUE_CAPABILITY_TRANSFER_IMAGE_BUFFER_INTEL (1 << 16)
-+#define CL_QUEUE_CAPABILITY_MARKER_INTEL (1 << 24)
-+#define CL_QUEUE_CAPABILITY_BARRIER_INTEL (1 << 25)
-+#define CL_QUEUE_CAPABILITY_KERNEL_INTEL (1 << 26)
-+
- #ifdef __cplusplus
- }
- #endif
-diff --git a/khronos-headers/CL/cl_gl.h b/khronos-headers/CL/cl_gl.h
-index b587f02..5ea0fd8 100644
---- a/khronos-headers/CL/cl_gl.h
-+++ b/khronos-headers/CL/cl_gl.h
-@@ -1,5 +1,5 @@
- /*******************************************************************************
-- * Copyright (c) 2008-2020 The Khronos Group Inc.
-+ * Copyright (c) 2008-2021 The Khronos Group Inc.
- *
- * Licensed under the Apache License, Version 2.0 (the "License");
- * you may not use this file except in compliance with the License.
-@@ -102,21 +102,21 @@ clEnqueueReleaseGLObjects(cl_command_queue command_queue,
-
-
- /* Deprecated OpenCL 1.1 APIs */
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
- clCreateFromGLTexture2D(cl_context context,
- cl_mem_flags flags,
- cl_GLenum target,
- cl_GLint miplevel,
- cl_GLuint texture,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--extern CL_API_ENTRY CL_EXT_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
-+extern CL_API_ENTRY CL_API_PREFIX__VERSION_1_1_DEPRECATED cl_mem CL_API_CALL
- clCreateFromGLTexture3D(cl_context context,
- cl_mem_flags flags,
- cl_GLenum target,
- cl_GLint miplevel,
- cl_GLuint texture,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
- /* cl_khr_gl_sharing extension */
-
-@@ -145,13 +145,23 @@ clGetGLContextInfoKHR(const cl_context_properties * properties,
- void * param_value,
- size_t * param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetGLContextInfoKHR_fn)(
-+typedef cl_int (CL_API_CALL *clGetGLContextInfoKHR_fn)(
- const cl_context_properties * properties,
- cl_gl_context_info param_name,
- size_t param_value_size,
- void * param_value,
- size_t * param_value_size_ret);
-
-+/*
-+ * cl_khr_gl_event extension
-+ */
-+#define CL_COMMAND_GL_FENCE_SYNC_OBJECT_KHR 0x200D
-+
-+extern CL_API_ENTRY cl_event CL_API_CALL
-+clCreateEventFromGLsyncKHR(cl_context context,
-+ cl_GLsync sync,
-+ cl_int * errcode_ret) CL_API_SUFFIX__VERSION_1_1;
-+
- #ifdef __cplusplus
- }
- #endif
-diff --git a/khronos-headers/CL/cl_gl_ext.h b/khronos-headers/CL/cl_gl_ext.h
-index 52107b1..8ec8181 100644
---- a/khronos-headers/CL/cl_gl_ext.h
-+++ b/khronos-headers/CL/cl_gl_ext.h
-@@ -1,5 +1,5 @@
- /*******************************************************************************
-- * Copyright (c) 2008-2020 The Khronos Group Inc.
-+ * Copyright (c) 2008-2021 The Khronos Group Inc.
- *
- * Licensed under the Apache License, Version 2.0 (the "License");
- * you may not use this file except in compliance with the License.
-@@ -14,27 +14,5 @@
- * limitations under the License.
- ******************************************************************************/
-
--#ifndef __OPENCL_CL_GL_EXT_H
--#define __OPENCL_CL_GL_EXT_H
--
--#ifdef __cplusplus
--extern "C" {
--#endif
--
- #include <CL/cl_gl.h>
--
--/*
-- * cl_khr_gl_event extension
-- */
--#define CL_COMMAND_GL_FENCE_SYNC_OBJECT_KHR 0x200D
--
--extern CL_API_ENTRY cl_event CL_API_CALL
--clCreateEventFromGLsyncKHR(cl_context context,
-- cl_GLsync sync,
-- cl_int * errcode_ret) CL_EXT_SUFFIX__VERSION_1_1;
--
--#ifdef __cplusplus
--}
--#endif
--
--#endif /* __OPENCL_CL_GL_EXT_H */
-+#pragma message("All OpenGL-related extensions have been moved into cl_gl.h. Please include cl_gl.h directly.")
-diff --git a/khronos-headers/CL/cl_icd.h b/khronos-headers/CL/cl_icd.h
-index 8ff8b94..d5ac1de 100644
---- a/khronos-headers/CL/cl_icd.h
-+++ b/khronos-headers/CL/cl_icd.h
-@@ -41,35 +41,35 @@ extern "C" {
- /* API function pointer definitions */
-
- // Platform APIs
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetPlatformIDs)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetPlatformIDs)(
- cl_uint num_entries, cl_platform_id *platforms,
- cl_uint *num_platforms) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetPlatformInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetPlatformInfo)(
- cl_platform_id platform, cl_platform_info param_name,
- size_t param_value_size, void *param_value,
- size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- // Device APIs
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetDeviceIDs)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetDeviceIDs)(
- cl_platform_id platform, cl_device_type device_type, cl_uint num_entries,
- cl_device_id *devices, cl_uint *num_devices) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetDeviceInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetDeviceInfo)(
- cl_device_id device, cl_device_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clCreateSubDevices)(
-+typedef cl_int(CL_API_CALL *cl_api_clCreateSubDevices)(
- cl_device_id in_device,
- const cl_device_partition_property *partition_properties,
- cl_uint num_entries, cl_device_id *out_devices, cl_uint *num_devices);
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainDevice)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainDevice)(
- cl_device_id device) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseDevice)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseDevice)(
- cl_device_id device) CL_API_SUFFIX__VERSION_1_2;
-
- #else
-@@ -81,36 +81,36 @@ typedef void *cl_api_clReleaseDevice;
- #endif
-
- // Context APIs
--typedef CL_API_ENTRY cl_context(CL_API_CALL *cl_api_clCreateContext)(
-+typedef cl_context(CL_API_CALL *cl_api_clCreateContext)(
- const cl_context_properties *properties, cl_uint num_devices,
- const cl_device_id *devices,
- void(CL_CALLBACK *pfn_notify)(const char *, const void *, size_t, void *),
- void *user_data, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_context(CL_API_CALL *cl_api_clCreateContextFromType)(
-+typedef cl_context(CL_API_CALL *cl_api_clCreateContextFromType)(
- const cl_context_properties *properties, cl_device_type device_type,
- void(CL_CALLBACK *pfn_notify)(const char *, const void *, size_t, void *),
- void *user_data, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainContext)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainContext)(
- cl_context context) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseContext)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseContext)(
- cl_context context) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetContextInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetContextInfo)(
- cl_context context, cl_context_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- // Command Queue APIs
--typedef CL_API_ENTRY cl_command_queue(CL_API_CALL *cl_api_clCreateCommandQueue)(
-+typedef cl_command_queue(CL_API_CALL *cl_api_clCreateCommandQueue)(
- cl_context context, cl_device_id device,
- cl_command_queue_properties properties,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_2_0
-
--typedef CL_API_ENTRY
-+typedef
- cl_command_queue(CL_API_CALL *cl_api_clCreateCommandQueueWithProperties)(
- cl_context /* context */, cl_device_id /* device */,
- const cl_queue_properties * /* properties */,
-@@ -122,25 +122,25 @@ typedef void *cl_api_clCreateCommandQueueWithProperties;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainCommandQueue)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainCommandQueue)(
- cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseCommandQueue)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseCommandQueue)(
- cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetCommandQueueInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetCommandQueueInfo)(
- cl_command_queue command_queue, cl_command_queue_info param_name,
- size_t param_value_size, void *param_value,
- size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- // Memory Object APIs
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateBuffer)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateBuffer)(
- cl_context context, cl_mem_flags flags, size_t size, void *host_ptr,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateImage)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateImage)(
- cl_context context, cl_mem_flags flags, const cl_image_format *image_format,
- const cl_image_desc *image_desc, void *host_ptr,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-@@ -153,17 +153,17 @@ typedef void *cl_api_clCreateImage;
-
- #ifdef CL_VERSION_3_0
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateBufferWithProperties)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateBufferWithProperties)(
- cl_context context, const cl_mem_properties *properties, cl_mem_flags flags,
- size_t size, void *host_ptr,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_3_0;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateImageWithProperties)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateImageWithProperties)(
- cl_context context, const cl_mem_properties *properties, cl_mem_flags flags,
- const cl_image_format *image_format, const cl_image_desc *image_desc,
- void *host_ptr, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_3_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL* cl_api_clSetContextDestructorCallback)(
-+typedef cl_int(CL_API_CALL* cl_api_clSetContextDestructorCallback)(
- cl_context context,
- void(CL_CALLBACK* pfn_notify)(cl_context context, void* user_data),
- void* user_data) CL_API_SUFFIX__VERSION_3_0;
-@@ -176,43 +176,43 @@ typedef void *cl_api_clSetContextDestructorCallback;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainMemObject)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainMemObject)(
- cl_mem memobj) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseMemObject)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseMemObject)(
- cl_mem memobj) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetSupportedImageFormats)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetSupportedImageFormats)(
- cl_context context, cl_mem_flags flags, cl_mem_object_type image_type,
- cl_uint num_entries, cl_image_format *image_formats,
- cl_uint *num_image_formats) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetMemObjectInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetMemObjectInfo)(
- cl_mem memobj, cl_mem_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetImageInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetImageInfo)(
- cl_mem image, cl_image_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_2_0
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreatePipe)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreatePipe)(
- cl_context /* context */, cl_mem_flags /* flags */,
- cl_uint /* pipe_packet_size */, cl_uint /* pipe_max_packets */,
- const cl_pipe_properties * /* properties */,
- cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetPipeInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetPipeInfo)(
- cl_mem /* pipe */, cl_pipe_info /* param_name */,
- size_t /* param_value_size */, void * /* param_value */,
- size_t * /* param_value_size_ret */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY void *(CL_API_CALL *cl_api_clSVMAlloc)(
-+typedef void *(CL_API_CALL *cl_api_clSVMAlloc)(
- cl_context /* context */, cl_svm_mem_flags /* flags */, size_t /* size */,
- unsigned int /* alignment */)CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY void(CL_API_CALL *cl_api_clSVMFree)(
-+typedef void(CL_API_CALL *cl_api_clSVMFree)(
- cl_context /* context */,
- void * /* svm_pointer */) CL_API_SUFFIX__VERSION_2_0;
-
-@@ -226,24 +226,24 @@ typedef void *cl_api_clSVMFree;
- #endif
-
- // Sampler APIs
--typedef CL_API_ENTRY cl_sampler(CL_API_CALL *cl_api_clCreateSampler)(
-+typedef cl_sampler(CL_API_CALL *cl_api_clCreateSampler)(
- cl_context context, cl_bool normalized_coords,
- cl_addressing_mode addressing_mode, cl_filter_mode filter_mode,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainSampler)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainSampler)(
- cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseSampler)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseSampler)(
- cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetSamplerInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetSamplerInfo)(
- cl_sampler sampler, cl_sampler_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_2_0
-
--typedef CL_API_ENTRY
-+typedef
- cl_sampler(CL_API_CALL *cl_api_clCreateSamplerWithProperties)(
- cl_context /* context */,
- const cl_sampler_properties * /* sampler_properties */,
-@@ -256,18 +256,18 @@ typedef void *cl_api_clCreateSamplerWithProperties;
- #endif
-
- // Program Object APIs
--typedef CL_API_ENTRY cl_program(CL_API_CALL *cl_api_clCreateProgramWithSource)(
-+typedef cl_program(CL_API_CALL *cl_api_clCreateProgramWithSource)(
- cl_context context, cl_uint count, const char **strings,
- const size_t *lengths, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_program(CL_API_CALL *cl_api_clCreateProgramWithBinary)(
-+typedef cl_program(CL_API_CALL *cl_api_clCreateProgramWithBinary)(
- cl_context context, cl_uint num_devices, const cl_device_id *device_list,
- const size_t *lengths, const unsigned char **binaries,
- cl_int *binary_status, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY
-+typedef
- cl_program(CL_API_CALL *cl_api_clCreateProgramWithBuiltInKernels)(
- cl_context context, cl_uint num_devices, const cl_device_id *device_list,
- const char *kernel_names, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-@@ -278,13 +278,13 @@ typedef void *cl_api_clCreateProgramWithBuiltInKernels;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainProgram)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainProgram)(
- cl_program program) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseProgram)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseProgram)(
- cl_program program) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clBuildProgram)(
-+typedef cl_int(CL_API_CALL *cl_api_clBuildProgram)(
- cl_program program, cl_uint num_devices, const cl_device_id *device_list,
- const char *options,
- void(CL_CALLBACK *pfn_notify)(cl_program program, void *user_data),
-@@ -292,14 +292,14 @@ typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clBuildProgram)(
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clCompileProgram)(
-+typedef cl_int(CL_API_CALL *cl_api_clCompileProgram)(
- cl_program program, cl_uint num_devices, const cl_device_id *device_list,
- const char *options, cl_uint num_input_headers,
- const cl_program *input_headers, const char **header_include_names,
- void(CL_CALLBACK *pfn_notify)(cl_program program, void *user_data),
- void *user_data) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_program(CL_API_CALL *cl_api_clLinkProgram)(
-+typedef cl_program(CL_API_CALL *cl_api_clLinkProgram)(
- cl_context context, cl_uint num_devices, const cl_device_id *device_list,
- const char *options, cl_uint num_input_programs,
- const cl_program *input_programs,
-@@ -315,12 +315,12 @@ typedef void *cl_api_clLinkProgram;
-
- #ifdef CL_VERSION_2_2
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clSetProgramSpecializationConstant)(
- cl_program program, cl_uint spec_id, size_t spec_size,
- const void *spec_value) CL_API_SUFFIX__VERSION_2_2;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetProgramReleaseCallback)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetProgramReleaseCallback)(
- cl_program program,
- void(CL_CALLBACK *pfn_notify)(cl_program program, void *user_data),
- void *user_data) CL_API_SUFFIX__VERSION_2_2;
-@@ -334,7 +334,7 @@ typedef void *cl_api_clSetProgramReleaseCallback;
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clUnloadPlatformCompiler)(
-+typedef cl_int(CL_API_CALL *cl_api_clUnloadPlatformCompiler)(
- cl_platform_id platform) CL_API_SUFFIX__VERSION_1_2;
-
- #else
-@@ -343,41 +343,41 @@ typedef void *cl_api_clUnloadPlatformCompiler;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetProgramInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetProgramInfo)(
- cl_program program, cl_program_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetProgramBuildInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetProgramBuildInfo)(
- cl_program program, cl_device_id device, cl_program_build_info param_name,
- size_t param_value_size, void *param_value,
- size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- // Kernel Object APIs
--typedef CL_API_ENTRY cl_kernel(CL_API_CALL *cl_api_clCreateKernel)(
-+typedef cl_kernel(CL_API_CALL *cl_api_clCreateKernel)(
- cl_program program, const char *kernel_name,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clCreateKernelsInProgram)(
-+typedef cl_int(CL_API_CALL *cl_api_clCreateKernelsInProgram)(
- cl_program program, cl_uint num_kernels, cl_kernel *kernels,
- cl_uint *num_kernels_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainKernel)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainKernel)(
- cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseKernel)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseKernel)(
- cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetKernelArg)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetKernelArg)(
- cl_kernel kernel, cl_uint arg_index, size_t arg_size,
- const void *arg_value) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetKernelInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetKernelInfo)(
- cl_kernel kernel, cl_kernel_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetKernelArgInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetKernelArgInfo)(
- cl_kernel kernel, cl_uint arg_indx, cl_kernel_arg_info param_name,
- size_t param_value_size, void *param_value,
- size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_2;
-@@ -388,28 +388,28 @@ typedef void *cl_api_clGetKernelArgInfo;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetKernelWorkGroupInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetKernelWorkGroupInfo)(
- cl_kernel kernel, cl_device_id device, cl_kernel_work_group_info param_name,
- size_t param_value_size, void *param_value,
- size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_2_0
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetKernelArgSVMPointer)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetKernelArgSVMPointer)(
- cl_kernel /* kernel */, cl_uint /* arg_index */,
- const void * /* arg_value */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetKernelExecInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetKernelExecInfo)(
- cl_kernel /* kernel */, cl_kernel_exec_info /* param_name */,
- size_t /* param_value_size */,
- const void * /* param_value */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetKernelSubGroupInfoKHR)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetKernelSubGroupInfoKHR)(
- cl_kernel /* in_kernel */, cl_device_id /*in_device*/,
- cl_kernel_sub_group_info /* param_name */, size_t /*input_value_size*/,
- const void * /*input_value*/, size_t /*param_value_size*/,
- void * /*param_value*/,
-- size_t * /*param_value_size_ret*/) CL_EXT_SUFFIX__VERSION_2_0;
-+ size_t * /*param_value_size_ret*/) CL_API_SUFFIX__VERSION_2_0;
-
- #else
-
-@@ -420,33 +420,33 @@ typedef void *cl_api_clGetKernelSubGroupInfoKHR;
- #endif
-
- // Event Object APIs
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clWaitForEvents)(
-+typedef cl_int(CL_API_CALL *cl_api_clWaitForEvents)(
- cl_uint num_events, const cl_event *event_list) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetEventInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetEventInfo)(
- cl_event event, cl_event_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainEvent)(cl_event event)
-+typedef cl_int(CL_API_CALL *cl_api_clRetainEvent)(cl_event event)
- CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseEvent)(cl_event event)
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseEvent)(cl_event event)
- CL_API_SUFFIX__VERSION_1_0;
-
- // Profiling APIs
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetEventProfilingInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetEventProfilingInfo)(
- cl_event event, cl_profiling_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
- // Flush and Finish APIs
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clFlush)(
-+typedef cl_int(CL_API_CALL *cl_api_clFlush)(
- cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clFinish)(
-+typedef cl_int(CL_API_CALL *cl_api_clFinish)(
- cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
-
- // Enqueued Commands APIs
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueReadBuffer)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueReadBuffer)(
- cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_read,
- size_t offset, size_t cb, void *ptr, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
-@@ -454,7 +454,7 @@ typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueReadBuffer)(
-
- #ifdef CL_VERSION_1_1
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueReadBufferRect)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueReadBufferRect)(
- cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_read,
- const size_t *buffer_origin, const size_t *host_origin,
- const size_t *region, size_t buffer_row_pitch, size_t buffer_slice_pitch,
-@@ -468,7 +468,7 @@ typedef void *cl_api_clEnqueueReadBufferRect;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueWriteBuffer)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueWriteBuffer)(
- cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_write,
- size_t offset, size_t cb, const void *ptr, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
-@@ -476,7 +476,7 @@ typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueWriteBuffer)(
-
- #ifdef CL_VERSION_1_1
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueWriteBufferRect)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueWriteBufferRect)(
- cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_read,
- const size_t *buffer_origin, const size_t *host_origin,
- const size_t *region, size_t buffer_row_pitch, size_t buffer_slice_pitch,
-@@ -492,7 +492,7 @@ typedef void *cl_api_clEnqueueWriteBufferRect;
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueFillBuffer)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueFillBuffer)(
- cl_command_queue command_queue, cl_mem buffer, const void *pattern,
- size_t pattern_size, size_t offset, size_t cb,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
-@@ -504,7 +504,7 @@ typedef void *cl_api_clEnqueueFillBuffer;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueCopyBuffer)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueCopyBuffer)(
- cl_command_queue command_queue, cl_mem src_buffer, cl_mem dst_buffer,
- size_t src_offset, size_t dst_offset, size_t cb,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
-@@ -512,7 +512,7 @@ typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueCopyBuffer)(
-
- #ifdef CL_VERSION_1_1
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueCopyBufferRect)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueCopyBufferRect)(
- cl_command_queue command_queue, cl_mem src_buffer, cl_mem dst_buffer,
- const size_t *src_origin, const size_t *dst_origin, const size_t *region,
- size_t src_row_pitch, size_t src_slice_pitch, size_t dst_row_pitch,
-@@ -526,14 +526,14 @@ typedef void *cl_api_clEnqueueCopyBufferRect;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueReadImage)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueReadImage)(
- cl_command_queue command_queue, cl_mem image, cl_bool blocking_read,
- const size_t *origin, const size_t *region, size_t row_pitch,
- size_t slice_pitch, void *ptr, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueWriteImage)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueWriteImage)(
- cl_command_queue command_queue, cl_mem image, cl_bool blocking_write,
- const size_t *origin, const size_t *region, size_t input_row_pitch,
- size_t input_slice_pitch, const void *ptr, cl_uint num_events_in_wait_list,
-@@ -542,7 +542,7 @@ typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueWriteImage)(
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueFillImage)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueFillImage)(
- cl_command_queue command_queue, cl_mem image, const void *fill_color,
- const size_t origin[3], const size_t region[3],
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
-@@ -554,45 +554,45 @@ typedef void *cl_api_clEnqueueFillImage;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueCopyImage)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueCopyImage)(
- cl_command_queue command_queue, cl_mem src_image, cl_mem dst_image,
- const size_t *src_origin, const size_t *dst_origin, const size_t *region,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueCopyImageToBuffer)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueCopyImageToBuffer)(
- cl_command_queue command_queue, cl_mem src_image, cl_mem dst_buffer,
- const size_t *src_origin, const size_t *region, size_t dst_offset,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueCopyBufferToImage)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueCopyBufferToImage)(
- cl_command_queue command_queue, cl_mem src_buffer, cl_mem dst_image,
- size_t src_offset, const size_t *dst_origin, const size_t *region,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY void *(CL_API_CALL *cl_api_clEnqueueMapBuffer)(
-+typedef void *(CL_API_CALL *cl_api_clEnqueueMapBuffer)(
- cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_map,
- cl_map_flags map_flags, size_t offset, size_t cb,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
- cl_event *event, cl_int *errcode_ret)CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY void *(CL_API_CALL *cl_api_clEnqueueMapImage)(
-+typedef void *(CL_API_CALL *cl_api_clEnqueueMapImage)(
- cl_command_queue command_queue, cl_mem image, cl_bool blocking_map,
- cl_map_flags map_flags, const size_t *origin, const size_t *region,
- size_t *image_row_pitch, size_t *image_slice_pitch,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
- cl_event *event, cl_int *errcode_ret)CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueUnmapMemObject)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueUnmapMemObject)(
- cl_command_queue command_queue, cl_mem memobj, void *mapped_ptr,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueMigrateMemObjects)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueMigrateMemObjects)(
- cl_command_queue command_queue, cl_uint num_mem_objects,
- const cl_mem *mem_objects, cl_mem_migration_flags flags,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
-@@ -604,19 +604,19 @@ typedef void *cl_api_clEnqueueMigrateMemObjects;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueNDRangeKernel)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueNDRangeKernel)(
- cl_command_queue command_queue, cl_kernel kernel, cl_uint work_dim,
- const size_t *global_work_offset, const size_t *global_work_size,
- const size_t *local_work_size, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueTask)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueTask)(
- cl_command_queue command_queue, cl_kernel kernel,
- cl_uint num_events_in_wait_list, const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueNativeKernel)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueNativeKernel)(
- cl_command_queue command_queue, void(CL_CALLBACK *user_func)(void *),
- void *args, size_t cb_args, cl_uint num_mem_objects, const cl_mem *mem_list,
- const void **args_mem_loc, cl_uint num_events_in_wait_list,
-@@ -625,17 +625,17 @@ typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueNativeKernel)(
-
- #ifdef CL_VERSION_1_2
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueMarkerWithWaitList)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueMarkerWithWaitList)(
- cl_command_queue command_queue, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueBarrierWithWaitList)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueBarrierWithWaitList)(
- cl_command_queue command_queue, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY void *(
-+typedef void *(
- CL_API_CALL *cl_api_clGetExtensionFunctionAddressForPlatform)(
- cl_platform_id platform,
- const char *function_name)CL_API_SUFFIX__VERSION_1_2;
-@@ -652,7 +652,7 @@ typedef void *cl_api_clGetExtensionFunctionAddressForPlatform;
-
- #ifdef CL_VERSION_2_0
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueSVMFree)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueSVMFree)(
- cl_command_queue /* command_queue */, cl_uint /* num_svm_pointers */,
- void ** /* svm_pointers */,
- void(CL_CALLBACK *pfn_free_func)(cl_command_queue /* queue */,
-@@ -663,28 +663,28 @@ typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueSVMFree)(
- const cl_event * /* event_wait_list */,
- cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueSVMMemcpy)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueSVMMemcpy)(
- cl_command_queue /* command_queue */, cl_bool /* blocking_copy */,
- void * /* dst_ptr */, const void * /* src_ptr */, size_t /* size */,
- cl_uint /* num_events_in_wait_list */,
- const cl_event * /* event_wait_list */,
- cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueSVMMemFill)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueSVMMemFill)(
- cl_command_queue /* command_queue */, void * /* svm_ptr */,
- const void * /* pattern */, size_t /* pattern_size */, size_t /* size */,
- cl_uint /* num_events_in_wait_list */,
- const cl_event * /* event_wait_list */,
- cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueSVMMap)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueSVMMap)(
- cl_command_queue /* command_queue */, cl_bool /* blocking_map */,
- cl_map_flags /* map_flags */, void * /* svm_ptr */, size_t /* size */,
- cl_uint /* num_events_in_wait_list */,
- const cl_event * /* event_wait_list */,
- cl_event * /* event */) CL_API_SUFFIX__VERSION_2_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueSVMUnmap)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueSVMUnmap)(
- cl_command_queue /* command_queue */, void * /* svm_ptr */,
- cl_uint /* num_events_in_wait_list */,
- const cl_event * /* event_wait_list */,
-@@ -701,119 +701,119 @@ typedef void *cl_api_clEnqueueSVMUnmap;
- #endif
-
- // Deprecated APIs
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetCommandQueueProperty)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetCommandQueueProperty)(
- cl_command_queue command_queue, cl_command_queue_properties properties,
- cl_bool enable, cl_command_queue_properties *old_properties)
-- CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED;
-+ CL_API_SUFFIX__VERSION_1_0_DEPRECATED;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateImage2D)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateImage2D)(
- cl_context context, cl_mem_flags flags, const cl_image_format *image_format,
- size_t image_width, size_t image_height, size_t image_row_pitch,
-- void *host_ptr, cl_int *errcode_ret) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ void *host_ptr, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateImage3D)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateImage3D)(
- cl_context context, cl_mem_flags flags, const cl_image_format *image_format,
- size_t image_width, size_t image_height, size_t image_depth,
- size_t image_row_pitch, size_t image_slice_pitch, void *host_ptr,
-- cl_int *errcode_ret) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clUnloadCompiler)(void)
-- CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+typedef cl_int(CL_API_CALL *cl_api_clUnloadCompiler)(void)
-+ CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueMarker)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueMarker)(
- cl_command_queue command_queue,
-- cl_event *event) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ cl_event *event) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueWaitForEvents)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueWaitForEvents)(
- cl_command_queue command_queue, cl_uint num_events,
-- const cl_event *event_list) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+ const cl_event *event_list) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueBarrier)(
-- cl_command_queue command_queue) CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueBarrier)(
-+ cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
--typedef CL_API_ENTRY void *(CL_API_CALL *cl_api_clGetExtensionFunctionAddress)(
-- const char *function_name)CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED;
-+typedef void *(CL_API_CALL *cl_api_clGetExtensionFunctionAddress)(
-+ const char *function_name)CL_API_SUFFIX__VERSION_1_1_DEPRECATED;
-
- // GL and other APIs
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromGLBuffer)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromGLBuffer)(
- cl_context context, cl_mem_flags flags, cl_GLuint bufobj,
- int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromGLTexture)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromGLTexture)(
- cl_context context, cl_mem_flags flags, cl_GLenum target, cl_GLint miplevel,
- cl_GLuint texture, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromGLTexture2D)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromGLTexture2D)(
- cl_context context, cl_mem_flags flags, cl_GLenum target, cl_GLint miplevel,
- cl_GLuint texture, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromGLTexture3D)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromGLTexture3D)(
- cl_context context, cl_mem_flags flags, cl_GLenum target, cl_GLint miplevel,
- cl_GLuint texture, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromGLRenderbuffer)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromGLRenderbuffer)(
- cl_context context, cl_mem_flags flags, cl_GLuint renderbuffer,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetGLObjectInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetGLObjectInfo)(
- cl_mem memobj, cl_gl_object_type *gl_object_type,
- cl_GLuint *gl_object_name) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetGLTextureInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetGLTextureInfo)(
- cl_mem memobj, cl_gl_texture_info param_name, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueAcquireGLObjects)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueAcquireGLObjects)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueReleaseGLObjects)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueReleaseGLObjects)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
- /* cl_khr_gl_sharing */
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetGLContextInfoKHR)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetGLContextInfoKHR)(
- const cl_context_properties *properties, cl_gl_context_info param_name,
- size_t param_value_size, void *param_value, size_t *param_value_size_ret);
-
- /* cl_khr_gl_event */
--typedef CL_API_ENTRY cl_event(CL_API_CALL *cl_api_clCreateEventFromGLsyncKHR)(
-+typedef cl_event(CL_API_CALL *cl_api_clCreateEventFromGLsyncKHR)(
- cl_context context, cl_GLsync sync, cl_int *errcode_ret);
-
- #if defined(_WIN32)
-
- /* cl_khr_d3d10_sharing */
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetDeviceIDsFromD3D10KHR)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetDeviceIDsFromD3D10KHR)(
- cl_platform_id platform, cl_d3d10_device_source_khr d3d_device_source,
- void *d3d_object, cl_d3d10_device_set_khr d3d_device_set,
- cl_uint num_entries, cl_device_id *devices,
- cl_uint *num_devices) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromD3D10BufferKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromD3D10BufferKHR)(
- cl_context context, cl_mem_flags flags, ID3D10Buffer *resource,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromD3D10Texture2DKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromD3D10Texture2DKHR)(
- cl_context context, cl_mem_flags flags, ID3D10Texture2D *resource,
- UINT subresource, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromD3D10Texture3DKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromD3D10Texture3DKHR)(
- cl_context context, cl_mem_flags flags, ID3D10Texture3D *resource,
- UINT subresource, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clEnqueueAcquireD3D10ObjectsKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clEnqueueReleaseD3D10ObjectsKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
-@@ -848,32 +848,32 @@ extern CL_API_ENTRY cl_int CL_API_CALL clEnqueueReleaseD3D10ObjectsKHR(
- const cl_event *event_wait_list, cl_event *event);
-
- /* cl_khr_d3d11_sharing */
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetDeviceIDsFromD3D11KHR)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetDeviceIDsFromD3D11KHR)(
- cl_platform_id platform, cl_d3d11_device_source_khr d3d_device_source,
- void *d3d_object, cl_d3d11_device_set_khr d3d_device_set,
- cl_uint num_entries, cl_device_id *devices,
- cl_uint *num_devices) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromD3D11BufferKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromD3D11BufferKHR)(
- cl_context context, cl_mem_flags flags, ID3D11Buffer *resource,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromD3D11Texture2DKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromD3D11Texture2DKHR)(
- cl_context context, cl_mem_flags flags, ID3D11Texture2D *resource,
- UINT subresource, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromD3D11Texture3DKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromD3D11Texture3DKHR)(
- cl_context context, cl_mem_flags flags, ID3D11Texture3D *resource,
- UINT subresource, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clEnqueueAcquireD3D11ObjectsKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clEnqueueReleaseD3D11ObjectsKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
-@@ -881,26 +881,26 @@ cl_int(CL_API_CALL *cl_api_clEnqueueReleaseD3D11ObjectsKHR)(
- cl_event *event) CL_API_SUFFIX__VERSION_1_2;
-
- /* cl_khr_dx9_media_sharing */
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clGetDeviceIDsFromDX9MediaAdapterKHR)(
- cl_platform_id platform, cl_uint num_media_adapters,
- cl_dx9_media_adapter_type_khr *media_adapters_type, void *media_adapters,
- cl_dx9_media_adapter_set_khr media_adapter_set, cl_uint num_entries,
- cl_device_id *devices, cl_uint *num_devices) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromDX9MediaSurfaceKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromDX9MediaSurfaceKHR)(
- cl_context context, cl_mem_flags flags,
- cl_dx9_media_adapter_type_khr adapter_type, void *surface_info,
- cl_uint plane, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clEnqueueAcquireDX9MediaSurfacesKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clEnqueueReleaseDX9MediaSurfacesKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
-@@ -987,29 +987,29 @@ typedef void *cl_api_clGetDeviceIDsFromDX9MediaAdapterKHR;
-
- #ifdef CL_VERSION_1_1
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetEventCallback)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetEventCallback)(
- cl_event /* event */, cl_int /* command_exec_callback_type */,
- void(CL_CALLBACK * /* pfn_notify */)(cl_event, cl_int, void *),
- void * /* user_data */) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateSubBuffer)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateSubBuffer)(
- cl_mem /* buffer */, cl_mem_flags /* flags */,
- cl_buffer_create_type /* buffer_create_type */,
- const void * /* buffer_create_info */,
- cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY
-+typedef
- cl_int(CL_API_CALL *cl_api_clSetMemObjectDestructorCallback)(
- cl_mem /* memobj */,
- void(CL_CALLBACK * /*pfn_notify*/)(cl_mem /* memobj */,
- void * /*user_data*/),
- void * /*user_data */) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_event(CL_API_CALL *cl_api_clCreateUserEvent)(
-+typedef cl_event(CL_API_CALL *cl_api_clCreateUserEvent)(
- cl_context /* context */,
- cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetUserEventStatus)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetUserEventStatus)(
- cl_event /* event */,
- cl_int /* execution_status */) CL_API_SUFFIX__VERSION_1_1;
-
-@@ -1023,68 +1023,68 @@ typedef void *cl_api_clSetUserEventStatus;
-
- #endif
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clCreateSubDevicesEXT)(
-+typedef cl_int(CL_API_CALL *cl_api_clCreateSubDevicesEXT)(
- cl_device_id in_device,
- const cl_device_partition_property_ext *partition_properties,
- cl_uint num_entries, cl_device_id *out_devices, cl_uint *num_devices);
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clRetainDeviceEXT)(
-+typedef cl_int(CL_API_CALL *cl_api_clRetainDeviceEXT)(
- cl_device_id device) CL_API_SUFFIX__VERSION_1_0;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clReleaseDeviceEXT)(
-+typedef cl_int(CL_API_CALL *cl_api_clReleaseDeviceEXT)(
- cl_device_id device) CL_API_SUFFIX__VERSION_1_0;
-
- /* cl_khr_egl_image */
--typedef CL_API_ENTRY cl_mem(CL_API_CALL *cl_api_clCreateFromEGLImageKHR)(
-+typedef cl_mem(CL_API_CALL *cl_api_clCreateFromEGLImageKHR)(
- cl_context context, CLeglDisplayKHR display, CLeglImageKHR image,
- cl_mem_flags flags, const cl_egl_image_properties_khr *properties,
- cl_int *errcode_ret);
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueAcquireEGLObjectsKHR)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueAcquireEGLObjectsKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list, cl_event *event);
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueReleaseEGLObjectsKHR)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueReleaseEGLObjectsKHR)(
- cl_command_queue command_queue, cl_uint num_objects,
- const cl_mem *mem_objects, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list, cl_event *event);
-
- /* cl_khr_egl_event */
--typedef CL_API_ENTRY cl_event(CL_API_CALL *cl_api_clCreateEventFromEGLSyncKHR)(
-+typedef cl_event(CL_API_CALL *cl_api_clCreateEventFromEGLSyncKHR)(
- cl_context context, CLeglSyncKHR sync, CLeglDisplayKHR display,
- cl_int *errcode_ret);
-
- #ifdef CL_VERSION_2_1
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clSetDefaultDeviceCommandQueue)(
-+typedef cl_int(CL_API_CALL *cl_api_clSetDefaultDeviceCommandQueue)(
- cl_context context, cl_device_id device,
- cl_command_queue command_queue) CL_API_SUFFIX__VERSION_2_1;
-
--typedef CL_API_ENTRY cl_program(CL_API_CALL *cl_api_clCreateProgramWithIL)(
-+typedef cl_program(CL_API_CALL *cl_api_clCreateProgramWithIL)(
- cl_context context, const void *il, size_t length,
- cl_int *errcode_ret) CL_API_SUFFIX__VERSION_2_1;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetKernelSubGroupInfo)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetKernelSubGroupInfo)(
- cl_kernel kernel, cl_device_id device, cl_kernel_sub_group_info param_name,
- size_t input_value_size, const void *input_value, size_t param_value_size,
- void *param_value, size_t *param_value_size_ret) CL_API_SUFFIX__VERSION_2_1;
-
--typedef CL_API_ENTRY cl_kernel(CL_API_CALL *cl_api_clCloneKernel)(
-+typedef cl_kernel(CL_API_CALL *cl_api_clCloneKernel)(
- cl_kernel source_kernel, cl_int *errcode_ret) CL_API_SUFFIX__VERSION_2_1;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clEnqueueSVMMigrateMem)(
-+typedef cl_int(CL_API_CALL *cl_api_clEnqueueSVMMigrateMem)(
- cl_command_queue command_queue, cl_uint num_svm_pointers,
- const void **svm_pointers, const size_t *sizes,
- cl_mem_migration_flags flags, cl_uint num_events_in_wait_list,
- const cl_event *event_wait_list,
- cl_event *event) CL_API_SUFFIX__VERSION_2_1;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetDeviceAndHostTimer)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetDeviceAndHostTimer)(
- cl_device_id device, cl_ulong *device_timestamp,
- cl_ulong *host_timestamp) CL_API_SUFFIX__VERSION_2_1;
-
--typedef CL_API_ENTRY cl_int(CL_API_CALL *cl_api_clGetHostTimer)(
-+typedef cl_int(CL_API_CALL *cl_api_clGetHostTimer)(
- cl_device_id device, cl_ulong *host_timestamp) CL_API_SUFFIX__VERSION_2_1;
-
- #else
-diff --git a/khronos-headers/CL/cl_layer.h b/khronos-headers/CL/cl_layer.h
-index b75e6bc..59dae75 100644
---- a/khronos-headers/CL/cl_layer.h
-+++ b/khronos-headers/CL/cl_layer.h
-@@ -36,7 +36,7 @@ clGetLayerInfo(cl_layer_info param_name,
- void *param_value,
- size_t *param_value_size_ret);
-
--CL_API_ENTRY typedef cl_int
-+typedef cl_int
- (CL_API_CALL *pfn_clGetLayerInfo)(cl_layer_info param_name,
- size_t param_value_size,
- void *param_value,
-@@ -48,7 +48,7 @@ clInitLayer(cl_uint num_entries,
- cl_uint *num_entries_ret,
- const cl_icd_dispatch **layer_dispatch_ret);
-
--CL_API_ENTRY typedef cl_int
-+typedef cl_int
- (CL_API_CALL *pfn_clInitLayer)(cl_uint num_entries,
- const cl_icd_dispatch *target_dispatch,
- cl_uint *num_entries_ret,
-diff --git a/khronos-headers/CL/cl_platform.h b/khronos-headers/CL/cl_platform.h
-index bed2370..8ae655d 100644
---- a/khronos-headers/CL/cl_platform.h
-+++ b/khronos-headers/CL/cl_platform.h
-@@ -24,13 +24,25 @@ extern "C" {
- #endif
-
- #if defined(_WIN32)
-- #define CL_API_ENTRY
-- #define CL_API_CALL __stdcall
-- #define CL_CALLBACK __stdcall
-+ #if !defined(CL_API_ENTRY)
-+ #define CL_API_ENTRY
-+ #endif
-+ #if !defined(CL_API_CALL)
-+ #define CL_API_CALL __stdcall
-+ #endif
-+ #if !defined(CL_CALLBACK)
-+ #define CL_CALLBACK __stdcall
-+ #endif
- #else
-- #define CL_API_ENTRY
-- #define CL_API_CALL
-- #define CL_CALLBACK
-+ #if !defined(CL_API_ENTRY)
-+ #define CL_API_ENTRY
-+ #endif
-+ #if !defined(CL_API_CALL)
-+ #define CL_API_CALL
-+ #endif
-+ #if !defined(CL_CALLBACK)
-+ #define CL_CALLBACK
-+ #endif
- #endif
-
- /*
-@@ -41,85 +53,94 @@ extern "C" {
- * deprecation but is deprecated in versions later than 1.1.
- */
-
--#define CL_API_SUFFIX__VERSION_1_0
--#define CL_EXT_SUFFIX__VERSION_1_0
--#define CL_API_SUFFIX__VERSION_1_1
--#define CL_EXT_SUFFIX__VERSION_1_1
--#define CL_API_SUFFIX__VERSION_1_2
--#define CL_EXT_SUFFIX__VERSION_1_2
--#define CL_API_SUFFIX__VERSION_2_0
--#define CL_EXT_SUFFIX__VERSION_2_0
--#define CL_API_SUFFIX__VERSION_2_1
--#define CL_EXT_SUFFIX__VERSION_2_1
--#define CL_API_SUFFIX__VERSION_2_2
--#define CL_EXT_SUFFIX__VERSION_2_2
--#define CL_API_SUFFIX__VERSION_3_0
--#define CL_EXT_SUFFIX__VERSION_3_0
--#define CL_API_SUFFIX__EXPERIMENTAL
--#define CL_EXT_SUFFIX__EXPERIMENTAL
-+#ifndef CL_API_SUFFIX_USER
-+#define CL_API_SUFFIX_USER
-+#endif
-+
-+#ifndef CL_API_PREFIX_USER
-+#define CL_API_PREFIX_USER
-+#endif
-+
-+#define CL_API_SUFFIX_COMMON CL_API_SUFFIX_USER
-+#define CL_API_PREFIX_COMMON CL_API_PREFIX_USER
-+
-+#define CL_API_SUFFIX__VERSION_1_0 CL_API_SUFFIX_COMMON
-+#define CL_API_SUFFIX__VERSION_1_1 CL_API_SUFFIX_COMMON
-+#define CL_API_SUFFIX__VERSION_1_2 CL_API_SUFFIX_COMMON
-+#define CL_API_SUFFIX__VERSION_2_0 CL_API_SUFFIX_COMMON
-+#define CL_API_SUFFIX__VERSION_2_1 CL_API_SUFFIX_COMMON
-+#define CL_API_SUFFIX__VERSION_2_2 CL_API_SUFFIX_COMMON
-+#define CL_API_SUFFIX__VERSION_3_0 CL_API_SUFFIX_COMMON
-+#define CL_API_SUFFIX__EXPERIMENTAL CL_API_SUFFIX_COMMON
-
-
- #ifdef __GNUC__
-- #define CL_EXT_SUFFIX_DEPRECATED __attribute__((deprecated))
-- #define CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX_DEPRECATED __attribute__((deprecated))
-+ #define CL_API_PREFIX_DEPRECATED
- #elif defined(_WIN32)
-- #define CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX_DEPRECATED __declspec(deprecated)
-+ #define CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX_DEPRECATED __declspec(deprecated)
- #else
-- #define CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX_DEPRECATED
- #endif
-
- #ifdef CL_USE_DEPRECATED_OPENCL_1_0_APIS
-- #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_1_0_DEPRECATED CL_API_SUFFIX_COMMON
-+ #define CL_API_PREFIX__VERSION_1_0_DEPRECATED CL_API_PREFIX_COMMON
- #else
-- #define CL_EXT_SUFFIX__VERSION_1_0_DEPRECATED CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_1_0_DEPRECATED CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_1_0_DEPRECATED CL_API_SUFFIX_COMMON CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX__VERSION_1_0_DEPRECATED CL_API_PREFIX_COMMON CL_API_PREFIX_DEPRECATED
- #endif
-
- #ifdef CL_USE_DEPRECATED_OPENCL_1_1_APIS
-- #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_1_1_DEPRECATED CL_API_SUFFIX_COMMON
-+ #define CL_API_PREFIX__VERSION_1_1_DEPRECATED CL_API_PREFIX_COMMON
- #else
-- #define CL_EXT_SUFFIX__VERSION_1_1_DEPRECATED CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_1_1_DEPRECATED CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_1_1_DEPRECATED CL_API_SUFFIX_COMMON CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX__VERSION_1_1_DEPRECATED CL_API_PREFIX_COMMON CL_API_PREFIX_DEPRECATED
- #endif
-
- #ifdef CL_USE_DEPRECATED_OPENCL_1_2_APIS
-- #define CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_1_2_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_1_2_DEPRECATED CL_API_SUFFIX_COMMON
-+ #define CL_API_PREFIX__VERSION_1_2_DEPRECATED CL_API_PREFIX_COMMON
- #else
-- #define CL_EXT_SUFFIX__VERSION_1_2_DEPRECATED CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_1_2_DEPRECATED CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_1_2_DEPRECATED CL_API_SUFFIX_COMMON CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX__VERSION_1_2_DEPRECATED CL_API_PREFIX_COMMON CL_API_PREFIX_DEPRECATED
- #endif
-
- #ifdef CL_USE_DEPRECATED_OPENCL_2_0_APIS
-- #define CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_2_0_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_2_0_DEPRECATED CL_API_SUFFIX_COMMON
-+ #define CL_API_PREFIX__VERSION_2_0_DEPRECATED CL_API_PREFIX_COMMON
- #else
-- #define CL_EXT_SUFFIX__VERSION_2_0_DEPRECATED CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_2_0_DEPRECATED CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_2_0_DEPRECATED CL_API_SUFFIX_COMMON CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX__VERSION_2_0_DEPRECATED CL_API_PREFIX_COMMON CL_API_PREFIX_DEPRECATED
- #endif
-
- #ifdef CL_USE_DEPRECATED_OPENCL_2_1_APIS
-- #define CL_EXT_SUFFIX__VERSION_2_1_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_2_1_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_2_1_DEPRECATED CL_API_SUFFIX_COMMON
-+ #define CL_API_PREFIX__VERSION_2_1_DEPRECATED CL_API_PREFIX_COMMON
- #else
-- #define CL_EXT_SUFFIX__VERSION_2_1_DEPRECATED CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_2_1_DEPRECATED CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_2_1_DEPRECATED CL_API_SUFFIX_COMMON CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX__VERSION_2_1_DEPRECATED CL_API_PREFIX_COMMON CL_API_PREFIX_DEPRECATED
- #endif
-
- #ifdef CL_USE_DEPRECATED_OPENCL_2_2_APIS
-- #define CL_EXT_SUFFIX__VERSION_2_2_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_2_2_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_2_2_DEPRECATED CL_API_SUFFIX_COMMON
-+ #define CL_API_PREFIX__VERSION_2_2_DEPRECATED CL_API_PREFIX_COMMON
- #else
-- #define CL_EXT_SUFFIX__VERSION_2_2_DEPRECATED CL_EXT_SUFFIX_DEPRECATED
-- #define CL_EXT_PREFIX__VERSION_2_2_DEPRECATED CL_EXT_PREFIX_DEPRECATED
-+ #define CL_API_SUFFIX__VERSION_2_2_DEPRECATED CL_API_SUFFIX_COMMON CL_API_SUFFIX_DEPRECATED
-+ #define CL_API_PREFIX__VERSION_2_2_DEPRECATED CL_API_PREFIX_COMMON CL_API_PREFIX_DEPRECATED
- #endif
-
- #if (defined (_WIN32) && defined(_MSC_VER))
-
-+/* intptr_t is used in cl.h and provided by stddef.h in Visual C++, but not in clang */
-+/* stdint.h was missing before Visual Studio 2010, include it for later versions and for clang */
-+#if defined(__clang__) || _MSC_VER >= 1600
-+ #include <stdint.h>
-+#endif
-+
- /* scalar types */
- typedef signed __int8 cl_char;
- typedef unsigned __int8 cl_uchar;
-diff --git a/khronos-headers/CL/cl_va_api_media_sharing_intel.h b/khronos-headers/CL/cl_va_api_media_sharing_intel.h
-index 7c4a4ba..7ba2ec8 100644
---- a/khronos-headers/CL/cl_va_api_media_sharing_intel.h
-+++ b/khronos-headers/CL/cl_va_api_media_sharing_intel.h
-@@ -68,16 +68,16 @@ clGetDeviceIDsFromVA_APIMediaAdapterINTEL(
- cl_va_api_device_set_intel media_adapter_set,
- cl_uint num_entries,
- cl_device_id* devices,
-- cl_uint* num_devices) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_uint* num_devices) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL * clGetDeviceIDsFromVA_APIMediaAdapterINTEL_fn)(
-+typedef cl_int (CL_API_CALL * clGetDeviceIDsFromVA_APIMediaAdapterINTEL_fn)(
- cl_platform_id platform,
- cl_va_api_device_source_intel media_adapter_type,
- void* media_adapter,
- cl_va_api_device_set_intel media_adapter_set,
- cl_uint num_entries,
- cl_device_id* devices,
-- cl_uint* num_devices) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_uint* num_devices) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_mem CL_API_CALL
- clCreateFromVA_APIMediaSurfaceINTEL(
-@@ -85,14 +85,14 @@ clCreateFromVA_APIMediaSurfaceINTEL(
- cl_mem_flags flags,
- VASurfaceID* surface,
- cl_uint plane,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_mem (CL_API_CALL * clCreateFromVA_APIMediaSurfaceINTEL_fn)(
-+typedef cl_mem (CL_API_CALL * clCreateFromVA_APIMediaSurfaceINTEL_fn)(
- cl_context context,
- cl_mem_flags flags,
- VASurfaceID* surface,
- cl_uint plane,
-- cl_int* errcode_ret) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueAcquireVA_APIMediaSurfacesINTEL(
-@@ -101,15 +101,15 @@ clEnqueueAcquireVA_APIMediaSurfacesINTEL(
- const cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueAcquireVA_APIMediaSurfacesINTEL_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueAcquireVA_APIMediaSurfacesINTEL_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_2;
-
- extern CL_API_ENTRY cl_int CL_API_CALL
- clEnqueueReleaseVA_APIMediaSurfacesINTEL(
-@@ -118,15 +118,15 @@ clEnqueueReleaseVA_APIMediaSurfacesINTEL(
- const cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_2;
-
--typedef CL_API_ENTRY cl_int (CL_API_CALL *clEnqueueReleaseVA_APIMediaSurfacesINTEL_fn)(
-+typedef cl_int (CL_API_CALL *clEnqueueReleaseVA_APIMediaSurfacesINTEL_fn)(
- cl_command_queue command_queue,
- cl_uint num_objects,
- const cl_mem* mem_objects,
- cl_uint num_events_in_wait_list,
- const cl_event* event_wait_list,
-- cl_event* event) CL_EXT_SUFFIX__VERSION_1_2;
-+ cl_event* event) CL_API_SUFFIX__VERSION_1_2;
-
- #ifdef __cplusplus
- }
-diff --git a/khronos-headers/CL/opencl.h b/khronos-headers/CL/opencl.h
-index 1c4e10c..ef8dd1e 100644
---- a/khronos-headers/CL/opencl.h
-+++ b/khronos-headers/CL/opencl.h
-@@ -1,5 +1,5 @@
- /*******************************************************************************
-- * Copyright (c) 2008-2020 The Khronos Group Inc.
-+ * Copyright (c) 2008-2021 The Khronos Group Inc.
- *
- * Licensed under the Apache License, Version 2.0 (the "License");
- * you may not use this file except in compliance with the License.
-@@ -23,7 +23,6 @@ extern "C" {
-
- #include <CL/cl.h>
- #include <CL/cl_gl.h>
--#include <CL/cl_gl_ext.h>
- #include <CL/cl_ext.h>
-
- #ifdef __cplusplus
-diff --git a/ocl_interface.yaml b/ocl_interface.yaml
-index 1e80f16..43a0e59 100644
---- a/ocl_interface.yaml
-+++ b/ocl_interface.yaml
-@@ -674,18 +674,18 @@
- const cl_device_partition_property_ext * /* properties */,
- cl_uint /*num_entries*/,
- cl_device_id * /*out_devices*/,
-- cl_uint * /*num_devices*/ ) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_uint * /*num_devices*/ ) CL_API_SUFFIX__VERSION_1_1;
- 90: |-
- CL_API_ENTRY cl_int CL_API_CALL
-- clRetainDeviceEXT( cl_device_id /*device*/ ) CL_EXT_SUFFIX__VERSION_1_1;
-+ clRetainDeviceEXT( cl_device_id /*device*/ ) CL_API_SUFFIX__VERSION_1_1;
- 91: |-
- CL_API_ENTRY cl_int CL_API_CALL
-- clReleaseDeviceEXT( cl_device_id /*device*/ ) CL_EXT_SUFFIX__VERSION_1_1;
-+ clReleaseDeviceEXT( cl_device_id /*device*/ ) CL_API_SUFFIX__VERSION_1_1;
- 92: |-
- CL_API_ENTRY cl_event CL_API_CALL
- clCreateEventFromGLsyncKHR(cl_context /* context */,
- cl_GLsync /* cl_GLsync */,
-- cl_int * /* errcode_ret */) CL_EXT_SUFFIX__VERSION_1_1;
-+ cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1;
- 93: |-
- CL_API_ENTRY cl_int CL_API_CALL
- clCreateSubDevices(cl_device_id /* in_device */,
-@@ -1016,7 +1016,7 @@
- const void * /*input_value*/,
- size_t /*param_value_size*/,
- void* /*param_value*/,
-- size_t* /*param_value_size_ret*/ ) CL_EXT_SUFFIX__VERSION_2_0;
-+ size_t* /*param_value_size_ret*/ ) CL_API_SUFFIX__VERSION_2_0;
- 137: |-
- CL_API_ENTRY cl_kernel CL_API_CALL
- clCloneKernel(cl_kernel /* source_kernel */,
-diff --git a/run_dummy_icd.c b/run_dummy_icd.c
-index 400c1b0..c064b19 100644
---- a/run_dummy_icd.c
-+++ b/run_dummy_icd.c
-@@ -39,7 +39,6 @@ SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
- # include <CL/cl_gl.h>
- # include <CL/cl_egl.h>
- # include <CL/cl_ext.h>
--# include <CL/cl_gl_ext.h>
- #pragma GCC diagnostic pop
- #include <string.h>
- #include "ocl_icd_debug.h"
---
-2.31.1
-