mirror of https://github.com/PCSX2/pcsx2.git
3rdparty: Remove opencl lib source files.
This commit is contained in:
lightningterror
parent
6529fa419f
commit
413d58df57
File diff suppressed because it is too large
Load Diff
File diff suppressed because it is too large
Load Diff
|
|
@ -1,126 +0,0 @@
|
||||||
/**********************************************************************************
|
|
||||||
* Copyright (c) 2008-2013 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.
|
|
||||||
**********************************************************************************/
|
|
||||||
|
|
||||||
/* $Revision: 11708 $ on $Date: 2010-06-13 23:36:24 -0700 (Sun, 13 Jun 2010) $ */
|
|
||||||
|
|
||||||
#ifndef __OPENCL_CL_D3D10_H
|
|
||||||
#define __OPENCL_CL_D3D10_H
|
|
||||||
|
|
||||||
#include <d3d10.h>
|
|
||||||
#include <CL/cl.h>
|
|
||||||
#include <CL/cl_platform.h>
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
extern "C" {
|
|
||||||
#endif
|
|
||||||
|
|
||||||
/******************************************************************************
|
|
||||||
* cl_khr_d3d10_sharing */
|
|
||||||
#define cl_khr_d3d10_sharing 1
|
|
||||||
|
|
||||||
typedef cl_uint cl_d3d10_device_source_khr;
|
|
||||||
typedef cl_uint cl_d3d10_device_set_khr;
|
|
||||||
|
|
||||||
/******************************************************************************/
|
|
||||||
|
|
||||||
/* Error Codes */
|
|
||||||
#define CL_INVALID_D3D10_DEVICE_KHR -1002
|
|
||||||
#define CL_INVALID_D3D10_RESOURCE_KHR -1003
|
|
||||||
#define CL_D3D10_RESOURCE_ALREADY_ACQUIRED_KHR -1004
|
|
||||||
#define CL_D3D10_RESOURCE_NOT_ACQUIRED_KHR -1005
|
|
||||||
|
|
||||||
/* cl_d3d10_device_source_nv */
|
|
||||||
#define CL_D3D10_DEVICE_KHR 0x4010
|
|
||||||
#define CL_D3D10_DXGI_ADAPTER_KHR 0x4011
|
|
||||||
|
|
||||||
/* cl_d3d10_device_set_nv */
|
|
||||||
#define CL_PREFERRED_DEVICES_FOR_D3D10_KHR 0x4012
|
|
||||||
#define CL_ALL_DEVICES_FOR_D3D10_KHR 0x4013
|
|
||||||
|
|
||||||
/* cl_context_info */
|
|
||||||
#define CL_CONTEXT_D3D10_DEVICE_KHR 0x4014
|
|
||||||
#define CL_CONTEXT_D3D10_PREFER_SHARED_RESOURCES_KHR 0x402C
|
|
||||||
|
|
||||||
/* cl_mem_info */
|
|
||||||
#define CL_MEM_D3D10_RESOURCE_KHR 0x4015
|
|
||||||
|
|
||||||
/* cl_image_info */
|
|
||||||
#define CL_IMAGE_D3D10_SUBRESOURCE_KHR 0x4016
|
|
||||||
|
|
||||||
/* cl_command_type */
|
|
||||||
#define CL_COMMAND_ACQUIRE_D3D10_OBJECTS_KHR 0x4017
|
|
||||||
#define CL_COMMAND_RELEASE_D3D10_OBJECTS_KHR 0x4018
|
|
||||||
|
|
||||||
/******************************************************************************/
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY cl_int (CL_API_CALL *clGetDeviceIDsFromD3D10KHR_fn)(
|
|
||||||
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 *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)(
|
|
||||||
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)(
|
|
||||||
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)(
|
|
||||||
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 *clEnqueueReleaseD3D10ObjectsKHR_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;
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
}
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#endif /* __OPENCL_CL_D3D10_H */
|
|
||||||
|
|
||||||
|
|
@ -1,458 +0,0 @@
|
||||||
/*******************************************************************************
|
|
||||||
* Copyright (c) 2008-2013 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.
|
|
||||||
******************************************************************************/
|
|
||||||
|
|
||||||
/* $Revision: 11928 $ on $Date: 2010-07-13 09:04:56 -0700 (Tue, 13 Jul 2010) $ */
|
|
||||||
|
|
||||||
/* cl_ext.h contains OpenCL extensions which don't have external */
|
|
||||||
/* (OpenGL, D3D) dependencies. */
|
|
||||||
|
|
||||||
#ifndef __CL_EXT_H
|
|
||||||
#define __CL_EXT_H
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
extern "C" {
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#ifdef __APPLE__
|
|
||||||
#include <OpenCL/cl.h>
|
|
||||||
#include <AvailabilityMacros.h>
|
|
||||||
#else
|
|
||||||
#include <CL/cl.h>
|
|
||||||
#endif
|
|
||||||
|
|
||||||
/* cl_khr_fp16 extension - no extension #define since it has no functions */
|
|
||||||
#define CL_DEVICE_HALF_FP_CONFIG 0x1033
|
|
||||||
|
|
||||||
/* Memory object destruction
|
|
||||||
*
|
|
||||||
* Apple extension for use to manage externally allocated buffers used with cl_mem objects with CL_MEM_USE_HOST_PTR
|
|
||||||
*
|
|
||||||
* Registers a user callback function that will be called when the memory object is deleted and its resources
|
|
||||||
* freed. Each call to clSetMemObjectCallbackFn registers the specified user callback function on a callback
|
|
||||||
* stack associated with memobj. The registered user callback functions are called in the reverse order in
|
|
||||||
* which they were registered. The user callback functions are called and then the memory object is deleted
|
|
||||||
* and its resources freed. This provides a mechanism for the application (and libraries) using memobj to be
|
|
||||||
* notified when the memory referenced by host_ptr, specified when the memory object is created and used as
|
|
||||||
* the storage bits for the memory object, can be reused or freed.
|
|
||||||
*
|
|
||||||
* The application may not call CL api's with the cl_mem object passed to the pfn_notify.
|
|
||||||
*
|
|
||||||
* Please check for the "cl_APPLE_SetMemObjectDestructor" extension using clGetDeviceInfo(CL_DEVICE_EXTENSIONS)
|
|
||||||
* before using.
|
|
||||||
*/
|
|
||||||
#define cl_APPLE_SetMemObjectDestructor 1
|
|
||||||
cl_int CL_API_ENTRY clSetMemObjectDestructorAPPLE( cl_mem /* memobj */,
|
|
||||||
void (* /*pfn_notify*/)( cl_mem /* memobj */, void* /*user_data*/),
|
|
||||||
void * /*user_data */ ) CL_EXT_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
|
|
||||||
/* Context Logging Functions
|
|
||||||
*
|
|
||||||
* The next three convenience functions are intended to be used as the pfn_notify parameter to clCreateContext().
|
|
||||||
* Please check for the "cl_APPLE_ContextLoggingFunctions" extension using clGetDeviceInfo(CL_DEVICE_EXTENSIONS)
|
|
||||||
* before using.
|
|
||||||
*
|
|
||||||
* clLogMessagesToSystemLog fowards on all log messages to the Apple System Logger
|
|
||||||
*/
|
|
||||||
#define cl_APPLE_ContextLoggingFunctions 1
|
|
||||||
extern void CL_API_ENTRY clLogMessagesToSystemLogAPPLE( const char * /* errstr */,
|
|
||||||
const void * /* private_info */,
|
|
||||||
size_t /* cb */,
|
|
||||||
void * /* user_data */ ) CL_EXT_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
/* clLogMessagesToStdout sends all log messages to the file descriptor stdout */
|
|
||||||
extern void CL_API_ENTRY clLogMessagesToStdoutAPPLE( const char * /* errstr */,
|
|
||||||
const void * /* private_info */,
|
|
||||||
size_t /* cb */,
|
|
||||||
void * /* user_data */ ) CL_EXT_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
/* clLogMessagesToStderr sends all log messages to the file descriptor stderr */
|
|
||||||
extern void CL_API_ENTRY clLogMessagesToStderrAPPLE( const char * /* errstr */,
|
|
||||||
const void * /* private_info */,
|
|
||||||
size_t /* cb */,
|
|
||||||
void * /* user_data */ ) CL_EXT_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
|
|
||||||
/************************
|
|
||||||
* cl_khr_icd extension *
|
|
||||||
************************/
|
|
||||||
#define cl_khr_icd 1
|
|
||||||
|
|
||||||
/* cl_platform_info */
|
|
||||||
#define CL_PLATFORM_ICD_SUFFIX_KHR 0x0920
|
|
||||||
|
|
||||||
/* Additional Error Codes */
|
|
||||||
#define CL_PLATFORM_NOT_FOUND_KHR -1001
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clIcdGetPlatformIDsKHR(cl_uint /* num_entries */,
|
|
||||||
cl_platform_id * /* platforms */,
|
|
||||||
cl_uint * /* num_platforms */);
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY cl_int (CL_API_CALL *clIcdGetPlatformIDsKHR_fn)(
|
|
||||||
cl_uint /* num_entries */,
|
|
||||||
cl_platform_id * /* platforms */,
|
|
||||||
cl_uint * /* num_platforms */);
|
|
||||||
|
|
||||||
|
|
||||||
/* Extension: cl_khr_image2D_buffer
|
|
||||||
*
|
|
||||||
* This extension allows a 2D image to be created from a cl_mem buffer without a copy.
|
|
||||||
* The type associated with a 2D image created from a buffer in an OpenCL program is image2d_t.
|
|
||||||
* Both the sampler and sampler-less read_image built-in functions are supported for 2D images
|
|
||||||
* and 2D images created from a buffer. Similarly, the write_image built-ins are also supported
|
|
||||||
* for 2D images created from a buffer.
|
|
||||||
*
|
|
||||||
* When the 2D image from buffer is created, the client must specify the width,
|
|
||||||
* height, image format (i.e. channel order and channel data type) and optionally the row pitch
|
|
||||||
*
|
|
||||||
* The pitch specified must be a multiple of CL_DEVICE_IMAGE_PITCH_ALIGNMENT pixels.
|
|
||||||
* The base address of the buffer must be aligned to CL_DEVICE_IMAGE_BASE_ADDRESS_ALIGNMENT pixels.
|
|
||||||
*/
|
|
||||||
|
|
||||||
/*************************************
|
|
||||||
* cl_khr_initalize_memory extension *
|
|
||||||
*************************************/
|
|
||||||
|
|
||||||
#define CL_CONTEXT_MEMORY_INITIALIZE_KHR 0x2030
|
|
||||||
|
|
||||||
|
|
||||||
/**************************************
|
|
||||||
* cl_khr_terminate_context extension *
|
|
||||||
**************************************/
|
|
||||||
|
|
||||||
#define CL_DEVICE_TERMINATE_CAPABILITY_KHR 0x2031
|
|
||||||
#define CL_CONTEXT_TERMINATE_KHR 0x2032
|
|
||||||
|
|
||||||
#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;
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY cl_int (CL_API_CALL *clTerminateContextKHR_fn)(cl_context /* context */) CL_EXT_SUFFIX__VERSION_1_2;
|
|
||||||
|
|
||||||
|
|
||||||
/*
|
|
||||||
* Extension: cl_khr_spir
|
|
||||||
*
|
|
||||||
* This extension adds support to create an OpenCL program object from a
|
|
||||||
* Standard Portable Intermediate Representation (SPIR) instance
|
|
||||||
*/
|
|
||||||
|
|
||||||
#define CL_DEVICE_SPIR_VERSIONS 0x40E0
|
|
||||||
#define CL_PROGRAM_BINARY_TYPE_INTERMEDIATE 0x40E1
|
|
||||||
|
|
||||||
|
|
||||||
/******************************************
|
|
||||||
* cl_nv_device_attribute_query extension *
|
|
||||||
******************************************/
|
|
||||||
/* cl_nv_device_attribute_query extension - no extension #define since it has no functions */
|
|
||||||
#define CL_DEVICE_COMPUTE_CAPABILITY_MAJOR_NV 0x4000
|
|
||||||
#define CL_DEVICE_COMPUTE_CAPABILITY_MINOR_NV 0x4001
|
|
||||||
#define CL_DEVICE_REGISTERS_PER_BLOCK_NV 0x4002
|
|
||||||
#define CL_DEVICE_WARP_SIZE_NV 0x4003
|
|
||||||
#define CL_DEVICE_GPU_OVERLAP_NV 0x4004
|
|
||||||
#define CL_DEVICE_KERNEL_EXEC_TIMEOUT_NV 0x4005
|
|
||||||
#define CL_DEVICE_INTEGRATED_MEMORY_NV 0x4006
|
|
||||||
|
|
||||||
/*********************************
|
|
||||||
* cl_amd_device_attribute_query *
|
|
||||||
*********************************/
|
|
||||||
#define CL_DEVICE_PROFILING_TIMER_OFFSET_AMD 0x4036
|
|
||||||
|
|
||||||
/*********************************
|
|
||||||
* cl_arm_printf extension
|
|
||||||
*********************************/
|
|
||||||
#define CL_PRINTF_CALLBACK_ARM 0x40B0
|
|
||||||
#define CL_PRINTF_BUFFERSIZE_ARM 0x40B1
|
|
||||||
|
|
||||||
/*********************************
|
|
||||||
* cl_intel_accelerator extension *
|
|
||||||
*********************************/
|
|
||||||
#define cl_intel_accelerator 1
|
|
||||||
#define cl_intel_motion_estimation 1
|
|
||||||
|
|
||||||
typedef struct _cl_accelerator_intel* cl_accelerator_intel;
|
|
||||||
typedef cl_uint cl_accelerator_type_intel;
|
|
||||||
typedef cl_uint cl_accelerator_info_intel;
|
|
||||||
|
|
||||||
typedef struct _cl_motion_estimation_desc_intel {
|
|
||||||
cl_uint mb_block_type;
|
|
||||||
cl_uint subpixel_mode;
|
|
||||||
cl_uint sad_adjust_mode;
|
|
||||||
cl_uint search_path_type;
|
|
||||||
} cl_motion_estimation_desc_intel;
|
|
||||||
|
|
||||||
/* Error Codes */
|
|
||||||
#define CL_INVALID_ACCELERATOR_INTEL -1094
|
|
||||||
#define CL_INVALID_ACCELERATOR_TYPE_INTEL -1095
|
|
||||||
#define CL_INVALID_ACCELERATOR_DESCRIPTOR_INTEL -1096
|
|
||||||
#define CL_ACCELERATOR_TYPE_NOT_SUPPORTED_INTEL -1097
|
|
||||||
|
|
||||||
/* Deprecated Error Codes */
|
|
||||||
#define CL_INVALID_ACCELERATOR_INTEL_DEPRECATED -6000
|
|
||||||
#define CL_INVALID_ACCELERATOR_TYPE_INTEL_DEPRECATED -6001
|
|
||||||
#define CL_INVALID_ACCELERATOR_DESCRIPTOR_INTEL_DEPRECATED -6002
|
|
||||||
#define CL_ACCELERATOR_TYPE_NOT_SUPPORTED_INTEL_DEPRECATED -6003
|
|
||||||
|
|
||||||
/* cl_accelerator_type_intel */
|
|
||||||
#define CL_ACCELERATOR_TYPE_MOTION_ESTIMATION_INTEL 0x0
|
|
||||||
|
|
||||||
/* cl_accelerator_info_intel */
|
|
||||||
#define CL_ACCELERATOR_DESCRIPTOR_INTEL 0x4090
|
|
||||||
#define CL_ACCELERATOR_REFERENCE_COUNT_INTEL 0x4091
|
|
||||||
#define CL_ACCELERATOR_CONTEXT_INTEL 0x4092
|
|
||||||
#define CL_ACCELERATOR_TYPE_INTEL 0x4093
|
|
||||||
|
|
||||||
/*cl_motion_detect_desc_intel flags */
|
|
||||||
#define CL_ME_MB_TYPE_16x16_INTEL 0x0
|
|
||||||
#define CL_ME_MB_TYPE_8x8_INTEL 0x1
|
|
||||||
#define CL_ME_MB_TYPE_4x4_INTEL 0x2
|
|
||||||
|
|
||||||
#define CL_ME_SUBPIXEL_MODE_INTEGER_INTEL 0x0
|
|
||||||
#define CL_ME_SUBPIXEL_MODE_HPEL_INTEL 0x1
|
|
||||||
#define CL_ME_SUBPIXEL_MODE_QPEL_INTEL 0x2
|
|
||||||
|
|
||||||
#define CL_ME_SAD_ADJUST_MODE_NONE_INTEL 0x0
|
|
||||||
#define CL_ME_SAD_ADJUST_MODE_HAAR_INTEL 0x1
|
|
||||||
|
|
||||||
#define CL_ME_SEARCH_PATH_RADIUS_2_2_INTEL 0x0
|
|
||||||
#define CL_ME_SEARCH_PATH_RADIUS_4_4_INTEL 0x1
|
|
||||||
#define CL_ME_SEARCH_PATH_RADIUS_16_12_INTEL 0x5
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_accelerator_intel CL_API_CALL
|
|
||||||
clCreateAcceleratorINTEL(
|
|
||||||
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;
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY 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;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clGetAcceleratorInfoINTEL
|
|
||||||
(
|
|
||||||
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;
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY 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;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clRetainAcceleratorINTEL(
|
|
||||||
cl_accelerator_intel /* accelerator */ ) CL_EXT_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;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clReleaseAcceleratorINTEL(
|
|
||||||
cl_accelerator_intel /* accelerator */ ) CL_EXT_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;
|
|
||||||
|
|
||||||
#ifdef CL_VERSION_1_1
|
|
||||||
/***********************************
|
|
||||||
* cl_ext_device_fission extension *
|
|
||||||
***********************************/
|
|
||||||
#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;
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY cl_int
|
|
||||||
(CL_API_CALL *clReleaseDeviceEXT_fn)( cl_device_id /*device*/ ) CL_EXT_SUFFIX__VERSION_1_1;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clRetainDeviceEXT( cl_device_id /*device*/ ) CL_EXT_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_ulong cl_device_partition_property_ext;
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
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;
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY 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_device_partition_property_ext */
|
|
||||||
#define CL_DEVICE_PARTITION_EQUALLY_EXT 0x4050
|
|
||||||
#define CL_DEVICE_PARTITION_BY_COUNTS_EXT 0x4051
|
|
||||||
#define CL_DEVICE_PARTITION_BY_NAMES_EXT 0x4052
|
|
||||||
#define CL_DEVICE_PARTITION_BY_NAMES_INTEL 0x4052
|
|
||||||
#define CL_DEVICE_PARTITION_BY_AFFINITY_DOMAIN_EXT 0x4053
|
|
||||||
|
|
||||||
/* clDeviceGetInfo selectors */
|
|
||||||
#define CL_DEVICE_PARENT_DEVICE_EXT 0x4054
|
|
||||||
#define CL_DEVICE_PARTITION_TYPES_EXT 0x4055
|
|
||||||
#define CL_DEVICE_AFFINITY_DOMAINS_EXT 0x4056
|
|
||||||
#define CL_DEVICE_REFERENCE_COUNT_EXT 0x4057
|
|
||||||
#define CL_DEVICE_PARTITION_STYLE_EXT 0x4058
|
|
||||||
|
|
||||||
/* error codes */
|
|
||||||
#define CL_DEVICE_PARTITION_FAILED_EXT -1057
|
|
||||||
#define CL_INVALID_PARTITION_COUNT_EXT -1058
|
|
||||||
#define CL_INVALID_PARTITION_NAME_EXT -1059
|
|
||||||
|
|
||||||
/* CL_AFFINITY_DOMAINs */
|
|
||||||
#define CL_AFFINITY_DOMAIN_L1_CACHE_EXT 0x1
|
|
||||||
#define CL_AFFINITY_DOMAIN_L2_CACHE_EXT 0x2
|
|
||||||
#define CL_AFFINITY_DOMAIN_L3_CACHE_EXT 0x3
|
|
||||||
#define CL_AFFINITY_DOMAIN_L4_CACHE_EXT 0x4
|
|
||||||
#define CL_AFFINITY_DOMAIN_NUMA_EXT 0x10
|
|
||||||
#define CL_AFFINITY_DOMAIN_NEXT_FISSIONABLE_EXT 0x100
|
|
||||||
|
|
||||||
/* cl_device_partition_property_ext list terminators */
|
|
||||||
#define CL_PROPERTIES_LIST_END_EXT ((cl_device_partition_property_ext) 0)
|
|
||||||
#define CL_PARTITION_BY_COUNTS_LIST_END_EXT ((cl_device_partition_property_ext) 0)
|
|
||||||
#define CL_PARTITION_BY_NAMES_LIST_END_EXT ((cl_device_partition_property_ext) 0 - 1)
|
|
||||||
#define CL_PARTITION_BY_NAMES_LIST_END_INTEL ((cl_device_partition_property_ext) 0 - 1)
|
|
||||||
|
|
||||||
#define CL_QUEUE_THREAD_LOCAL_EXEC_ENABLE_INTEL (1 << 31)
|
|
||||||
|
|
||||||
|
|
||||||
/*********************************
|
|
||||||
* cl_qcom_ext_host_ptr extension
|
|
||||||
*********************************/
|
|
||||||
|
|
||||||
#define CL_MEM_EXT_HOST_PTR_QCOM (1 << 29)
|
|
||||||
|
|
||||||
#define CL_DEVICE_EXT_MEM_PADDING_IN_BYTES_QCOM 0x40A0
|
|
||||||
#define CL_DEVICE_PAGE_SIZE_QCOM 0x40A1
|
|
||||||
#define CL_IMAGE_ROW_ALIGNMENT_QCOM 0x40A2
|
|
||||||
#define CL_IMAGE_SLICE_ALIGNMENT_QCOM 0x40A3
|
|
||||||
#define CL_MEM_HOST_UNCACHED_QCOM 0x40A4
|
|
||||||
#define CL_MEM_HOST_WRITEBACK_QCOM 0x40A5
|
|
||||||
#define CL_MEM_HOST_WRITETHROUGH_QCOM 0x40A6
|
|
||||||
#define CL_MEM_HOST_WRITE_COMBINING_QCOM 0x40A7
|
|
||||||
|
|
||||||
typedef cl_uint cl_image_pitch_info_qcom;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clGetDeviceImageInfoQCOM(cl_device_id device,
|
|
||||||
size_t image_width,
|
|
||||||
size_t image_height,
|
|
||||||
const cl_image_format *image_format,
|
|
||||||
cl_image_pitch_info_qcom param_name,
|
|
||||||
size_t param_value_size,
|
|
||||||
void *param_value,
|
|
||||||
size_t *param_value_size_ret);
|
|
||||||
|
|
||||||
typedef struct _cl_mem_ext_host_ptr
|
|
||||||
{
|
|
||||||
/* Type of external memory allocation. */
|
|
||||||
/* Legal values will be defined in layered extensions. */
|
|
||||||
cl_uint allocation_type;
|
|
||||||
|
|
||||||
/* Host cache policy for this external memory allocation. */
|
|
||||||
cl_uint host_cache_policy;
|
|
||||||
|
|
||||||
} cl_mem_ext_host_ptr;
|
|
||||||
|
|
||||||
/*********************************
|
|
||||||
* cl_qcom_ion_host_ptr extension
|
|
||||||
*********************************/
|
|
||||||
|
|
||||||
#define CL_MEM_ION_HOST_PTR_QCOM 0x40A8
|
|
||||||
|
|
||||||
typedef struct _cl_mem_ion_host_ptr
|
|
||||||
{
|
|
||||||
/* Type of external memory allocation. */
|
|
||||||
/* Must be CL_MEM_ION_HOST_PTR_QCOM for ION allocations. */
|
|
||||||
cl_mem_ext_host_ptr ext_host_ptr;
|
|
||||||
|
|
||||||
/* ION file descriptor */
|
|
||||||
int ion_filedesc;
|
|
||||||
|
|
||||||
/* Host pointer to the ION allocated memory */
|
|
||||||
void* ion_hostptr;
|
|
||||||
|
|
||||||
} cl_mem_ion_host_ptr;
|
|
||||||
|
|
||||||
#endif /* CL_VERSION_1_1 */
|
|
||||||
|
|
||||||
|
|
||||||
#ifdef CL_VERSION_2_0
|
|
||||||
/*********************************
|
|
||||||
* cl_khr_sub_groups extension
|
|
||||||
*********************************/
|
|
||||||
#define cl_khr_sub_groups 1
|
|
||||||
|
|
||||||
typedef cl_uint cl_kernel_sub_group_info;
|
|
||||||
|
|
||||||
/* cl_khr_sub_group_info */
|
|
||||||
#define CL_KERNEL_MAX_SUB_GROUP_SIZE_FOR_NDRANGE_KHR 0x2033
|
|
||||||
#define CL_KERNEL_SUB_GROUP_COUNT_FOR_NDRANGE_KHR 0x2034
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clGetKernelSubGroupInfoKHR(cl_kernel /* in_kernel */,
|
|
||||||
cl_device_id /*in_device*/,
|
|
||||||
const 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;
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY cl_int
|
|
||||||
( CL_API_CALL * clGetKernelSubGroupInfoKHR_fn)(cl_kernel /* in_kernel */,
|
|
||||||
cl_device_id /*in_device*/,
|
|
||||||
const 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;
|
|
||||||
#endif /* CL_VERSION_2_0 */
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
}
|
|
||||||
#endif
|
|
||||||
|
|
||||||
|
|
||||||
#endif /* __CL_EXT_H */
|
|
||||||
|
|
@ -1,162 +0,0 @@
|
||||||
/**********************************************************************************
|
|
||||||
* Copyright (c) 2008 - 2013 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_GL_H
|
|
||||||
#define __OPENCL_CL_GL_H
|
|
||||||
|
|
||||||
#ifdef __APPLE__
|
|
||||||
#include <OpenCL/cl.h>
|
|
||||||
#else
|
|
||||||
#include <CL/cl.h>
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
extern "C" {
|
|
||||||
#endif
|
|
||||||
|
|
||||||
typedef cl_uint cl_gl_object_type;
|
|
||||||
typedef cl_uint cl_gl_texture_info;
|
|
||||||
typedef cl_uint cl_gl_platform_info;
|
|
||||||
typedef struct __GLsync *cl_GLsync;
|
|
||||||
|
|
||||||
/* cl_gl_object_type = 0x2000 - 0x200F enum values are currently taken */
|
|
||||||
#define CL_GL_OBJECT_BUFFER 0x2000
|
|
||||||
#define CL_GL_OBJECT_TEXTURE2D 0x2001
|
|
||||||
#define CL_GL_OBJECT_TEXTURE3D 0x2002
|
|
||||||
#define CL_GL_OBJECT_RENDERBUFFER 0x2003
|
|
||||||
#define CL_GL_OBJECT_TEXTURE2D_ARRAY 0x200E
|
|
||||||
#define CL_GL_OBJECT_TEXTURE1D 0x200F
|
|
||||||
#define CL_GL_OBJECT_TEXTURE1D_ARRAY 0x2010
|
|
||||||
#define CL_GL_OBJECT_TEXTURE_BUFFER 0x2011
|
|
||||||
|
|
||||||
/* cl_gl_texture_info */
|
|
||||||
#define CL_GL_TEXTURE_TARGET 0x2004
|
|
||||||
#define CL_GL_MIPMAP_LEVEL 0x2005
|
|
||||||
#define CL_GL_NUM_SAMPLES 0x2012
|
|
||||||
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_mem CL_API_CALL
|
|
||||||
clCreateFromGLBuffer(cl_context /* context */,
|
|
||||||
cl_mem_flags /* flags */,
|
|
||||||
cl_GLuint /* bufobj */,
|
|
||||||
int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_mem CL_API_CALL
|
|
||||||
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;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_mem CL_API_CALL
|
|
||||||
clCreateFromGLRenderbuffer(cl_context /* context */,
|
|
||||||
cl_mem_flags /* flags */,
|
|
||||||
cl_GLuint /* renderbuffer */,
|
|
||||||
cl_int * /* errcode_ret */) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
clGetGLObjectInfo(cl_mem /* memobj */,
|
|
||||||
cl_gl_object_type * /* gl_object_type */,
|
|
||||||
cl_GLuint * /* gl_object_name */) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
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;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
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;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
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;
|
|
||||||
|
|
||||||
|
|
||||||
/* Deprecated OpenCL 1.1 APIs */
|
|
||||||
extern CL_API_ENTRY CL_EXT_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;
|
|
||||||
|
|
||||||
extern CL_API_ENTRY CL_EXT_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_khr_gl_sharing extension */
|
|
||||||
|
|
||||||
#define cl_khr_gl_sharing 1
|
|
||||||
|
|
||||||
typedef cl_uint cl_gl_context_info;
|
|
||||||
|
|
||||||
/* Additional Error Codes */
|
|
||||||
#define CL_INVALID_GL_SHAREGROUP_REFERENCE_KHR -1000
|
|
||||||
|
|
||||||
/* cl_gl_context_info */
|
|
||||||
#define CL_CURRENT_DEVICE_FOR_GL_CONTEXT_KHR 0x2006
|
|
||||||
#define CL_DEVICES_FOR_GL_CONTEXT_KHR 0x2007
|
|
||||||
|
|
||||||
/* Additional cl_context_properties */
|
|
||||||
#define CL_GL_CONTEXT_KHR 0x2008
|
|
||||||
#define CL_EGL_DISPLAY_KHR 0x2009
|
|
||||||
#define CL_GLX_DISPLAY_KHR 0x200A
|
|
||||||
#define CL_WGL_HDC_KHR 0x200B
|
|
||||||
#define CL_CGL_SHAREGROUP_KHR 0x200C
|
|
||||||
|
|
||||||
extern CL_API_ENTRY cl_int CL_API_CALL
|
|
||||||
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_API_SUFFIX__VERSION_1_0;
|
|
||||||
|
|
||||||
typedef CL_API_ENTRY 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);
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
}
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#endif /* __OPENCL_CL_GL_H */
|
|
||||||
|
|
@ -1,69 +0,0 @@
|
||||||
/**********************************************************************************
|
|
||||||
* Copyright (c) 2008-2013 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.
|
|
||||||
**********************************************************************************/
|
|
||||||
|
|
||||||
/* $Revision: 11708 $ on $Date: 2010-06-13 23:36:24 -0700 (Sun, 13 Jun 2010) $ */
|
|
||||||
|
|
||||||
/* cl_gl_ext.h contains vendor (non-KHR) OpenCL extensions which have */
|
|
||||||
/* OpenGL dependencies. */
|
|
||||||
|
|
||||||
#ifndef __OPENCL_CL_GL_EXT_H
|
|
||||||
#define __OPENCL_CL_GL_EXT_H
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
extern "C" {
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#ifdef __APPLE__
|
|
||||||
#include <OpenCL/cl_gl.h>
|
|
||||||
#else
|
|
||||||
#include <CL/cl_gl.h>
|
|
||||||
#endif
|
|
||||||
|
|
||||||
/*
|
|
||||||
* For each extension, follow this template
|
|
||||||
* cl_VEN_extname extension */
|
|
||||||
/* #define cl_VEN_extname 1
|
|
||||||
* ... define new types, if any
|
|
||||||
* ... define new tokens, if any
|
|
||||||
* ... define new APIs, if any
|
|
||||||
*
|
|
||||||
* If you need GLtypes here, mirror them with a cl_GLtype, rather than including a GL header
|
|
||||||
* This allows us to avoid having to decide whether to include GL headers or GLES here.
|
|
||||||
*/
|
|
||||||
|
|
||||||
/*
|
|
||||||
* cl_khr_gl_event extension
|
|
||||||
* See section 9.9 in the OpenCL 1.1 spec for more information
|
|
||||||
*/
|
|
||||||
#define CL_COMMAND_GL_FENCE_SYNC_OBJECT_KHR 0x200D
|
|
||||||
|
|
||||||
extern 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;
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
}
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#endif /* __OPENCL_CL_GL_EXT_H */
|
|
||||||
File diff suppressed because it is too large
Load Diff
|
|
@ -1,54 +0,0 @@
|
||||||
/*******************************************************************************
|
|
||||||
* Copyright (c) 2008-2013 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.
|
|
||||||
******************************************************************************/
|
|
||||||
|
|
||||||
/* $Revision: 11708 $ on $Date: 2010-06-13 23:36:24 -0700 (Sun, 13 Jun 2010) $ */
|
|
||||||
|
|
||||||
#ifndef __OPENCL_H
|
|
||||||
#define __OPENCL_H
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
extern "C" {
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#ifdef __APPLE__
|
|
||||||
|
|
||||||
#include <OpenCL/cl.h>
|
|
||||||
#include <OpenCL/cl_gl.h>
|
|
||||||
#include <OpenCL/cl_gl_ext.h>
|
|
||||||
#include <OpenCL/cl_ext.h>
|
|
||||||
|
|
||||||
#else
|
|
||||||
|
|
||||||
#include <CL/cl.h>
|
|
||||||
#include <CL/cl_gl.h>
|
|
||||||
#include <CL/cl_gl_ext.h>
|
|
||||||
#include <CL/cl_ext.h>
|
|
||||||
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#ifdef __cplusplus
|
|
||||||
}
|
|
||||||
#endif
|
|
||||||
|
|
||||||
#endif /* __OPENCL_H */
|
|
||||||
|
|
||||||
|
|
@ -1,824 +0,0 @@
|
||||||
#include "CL/cl.h"
|
|
||||||
|
|
||||||
typedef cl_int (CL_API_CALL * clGetPlatformIDsPtr)(cl_uint num_entries, cl_platform_id* platforms, cl_uint* num_platforms) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clGetPlatformInfoPtr)(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 * clGetDeviceIDsPtr)(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 * clGetDeviceInfoPtr)(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_int (CL_API_CALL * clCreateSubDevicesPtr)(cl_device_id in_device, const cl_device_partition_property* properties, cl_uint num_devices, cl_device_id* out_devices, cl_uint* num_devices_ret) CL_API_SUFFIX__VERSION_1_2;
|
|
||||||
typedef cl_int (CL_API_CALL * clRetainDevicePtr)(cl_device_id device) CL_API_SUFFIX__VERSION_1_2;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseDevicePtr)(cl_device_id device) CL_API_SUFFIX__VERSION_1_2;
|
|
||||||
typedef cl_context (CL_API_CALL * clCreateContextPtr)(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 * clCreateContextFromTypePtr)(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 * clRetainContextPtr)(cl_context context) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseContextPtr)(cl_context context) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clGetContextInfoPtr)(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 * clCreateCommandQueueWithPropertiesPtr)(cl_context context, cl_device_id device, const cl_queue_properties* properties, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_2_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clRetainCommandQueuePtr)(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseCommandQueuePtr)(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clGetCommandQueueInfoPtr)(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_mem (CL_API_CALL * clCreateBufferPtr)(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 * clCreateSubBufferPtr)(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 * clCreateImagePtr)(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_mem (CL_API_CALL * clCreatePipePtr)(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 * clRetainMemObjectPtr)(cl_mem memobj) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseMemObjectPtr)(cl_mem memobj) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clGetSupportedImageFormatsPtr)(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 * clGetMemObjectInfoPtr)(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 * clGetImageInfoPtr)(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 * clGetPipeInfoPtr)(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 * clSetMemObjectDestructorCallbackPtr)(cl_mem memobj, void (CL_CALLBACK* pfn_notify)(cl_mem memobj, void* user_data), void* user_data) CL_API_SUFFIX__VERSION_1_1;
|
|
||||||
typedef void* (CL_API_CALL * clSVMAllocPtr)(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 * clSVMFreePtr)(cl_context context, void* svm_pointer) CL_API_SUFFIX__VERSION_2_0;
|
|
||||||
typedef cl_sampler (CL_API_CALL * clCreateSamplerWithPropertiesPtr)(cl_context context, const cl_sampler_properties* normalized_coords, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_2_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clRetainSamplerPtr)(cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseSamplerPtr)(cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clGetSamplerInfoPtr)(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;
|
|
||||||
typedef cl_program (CL_API_CALL * clCreateProgramWithSourcePtr)(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 * clCreateProgramWithBinaryPtr)(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_program (CL_API_CALL * clCreateProgramWithBuiltInKernelsPtr)(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 * clRetainProgramPtr)(cl_program program) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseProgramPtr)(cl_program program) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clBuildProgramPtr)(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 * clCompileProgramPtr)(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 * clLinkProgramPtr)(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 * clUnloadPlatformCompilerPtr)(cl_platform_id platform) CL_API_SUFFIX__VERSION_1_2;
|
|
||||||
typedef cl_int (CL_API_CALL * clGetProgramInfoPtr)(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 * clGetProgramBuildInfoPtr)(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;
|
|
||||||
typedef cl_kernel (CL_API_CALL * clCreateKernelPtr)(cl_program program, const char* kernel_name, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clCreateKernelsInProgramPtr)(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 * clRetainKernelPtr)(cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseKernelPtr)(cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clSetKernelArgPtr)(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 * clSetKernelArgSVMPointerPtr)(cl_kernel kernel, cl_uint arg_index, const void* arg_value) CL_API_SUFFIX__VERSION_2_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clSetKernelExecInfoPtr)(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 * clGetKernelInfoPtr)(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 * clGetKernelArgInfoPtr)(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 * clGetKernelWorkGroupInfoPtr)(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;
|
|
||||||
typedef cl_int (CL_API_CALL * clWaitForEventsPtr)(cl_uint num_events, const cl_event* event_list) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clGetEventInfoPtr)(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 * clCreateUserEventPtr)(cl_context context, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_1;
|
|
||||||
typedef cl_int (CL_API_CALL * clRetainEventPtr)(cl_event event) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clReleaseEventPtr)(cl_event event) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clSetUserEventStatusPtr)(cl_event event, cl_int execution_status) CL_API_SUFFIX__VERSION_1_1;
|
|
||||||
typedef cl_int (CL_API_CALL * clSetEventCallbackPtr)(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_int (CL_API_CALL * clGetEventProfilingInfoPtr)(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;
|
|
||||||
typedef cl_int (CL_API_CALL * clFlushPtr)(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clFinishPtr)(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clEnqueueReadBufferPtr)(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_read, size_t offset, size_t size, 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 * clEnqueueReadBufferRectPtr)(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 * clEnqueueWriteBufferPtr)(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_write, size_t offset, size_t size, 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 * clEnqueueWriteBufferRectPtr)(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_write, 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 * clEnqueueFillBufferPtr)(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 * clEnqueueCopyBufferPtr)(cl_command_queue command_queue, cl_mem src_buffer, cl_mem dst_buffer, size_t src_offset, size_t dst_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_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clEnqueueCopyBufferRectPtr)(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 * clEnqueueReadImagePtr)(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_int (CL_API_CALL * clEnqueueWriteImagePtr)(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) CL_API_SUFFIX__VERSION_1_0;
|
|
||||||
typedef cl_int (CL_API_CALL * clEnqueueFillImagePtr)(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 * clEnqueueCopyImagePtr)(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_int (CL_API_CALL * clEnqueueCopyImageToBufferPtr)(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_int (CL_API_CALL * clEnqueueCopyBufferToImagePtr)(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 void* (CL_API_CALL * clEnqueueMapBufferPtr)(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_map, cl_map_flags map_flags, size_t offset, size_t size, 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 * clEnqueueMapImagePtr)(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_int (CL_API_CALL * clEnqueueUnmapMemObjectPtr)(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 * clEnqueueMigrateMemObjectsPtr)(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 * clEnqueueNDRangeKernelPtr)(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 * clEnqueueNativeKernelPtr)(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 * clEnqueueMarkerWithWaitListPtr)(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 * clEnqueueBarrierWithWaitListPtr)(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 * clEnqueueSVMFreePtr)(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 * clEnqueueSVMMemcpyPtr)(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 * clEnqueueSVMMemFillPtr)(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 * clEnqueueSVMMapPtr)(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 * clEnqueueSVMUnmapPtr)(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 void* (CL_API_CALL * clGetExtensionFunctionAddressForPlatformPtr)(cl_platform_id platform, const char* func_name) CL_API_SUFFIX__VERSION_1_2;
|
|
||||||
typedef cl_mem (CL_API_CALL * clCreateImage2DPtr)(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);
|
|
||||||
typedef cl_mem (CL_API_CALL * clCreateImage3DPtr)(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);
|
|
||||||
typedef cl_int (CL_API_CALL * clEnqueueMarkerPtr)(cl_command_queue command_queue, cl_event* event);
|
|
||||||
typedef cl_int (CL_API_CALL * clEnqueueWaitForEventsPtr)(cl_command_queue command_queue, cl_uint num_events, const cl_event* event_list);
|
|
||||||
typedef cl_int (CL_API_CALL * clEnqueueBarrierPtr)(cl_command_queue command_queue);
|
|
||||||
typedef cl_int (CL_API_CALL * clUnloadCompilerPtr)(void);
|
|
||||||
typedef void* (CL_API_CALL * clGetExtensionFunctionAddressPtr)(const char* func_name);
|
|
||||||
typedef cl_command_queue (CL_API_CALL * clCreateCommandQueuePtr)(cl_context context, cl_device_id device, cl_command_queue_properties properties, cl_int* errcode_ret);
|
|
||||||
typedef cl_sampler (CL_API_CALL * clCreateSamplerPtr)(cl_context context, cl_bool normalized_coords, cl_addressing_mode addressing_mode, cl_filter_mode filter_mode, cl_int* errcode_ret);
|
|
||||||
typedef cl_int (CL_API_CALL * clEnqueueTaskPtr)(cl_command_queue command_queue, cl_kernel kernel, cl_uint num_events_in_wait_list, const cl_event* event_wait_list, cl_event* event);
|
|
||||||
|
|
||||||
static clGetPlatformIDsPtr cl_GetPlatformIDs = NULL;
|
|
||||||
static clGetPlatformInfoPtr cl_GetPlatformInfo = NULL;
|
|
||||||
static clGetDeviceIDsPtr cl_GetDeviceIDs = NULL;
|
|
||||||
static clGetDeviceInfoPtr cl_GetDeviceInfo = NULL;
|
|
||||||
static clCreateSubDevicesPtr cl_CreateSubDevices = NULL;
|
|
||||||
static clRetainDevicePtr cl_RetainDevice = NULL;
|
|
||||||
static clReleaseDevicePtr cl_ReleaseDevice = NULL;
|
|
||||||
static clCreateContextPtr cl_CreateContext = NULL;
|
|
||||||
static clCreateContextFromTypePtr cl_CreateContextFromType = NULL;
|
|
||||||
static clRetainContextPtr cl_RetainContext = NULL;
|
|
||||||
static clReleaseContextPtr cl_ReleaseContext = NULL;
|
|
||||||
static clGetContextInfoPtr cl_GetContextInfo = NULL;
|
|
||||||
static clCreateCommandQueueWithPropertiesPtr cl_CreateCommandQueueWithProperties = NULL;
|
|
||||||
static clRetainCommandQueuePtr cl_RetainCommandQueue = NULL;
|
|
||||||
static clReleaseCommandQueuePtr cl_ReleaseCommandQueue = NULL;
|
|
||||||
static clGetCommandQueueInfoPtr cl_GetCommandQueueInfo = NULL;
|
|
||||||
static clCreateBufferPtr cl_CreateBuffer = NULL;
|
|
||||||
static clCreateSubBufferPtr cl_CreateSubBuffer = NULL;
|
|
||||||
static clCreateImagePtr cl_CreateImage = NULL;
|
|
||||||
static clCreatePipePtr cl_CreatePipe = NULL;
|
|
||||||
static clRetainMemObjectPtr cl_RetainMemObject = NULL;
|
|
||||||
static clReleaseMemObjectPtr cl_ReleaseMemObject = NULL;
|
|
||||||
static clGetSupportedImageFormatsPtr cl_GetSupportedImageFormats = NULL;
|
|
||||||
static clGetMemObjectInfoPtr cl_GetMemObjectInfo = NULL;
|
|
||||||
static clGetImageInfoPtr cl_GetImageInfo = NULL;
|
|
||||||
static clGetPipeInfoPtr cl_GetPipeInfo = NULL;
|
|
||||||
static clSetMemObjectDestructorCallbackPtr cl_SetMemObjectDestructorCallback = NULL;
|
|
||||||
static clSVMAllocPtr cl_SVMAlloc = NULL;
|
|
||||||
static clSVMFreePtr cl_SVMFree = NULL;
|
|
||||||
static clCreateSamplerWithPropertiesPtr cl_CreateSamplerWithProperties = NULL;
|
|
||||||
static clRetainSamplerPtr cl_RetainSampler = NULL;
|
|
||||||
static clReleaseSamplerPtr cl_ReleaseSampler = NULL;
|
|
||||||
static clGetSamplerInfoPtr cl_GetSamplerInfo = NULL;
|
|
||||||
static clCreateProgramWithSourcePtr cl_CreateProgramWithSource = NULL;
|
|
||||||
static clCreateProgramWithBinaryPtr cl_CreateProgramWithBinary = NULL;
|
|
||||||
static clCreateProgramWithBuiltInKernelsPtr cl_CreateProgramWithBuiltInKernels = NULL;
|
|
||||||
static clRetainProgramPtr cl_RetainProgram = NULL;
|
|
||||||
static clReleaseProgramPtr cl_ReleaseProgram = NULL;
|
|
||||||
static clBuildProgramPtr cl_BuildProgram = NULL;
|
|
||||||
static clCompileProgramPtr cl_CompileProgram = NULL;
|
|
||||||
static clLinkProgramPtr cl_LinkProgram = NULL;
|
|
||||||
static clUnloadPlatformCompilerPtr cl_UnloadPlatformCompiler = NULL;
|
|
||||||
static clGetProgramInfoPtr cl_GetProgramInfo = NULL;
|
|
||||||
static clGetProgramBuildInfoPtr cl_GetProgramBuildInfo = NULL;
|
|
||||||
static clCreateKernelPtr cl_CreateKernel = NULL;
|
|
||||||
static clCreateKernelsInProgramPtr cl_CreateKernelsInProgram = NULL;
|
|
||||||
static clRetainKernelPtr cl_RetainKernel = NULL;
|
|
||||||
static clReleaseKernelPtr cl_ReleaseKernel = NULL;
|
|
||||||
static clSetKernelArgPtr cl_SetKernelArg = NULL;
|
|
||||||
static clSetKernelArgSVMPointerPtr cl_SetKernelArgSVMPointer = NULL;
|
|
||||||
static clSetKernelExecInfoPtr cl_SetKernelExecInfo = NULL;
|
|
||||||
static clGetKernelInfoPtr cl_GetKernelInfo = NULL;
|
|
||||||
static clGetKernelArgInfoPtr cl_GetKernelArgInfo = NULL;
|
|
||||||
static clGetKernelWorkGroupInfoPtr cl_GetKernelWorkGroupInfo = NULL;
|
|
||||||
static clWaitForEventsPtr cl_WaitForEvents = NULL;
|
|
||||||
static clGetEventInfoPtr cl_GetEventInfo = NULL;
|
|
||||||
static clCreateUserEventPtr cl_CreateUserEvent = NULL;
|
|
||||||
static clRetainEventPtr cl_RetainEvent = NULL;
|
|
||||||
static clReleaseEventPtr cl_ReleaseEvent = NULL;
|
|
||||||
static clSetUserEventStatusPtr cl_SetUserEventStatus = NULL;
|
|
||||||
static clSetEventCallbackPtr cl_SetEventCallback = NULL;
|
|
||||||
static clGetEventProfilingInfoPtr cl_GetEventProfilingInfo = NULL;
|
|
||||||
static clFlushPtr cl_Flush = NULL;
|
|
||||||
static clFinishPtr cl_Finish = NULL;
|
|
||||||
static clEnqueueReadBufferPtr cl_EnqueueReadBuffer = NULL;
|
|
||||||
static clEnqueueReadBufferRectPtr cl_EnqueueReadBufferRect = NULL;
|
|
||||||
static clEnqueueWriteBufferPtr cl_EnqueueWriteBuffer = NULL;
|
|
||||||
static clEnqueueWriteBufferRectPtr cl_EnqueueWriteBufferRect = NULL;
|
|
||||||
static clEnqueueFillBufferPtr cl_EnqueueFillBuffer = NULL;
|
|
||||||
static clEnqueueCopyBufferPtr cl_EnqueueCopyBuffer = NULL;
|
|
||||||
static clEnqueueCopyBufferRectPtr cl_EnqueueCopyBufferRect = NULL;
|
|
||||||
static clEnqueueReadImagePtr cl_EnqueueReadImage = NULL;
|
|
||||||
static clEnqueueWriteImagePtr cl_EnqueueWriteImage = NULL;
|
|
||||||
static clEnqueueFillImagePtr cl_EnqueueFillImage = NULL;
|
|
||||||
static clEnqueueCopyImagePtr cl_EnqueueCopyImage = NULL;
|
|
||||||
static clEnqueueCopyImageToBufferPtr cl_EnqueueCopyImageToBuffer = NULL;
|
|
||||||
static clEnqueueCopyBufferToImagePtr cl_EnqueueCopyBufferToImage = NULL;
|
|
||||||
static clEnqueueMapBufferPtr cl_EnqueueMapBuffer = NULL;
|
|
||||||
static clEnqueueMapImagePtr cl_EnqueueMapImage = NULL;
|
|
||||||
static clEnqueueUnmapMemObjectPtr cl_EnqueueUnmapMemObject = NULL;
|
|
||||||
static clEnqueueMigrateMemObjectsPtr cl_EnqueueMigrateMemObjects = NULL;
|
|
||||||
static clEnqueueNDRangeKernelPtr cl_EnqueueNDRangeKernel = NULL;
|
|
||||||
static clEnqueueNativeKernelPtr cl_EnqueueNativeKernel = NULL;
|
|
||||||
static clEnqueueMarkerWithWaitListPtr cl_EnqueueMarkerWithWaitList = NULL;
|
|
||||||
static clEnqueueBarrierWithWaitListPtr cl_EnqueueBarrierWithWaitList = NULL;
|
|
||||||
static clEnqueueSVMFreePtr cl_EnqueueSVMFree = NULL;
|
|
||||||
static clEnqueueSVMMemcpyPtr cl_EnqueueSVMMemcpy = NULL;
|
|
||||||
static clEnqueueSVMMemFillPtr cl_EnqueueSVMMemFill = NULL;
|
|
||||||
static clEnqueueSVMMapPtr cl_EnqueueSVMMap = NULL;
|
|
||||||
static clEnqueueSVMUnmapPtr cl_EnqueueSVMUnmap = NULL;
|
|
||||||
static clGetExtensionFunctionAddressForPlatformPtr cl_GetExtensionFunctionAddressForPlatform = NULL;
|
|
||||||
static clCreateImage2DPtr cl_CreateImage2D = NULL;
|
|
||||||
static clCreateImage3DPtr cl_CreateImage3D = NULL;
|
|
||||||
static clEnqueueMarkerPtr cl_EnqueueMarker = NULL;
|
|
||||||
static clEnqueueWaitForEventsPtr cl_EnqueueWaitForEvents = NULL;
|
|
||||||
static clEnqueueBarrierPtr cl_EnqueueBarrier = NULL;
|
|
||||||
static clUnloadCompilerPtr cl_UnloadCompiler = NULL;
|
|
||||||
static clGetExtensionFunctionAddressPtr cl_GetExtensionFunctionAddress = NULL;
|
|
||||||
static clCreateCommandQueuePtr cl_CreateCommandQueue = NULL;
|
|
||||||
static clCreateSamplerPtr cl_CreateSampler = NULL;
|
|
||||||
static clEnqueueTaskPtr cl_EnqueueTask = NULL;
|
|
||||||
|
|
||||||
#include <Windows.h>
|
|
||||||
|
|
||||||
static struct Loader
|
|
||||||
{
|
|
||||||
struct Loader()
|
|
||||||
{
|
|
||||||
HMODULE hModule = LoadLibrary("OpenCL.dll");
|
|
||||||
|
|
||||||
if(hModule == NULL) return;
|
|
||||||
|
|
||||||
*(void**)&cl_GetPlatformIDs = GetProcAddress(hModule, "clGetPlatformIDs");
|
|
||||||
*(void**)&cl_GetPlatformInfo = GetProcAddress(hModule, "clGetPlatformInfo");
|
|
||||||
*(void**)&cl_GetDeviceIDs = GetProcAddress(hModule, "clGetDeviceIDs");
|
|
||||||
*(void**)&cl_GetDeviceInfo = GetProcAddress(hModule, "clGetDeviceInfo");
|
|
||||||
*(void**)&cl_CreateSubDevices = GetProcAddress(hModule, "clCreateSubDevices");
|
|
||||||
*(void**)&cl_RetainDevice = GetProcAddress(hModule, "clRetainDevice");
|
|
||||||
*(void**)&cl_ReleaseDevice = GetProcAddress(hModule, "clReleaseDevice");
|
|
||||||
*(void**)&cl_CreateContext = GetProcAddress(hModule, "clCreateContext");
|
|
||||||
*(void**)&cl_CreateContextFromType = GetProcAddress(hModule, "clCreateContextFromType");
|
|
||||||
*(void**)&cl_RetainContext = GetProcAddress(hModule, "clRetainContext");
|
|
||||||
*(void**)&cl_ReleaseContext = GetProcAddress(hModule, "clReleaseContext");
|
|
||||||
*(void**)&cl_GetContextInfo = GetProcAddress(hModule, "clGetContextInfo");
|
|
||||||
*(void**)&cl_CreateCommandQueueWithProperties = GetProcAddress(hModule, "clCreateCommandQueueWithProperties");
|
|
||||||
*(void**)&cl_RetainCommandQueue = GetProcAddress(hModule, "clRetainCommandQueue");
|
|
||||||
*(void**)&cl_ReleaseCommandQueue = GetProcAddress(hModule, "clReleaseCommandQueue");
|
|
||||||
*(void**)&cl_GetCommandQueueInfo = GetProcAddress(hModule, "clGetCommandQueueInfo");
|
|
||||||
*(void**)&cl_CreateBuffer = GetProcAddress(hModule, "clCreateBuffer");
|
|
||||||
*(void**)&cl_CreateSubBuffer = GetProcAddress(hModule, "clCreateSubBuffer");
|
|
||||||
*(void**)&cl_CreateImage = GetProcAddress(hModule, "clCreateImage");
|
|
||||||
*(void**)&cl_CreatePipe = GetProcAddress(hModule, "clCreatePipe");
|
|
||||||
*(void**)&cl_RetainMemObject = GetProcAddress(hModule, "clRetainMemObject");
|
|
||||||
*(void**)&cl_ReleaseMemObject = GetProcAddress(hModule, "clReleaseMemObject");
|
|
||||||
*(void**)&cl_GetSupportedImageFormats = GetProcAddress(hModule, "clGetSupportedImageFormats");
|
|
||||||
*(void**)&cl_GetMemObjectInfo = GetProcAddress(hModule, "clGetMemObjectInfo");
|
|
||||||
*(void**)&cl_GetImageInfo = GetProcAddress(hModule, "clGetImageInfo");
|
|
||||||
*(void**)&cl_GetPipeInfo = GetProcAddress(hModule, "clGetPipeInfo");
|
|
||||||
*(void**)&cl_SetMemObjectDestructorCallback = GetProcAddress(hModule, "clSetMemObjectDestructorCallback");
|
|
||||||
*(void**)&cl_SVMAlloc = GetProcAddress(hModule, "clSVMAlloc");
|
|
||||||
*(void**)&cl_SVMFree = GetProcAddress(hModule, "clSVMFree");
|
|
||||||
*(void**)&cl_CreateSamplerWithProperties = GetProcAddress(hModule, "clCreateSamplerWithProperties");
|
|
||||||
*(void**)&cl_RetainSampler = GetProcAddress(hModule, "clRetainSampler");
|
|
||||||
*(void**)&cl_ReleaseSampler = GetProcAddress(hModule, "clReleaseSampler");
|
|
||||||
*(void**)&cl_GetSamplerInfo = GetProcAddress(hModule, "clGetSamplerInfo");
|
|
||||||
*(void**)&cl_CreateProgramWithSource = GetProcAddress(hModule, "clCreateProgramWithSource");
|
|
||||||
*(void**)&cl_CreateProgramWithBinary = GetProcAddress(hModule, "clCreateProgramWithBinary");
|
|
||||||
*(void**)&cl_CreateProgramWithBuiltInKernels = GetProcAddress(hModule, "clCreateProgramWithBuiltInKernels");
|
|
||||||
*(void**)&cl_RetainProgram = GetProcAddress(hModule, "clRetainProgram");
|
|
||||||
*(void**)&cl_ReleaseProgram = GetProcAddress(hModule, "clReleaseProgram");
|
|
||||||
*(void**)&cl_BuildProgram = GetProcAddress(hModule, "clBuildProgram");
|
|
||||||
*(void**)&cl_CompileProgram = GetProcAddress(hModule, "clCompileProgram");
|
|
||||||
*(void**)&cl_LinkProgram = GetProcAddress(hModule, "clLinkProgram");
|
|
||||||
*(void**)&cl_UnloadPlatformCompiler = GetProcAddress(hModule, "clUnloadPlatformCompiler");
|
|
||||||
*(void**)&cl_GetProgramInfo = GetProcAddress(hModule, "clGetProgramInfo");
|
|
||||||
*(void**)&cl_GetProgramBuildInfo = GetProcAddress(hModule, "clGetProgramBuildInfo");
|
|
||||||
*(void**)&cl_CreateKernel = GetProcAddress(hModule, "clCreateKernel");
|
|
||||||
*(void**)&cl_CreateKernelsInProgram = GetProcAddress(hModule, "clCreateKernelsInProgram");
|
|
||||||
*(void**)&cl_RetainKernel = GetProcAddress(hModule, "clRetainKernel");
|
|
||||||
*(void**)&cl_ReleaseKernel = GetProcAddress(hModule, "clReleaseKernel");
|
|
||||||
*(void**)&cl_SetKernelArg = GetProcAddress(hModule, "clSetKernelArg");
|
|
||||||
*(void**)&cl_SetKernelArgSVMPointer = GetProcAddress(hModule, "clSetKernelArgSVMPointer");
|
|
||||||
*(void**)&cl_SetKernelExecInfo = GetProcAddress(hModule, "clSetKernelExecInfo");
|
|
||||||
*(void**)&cl_GetKernelInfo = GetProcAddress(hModule, "clGetKernelInfo");
|
|
||||||
*(void**)&cl_GetKernelArgInfo = GetProcAddress(hModule, "clGetKernelArgInfo");
|
|
||||||
*(void**)&cl_GetKernelWorkGroupInfo = GetProcAddress(hModule, "clGetKernelWorkGroupInfo");
|
|
||||||
*(void**)&cl_WaitForEvents = GetProcAddress(hModule, "clWaitForEvents");
|
|
||||||
*(void**)&cl_GetEventInfo = GetProcAddress(hModule, "clGetEventInfo");
|
|
||||||
*(void**)&cl_CreateUserEvent = GetProcAddress(hModule, "clCreateUserEvent");
|
|
||||||
*(void**)&cl_RetainEvent = GetProcAddress(hModule, "clRetainEvent");
|
|
||||||
*(void**)&cl_ReleaseEvent = GetProcAddress(hModule, "clReleaseEvent");
|
|
||||||
*(void**)&cl_SetUserEventStatus = GetProcAddress(hModule, "clSetUserEventStatus");
|
|
||||||
*(void**)&cl_SetEventCallback = GetProcAddress(hModule, "clSetEventCallback");
|
|
||||||
*(void**)&cl_GetEventProfilingInfo = GetProcAddress(hModule, "clGetEventProfilingInfo");
|
|
||||||
*(void**)&cl_Flush = GetProcAddress(hModule, "clFlush");
|
|
||||||
*(void**)&cl_Finish = GetProcAddress(hModule, "clFinish");
|
|
||||||
*(void**)&cl_EnqueueReadBuffer = GetProcAddress(hModule, "clEnqueueReadBuffer");
|
|
||||||
*(void**)&cl_EnqueueReadBufferRect = GetProcAddress(hModule, "clEnqueueReadBufferRect");
|
|
||||||
*(void**)&cl_EnqueueWriteBuffer = GetProcAddress(hModule, "clEnqueueWriteBuffer");
|
|
||||||
*(void**)&cl_EnqueueWriteBufferRect = GetProcAddress(hModule, "clEnqueueWriteBufferRect");
|
|
||||||
*(void**)&cl_EnqueueFillBuffer = GetProcAddress(hModule, "clEnqueueFillBuffer");
|
|
||||||
*(void**)&cl_EnqueueCopyBuffer = GetProcAddress(hModule, "clEnqueueCopyBuffer");
|
|
||||||
*(void**)&cl_EnqueueCopyBufferRect = GetProcAddress(hModule, "clEnqueueCopyBufferRect");
|
|
||||||
*(void**)&cl_EnqueueReadImage = GetProcAddress(hModule, "clEnqueueReadImage");
|
|
||||||
*(void**)&cl_EnqueueWriteImage = GetProcAddress(hModule, "clEnqueueWriteImage");
|
|
||||||
*(void**)&cl_EnqueueFillImage = GetProcAddress(hModule, "clEnqueueFillImage");
|
|
||||||
*(void**)&cl_EnqueueCopyImage = GetProcAddress(hModule, "clEnqueueCopyImage");
|
|
||||||
*(void**)&cl_EnqueueCopyImageToBuffer = GetProcAddress(hModule, "clEnqueueCopyImageToBuffer");
|
|
||||||
*(void**)&cl_EnqueueCopyBufferToImage = GetProcAddress(hModule, "clEnqueueCopyBufferToImage");
|
|
||||||
*(void**)&cl_EnqueueMapBuffer = GetProcAddress(hModule, "clEnqueueMapBuffer");
|
|
||||||
*(void**)&cl_EnqueueMapImage = GetProcAddress(hModule, "clEnqueueMapImage");
|
|
||||||
*(void**)&cl_EnqueueUnmapMemObject = GetProcAddress(hModule, "clEnqueueUnmapMemObject");
|
|
||||||
*(void**)&cl_EnqueueMigrateMemObjects = GetProcAddress(hModule, "clEnqueueMigrateMemObjects");
|
|
||||||
*(void**)&cl_EnqueueNDRangeKernel = GetProcAddress(hModule, "clEnqueueNDRangeKernel");
|
|
||||||
*(void**)&cl_EnqueueNativeKernel = GetProcAddress(hModule, "clEnqueueNativeKernel");
|
|
||||||
*(void**)&cl_EnqueueMarkerWithWaitList = GetProcAddress(hModule, "clEnqueueMarkerWithWaitList");
|
|
||||||
*(void**)&cl_EnqueueBarrierWithWaitList = GetProcAddress(hModule, "clEnqueueBarrierWithWaitList");
|
|
||||||
*(void**)&cl_EnqueueSVMFree = GetProcAddress(hModule, "clEnqueueSVMFree");
|
|
||||||
*(void**)&cl_EnqueueSVMMemcpy = GetProcAddress(hModule, "clEnqueueSVMMemcpy");
|
|
||||||
*(void**)&cl_EnqueueSVMMemFill = GetProcAddress(hModule, "clEnqueueSVMMemFill");
|
|
||||||
*(void**)&cl_EnqueueSVMMap = GetProcAddress(hModule, "clEnqueueSVMMap");
|
|
||||||
*(void**)&cl_EnqueueSVMUnmap = GetProcAddress(hModule, "clEnqueueSVMUnmap");
|
|
||||||
*(void**)&cl_GetExtensionFunctionAddressForPlatform = GetProcAddress(hModule, "clGetExtensionFunctionAddressForPlatform");
|
|
||||||
*(void**)&cl_CreateImage2D = GetProcAddress(hModule, "clCreateImage2D");
|
|
||||||
*(void**)&cl_CreateImage3D = GetProcAddress(hModule, "clCreateImage3D");
|
|
||||||
*(void**)&cl_EnqueueMarker = GetProcAddress(hModule, "clEnqueueMarker");
|
|
||||||
*(void**)&cl_EnqueueWaitForEvents = GetProcAddress(hModule, "clEnqueueWaitForEvents");
|
|
||||||
*(void**)&cl_EnqueueBarrier = GetProcAddress(hModule, "clEnqueueBarrier");
|
|
||||||
*(void**)&cl_UnloadCompiler = GetProcAddress(hModule, "clUnloadCompiler");
|
|
||||||
*(void**)&cl_GetExtensionFunctionAddress = GetProcAddress(hModule, "clGetExtensionFunctionAddress");
|
|
||||||
*(void**)&cl_CreateCommandQueue = GetProcAddress(hModule, "clCreateCommandQueue");
|
|
||||||
*(void**)&cl_CreateSampler = GetProcAddress(hModule, "clCreateSampler");
|
|
||||||
*(void**)&cl_EnqueueTask = GetProcAddress(hModule, "clEnqueueTask");
|
|
||||||
}
|
|
||||||
} s_loader;
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clGetPlatformIDs(cl_uint num_entries, cl_platform_id* platforms, cl_uint* num_platforms) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetPlatformIDs(num_entries, platforms, num_platforms);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetPlatformInfo(platform, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetDeviceIDs(platform, device_type, num_entries, devices, num_devices);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetDeviceInfo(device, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clCreateSubDevices(cl_device_id in_device, const cl_device_partition_property* properties, cl_uint num_devices, cl_device_id* out_devices, cl_uint* num_devices_ret) CL_API_SUFFIX__VERSION_1_2
|
|
||||||
{
|
|
||||||
return cl_CreateSubDevices(in_device, properties, num_devices, out_devices, num_devices_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainDevice(cl_device_id device) CL_API_SUFFIX__VERSION_1_2
|
|
||||||
{
|
|
||||||
return cl_RetainDevice(device);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseDevice(cl_device_id device) CL_API_SUFFIX__VERSION_1_2
|
|
||||||
{
|
|
||||||
return cl_ReleaseDevice(device);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_CreateContext(properties, num_devices, devices, pfn_notify, user_data, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_CreateContextFromType(properties, device_type, pfn_notify, user_data, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainContext(cl_context context) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_RetainContext(context);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseContext(cl_context context) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_ReleaseContext(context);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetContextInfo(context, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_command_queue CL_API_CALL clCreateCommandQueueWithProperties(cl_context context, cl_device_id device, const cl_queue_properties* properties, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_2_0
|
|
||||||
{
|
|
||||||
return cl_CreateCommandQueueWithProperties(context, device, properties, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainCommandQueue(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_RetainCommandQueue(command_queue);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseCommandQueue(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_ReleaseCommandQueue(command_queue);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetCommandQueueInfo(command_queue, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_mem CL_API_CALL clCreateBuffer(cl_context context, cl_mem_flags flags, size_t size, void* host_ptr, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_CreateBuffer(context, flags, size, host_ptr, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_mem CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_CreateSubBuffer(buffer, flags, buffer_create_type, buffer_create_info, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_mem CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_CreateImage(context, flags, image_format, image_desc, host_ptr, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_mem CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_CreatePipe(context, flags, pipe_packet_size, pipe_max_packets, properties, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainMemObject(cl_mem memobj) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_RetainMemObject(memobj);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseMemObject(cl_mem memobj) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_ReleaseMemObject(memobj);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetSupportedImageFormats(context, flags, image_type, num_entries, image_formats, num_image_formats);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetMemObjectInfo(memobj, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetImageInfo(image, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_GetPipeInfo(pipe, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clSetMemObjectDestructorCallback(cl_mem memobj, void (CL_CALLBACK* pfn_notify)(cl_mem memobj, void* user_data), void* user_data) CL_API_SUFFIX__VERSION_1_1
|
|
||||||
{
|
|
||||||
return cl_SetMemObjectDestructorCallback(memobj, pfn_notify, user_data);
|
|
||||||
}
|
|
||||||
|
|
||||||
void* CL_API_CALL clSVMAlloc(cl_context context, cl_svm_mem_flags flags, size_t size, cl_uint alignment) CL_API_SUFFIX__VERSION_2_0
|
|
||||||
{
|
|
||||||
return cl_SVMAlloc(context, flags, size, alignment);
|
|
||||||
}
|
|
||||||
|
|
||||||
void CL_API_CALL clSVMFree(cl_context context, void* svm_pointer) CL_API_SUFFIX__VERSION_2_0
|
|
||||||
{
|
|
||||||
cl_SVMFree(context, svm_pointer);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_sampler CL_API_CALL clCreateSamplerWithProperties(cl_context context, const cl_sampler_properties* normalized_coords, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_2_0
|
|
||||||
{
|
|
||||||
return cl_CreateSamplerWithProperties(context, normalized_coords, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainSampler(cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_RetainSampler(sampler);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseSampler(cl_sampler sampler) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_ReleaseSampler(sampler);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetSamplerInfo(sampler, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_program CL_API_CALL clCreateProgramWithSource(cl_context context, cl_uint count, const char** strings, const size_t* lengths, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_CreateProgramWithSource(context, count, strings, lengths, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_CreateProgramWithBinary(context, num_devices, device_list, lengths, binaries, binary_status, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_program CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_CreateProgramWithBuiltInKernels(context, num_devices, device_list, kernel_names, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainProgram(cl_program program) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_RetainProgram(program);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseProgram(cl_program program) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_ReleaseProgram(program);
|
|
||||||
}
|
|
||||||
|
|
||||||
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* user_data), void* user_data) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_BuildProgram(program, num_devices, device_list, options, pfn_notify, user_data);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_CompileProgram(program, num_devices, device_list, options, num_input_headers, input_headers, header_include_names, pfn_notify, user_data);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_program CL_API_CALL 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, void (CL_CALLBACK* pfn_notify)(cl_program program, void* user_data), void* user_data, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_2
|
|
||||||
{
|
|
||||||
return cl_LinkProgram(context, num_devices, device_list, options, num_input_programs, input_programs, pfn_notify, user_data, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clUnloadPlatformCompiler(cl_platform_id platform) CL_API_SUFFIX__VERSION_1_2
|
|
||||||
{
|
|
||||||
return cl_UnloadPlatformCompiler(platform);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetProgramInfo(program, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetProgramBuildInfo(program, device, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_kernel CL_API_CALL clCreateKernel(cl_program program, const char* kernel_name, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_CreateKernel(program, kernel_name, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clCreateKernelsInProgram(cl_program program, cl_uint num_kernels, cl_kernel* kernels, cl_uint* num_kernels_ret) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_CreateKernelsInProgram(program, num_kernels, kernels, num_kernels_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainKernel(cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_RetainKernel(kernel);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseKernel(cl_kernel kernel) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_ReleaseKernel(kernel);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clSetKernelArg(cl_kernel kernel, cl_uint arg_index, size_t arg_size, const void* arg_value) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_SetKernelArg(kernel, arg_index, arg_size, arg_value);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clSetKernelArgSVMPointer(cl_kernel kernel, cl_uint arg_index, const void* arg_value) CL_API_SUFFIX__VERSION_2_0
|
|
||||||
{
|
|
||||||
return cl_SetKernelArgSVMPointer(kernel, arg_index, arg_value);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_SetKernelExecInfo(kernel, param_name, param_value_size, param_value);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetKernelInfo(kernel, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_GetKernelArgInfo(kernel, arg_indx, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetKernelWorkGroupInfo(kernel, device, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clWaitForEvents(cl_uint num_events, const cl_event* event_list) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_WaitForEvents(num_events, event_list);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetEventInfo(event, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_event CL_API_CALL clCreateUserEvent(cl_context context, cl_int* errcode_ret) CL_API_SUFFIX__VERSION_1_1
|
|
||||||
{
|
|
||||||
return cl_CreateUserEvent(context, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clRetainEvent(cl_event event) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_RetainEvent(event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clReleaseEvent(cl_event event) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_ReleaseEvent(event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clSetUserEventStatus(cl_event event, cl_int execution_status) CL_API_SUFFIX__VERSION_1_1
|
|
||||||
{
|
|
||||||
return cl_SetUserEventStatus(event, execution_status);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_SetEventCallback(event, command_exec_callback_type, pfn_notify, user_data);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_GetEventProfilingInfo(event, param_name, param_value_size, param_value, param_value_size_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clFlush(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_Flush(command_queue);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clFinish(cl_command_queue command_queue) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_Finish(command_queue);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueReadBuffer(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_read, size_t offset, size_t size, void* ptr, cl_uint num_events_in_wait_list, const cl_event* event_wait_list, cl_event* event) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueReadBuffer(command_queue, buffer, blocking_read, offset, size, ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueReadBufferRect(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
|
|
||||||
{
|
|
||||||
return cl_EnqueueReadBufferRect(command_queue, buffer, blocking_read, buffer_offset, host_offset, region, buffer_row_pitch, buffer_slice_pitch, host_row_pitch, host_slice_pitch, ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueWriteBuffer(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_write, size_t offset, size_t size, 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueWriteBuffer(command_queue, buffer, blocking_write, offset, size, ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueWriteBufferRect(cl_command_queue command_queue, cl_mem buffer, cl_bool blocking_write, 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueWriteBufferRect(command_queue, buffer, blocking_write, buffer_offset, host_offset, region, buffer_row_pitch, buffer_slice_pitch, host_row_pitch, host_slice_pitch, ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueFillBuffer(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
|
|
||||||
{
|
|
||||||
return cl_EnqueueFillBuffer(command_queue, buffer, pattern, pattern_size, offset, size, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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 size, cl_uint num_events_in_wait_list, const cl_event* event_wait_list, cl_event* event) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueCopyBuffer(command_queue, src_buffer, dst_buffer, src_offset, dst_offset, size, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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, 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueCopyBufferRect(command_queue, src_buffer, dst_buffer, src_origin, dst_origin, region, src_row_pitch, src_slice_pitch, dst_row_pitch, dst_slice_pitch, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueReadImage(command_queue, image, blocking_read, origin, region, row_pitch, slice_pitch, ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueWriteImage(command_queue, image, blocking_write, origin, region, input_row_pitch, input_slice_pitch, ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueFillImage(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
|
|
||||||
{
|
|
||||||
return cl_EnqueueFillImage(command_queue, image, fill_color, origin, region, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueCopyImage(command_queue, src_image, dst_image, src_origin, dst_origin, region, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueCopyImageToBuffer(command_queue, src_image, dst_buffer, src_origin, region, dst_offset, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueCopyBufferToImage(command_queue, src_buffer, dst_image, src_offset, dst_origin, region, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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 size, 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueMapBuffer(command_queue, buffer, blocking_map, map_flags, offset, size, num_events_in_wait_list, event_wait_list, event, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueMapImage(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);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueUnmapMemObject(command_queue, memobj, mapped_ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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, cl_event* event) CL_API_SUFFIX__VERSION_1_2
|
|
||||||
{
|
|
||||||
return cl_EnqueueMigrateMemObjects(command_queue, num_mem_objects, mem_objects, flags, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
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) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueNDRangeKernel(command_queue, kernel, work_dim, global_work_offset, global_work_size, local_work_size, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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, const cl_event* event_wait_list, cl_event* event) CL_API_SUFFIX__VERSION_1_0
|
|
||||||
{
|
|
||||||
return cl_EnqueueNativeKernel(command_queue, user_func, args, cb_args, num_mem_objects, mem_list, args_mem_loc, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueMarkerWithWaitList(command_queue, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueBarrierWithWaitList(command_queue, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueSVMFree(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
|
|
||||||
{
|
|
||||||
return cl_EnqueueSVMFree(command_queue, num_svm_pointers, svm_pointers, pfn_free_func, user_data, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueSVMMemcpy(command_queue, blocking_copy, dst_ptr, src_ptr, size, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL 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
|
|
||||||
{
|
|
||||||
return cl_EnqueueSVMMemFill(command_queue, svm_ptr, pattern, pattern_size, size, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueSVMMap(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
|
|
||||||
{
|
|
||||||
return cl_EnqueueSVMMap(command_queue, blocking_map, flags, svm_ptr, size, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueSVMUnmap(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
|
|
||||||
{
|
|
||||||
return cl_EnqueueSVMUnmap(command_queue, svm_ptr, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
void* CL_API_CALL clGetExtensionFunctionAddressForPlatform(cl_platform_id platform, const char* func_name) CL_API_SUFFIX__VERSION_1_2
|
|
||||||
{
|
|
||||||
return cl_GetExtensionFunctionAddressForPlatform(platform, func_name);
|
|
||||||
}
|
|
||||||
|
|
||||||
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)
|
|
||||||
{
|
|
||||||
return cl_CreateImage2D(context, flags, image_format, image_width, image_height, image_row_pitch, host_ptr, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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)
|
|
||||||
{
|
|
||||||
return cl_CreateImage3D(context, flags, image_format, image_width, image_height, image_depth, image_row_pitch, image_slice_pitch, host_ptr, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueMarker(cl_command_queue command_queue, cl_event* event)
|
|
||||||
{
|
|
||||||
return cl_EnqueueMarker(command_queue, event);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueWaitForEvents(cl_command_queue command_queue, cl_uint num_events, const cl_event* event_list)
|
|
||||||
{
|
|
||||||
return cl_EnqueueWaitForEvents(command_queue, num_events, event_list);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clEnqueueBarrier(cl_command_queue command_queue)
|
|
||||||
{
|
|
||||||
return cl_EnqueueBarrier(command_queue);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_int CL_API_CALL clUnloadCompiler(void)
|
|
||||||
{
|
|
||||||
return cl_UnloadCompiler();
|
|
||||||
}
|
|
||||||
|
|
||||||
void* CL_API_CALL clGetExtensionFunctionAddress(const char* func_name)
|
|
||||||
{
|
|
||||||
return cl_GetExtensionFunctionAddress(func_name);
|
|
||||||
}
|
|
||||||
|
|
||||||
cl_command_queue CL_API_CALL clCreateCommandQueue(cl_context context, cl_device_id device, cl_command_queue_properties properties, cl_int* errcode_ret)
|
|
||||||
{
|
|
||||||
return cl_CreateCommandQueue(context, device, properties, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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)
|
|
||||||
{
|
|
||||||
return cl_CreateSampler(context, normalized_coords, addressing_mode, filter_mode, errcode_ret);
|
|
||||||
}
|
|
||||||
|
|
||||||
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)
|
|
||||||
{
|
|
||||||
return cl_EnqueueTask(command_queue, kernel, num_events_in_wait_list, event_wait_list, event);
|
|
||||||
}
|
|
||||||
|
|
@ -1,62 +0,0 @@
|
||||||
<?xml version="1.0" encoding="utf-8"?>
|
|
||||||
<Project DefaultTargets="Build" xmlns="http://schemas.microsoft.com/developer/msbuild/2003">
|
|
||||||
<ItemGroup Label="ProjectConfigurations">
|
|
||||||
<ProjectConfiguration Include="Debug|Win32">
|
|
||||||
<Configuration>Debug</Configuration>
|
|
||||||
<Platform>Win32</Platform>
|
|
||||||
</ProjectConfiguration>
|
|
||||||
<ProjectConfiguration Include="Debug|x64">
|
|
||||||
<Configuration>Debug</Configuration>
|
|
||||||
<Platform>x64</Platform>
|
|
||||||
</ProjectConfiguration>
|
|
||||||
<ProjectConfiguration Include="Release|Win32">
|
|
||||||
<Configuration>Release</Configuration>
|
|
||||||
<Platform>Win32</Platform>
|
|
||||||
</ProjectConfiguration>
|
|
||||||
<ProjectConfiguration Include="Release|x64">
|
|
||||||
<Configuration>Release</Configuration>
|
|
||||||
<Platform>x64</Platform>
|
|
||||||
</ProjectConfiguration>
|
|
||||||
</ItemGroup>
|
|
||||||
<Import Project="$(SolutionDir)common\vsprops\WinSDK.props" />
|
|
||||||
<PropertyGroup Label="Globals">
|
|
||||||
<ProjectGuid>{D80D4A75-C385-41BD-AE62-83D2E2B595A7}</ProjectGuid>
|
|
||||||
</PropertyGroup>
|
|
||||||
<Import Project="$(VCTargetsPath)\Microsoft.Cpp.Default.props" />
|
|
||||||
<PropertyGroup Label="Configuration">
|
|
||||||
<ConfigurationType>StaticLibrary</ConfigurationType>
|
|
||||||
<PlatformToolset>$(DefaultPlatformToolset)</PlatformToolset>
|
|
||||||
<CharacterSet>MultiByte</CharacterSet>
|
|
||||||
<WholeProgramOptimization Condition="$(Configuration.Contains(Release))">true</WholeProgramOptimization>
|
|
||||||
<UseDebugLibraries Condition="$(Configuration.Contains(Debug))">true</UseDebugLibraries>
|
|
||||||
<UseDebugLibraries Condition="!$(Configuration.Contains(Debug))">false</UseDebugLibraries>
|
|
||||||
</PropertyGroup>
|
|
||||||
<Import Project="$(VCTargetsPath)\Microsoft.Cpp.props" />
|
|
||||||
<ImportGroup Label="ExtensionSettings" />
|
|
||||||
<ImportGroup Label="PropertySheets">
|
|
||||||
<Import Project="..\DefaultProjectRootDir.props" />
|
|
||||||
<Import Project="..\3rdparty.props" />
|
|
||||||
<Import Condition="$(Configuration.Contains(Debug))" Project="..\..\common\vsprops\CodeGen_Debug.props" />
|
|
||||||
<Import Condition="$(Configuration.Contains(Release))" Project="..\..\common\vsprops\CodeGen_Release.props" />
|
|
||||||
<Import Condition="!$(Configuration.Contains(Release))" Project="..\..\common\vsprops\IncrementalLinking.props" />
|
|
||||||
</ImportGroup>
|
|
||||||
<PropertyGroup Label="UserMacros" />
|
|
||||||
<PropertyGroup>
|
|
||||||
<CodeAnalysisRuleSet>AllRules.ruleset</CodeAnalysisRuleSet>
|
|
||||||
</PropertyGroup>
|
|
||||||
<ItemGroup>
|
|
||||||
<ClInclude Include="CL\cl.h" />
|
|
||||||
<ClInclude Include="CL\cl.hpp" />
|
|
||||||
<ClInclude Include="CL\cl_d3d10.h" />
|
|
||||||
<ClInclude Include="CL\cl_ext.h" />
|
|
||||||
<ClInclude Include="CL\cl_gl.h" />
|
|
||||||
<ClInclude Include="CL\cl_gl_ext.h" />
|
|
||||||
<ClInclude Include="CL\cl_platform.h" />
|
|
||||||
<ClInclude Include="CL\opencl.h" />
|
|
||||||
</ItemGroup>
|
|
||||||
<ItemGroup>
|
|
||||||
<ClCompile Include="opencl.cpp" />
|
|
||||||
</ItemGroup>
|
|
||||||
<Import Project="$(VCTargetsPath)\Microsoft.Cpp.targets" />
|
|
||||||
<ImportGroup Label="ExtensionTargets" />
|
|
||||||
</Project>
|
|
||||||
|
|
@ -1,48 +0,0 @@
|
||||||
<?xml version="1.0" encoding="utf-8"?>
|
|
||||||
<Project ToolsVersion="4.0" xmlns="http://schemas.microsoft.com/developer/msbuild/2003">
|
|
||||||
<ItemGroup>
|
|
||||||
<Filter Include="Source Files">
|
|
||||||
<UniqueIdentifier>{4FC737F1-C7A5-4376-A066-2A32D752A2FF}</UniqueIdentifier>
|
|
||||||
<Extensions>cpp;c;cc;cxx;def;odl;idl;hpj;bat;asm;asmx</Extensions>
|
|
||||||
</Filter>
|
|
||||||
<Filter Include="Header Files">
|
|
||||||
<UniqueIdentifier>{93995380-89BD-4b04-88EB-625FBE52EBFB}</UniqueIdentifier>
|
|
||||||
<Extensions>h;hh;hpp;hxx;hm;inl;inc;xsd</Extensions>
|
|
||||||
</Filter>
|
|
||||||
<Filter Include="Resource Files">
|
|
||||||
<UniqueIdentifier>{67DA6AB6-F800-4c08-8B7A-83BB121AAD01}</UniqueIdentifier>
|
|
||||||
<Extensions>rc;ico;cur;bmp;dlg;rc2;rct;bin;rgs;gif;jpg;jpeg;jpe;resx;tiff;tif;png;wav;mfcribbon-ms</Extensions>
|
|
||||||
</Filter>
|
|
||||||
</ItemGroup>
|
|
||||||
<ItemGroup>
|
|
||||||
<ClInclude Include="CL\cl.h">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
<ClInclude Include="CL\cl.hpp">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
<ClInclude Include="CL\cl_d3d10.h">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
<ClInclude Include="CL\cl_ext.h">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
<ClInclude Include="CL\cl_gl.h">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
<ClInclude Include="CL\cl_gl_ext.h">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
<ClInclude Include="CL\cl_platform.h">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
<ClInclude Include="CL\opencl.h">
|
|
||||||
<Filter>Header Files</Filter>
|
|
||||||
</ClInclude>
|
|
||||||
</ItemGroup>
|
|
||||||
<ItemGroup>
|
|
||||||
<ClCompile Include="opencl.cpp">
|
|
||||||
<Filter>Source Files</Filter>
|
|
||||||
</ClCompile>
|
|
||||||
</ItemGroup>
|
|
||||||
</Project>
|
|
||||||
Loading…
Reference in New Issue