/*******************************************************************************
 * Copyright (c) 2008-2010 The Khronos Group Inc.
 *
 * Permission is hereby granted, free of charge, to any person obtaining a
 * copy of this software and/or associated documentation files (the
 * "Materials"), to deal in the Materials without restriction, including
 * without limitation the rights to use, copy, modify, merge, publish,
 * distribute, sublicense, and/or sell copies of the Materials, and to
 * permit persons to whom the Materials are furnished to do so, subject to
 * the following conditions:
 *
 * The above copyright notice and this permission notice shall be included
 * in all copies or substantial portions of the Materials.
 *
 * THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
 * EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
 * MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
 * IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY
 * CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT,
 * TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE
 * MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS.
 ******************************************************************************/

#ifndef __OPENCL_CL_ICD_H
#define __OPENCL_CL_ICD_H

#include <CL/cl.h>
#include <CL/cl_gl.h>

#define cl_khr_icd 1

#ifdef __cplusplus
extern "C" {
#endif /* __cplusplus */

typedef cl_int (CL_API_CALL * clGetPlatformIDs_fn)(
    cl_uint          /* num_entries */,
    cl_platform_id * /* platforms */,
    cl_uint *        /* num_platforms */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetPlatformInfo_fn)(
    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;

typedef cl_int (CL_API_CALL * clGetDeviceIDs_fn)(
    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_int (CL_API_CALL * clGetDeviceInfo_fn)(
    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;

typedef cl_context (CL_API_CALL * clCreateContext_fn)(
    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_context (CL_API_CALL * clCreateContextFromType_fn)(
    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_int (CL_API_CALL * clRetainContext_fn)(
    cl_context /* context */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clReleaseContext_fn)(
    cl_context /* context */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetContextInfo_fn)(
    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;

typedef cl_command_queue (CL_API_CALL * clCreateCommandQueue_fn)(
    cl_context                     /* context */,
    cl_device_id                   /* device */,
    cl_command_queue_properties    /* properties */,
    cl_int *                       /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clRetainCommandQueue_fn)(
    cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clReleaseCommandQueue_fn)(
    cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetCommandQueueInfo_fn)(
    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;

typedef cl_int (CL_API_CALL * clSetCommandQueueProperty_fn)(
    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*/;

typedef cl_mem (CL_API_CALL * clCreateBuffer_fn)(
    cl_context   /* context */,
    cl_mem_flags /* flags */,
    size_t       /* size */,
    void *       /* host_ptr */,
    cl_int *     /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_mem (CL_API_CALL * clCreateSubBuffer_fn)(
    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_mem (CL_API_CALL * clCreateImage2D_fn)(
    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_API_SUFFIX__VERSION_1_0;

typedef cl_mem (CL_API_CALL * clCreateImage3D_fn)(
    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_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clRetainMemObject_fn)(
    cl_mem /* memobj */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clReleaseMemObject_fn)(
    cl_mem /* memobj */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetSupportedImageFormats_fn)(
    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_int (CL_API_CALL * clGetMemObjectInfo_fn)(
    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_int (CL_API_CALL * clGetImageInfo_fn)(
    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;

typedef cl_int (CL_API_CALL * clSetMemObjectDestructorCallback_fn)(
      cl_mem /* memobj */,
      void (CL_CALLBACK * /*pfn_notify*/)( cl_mem /* memobj */, void* /*user_data*/),
      void * /*user_data */ ) CL_API_SUFFIX__VERSION_1_1;

/* Sampler APIs  */
typedef cl_sampler (CL_API_CALL * clCreateSampler_fn)(
    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_int (CL_API_CALL * clRetainSampler_fn)(
    cl_sampler /* sampler */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clReleaseSampler_fn)(
    cl_sampler /* sampler */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetSamplerInfo_fn)(
    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;

/* Program Object APIs  */
typedef cl_program (CL_API_CALL * clCreateProgramWithSource_fn)(
    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_program (CL_API_CALL * clCreateProgramWithBinary_fn)(
    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;

typedef cl_int (CL_API_CALL * clRetainProgram_fn)(
    cl_program /* program */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clReleaseProgram_fn)(
    cl_program /* program */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clBuildProgram_fn)(
    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 */),
    void *               /* user_data */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clUnloadCompiler_fn)(void) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetProgramInfo_fn)(
    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_int (CL_API_CALL * clGetProgramBuildInfo_fn)(
    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_kernel (CL_API_CALL * clCreateKernel_fn)(
    cl_program      /* program */,
    const char *    /* kernel_name */,
    cl_int *        /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clCreateKernelsInProgram_fn)(
    cl_program     /* program */,
    cl_uint        /* num_kernels */,
    cl_kernel *    /* kernels */,
    cl_uint *      /* num_kernels_ret */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clRetainKernel_fn)(
    cl_kernel    /* kernel */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clReleaseKernel_fn)(
    cl_kernel   /* kernel */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clSetKernelArg_fn)(
    cl_kernel    /* kernel */,
    cl_uint      /* arg_index */,
    size_t       /* arg_size */,
    const void * /* arg_value */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetKernelInfo_fn)(
    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;

typedef cl_int (CL_API_CALL * clGetKernelWorkGroupInfo_fn)(
    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;

/* Event Object APIs  */
typedef cl_int (CL_API_CALL * clWaitForEvents_fn)(
    cl_uint             /* num_events */,
    const cl_event *    /* event_list */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetEventInfo_fn)(
    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_event (CL_API_CALL * clCreateUserEvent_fn)(
    cl_context    /* context */,
    cl_int *      /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1;

typedef cl_int (CL_API_CALL * clRetainEvent_fn)(
    cl_event /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clReleaseEvent_fn)(
    cl_event /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clSetUserEventStatus_fn)(
    cl_event   /* event */,
                     cl_int     /* execution_status */) CL_API_SUFFIX__VERSION_1_1;

typedef cl_int (CL_API_CALL * clSetEventCallback_fn)(
     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;

/* Profiling APIs  */
typedef cl_int (CL_API_CALL * clGetEventProfilingInfo_fn)(
    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_int (CL_API_CALL * clFlush_fn)(
    cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clFinish_fn)(
    cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;

/* Enqueued Commands APIs */
typedef cl_int (CL_API_CALL * clEnqueueReadBuffer_fn)(
    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 */,
    cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueReadBufferRect_fn)(
    cl_command_queue    /* command_queue */,
    cl_mem              /* buffer */,
    cl_bool             /* blocking_read */,
    const size_t *      /* buffer_offset */,
    const size_t *      /* host_offset */,
    const size_t *      /* region */,
    size_t              /* buffer_row_pitch */,
    size_t              /* buffer_slice_pitch */,
    size_t              /* host_row_pitch */,
    size_t              /* host_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_1;

typedef cl_int (CL_API_CALL * clEnqueueWriteBuffer_fn)(
    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 */,
    cl_event *         /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueWriteBufferRect_fn)(
    cl_command_queue    /* command_queue */,
    cl_mem              /* buffer */,
    cl_bool             /* blocking_read */,
    const size_t *      /* buffer_offset */,
    const size_t *      /* host_offset */,
    const size_t *      /* region */,
    size_t              /* buffer_row_pitch */,
    size_t              /* buffer_slice_pitch */,
    size_t              /* host_row_pitch */,
    size_t              /* host_slice_pitch */,
    const void *        /* ptr */,
    cl_uint             /* num_events_in_wait_list */,
    const cl_event *    /* event_wait_list */,
    cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_1;

typedef cl_int (CL_API_CALL * clEnqueueCopyBuffer_fn)(
    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 */,
    cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueCopyBufferRect_fn)(
    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 */,
    size_t              /* dst_slice_pitch */,
    cl_uint             /* num_events_in_wait_list */,
    const cl_event *    /* event_wait_list */,
    cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_1;

typedef cl_int (CL_API_CALL * clEnqueueReadImage_fn)(
    cl_command_queue     /* command_queue */,
    cl_mem               /* image */,
    cl_bool              /* blocking_read */,
    const size_t *       /* origin[3] */,
    const size_t *       /* region[3] */,
    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_int (CL_API_CALL * clEnqueueWriteImage_fn)(
    cl_command_queue    /* command_queue */,
    cl_mem              /* image */,
    cl_bool             /* blocking_write */,
    const size_t *      /* origin[3] */,
    const size_t *      /* region[3] */,
    size_t              /* input_row_pitch */,
    size_t              /* input_slice_pitch */,
    const 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_int (CL_API_CALL * clEnqueueCopyImage_fn)(
    cl_command_queue     /* command_queue */,
    cl_mem               /* src_image */,
    cl_mem               /* dst_image */,
    const size_t *       /* src_origin[3] */,
    const size_t *       /* dst_origin[3] */,
    const size_t *       /* region[3] */,
    cl_uint              /* num_events_in_wait_list */,
    const cl_event *     /* event_wait_list */,
    cl_event *           /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueCopyImageToBuffer_fn)(
    cl_command_queue /* command_queue */,
    cl_mem           /* src_image */,
    cl_mem           /* dst_buffer */,
    const size_t *   /* src_origin[3] */,
    const size_t *   /* region[3] */,
    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_int (CL_API_CALL * clEnqueueCopyBufferToImage_fn)(
    cl_command_queue /* command_queue */,
    cl_mem           /* src_buffer */,
    cl_mem           /* dst_image */,
    size_t           /* src_offset */,
    const size_t *   /* dst_origin[3] */,
    const size_t *   /* region[3] */,
    cl_uint          /* num_events_in_wait_list */,
    const cl_event * /* event_wait_list */,
    cl_event *       /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef void * (CL_API_CALL * clEnqueueMapBuffer_fn)(
    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 void * (CL_API_CALL * clEnqueueMapImage_fn)(
    cl_command_queue  /* command_queue */,
    cl_mem            /* image */,
    cl_bool           /* blocking_map */,
    cl_map_flags      /* map_flags */,
    const size_t *    /* origin[3] */,
    const size_t *    /* region[3] */,
    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_int (CL_API_CALL * clEnqueueUnmapMemObject_fn)(
    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;

typedef cl_int (CL_API_CALL * clEnqueueNDRangeKernel_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 */,
    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_int (CL_API_CALL * clEnqueueTask_fn)(
    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_int (CL_API_CALL * clEnqueueNativeKernel_fn)(
    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 */,
    const cl_event *  /* event_wait_list */,
    cl_event *        /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueMarker_fn)(
    cl_command_queue    /* command_queue */,
    cl_event *          /* event */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueWaitForEvents_fn)(
    cl_command_queue /* command_queue */,
    cl_uint          /* num_events */,
    const cl_event * /* event_list */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueBarrier_fn)(
    cl_command_queue /* command_queue */) CL_API_SUFFIX__VERSION_1_0;

typedef void * (CL_API_CALL * clGetExtensionFunctionAddress_fn)(
    const char * /* func_name */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_mem (CL_API_CALL * clCreateFromGLBuffer_fn)(
    cl_context     /* context */,
    cl_mem_flags   /* flags */,
    cl_GLuint      /* bufobj */,
    int *          /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_mem (CL_API_CALL * clCreateFromGLTexture2D_fn)(
    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_mem (CL_API_CALL * clCreateFromGLTexture3D_fn)(
    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_mem (CL_API_CALL * clCreateFromGLRenderbuffer_fn)(
    cl_context   /* context */,
    cl_mem_flags /* flags */,
    cl_GLuint    /* renderbuffer */,
    cl_int *     /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetGLObjectInfo_fn)(
    cl_mem                /* memobj */,
    cl_gl_object_type *   /* gl_object_type */,
    cl_GLuint *              /* gl_object_name */) CL_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clGetGLTextureInfo_fn)(
    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_event (CL_API_CALL * clCreateEventFromGLsyncKHR_fn) (
    cl_context           /* context */,
    cl_GLsync            /* cl_GLsync */,
    cl_int *             /* errcode_ret */) CL_API_SUFFIX__VERSION_1_1;

typedef cl_int (CL_API_CALL * clEnqueueAcquireGLObjects_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_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clEnqueueReleaseGLObjects_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_API_SUFFIX__VERSION_1_0;

typedef cl_int (CL_API_CALL * clCreateSubDevices_fn)(
    cl_device_id        /* in_device */,
    const cl_device_partition_property * /* properties */,
    cl_uint             /* num_entries */,
    cl_device_id *      /* out_devices */,
    cl_uint *           /* num_devices */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_int (CL_API_CALL * clRetainDevice_fn)(
    cl_device_id            /* device */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_int (CL_API_CALL * clReleaseDevice_fn)(
    cl_device_id            /* device */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_mem (CL_API_CALL * clCreateImage_fn)(
    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;

typedef cl_program (CL_API_CALL * clCreateProgramWithBuiltInKernels_fn)(
    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;

typedef cl_int (CL_API_CALL * clCompileProgram_fn)(
    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_program (CL_API_CALL * clLinkProgram_fn)(
    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 */,
    void (CL_CALLBACK *pfn_notify)(cl_program program, void *user_data),
    void *                  /* user_data */,
    cl_int *                /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_int (CL_API_CALL * clUnloadPlatformCompiler_fn)(
    cl_platform_id          /* platform */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_int (CL_API_CALL * clGetKernelArgInfo_fn)(
    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;

typedef cl_int (CL_API_CALL * clEnqueueFillBuffer_fn)(
    cl_command_queue        /* command_queue */,
    cl_mem                  /* buffer */,
    const void *            /* pattern */,
    size_t                  /* pattern_size */,
    size_t                  /* offset */,
    size_t                  /* size */,
    cl_uint                 /* num_events_in_wait_list */,
    const cl_event *        /* event_wait_list */,
    cl_event *              /* event */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_int (CL_API_CALL * clEnqueueFillImage_fn)(
    cl_command_queue        /* command_queue */,
    cl_mem                  /* image */,
    const void *            /* fill_color */,
    const size_t *          /* 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_2;

typedef cl_int (CL_API_CALL * clEnqueueMigrateMemObjects_fn)(
    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 */,
    cl_event *              /* event */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_int (CL_API_CALL * clEnqueueMarkerWithWaitList_fn)(
    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_int (CL_API_CALL * clEnqueueBarrierWithWaitList_fn)(
    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 void* (CL_API_CALL * clGetExtensionFunctionAddressForPlatform_fn)(
    cl_platform_id          /* platform */,
    const char *            /* funcname */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_mem (CL_API_CALL * clCreateFromGLTexture_fn)(
    cl_context              /* context */,
    cl_mem_flags            /* flags */,
    cl_GLenum               /* texture_target */,
    cl_GLint                /* miplevel */,
    cl_GLuint               /* texture */,
    cl_int *                /* errcode_ret */) CL_API_SUFFIX__VERSION_1_2;

typedef cl_command_queue (CL_API_CALL * clCreateCommandQueueWithProperties_fn)(
    cl_context                  /* context */,
    cl_device_id                /* device */,
    const cl_queue_properties * /* properties */,
    cl_int *                    /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0;

typedef cl_sampler (CL_API_CALL * clCreateSamplerWithProperties_fn)(
    cl_context                    /* context */,
    const cl_sampler_properties * /* properties */,
    cl_int *                      /* errcode_ret */) CL_API_SUFFIX__VERSION_2_0;

typedef void * (CL_API_CALL * clSVMAlloc_fn)(
    cl_context              /* context */,
    cl_svm_mem_flags        /* flags */,
    size_t                  /* size */,
    cl_uint                 /* alignment */) CL_API_SUFFIX__VERSION_2_0;

typedef void (CL_API_CALL * clSVMFree_fn)(
    cl_context              /* context */,
    void *                  /* svm_pointer */) CL_API_SUFFIX__VERSION_2_0;

typedef cl_int (CL_API_CALL * clSetKernelArgSVMPointer_fn)(
    cl_kernel               /* kernel */,
    cl_uint                 /*  arg_index */,
    const void *            /* arg_value */) CL_API_SUFFIX__VERSION_2_0;

typedef cl_int (CL_API_CALL * clSetKernelExecInfo_fn)(
    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_int (CL_API_CALL * clEnqueueSVMFree_fn)(
    cl_command_queue       /* command_queue */,
    cl_uint                /* num_svm_pointers */,
    void *[]               /* svm_pointers */,
    void (CL_CALLBACK *    /* pfn_free_func */)(cl_command_queue /* queue */,
                                                cl_uint          /* num_svm_pointers */,
                                                void *[]         /* svm_pointers */,
                                                void *           /* user_data */),
    void *                 /* user_data */,
    cl_uint                /* num_events_in_wait_list */,
    const cl_event *       /* event_wait_list */,
    cl_event *             /* event */) CL_API_SUFFIX__VERSION_2_0;

typedef cl_int (CL_API_CALL * clEnqueueSVMMemcpy_fn)(
    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_int (CL_API_CALL * clEnqueueSVMMemFill_fn)(
    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_int (CL_API_CALL * clEnqueueSVMMap_fn)(
    cl_command_queue       /* command_queue */,
    cl_bool                /* blocking_map */,
    cl_map_flags           /* 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_int (CL_API_CALL * clEnqueueSVMUnmap_fn)(
    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_API_SUFFIX__VERSION_2_0;

typedef cl_mem (CL_API_CALL * clCreatePipe_fn)(
    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_int (CL_API_CALL * clGetPipeInfo_fn)(
    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_int (CL_API_CALL * clGetKernelSubGroupInfoKHR_fn)(
    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_0;


typedef struct _cl_icd_dispatch_table
{
    /* OpenCL 1.0 */
    clGetPlatformIDs_fn           GetPlatformIDs;
    clGetPlatformInfo_fn          GetPlatformInfo;
    clGetDeviceIDs_fn             GetDeviceIDs;
    clGetDeviceInfo_fn            GetDeviceInfo;
    clCreateContext_fn            CreateContext;
    clCreateContextFromType_fn    CreateContextFromType;
    clRetainContext_fn            RetainContext;
    clReleaseContext_fn           ReleaseContext;
    clGetContextInfo_fn           GetContextInfo;
    clCreateCommandQueue_fn       CreateCommandQueue;
    clRetainCommandQueue_fn       RetainCommandQueue;
    clReleaseCommandQueue_fn      ReleaseCommandQueue;
    clGetCommandQueueInfo_fn      GetCommandQueueInfo;
    clSetCommandQueueProperty_fn  SetCommandQueueProperty;
    clCreateBuffer_fn             CreateBuffer;
    clCreateImage2D_fn            CreateImage2D;
    clCreateImage3D_fn            CreateImage3D;
    clRetainMemObject_fn          RetainMemObject;
    clReleaseMemObject_fn         ReleaseMemObject;
    clGetSupportedImageFormats_fn GetSupportedImageFormats;
    clGetMemObjectInfo_fn         GetMemObjectInfo;
    clGetImageInfo_fn             GetImageInfo;
    clCreateSampler_fn            CreateSampler;
    clRetainSampler_fn            RetainSampler;
    clReleaseSampler_fn           ReleaseSampler;
    clGetSamplerInfo_fn           GetSamplerInfo;
    clCreateProgramWithSource_fn  CreateProgramWithSource;
    clCreateProgramWithBinary_fn  CreateProgramWithBinary;
    clRetainProgram_fn            RetainProgram;
    clReleaseProgram_fn           ReleaseProgram;
    clBuildProgram_fn             BuildProgram;
    clUnloadCompiler_fn           UnloadCompiler;
    clGetProgramInfo_fn           GetProgramInfo;
    clGetProgramBuildInfo_fn      GetProgramBuildInfo;
    clCreateKernel_fn             CreateKernel;
    clCreateKernelsInProgram_fn   CreateKernelsInProgram;
    clRetainKernel_fn             RetainKernel;
    clReleaseKernel_fn            ReleaseKernel;
    clSetKernelArg_fn             SetKernelArg;
    clGetKernelInfo_fn            GetKernelInfo;
    clGetKernelWorkGroupInfo_fn   GetKernelWorkGroupInfo;
    clWaitForEvents_fn            WaitForEvents;
    clGetEventInfo_fn             GetEventInfo;
    clRetainEvent_fn              RetainEvent;
    clReleaseEvent_fn             ReleaseEvent;
    clGetEventProfilingInfo_fn    GetEventProfilingInfo;
    clFlush_fn                    Flush;
    clFinish_fn                   Finish;
    clEnqueueReadBuffer_fn        EnqueueReadBuffer;
    clEnqueueWriteBuffer_fn       EnqueueWriteBuffer;
    clEnqueueCopyBuffer_fn        EnqueueCopyBuffer;
    clEnqueueReadImage_fn         EnqueueReadImage;
    clEnqueueWriteImage_fn        EnqueueWriteImage;
    clEnqueueCopyImage_fn         EnqueueCopyImage;
    clEnqueueCopyImageToBuffer_fn EnqueueCopyImageToBuffer;
    clEnqueueCopyBufferToImage_fn EnqueueCopyBufferToImage;
    clEnqueueMapBuffer_fn         EnqueueMapBuffer;
    clEnqueueMapImage_fn          EnqueueMapImage;
    clEnqueueUnmapMemObject_fn    EnqueueUnmapMemObject;
    clEnqueueNDRangeKernel_fn     EnqueueNDRangeKernel;
    clEnqueueTask_fn              EnqueueTask;
    clEnqueueNativeKernel_fn      EnqueueNativeKernel;
    clEnqueueMarker_fn            EnqueueMarker;
    clEnqueueWaitForEvents_fn     EnqueueWaitForEvents;
    clEnqueueBarrier_fn           EnqueueBarrier;
    clGetExtensionFunctionAddress_fn GetExtensionFunctionAddress;
    clCreateFromGLBuffer_fn       CreateFromGLBuffer;
    clCreateFromGLTexture2D_fn    CreateFromGLTexture2D;
    clCreateFromGLTexture3D_fn    CreateFromGLTexture3D;
    clCreateFromGLRenderbuffer_fn CreateFromGLRenderbuffer;
    clGetGLObjectInfo_fn          GetGLObjectInfo;
    clGetGLTextureInfo_fn         GetGLTextureInfo;
    clEnqueueAcquireGLObjects_fn  EnqueueAcquireGLObjects;
    clEnqueueReleaseGLObjects_fn  EnqueueReleaseGLObjects;
    clGetGLContextInfoKHR_fn      GetGLContextInfoKHR;
    void*                         _reservedForD3D10KHR[6];
    /* OpenCL 1.1 */
    clSetEventCallback_fn         SetEventCallback;
    clCreateSubBuffer_fn          CreateSubBuffer;
    clSetMemObjectDestructorCallback_fn SetMemObjectDestructorCallback;
    clCreateUserEvent_fn          CreateUserEvent;
    clSetUserEventStatus_fn       SetUserEventStatus;
    clEnqueueReadBufferRect_fn    EnqueueReadBufferRect;
    clEnqueueWriteBufferRect_fn   EnqueueWriteBufferRect;
    clEnqueueCopyBufferRect_fn    EnqueueCopyBufferRect;

    void*                         _reservedForDeviceFissionEXT[3];
    clCreateEventFromGLsyncKHR_fn CreateEventFromGLsyncKHR;

    /* OpenCL 1.2 */
    clCreateSubDevices_fn                   CreateSubDevices;
    clRetainDevice_fn                       RetainDevice;
    clReleaseDevice_fn                      ReleaseDevice;
    clCreateImage_fn                        CreateImage;
    clCreateProgramWithBuiltInKernels_fn    CreateProgramWithBuiltInKernels;
    clCompileProgram_fn                     CompileProgram;
    clLinkProgram_fn                        LinkProgram;
    clUnloadPlatformCompiler_fn             UnloadPlatformCompiler;
    clGetKernelArgInfo_fn                   GetKernelArgInfo;
    clEnqueueFillBuffer_fn                  EnqueueFillBuffer;
    clEnqueueFillImage_fn                   EnqueueFillImage;
    clEnqueueMigrateMemObjects_fn           EnqueueMigrateMemObjects;
    clEnqueueMarkerWithWaitList_fn          EnqueueMarkerWithWaitList;
    clEnqueueBarrierWithWaitList_fn         EnqueueBarrierWithWaitList;
    clGetExtensionFunctionAddressForPlatform_fn GetExtensionFunctionAddressForPlatform;
    clCreateFromGLTexture_fn                CreateFromGLTexture;

    /* cl_khr_d3d11_sharing, cl_khr_dx9_media_sharing */
    void*                         _reservedD3DExtensions[10];

    /* cl_khr_egl_image, cl_khr_egl_event */
    void*                         _reservedEGLExtensions[4];

    /* OpenCL 2.0 */
    clCreateCommandQueueWithProperties_fn   CreateCommandQueueWithProperties;
    clCreatePipe_fn                         CreatePipe;
    clGetPipeInfo_fn                        GetPipeInfo;
    clSVMAlloc_fn                           SVMAlloc;
    clSVMFree_fn                            SVMFree;
    clEnqueueSVMFree_fn                     EnqueueSVMFree;
    clEnqueueSVMMemcpy_fn                   EnqueueSVMMemcpy;
    clEnqueueSVMMemFill_fn                  EnqueueSVMMemFill;
    clEnqueueSVMMap_fn                      EnqueueSVMMap;
    clEnqueueSVMUnmap_fn                    EnqueueSVMUnmap;
    clCreateSamplerWithProperties_fn        CreateSamplerWithProperties;
    clSetKernelArgSVMPointer_fn             SetKernelArgSVMPointer;
    clSetKernelExecInfo_fn                  SetKernelExecInfo;

    clGetKernelSubGroupInfoKHR_fn           GetKernelSubGroupInfoKHR;
    clTerminateContextKHR_fn                TerminateContextKHR;
} cl_icd_dispatch_table;

#ifdef __cplusplus
}
#endif /* __cplusplus */

#endif /* __OPENCL_CL_ICD_H */