diff options
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.patch | 2434 |
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 6912d7d2b..000000000 --- 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 - |