2010-06-29 02:23:09 +00:00
// Automatically generated by generateClRun.pl
# include "dynamiclib.h"
# include "../include/CL/cl.h"
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetPlatformIDs_ptr ) ( cl_uint , cl_platform_id * , cl_uint * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetPlatformIDs ( cl_uint num_entries , cl_platform_id * platforms , cl_uint * num_platforms ) {
if ( ! clGetPlatformIDs_ptr ) clGetPlatformIDs_ptr = getFunction ( " clGetPlatformIDs " ) ;
return ( * clGetPlatformIDs_ptr ) ( num_entries , platforms , num_platforms ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetPlatformInfo_ptr ) ( cl_platform_id , cl_platform_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetPlatformInfo ( cl_platform_id platform , cl_platform_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetPlatformInfo_ptr ) clGetPlatformInfo_ptr = getFunction ( " clGetPlatformInfo " ) ;
return ( * clGetPlatformInfo_ptr ) ( platform , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetDeviceIDs_ptr ) ( cl_platform_id , cl_device_type , cl_uint , cl_device_id * , cl_uint * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetDeviceIDs ( cl_platform_id platform , cl_device_type device_type , cl_uint num_entries , cl_device_id * devices , cl_uint * num_devices ) {
if ( ! clGetDeviceIDs_ptr ) clGetDeviceIDs_ptr = getFunction ( " clGetDeviceIDs " ) ;
return ( * clGetDeviceIDs_ptr ) ( platform , device_type , num_entries , devices , num_devices ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetDeviceInfo_ptr ) ( cl_device_id , cl_device_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetDeviceInfo ( cl_device_id device , cl_device_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetDeviceInfo_ptr ) clGetDeviceInfo_ptr = getFunction ( " clGetDeviceInfo " ) ;
return ( * clGetDeviceInfo_ptr ) ( device , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_context ( CL_API_CALL * clCreateContext_ptr ) ( const cl_context_properties * , cl_uint , const cl_device_id * , void ( CL_CALLBACK * ) ( const char * , const void * , size_t , void * ) , void * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_context CL_API_CALL 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 ) {
if ( ! clCreateContext_ptr ) clCreateContext_ptr = getFunction ( " clCreateContext " ) ;
return ( * clCreateContext_ptr ) ( properties , num_devices , devices , pfn_notify , user_data , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_context ( CL_API_CALL * clCreateContextFromType_ptr ) ( const cl_context_properties * , cl_device_type , void ( CL_CALLBACK * ) ( const char * , const void * , size_t , void * ) , void * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_context CL_API_CALL 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 ) {
if ( ! clCreateContextFromType_ptr ) clCreateContextFromType_ptr = getFunction ( " clCreateContextFromType " ) ;
return ( * clCreateContextFromType_ptr ) ( properties , device_type , pfn_notify , user_data , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clRetainContext_ptr ) ( cl_context ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clRetainContext ( cl_context context ) {
if ( ! clRetainContext_ptr ) clRetainContext_ptr = getFunction ( " clRetainContext " ) ;
return ( * clRetainContext_ptr ) ( context ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clReleaseContext_ptr ) ( cl_context ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clReleaseContext ( cl_context context ) {
if ( ! clReleaseContext_ptr ) clReleaseContext_ptr = getFunction ( " clReleaseContext " ) ;
return ( * clReleaseContext_ptr ) ( context ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetContextInfo_ptr ) ( cl_context , cl_context_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetContextInfo ( cl_context context , cl_context_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetContextInfo_ptr ) clGetContextInfo_ptr = getFunction ( " clGetContextInfo " ) ;
return ( * clGetContextInfo_ptr ) ( context , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_command_queue ( CL_API_CALL * clCreateCommandQueue_ptr ) ( cl_context , cl_device_id , cl_command_queue_properties , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_command_queue CL_API_CALL clCreateCommandQueue ( cl_context context , cl_device_id device , cl_command_queue_properties properties , cl_int * errcode_ret ) {
if ( ! clCreateCommandQueue_ptr ) clCreateCommandQueue_ptr = getFunction ( " clCreateCommandQueue " ) ;
return ( * clCreateCommandQueue_ptr ) ( context , device , properties , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clRetainCommandQueue_ptr ) ( cl_command_queue ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clRetainCommandQueue ( cl_command_queue command_queue ) {
if ( ! clRetainCommandQueue_ptr ) clRetainCommandQueue_ptr = getFunction ( " clRetainCommandQueue " ) ;
return ( * clRetainCommandQueue_ptr ) ( command_queue ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clReleaseCommandQueue_ptr ) ( cl_command_queue ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clReleaseCommandQueue ( cl_command_queue command_queue ) {
if ( ! clReleaseCommandQueue_ptr ) clReleaseCommandQueue_ptr = getFunction ( " clReleaseCommandQueue " ) ;
return ( * clReleaseCommandQueue_ptr ) ( command_queue ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetCommandQueueInfo_ptr ) ( cl_command_queue , cl_command_queue_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clGetCommandQueueInfo_ptr ) clGetCommandQueueInfo_ptr = getFunction ( " clGetCommandQueueInfo " ) ;
return ( * clGetCommandQueueInfo_ptr ) ( command_queue , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clSetCommandQueueProperty_ptr ) ( cl_command_queue , cl_command_queue_properties , cl_bool , cl_command_queue_properties * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clSetCommandQueueProperty ( cl_command_queue command_queue , cl_command_queue_properties properties , cl_bool enable , cl_command_queue_properties * old_properties ) {
if ( ! clSetCommandQueueProperty_ptr ) clSetCommandQueueProperty_ptr = getFunction ( " clSetCommandQueueProperty " ) ;
return ( * clSetCommandQueueProperty_ptr ) ( command_queue , properties , enable , old_properties ) ;
}
2010-07-18 14:18:37 +00:00
static cl_mem ( CL_API_CALL * clCreateBuffer_ptr ) ( cl_context , cl_mem_flags , size_t , void * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_mem CL_API_CALL clCreateBuffer ( cl_context context , cl_mem_flags flags , size_t size , void * host_ptr , cl_int * errcode_ret ) {
if ( ! clCreateBuffer_ptr ) clCreateBuffer_ptr = getFunction ( " clCreateBuffer " ) ;
return ( * clCreateBuffer_ptr ) ( context , flags , size , host_ptr , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_mem ( CL_API_CALL * clCreateImage2D_ptr ) ( cl_context , cl_mem_flags , const cl_image_format * , size_t , size_t , size_t , void * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_mem CL_API_CALL 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 ) {
if ( ! clCreateImage2D_ptr ) clCreateImage2D_ptr = getFunction ( " clCreateImage2D " ) ;
return ( * clCreateImage2D_ptr ) ( context , flags , image_format , image_width , image_height , image_row_pitch , host_ptr , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_mem ( CL_API_CALL * clCreateImage3D_ptr ) ( cl_context , cl_mem_flags , const cl_image_format * , size_t , size_t , size_t , size_t , size_t , void * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_mem CL_API_CALL 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 ) {
if ( ! clCreateImage3D_ptr ) clCreateImage3D_ptr = getFunction ( " clCreateImage3D " ) ;
return ( * clCreateImage3D_ptr ) ( context , flags , image_format , image_width , image_height , image_depth , image_row_pitch , image_slice_pitch , host_ptr , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clRetainMemObject_ptr ) ( cl_mem ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clRetainMemObject ( cl_mem memobj ) {
if ( ! clRetainMemObject_ptr ) clRetainMemObject_ptr = getFunction ( " clRetainMemObject " ) ;
return ( * clRetainMemObject_ptr ) ( memobj ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clReleaseMemObject_ptr ) ( cl_mem ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clReleaseMemObject ( cl_mem memobj ) {
if ( ! clReleaseMemObject_ptr ) clReleaseMemObject_ptr = getFunction ( " clReleaseMemObject " ) ;
return ( * clReleaseMemObject_ptr ) ( memobj ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetSupportedImageFormats_ptr ) ( cl_context , cl_mem_flags , cl_mem_object_type , cl_uint , cl_image_format * , cl_uint * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clGetSupportedImageFormats_ptr ) clGetSupportedImageFormats_ptr = getFunction ( " clGetSupportedImageFormats " ) ;
return ( * clGetSupportedImageFormats_ptr ) ( context , flags , image_type , num_entries , image_formats , num_image_formats ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetMemObjectInfo_ptr ) ( cl_mem , cl_mem_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetMemObjectInfo ( cl_mem memobj , cl_mem_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetMemObjectInfo_ptr ) clGetMemObjectInfo_ptr = getFunction ( " clGetMemObjectInfo " ) ;
return ( * clGetMemObjectInfo_ptr ) ( memobj , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetImageInfo_ptr ) ( cl_mem , cl_image_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetImageInfo ( cl_mem image , cl_image_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetImageInfo_ptr ) clGetImageInfo_ptr = getFunction ( " clGetImageInfo " ) ;
return ( * clGetImageInfo_ptr ) ( image , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_sampler ( CL_API_CALL * clCreateSampler_ptr ) ( cl_context , cl_bool , cl_addressing_mode , cl_filter_mode , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
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 ) {
if ( ! clCreateSampler_ptr ) clCreateSampler_ptr = getFunction ( " clCreateSampler " ) ;
return ( * clCreateSampler_ptr ) ( context , normalized_coords , addressing_mode , filter_mode , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clRetainSampler_ptr ) ( cl_sampler ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clRetainSampler ( cl_sampler sampler ) {
if ( ! clRetainSampler_ptr ) clRetainSampler_ptr = getFunction ( " clRetainSampler " ) ;
return ( * clRetainSampler_ptr ) ( sampler ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clReleaseSampler_ptr ) ( cl_sampler ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clReleaseSampler ( cl_sampler sampler ) {
if ( ! clReleaseSampler_ptr ) clReleaseSampler_ptr = getFunction ( " clReleaseSampler " ) ;
return ( * clReleaseSampler_ptr ) ( sampler ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetSamplerInfo_ptr ) ( cl_sampler , cl_sampler_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetSamplerInfo ( cl_sampler sampler , cl_sampler_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetSamplerInfo_ptr ) clGetSamplerInfo_ptr = getFunction ( " clGetSamplerInfo " ) ;
return ( * clGetSamplerInfo_ptr ) ( sampler , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_program ( CL_API_CALL * clCreateProgramWithSource_ptr ) ( cl_context , cl_uint , const char * * , const size_t * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_program CL_API_CALL clCreateProgramWithSource ( cl_context context , cl_uint count , const char * * strings , const size_t * lengths , cl_int * errcode_ret ) {
if ( ! clCreateProgramWithSource_ptr ) clCreateProgramWithSource_ptr = getFunction ( " clCreateProgramWithSource " ) ;
return ( * clCreateProgramWithSource_ptr ) ( context , count , strings , lengths , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_program ( CL_API_CALL * clCreateProgramWithBinary_ptr ) ( cl_context , cl_uint , const cl_device_id * , const size_t * , const unsigned char * * , cl_int * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_program CL_API_CALL 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 ) {
if ( ! clCreateProgramWithBinary_ptr ) clCreateProgramWithBinary_ptr = getFunction ( " clCreateProgramWithBinary " ) ;
return ( * clCreateProgramWithBinary_ptr ) ( context , num_devices , device_list , lengths , binaries , binary_status , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clRetainProgram_ptr ) ( cl_program ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clRetainProgram ( cl_program program ) {
if ( ! clRetainProgram_ptr ) clRetainProgram_ptr = getFunction ( " clRetainProgram " ) ;
return ( * clRetainProgram_ptr ) ( program ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clReleaseProgram_ptr ) ( cl_program ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clReleaseProgram ( cl_program program ) {
if ( ! clReleaseProgram_ptr ) clReleaseProgram_ptr = getFunction ( " clReleaseProgram " ) ;
return ( * clReleaseProgram_ptr ) ( program ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clBuildProgram_ptr ) ( cl_program , cl_uint , const cl_device_id * , const char * , void ( CL_CALLBACK * /* pfn_notify */ ) ( cl_program /* program */ , void * ) , void * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 * ) , void * user_data ) {
if ( ! clBuildProgram_ptr ) clBuildProgram_ptr = getFunction ( " clBuildProgram " ) ;
return ( * clBuildProgram_ptr ) ( program , num_devices , device_list , options , pfn_notify , user_data ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clUnloadCompiler_ptr ) ( void ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clUnloadCompiler ( void ) {
if ( ! clUnloadCompiler_ptr ) clUnloadCompiler_ptr = getFunction ( " clUnloadCompiler " ) ;
return ( * clUnloadCompiler_ptr ) ( ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetProgramInfo_ptr ) ( cl_program , cl_program_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetProgramInfo ( cl_program program , cl_program_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetProgramInfo_ptr ) clGetProgramInfo_ptr = getFunction ( " clGetProgramInfo " ) ;
return ( * clGetProgramInfo_ptr ) ( program , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetProgramBuildInfo_ptr ) ( cl_program , cl_device_id , cl_program_build_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clGetProgramBuildInfo_ptr ) clGetProgramBuildInfo_ptr = getFunction ( " clGetProgramBuildInfo " ) ;
return ( * clGetProgramBuildInfo_ptr ) ( program , device , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_kernel ( CL_API_CALL * clCreateKernel_ptr ) ( cl_program , const char * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_kernel CL_API_CALL clCreateKernel ( cl_program program , const char * kernel_name , cl_int * errcode_ret ) {
if ( ! clCreateKernel_ptr ) clCreateKernel_ptr = getFunction ( " clCreateKernel " ) ;
return ( * clCreateKernel_ptr ) ( program , kernel_name , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clCreateKernelsInProgram_ptr ) ( cl_program , cl_uint , cl_kernel * , cl_uint * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clCreateKernelsInProgram ( cl_program program , cl_uint num_kernels , cl_kernel * kernels , cl_uint * num_kernels_ret ) {
if ( ! clCreateKernelsInProgram_ptr ) clCreateKernelsInProgram_ptr = getFunction ( " clCreateKernelsInProgram " ) ;
return ( * clCreateKernelsInProgram_ptr ) ( program , num_kernels , kernels , num_kernels_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clRetainKernel_ptr ) ( cl_kernel ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clRetainKernel ( cl_kernel kernel ) {
if ( ! clRetainKernel_ptr ) clRetainKernel_ptr = getFunction ( " clRetainKernel " ) ;
return ( * clRetainKernel_ptr ) ( kernel ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clReleaseKernel_ptr ) ( cl_kernel ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clReleaseKernel ( cl_kernel kernel ) {
if ( ! clReleaseKernel_ptr ) clReleaseKernel_ptr = getFunction ( " clReleaseKernel " ) ;
return ( * clReleaseKernel_ptr ) ( kernel ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clSetKernelArg_ptr ) ( cl_kernel , cl_uint , size_t , const void * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clSetKernelArg ( cl_kernel kernel , cl_uint arg_index , size_t arg_size , const void * arg_value ) {
if ( ! clSetKernelArg_ptr ) clSetKernelArg_ptr = getFunction ( " clSetKernelArg " ) ;
return ( * clSetKernelArg_ptr ) ( kernel , arg_index , arg_size , arg_value ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetKernelInfo_ptr ) ( cl_kernel , cl_kernel_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetKernelInfo ( cl_kernel kernel , cl_kernel_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetKernelInfo_ptr ) clGetKernelInfo_ptr = getFunction ( " clGetKernelInfo " ) ;
return ( * clGetKernelInfo_ptr ) ( kernel , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetKernelWorkGroupInfo_ptr ) ( cl_kernel , cl_device_id , cl_kernel_work_group_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clGetKernelWorkGroupInfo_ptr ) clGetKernelWorkGroupInfo_ptr = getFunction ( " clGetKernelWorkGroupInfo " ) ;
return ( * clGetKernelWorkGroupInfo_ptr ) ( kernel , device , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clWaitForEvents_ptr ) ( cl_uint , const cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clWaitForEvents ( cl_uint num_events , const cl_event * event_list ) {
if ( ! clWaitForEvents_ptr ) clWaitForEvents_ptr = getFunction ( " clWaitForEvents " ) ;
return ( * clWaitForEvents_ptr ) ( num_events , event_list ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetEventInfo_ptr ) ( cl_event , cl_event_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetEventInfo ( cl_event event , cl_event_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetEventInfo_ptr ) clGetEventInfo_ptr = getFunction ( " clGetEventInfo " ) ;
return ( * clGetEventInfo_ptr ) ( event , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clRetainEvent_ptr ) ( cl_event ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clRetainEvent ( cl_event event ) {
if ( ! clRetainEvent_ptr ) clRetainEvent_ptr = getFunction ( " clRetainEvent " ) ;
return ( * clRetainEvent_ptr ) ( event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clReleaseEvent_ptr ) ( cl_event ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clReleaseEvent ( cl_event event ) {
if ( ! clReleaseEvent_ptr ) clReleaseEvent_ptr = getFunction ( " clReleaseEvent " ) ;
return ( * clReleaseEvent_ptr ) ( event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clGetEventProfilingInfo_ptr ) ( cl_event , cl_profiling_info , size_t , void * , size_t * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clGetEventProfilingInfo ( cl_event event , cl_profiling_info param_name , size_t param_value_size , void * param_value , size_t * param_value_size_ret ) {
if ( ! clGetEventProfilingInfo_ptr ) clGetEventProfilingInfo_ptr = getFunction ( " clGetEventProfilingInfo " ) ;
return ( * clGetEventProfilingInfo_ptr ) ( event , param_name , param_value_size , param_value , param_value_size_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clFlush_ptr ) ( cl_command_queue ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clFlush ( cl_command_queue command_queue ) {
if ( ! clFlush_ptr ) clFlush_ptr = getFunction ( " clFlush " ) ;
return ( * clFlush_ptr ) ( command_queue ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clFinish_ptr ) ( cl_command_queue ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clFinish ( cl_command_queue command_queue ) {
if ( ! clFinish_ptr ) clFinish_ptr = getFunction ( " clFinish " ) ;
return ( * clFinish_ptr ) ( command_queue ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueReadBuffer_ptr ) ( cl_command_queue , cl_mem , cl_bool , size_t , size_t , void * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 , cl_event * event ) {
if ( ! clEnqueueReadBuffer_ptr ) clEnqueueReadBuffer_ptr = getFunction ( " clEnqueueReadBuffer " ) ;
return ( * clEnqueueReadBuffer_ptr ) ( command_queue , buffer , blocking_read , offset , cb , ptr , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueWriteBuffer_ptr ) ( cl_command_queue , cl_mem , cl_bool , size_t , size_t , const void * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 , cl_event * event ) {
if ( ! clEnqueueWriteBuffer_ptr ) clEnqueueWriteBuffer_ptr = getFunction ( " clEnqueueWriteBuffer " ) ;
return ( * clEnqueueWriteBuffer_ptr ) ( command_queue , buffer , blocking_write , offset , cb , ptr , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueCopyBuffer_ptr ) ( cl_command_queue , cl_mem , cl_mem , size_t , size_t , size_t , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 , cl_event * event ) {
if ( ! clEnqueueCopyBuffer_ptr ) clEnqueueCopyBuffer_ptr = getFunction ( " clEnqueueCopyBuffer " ) ;
return ( * clEnqueueCopyBuffer_ptr ) ( command_queue , src_buffer , dst_buffer , src_offset , dst_offset , cb , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueReadImage_ptr ) ( cl_command_queue , cl_mem , cl_bool , const size_t * , const size_t * , size_t , size_t , void * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clEnqueueReadImage_ptr ) clEnqueueReadImage_ptr = getFunction ( " clEnqueueReadImage " ) ;
return ( * clEnqueueReadImage_ptr ) ( command_queue , image , blocking_read , origin , region , row_pitch , slice_pitch , ptr , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueWriteImage_ptr ) ( cl_command_queue , cl_mem , cl_bool , const size_t * , const size_t * , size_t , size_t , const void * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 , const cl_event * event_wait_list , cl_event * event ) {
if ( ! clEnqueueWriteImage_ptr ) clEnqueueWriteImage_ptr = getFunction ( " clEnqueueWriteImage " ) ;
return ( * clEnqueueWriteImage_ptr ) ( command_queue , image , blocking_write , origin , region , input_row_pitch , input_slice_pitch , ptr , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueCopyImage_ptr ) ( cl_command_queue , cl_mem , cl_mem , const size_t * , const size_t * , const size_t * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clEnqueueCopyImage_ptr ) clEnqueueCopyImage_ptr = getFunction ( " clEnqueueCopyImage " ) ;
return ( * clEnqueueCopyImage_ptr ) ( command_queue , src_image , dst_image , src_origin , dst_origin , region , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueCopyImageToBuffer_ptr ) ( cl_command_queue , cl_mem , cl_mem , const size_t * , const size_t * , size_t , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clEnqueueCopyImageToBuffer_ptr ) clEnqueueCopyImageToBuffer_ptr = getFunction ( " clEnqueueCopyImageToBuffer " ) ;
return ( * clEnqueueCopyImageToBuffer_ptr ) ( command_queue , src_image , dst_buffer , src_origin , region , dst_offset , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueCopyBufferToImage_ptr ) ( cl_command_queue , cl_mem , cl_mem , size_t , const size_t * , const size_t * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clEnqueueCopyBufferToImage_ptr ) clEnqueueCopyBufferToImage_ptr = getFunction ( " clEnqueueCopyBufferToImage " ) ;
return ( * clEnqueueCopyBufferToImage_ptr ) ( command_queue , src_buffer , dst_image , src_offset , dst_origin , region , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static void * ( CL_API_CALL * clEnqueueMapBuffer_ptr ) ( cl_command_queue , cl_mem , cl_bool , cl_map_flags , size_t , size_t , cl_uint , const cl_event * , cl_event * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
void * CL_API_CALL 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 ) {
if ( ! clEnqueueMapBuffer_ptr ) clEnqueueMapBuffer_ptr = getFunction ( " clEnqueueMapBuffer " ) ;
return ( * clEnqueueMapBuffer_ptr ) ( command_queue , buffer , blocking_map , map_flags , offset , cb , num_events_in_wait_list , event_wait_list , event , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static void * ( CL_API_CALL * clEnqueueMapImage_ptr ) ( cl_command_queue , cl_mem , cl_bool , cl_map_flags , const size_t * , const size_t * , size_t * , size_t * , cl_uint , const cl_event * , cl_event * , cl_int * ) = NULL ;
2010-06-29 02:23:09 +00:00
void * CL_API_CALL 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 ) {
if ( ! clEnqueueMapImage_ptr ) clEnqueueMapImage_ptr = getFunction ( " clEnqueueMapImage " ) ;
return ( * clEnqueueMapImage_ptr ) ( command_queue , image , blocking_map , map_flags , origin , region , image_row_pitch , image_slice_pitch , num_events_in_wait_list , event_wait_list , event , errcode_ret ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueUnmapMemObject_ptr ) ( cl_command_queue , cl_mem , void * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clEnqueueUnmapMemObject_ptr ) clEnqueueUnmapMemObject_ptr = getFunction ( " clEnqueueUnmapMemObject " ) ;
return ( * clEnqueueUnmapMemObject_ptr ) ( command_queue , memobj , mapped_ptr , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueNDRangeKernel_ptr ) ( cl_command_queue , cl_kernel , cl_uint , const size_t * , const size_t * , const size_t * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL 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 ) {
if ( ! clEnqueueNDRangeKernel_ptr ) clEnqueueNDRangeKernel_ptr = getFunction ( " clEnqueueNDRangeKernel " ) ;
return ( * clEnqueueNDRangeKernel_ptr ) ( command_queue , kernel , work_dim , global_work_offset , global_work_size , local_work_size , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueTask_ptr ) ( cl_command_queue , cl_kernel , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
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 ) {
if ( ! clEnqueueTask_ptr ) clEnqueueTask_ptr = getFunction ( " clEnqueueTask " ) ;
return ( * clEnqueueTask_ptr ) ( command_queue , kernel , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueNativeKernel_ptr ) ( cl_command_queue , void ( * ) ( void * ) , void * , size_t , cl_uint , const cl_mem * , const void * * , cl_uint , const cl_event * , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clEnqueueNativeKernel ( cl_command_queue command_queue , void ( * 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 ) {
if ( ! clEnqueueNativeKernel_ptr ) clEnqueueNativeKernel_ptr = getFunction ( " clEnqueueNativeKernel " ) ;
return ( * clEnqueueNativeKernel_ptr ) ( command_queue , user_func , args , cb_args , num_mem_objects , mem_list , args_mem_loc , num_events_in_wait_list , event_wait_list , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueMarker_ptr ) ( cl_command_queue , cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clEnqueueMarker ( cl_command_queue command_queue , cl_event * event ) {
if ( ! clEnqueueMarker_ptr ) clEnqueueMarker_ptr = getFunction ( " clEnqueueMarker " ) ;
return ( * clEnqueueMarker_ptr ) ( command_queue , event ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueWaitForEvents_ptr ) ( cl_command_queue , cl_uint , const cl_event * ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clEnqueueWaitForEvents ( cl_command_queue command_queue , cl_uint num_events , const cl_event * event_list ) {
if ( ! clEnqueueWaitForEvents_ptr ) clEnqueueWaitForEvents_ptr = getFunction ( " clEnqueueWaitForEvents " ) ;
return ( * clEnqueueWaitForEvents_ptr ) ( command_queue , num_events , event_list ) ;
}
2010-07-18 14:18:37 +00:00
static cl_int ( CL_API_CALL * clEnqueueBarrier_ptr ) ( cl_command_queue ) = NULL ;
2010-06-29 02:23:09 +00:00
cl_int CL_API_CALL clEnqueueBarrier ( cl_command_queue command_queue ) {
if ( ! clEnqueueBarrier_ptr ) clEnqueueBarrier_ptr = getFunction ( " clEnqueueBarrier " ) ;
return ( * clEnqueueBarrier_ptr ) ( command_queue ) ;
}
2010-07-18 14:18:37 +00:00
static void * ( CL_API_CALL * clGetExtensionFunctionAddress_ptr ) ( const char * ) = NULL ;
2010-06-29 02:23:09 +00:00
void * CL_API_CALL clGetExtensionFunctionAddress ( const char * func_name ) {
if ( ! clGetExtensionFunctionAddress_ptr ) clGetExtensionFunctionAddress_ptr = getFunction ( " clGetExtensionFunctionAddress " ) ;
return ( * clGetExtensionFunctionAddress_ptr ) ( func_name ) ;
}