4012 lines
110 KiB
C++
4012 lines
110 KiB
C++
|
/*******************************************************************************
|
||
|
* Copyright (c) 2008-2010 The Khronos Group Inc.
|
||
|
*
|
||
|
* Permission is hereby granted, free of charge, to any person obtaining a
|
||
|
* copy of this software and/or associated documentation files (the
|
||
|
* "Materials"), to deal in the Materials without restriction, including
|
||
|
* without limitation the rights to use, copy, modify, merge, publish,
|
||
|
* distribute, sublicense, and/or sell copies of the Materials, and to
|
||
|
* permit persons to whom the Materials are furnished to do so, subject to
|
||
|
* the following conditions:
|
||
|
*
|
||
|
* The above copyright notice and this permission notice shall be included
|
||
|
* in all copies or substantial portions of the Materials.
|
||
|
*
|
||
|
* THE MATERIALS ARE PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND,
|
||
|
* EXPRESS OR IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF
|
||
|
* MERCHANTABILITY, FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.
|
||
|
* IN NO EVENT SHALL THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY
|
||
|
* CLAIM, DAMAGES OR OTHER LIABILITY, WHETHER IN AN ACTION OF CONTRACT,
|
||
|
* TORT OR OTHERWISE, ARISING FROM, OUT OF OR IN CONNECTION WITH THE
|
||
|
* MATERIALS OR THE USE OR OTHER DEALINGS IN THE MATERIALS.
|
||
|
******************************************************************************/
|
||
|
|
||
|
/*! \file
|
||
|
*
|
||
|
* \brief C++ bindings for OpenCL 1.0 (rev 48) and OpenCL 1.1 (rev 33)
|
||
|
* \author Benedict R. Gaster and Laurent Morichetti
|
||
|
*
|
||
|
* Additions and fixes from Brian Cole, March 3rd 2010.
|
||
|
*
|
||
|
* \version 1.1
|
||
|
* \date June 2010
|
||
|
*
|
||
|
* Optional extension support
|
||
|
*
|
||
|
* cl
|
||
|
* cl_ext_device_fission
|
||
|
* #define USE_CL_DEVICE_FISSION
|
||
|
*/
|
||
|
|
||
|
/*! \mainpage
|
||
|
* \section intro Introduction
|
||
|
* For many large applications C++ is the language of choice and so it seems
|
||
|
* reasonable to define C++ bindings for OpenCL.
|
||
|
*
|
||
|
*
|
||
|
* The interface is contained with a single C++ header file \em cl.hpp and all
|
||
|
* definitions are contained within the namespace \em cl. There is no additional
|
||
|
* requirement to include \em cl.h and to use either the C++ or original C
|
||
|
* bindings it is enough to simply include \em cl.hpp.
|
||
|
*
|
||
|
* The bindings themselves are lightweight and correspond closely to the
|
||
|
* underlying C API. Using the C++ bindings introduces no additional execution
|
||
|
* overhead.
|
||
|
*
|
||
|
* For detail documentation on the bindings see:
|
||
|
*
|
||
|
* The OpenCL C++ Wrapper API 1.1 (revision 04)
|
||
|
* http://www.khronos.org/registry/cl/specs/opencl-cplusplus-1.1.pdf
|
||
|
*
|
||
|
* \section example Example
|
||
|
*
|
||
|
* The following example shows a general use case for the C++
|
||
|
* bindings, including support for the optional exception feature and
|
||
|
* also the supplied vector and string classes, see following sections for
|
||
|
* decriptions of these features.
|
||
|
*
|
||
|
* \code
|
||
|
* #define __CL_ENABLE_EXCEPTIONS
|
||
|
*
|
||
|
* #if defined(__APPLE__) || defined(__MACOSX)
|
||
|
* #include <OpenCL/cl.hpp>
|
||
|
* #else
|
||
|
* #include <CL/cl.hpp>
|
||
|
* #endif
|
||
|
* #include <cstdio>
|
||
|
* #include <cstdlib>
|
||
|
* #include <iostream>
|
||
|
*
|
||
|
* const char * helloStr = "__kernel void "
|
||
|
* "hello(void) "
|
||
|
* "{ "
|
||
|
* " "
|
||
|
* "} ";
|
||
|
*
|
||
|
* int
|
||
|
* main(void)
|
||
|
* {
|
||
|
* cl_int err = CL_SUCCESS;
|
||
|
* try {
|
||
|
*
|
||
|
* std::vector<cl::Platform> platforms;
|
||
|
* cl::Platform::get(&platforms);
|
||
|
* if (platforms.size() == 0) {
|
||
|
* std::cout << "Platform size 0\n";
|
||
|
* return -1;
|
||
|
* }
|
||
|
*
|
||
|
* cl_context_properties properties[] =
|
||
|
* { CL_CONTEXT_PLATFORM, (cl_context_properties)(platforms[0])(), 0};
|
||
|
* cl::Context context(CL_DEVICE_TYPE_CPU, properties);
|
||
|
*
|
||
|
* std::vector<cl::Device> devices = context.getInfo<CL_CONTEXT_DEVICES>();
|
||
|
*
|
||
|
* cl::Program::Sources source(1,
|
||
|
* std::make_pair(helloStr,strlen(helloStr)));
|
||
|
* cl::Program program_ = cl::Program(context, source);
|
||
|
* program_.build(devices);
|
||
|
*
|
||
|
* cl::Kernel kernel(program_, "hello", &err);
|
||
|
*
|
||
|
* cl::Event event;
|
||
|
* cl::CommandQueue queue(context, devices[0], 0, &err);
|
||
|
* queue.enqueueNDRangeKernel(
|
||
|
* kernel,
|
||
|
* cl::NullRange,
|
||
|
* cl::NDRange(4,4),
|
||
|
* cl::NullRange,
|
||
|
* NULL,
|
||
|
* &event);
|
||
|
*
|
||
|
* event.wait();
|
||
|
* }
|
||
|
* catch (cl::Error err) {
|
||
|
* std::cerr
|
||
|
* << "ERROR: "
|
||
|
* << err.what()
|
||
|
* << "("
|
||
|
* << err.err()
|
||
|
* << ")"
|
||
|
* << std::endl;
|
||
|
* }
|
||
|
*
|
||
|
* return EXIT_SUCCESS;
|
||
|
* }
|
||
|
*
|
||
|
* \endcode
|
||
|
*
|
||
|
*/
|
||
|
#ifndef CL_HPP_
|
||
|
#define CL_HPP_
|
||
|
|
||
|
#ifdef _WIN32
|
||
|
#include <windows.h>
|
||
|
#include <malloc.h>
|
||
|
#if defined(USE_DX_INTEROP)
|
||
|
#include <CL/cl_d3d10.h>
|
||
|
#endif
|
||
|
#endif // _WIN32
|
||
|
|
||
|
//
|
||
|
#if defined(USE_CL_DEVICE_FISSION)
|
||
|
#include <CL/cl_ext.h>
|
||
|
#endif
|
||
|
|
||
|
#if defined(__APPLE__) || defined(__MACOSX)
|
||
|
#include <OpenGL/OpenGL.h>
|
||
|
#include <OpenCL/opencl.h>
|
||
|
#else
|
||
|
#include <GL/gl.h>
|
||
|
#include <CL/opencl.h>
|
||
|
#endif // !__APPLE__
|
||
|
|
||
|
#if !defined(CL_CALLBACK)
|
||
|
#define CL_CALLBACK
|
||
|
#endif //CL_CALLBACK
|
||
|
|
||
|
#include <utility>
|
||
|
|
||
|
#if !defined(__NO_STD_VECTOR)
|
||
|
#include <vector>
|
||
|
#endif
|
||
|
|
||
|
#if !defined(__NO_STD_STRING)
|
||
|
#include <string>
|
||
|
#endif
|
||
|
|
||
|
#if defined(linux) || defined(__APPLE__) || defined(__MACOSX)
|
||
|
# include <alloca.h>
|
||
|
#endif // linux
|
||
|
|
||
|
#include <cstring>
|
||
|
|
||
|
/*! \namespace cl
|
||
|
*
|
||
|
* \brief The OpenCL C++ bindings are defined within this namespace.
|
||
|
*
|
||
|
*/
|
||
|
namespace cl {
|
||
|
|
||
|
#define __INIT_CL_EXT_FCN_PTR(name) \
|
||
|
if(!pfn_##name) { \
|
||
|
pfn_##name = (PFN_##name) \
|
||
|
clGetExtensionFunctionAddress(#name); \
|
||
|
if(!pfn_##name) { \
|
||
|
} \
|
||
|
}
|
||
|
|
||
|
class Program;
|
||
|
class Device;
|
||
|
class Context;
|
||
|
class CommandQueue;
|
||
|
class Memory;
|
||
|
|
||
|
#if defined(__CL_ENABLE_EXCEPTIONS)
|
||
|
#include <exception>
|
||
|
/*! \class Error
|
||
|
* \brief Exception class
|
||
|
*/
|
||
|
class Error : public std::exception
|
||
|
{
|
||
|
private:
|
||
|
cl_int err_;
|
||
|
const char * errStr_;
|
||
|
public:
|
||
|
/*! Create a new CL error exception for a given error code
|
||
|
* and corresponding message.
|
||
|
*/
|
||
|
Error(cl_int err, const char * errStr = NULL) : err_(err), errStr_(errStr)
|
||
|
{}
|
||
|
|
||
|
~Error() throw() {}
|
||
|
|
||
|
/*! \brief Get error string associated with exception
|
||
|
*
|
||
|
* \return A memory pointer to the error message string.
|
||
|
*/
|
||
|
virtual const char * what() const throw ()
|
||
|
{
|
||
|
if (errStr_ == NULL) {
|
||
|
return "empty";
|
||
|
}
|
||
|
else {
|
||
|
return errStr_;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
/*! \brief Get error code associated with exception
|
||
|
*
|
||
|
* \return The error code.
|
||
|
*/
|
||
|
const cl_int err(void) const { return err_; }
|
||
|
};
|
||
|
|
||
|
#define __ERR_STR(x) #x
|
||
|
#else
|
||
|
#define __ERR_STR(x) NULL
|
||
|
#endif // __CL_ENABLE_EXCEPTIONS
|
||
|
|
||
|
//! \cond DOXYGEN_DETAIL
|
||
|
#if !defined(__CL_USER_OVERRIDE_ERROR_STRINGS)
|
||
|
#define __GET_DEVICE_INFO_ERR __ERR_STR(clgetDeviceInfo)
|
||
|
#define __GET_PLATFORM_INFO_ERR __ERR_STR(clGetPlatformInfo)
|
||
|
#define __GET_DEVICE_IDS_ERR __ERR_STR(clGetDeviceIDs)
|
||
|
#define __GET_PLATFORM_IDS_ERR __ERR_STR(clGetPlatformIDs)
|
||
|
#define __GET_CONTEXT_INFO_ERR __ERR_STR(clGetContextInfo)
|
||
|
#define __GET_EVENT_INFO_ERR __ERR_STR(clGetEventInfo)
|
||
|
#define __GET_EVENT_PROFILE_INFO_ERR __ERR_STR(clGetEventProfileInfo)
|
||
|
#define __GET_MEM_OBJECT_INFO_ERR __ERR_STR(clGetMemObjectInfo)
|
||
|
#define __GET_IMAGE_INFO_ERR __ERR_STR(clGetImageInfo)
|
||
|
#define __GET_SAMPLER_INFO_ERR __ERR_STR(clGetSamplerInfo)
|
||
|
#define __GET_KERNEL_INFO_ERR __ERR_STR(clGetKernelInfo)
|
||
|
#define __GET_KERNEL_WORK_GROUP_INFO_ERR __ERR_STR(clGetKernelWorkGroupInfo)
|
||
|
#define __GET_PROGRAM_INFO_ERR __ERR_STR(clGetProgramInfo)
|
||
|
#define __GET_PROGRAM_BUILD_INFO_ERR __ERR_STR(clGetProgramBuildInfo)
|
||
|
#define __GET_COMMAND_QUEUE_INFO_ERR __ERR_STR(clGetCommandQueueInfo)
|
||
|
|
||
|
#define __CREATE_CONTEXT_FROM_TYPE_ERR __ERR_STR(clCreateContextFromType)
|
||
|
#define __GET_SUPPORTED_IMAGE_FORMATS_ERR __ERR_STR(clGetSupportedImageFormats)
|
||
|
|
||
|
#define __CREATE_BUFFER_ERR __ERR_STR(clCreateBuffer)
|
||
|
#define __CREATE_SUBBUFFER_ERR __ERR_STR(clCreateSubBuffer)
|
||
|
#define __CREATE_GL_BUFFER_ERR __ERR_STR(clCreateFromGLBuffer)
|
||
|
#define __GET_GL_OBJECT_INFO_ERR __ERR_STR(clGetGLObjectInfo)
|
||
|
#define __CREATE_IMAGE2D_ERR __ERR_STR(clCreateImage2D)
|
||
|
#define __CREATE_IMAGE3D_ERR __ERR_STR(clCreateImage3D)
|
||
|
#define __CREATE_SAMPLER_ERR __ERR_STR(clCreateSampler)
|
||
|
#define __SET_MEM_OBJECT_DESTRUCTOR_CALLBACK_ERR __ERR_STR(clSetMemObjectDestructorCallback)
|
||
|
|
||
|
#define __CREATE_USER_EVENT_ERR __ERR_STR(clCreateUserEvent)
|
||
|
#define __SET_USER_EVENT_STATUS_ERR __ERR_STR(clSetUserEventStatus)
|
||
|
#define __SET_EVENT_CALLBACK_ERR __ERR_STR(clSetEventCallback)
|
||
|
#define __WAIT_FOR_EVENTS_ERR __ERR_STR(clWaitForEvents)
|
||
|
|
||
|
#define __CREATE_KERNEL_ERR __ERR_STR(clCreateKernel)
|
||
|
#define __SET_KERNEL_ARGS_ERR __ERR_STR(clSetKernelArg)
|
||
|
#define __CREATE_PROGRAM_WITH_SOURCE_ERR __ERR_STR(clCreateProgramWithSource)
|
||
|
#define __CREATE_PROGRAM_WITH_BINARY_ERR __ERR_STR(clCreateProgramWithBinary)
|
||
|
#define __BUILD_PROGRAM_ERR __ERR_STR(clBuildProgram)
|
||
|
#define __CREATE_KERNELS_IN_PROGRAM_ERR __ERR_STR(clCreateKernelsInProgram)
|
||
|
|
||
|
#define __CREATE_COMMAND_QUEUE_ERR __ERR_STR(clCreateCommandQueue)
|
||
|
#define __SET_COMMAND_QUEUE_PROPERTY_ERR __ERR_STR(clSetCommandQueueProperty)
|
||
|
#define __ENQUEUE_READ_BUFFER_ERR __ERR_STR(clEnqueueReadBuffer)
|
||
|
#define __ENQUEUE_READ_BUFFER_RECT_ERR __ERR_STR(clEnqueueReadBufferRect)
|
||
|
#define __ENQUEUE_WRITE_BUFFER_ERR __ERR_STR(clEnqueueWriteBuffer)
|
||
|
#define __ENQUEUE_WRITE_BUFFER_RECT_ERR __ERR_STR(clEnqueueWriteBufferRect)
|
||
|
#define __ENQEUE_COPY_BUFFER_ERR __ERR_STR(clEnqueueCopyBuffer)
|
||
|
#define __ENQEUE_COPY_BUFFER_RECT_ERR __ERR_STR(clEnqueueCopyBufferRect)
|
||
|
#define __ENQUEUE_READ_IMAGE_ERR __ERR_STR(clEnqueueReadImage)
|
||
|
#define __ENQUEUE_WRITE_IMAGE_ERR __ERR_STR(clEnqueueWriteImage)
|
||
|
#define __ENQUEUE_COPY_IMAGE_ERR __ERR_STR(clEnqueueCopyImage)
|
||
|
#define __ENQUEUE_COPY_IMAGE_TO_BUFFER_ERR __ERR_STR(clEnqueueCopyImageToBuffer)
|
||
|
#define __ENQUEUE_COPY_BUFFER_TO_IMAGE_ERR __ERR_STR(clEnqueueCopyBufferToImage)
|
||
|
#define __ENQUEUE_MAP_BUFFER_ERR __ERR_STR(clEnqueueMapBuffer)
|
||
|
#define __ENQUEUE_MAP_IMAGE_ERR __ERR_STR(clEnqueueMapImage)
|
||
|
#define __ENQUEUE_UNMAP_MEM_OBJECT_ERR __ERR_STR(clEnqueueUnMapMemObject)
|
||
|
#define __ENQUEUE_NDRANGE_KERNEL_ERR __ERR_STR(clEnqueueNDRangeKernel)
|
||
|
#define __ENQUEUE_TASK_ERR __ERR_STR(clEnqueueTask)
|
||
|
#define __ENQUEUE_NATIVE_KERNEL __ERR_STR(clEnqueueNativeKernel)
|
||
|
#define __ENQUEUE_MARKER_ERR __ERR_STR(clEnqueueMarker)
|
||
|
#define __ENQUEUE_WAIT_FOR_EVENTS_ERR __ERR_STR(clEnqueueWaitForEvents)
|
||
|
#define __ENQUEUE_BARRIER_ERR __ERR_STR(clEnqueueBarrier)
|
||
|
|
||
|
#define __ENQUEUE_ACQUIRE_GL_ERR __ERR_STR(clEnqueueAcquireGLObjects)
|
||
|
#define __ENQUEUE_RELEASE_GL_ERR __ERR_STR(clEnqueueReleaseGLObjects)
|
||
|
|
||
|
#define __UNLOAD_COMPILER_ERR __ERR_STR(clUnloadCompiler)
|
||
|
|
||
|
#define __FLUSH_ERR __ERR_STR(clFlush)
|
||
|
#define __FINISH_ERR __ERR_STR(clFinish)
|
||
|
|
||
|
#define __CREATE_SUB_DEVICES __ERR_STR(clCreateSubDevicesEXT)
|
||
|
#endif // __CL_USER_OVERRIDE_ERROR_STRINGS
|
||
|
//! \endcond
|
||
|
|
||
|
/*! \class string
|
||
|
* \brief Simple string class, that provides a limited subset of std::string
|
||
|
* functionality but avoids many of the issues that come with that class.
|
||
|
*/
|
||
|
class string
|
||
|
{
|
||
|
private:
|
||
|
::size_t size_;
|
||
|
char * str_;
|
||
|
public:
|
||
|
string(void) : size_(0), str_(NULL)
|
||
|
{
|
||
|
}
|
||
|
|
||
|
string(char * str, ::size_t size) :
|
||
|
size_(size),
|
||
|
str_(NULL)
|
||
|
{
|
||
|
str_ = new char[size_+1];
|
||
|
if (str_ != NULL) {
|
||
|
memcpy(str_, str, size_ * sizeof(char));
|
||
|
str_[size_] = '\0';
|
||
|
}
|
||
|
else {
|
||
|
size_ = 0;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
string(char * str) :
|
||
|
str_(NULL)
|
||
|
{
|
||
|
size_= ::strlen(str);
|
||
|
str_ = new char[size_ + 1];
|
||
|
if (str_ != NULL) {
|
||
|
memcpy(str_, str, (size_ + 1) * sizeof(char));
|
||
|
}
|
||
|
else {
|
||
|
size_ = 0;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
string& operator=(const string& rhs)
|
||
|
{
|
||
|
if (this == &rhs) {
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
if (rhs.size_ == 0 || rhs.str_ == NULL) {
|
||
|
size_ = 0;
|
||
|
str_ = NULL;
|
||
|
}
|
||
|
else {
|
||
|
size_ = rhs.size_;
|
||
|
str_ = new char[size_ + 1];
|
||
|
if (str_ != NULL) {
|
||
|
memcpy(str_, rhs.str_, (size_ + 1) * sizeof(char));
|
||
|
}
|
||
|
else {
|
||
|
size_ = 0;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
string(const string& rhs)
|
||
|
{
|
||
|
*this = rhs;
|
||
|
}
|
||
|
|
||
|
~string()
|
||
|
{
|
||
|
if (str_ != NULL) {
|
||
|
delete[] str_;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
::size_t size(void) const { return size_; }
|
||
|
::size_t length(void) const { return size(); }
|
||
|
|
||
|
const char * c_str(void) const { return (str_) ? str_ : "";}
|
||
|
};
|
||
|
|
||
|
#if !defined(__USE_DEV_STRING) && !defined(__NO_STD_STRING)
|
||
|
#include <string>
|
||
|
typedef std::string STRING_CLASS;
|
||
|
#elif !defined(__USE_DEV_STRING)
|
||
|
typedef cl::string STRING_CLASS;
|
||
|
#endif
|
||
|
|
||
|
#if !defined(__USE_DEV_VECTOR) && !defined(__NO_STD_VECTOR)
|
||
|
#include <vector>
|
||
|
#define VECTOR_CLASS std::vector
|
||
|
#elif !defined(__USE_DEV_VECTOR)
|
||
|
#define VECTOR_CLASS cl::vector
|
||
|
#endif
|
||
|
|
||
|
#if !defined(__MAX_DEFAULT_VECTOR_SIZE)
|
||
|
#define __MAX_DEFAULT_VECTOR_SIZE 10
|
||
|
#endif
|
||
|
|
||
|
/*! \class vector
|
||
|
* \brief Fixed sized vector implementation that mirroring
|
||
|
* std::vector functionality.
|
||
|
*/
|
||
|
template <typename T, unsigned int N = __MAX_DEFAULT_VECTOR_SIZE>
|
||
|
class vector
|
||
|
{
|
||
|
private:
|
||
|
T data_[N];
|
||
|
unsigned int size_;
|
||
|
bool empty_;
|
||
|
public:
|
||
|
vector() :
|
||
|
size_(-1),
|
||
|
empty_(true)
|
||
|
{}
|
||
|
|
||
|
~vector() {}
|
||
|
|
||
|
unsigned int size(void) const
|
||
|
{
|
||
|
return size_ + 1;
|
||
|
}
|
||
|
|
||
|
void clear()
|
||
|
{
|
||
|
size_ = -1;
|
||
|
empty_ = true;
|
||
|
}
|
||
|
|
||
|
void push_back (const T& x)
|
||
|
{
|
||
|
if (size() < N) {
|
||
|
size_++;
|
||
|
data_[size_] = x;
|
||
|
empty_ = false;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
void pop_back(void)
|
||
|
{
|
||
|
if (!empty_) {
|
||
|
data_[size_].~T();
|
||
|
size_--;
|
||
|
if (size_ == -1) {
|
||
|
empty_ = true;
|
||
|
}
|
||
|
}
|
||
|
}
|
||
|
|
||
|
vector(const vector<T, N>& vec) :
|
||
|
size_(vec.size_),
|
||
|
empty_(vec.empty_)
|
||
|
{
|
||
|
if (!empty_) {
|
||
|
memcpy(&data_[0], &vec.data_[0], size() * sizeof(T));
|
||
|
}
|
||
|
}
|
||
|
|
||
|
vector(unsigned int size, const T& val = T()) :
|
||
|
size_(-1),
|
||
|
empty_(true)
|
||
|
{
|
||
|
for (unsigned int i = 0; i < size; i++) {
|
||
|
push_back(val);
|
||
|
}
|
||
|
}
|
||
|
|
||
|
vector<T, N>& operator=(const vector<T, N>& rhs)
|
||
|
{
|
||
|
if (this == &rhs) {
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
size_ = rhs.size_;
|
||
|
empty_ = rhs.empty_;
|
||
|
|
||
|
if (!empty_) {
|
||
|
memcpy(&data_[0], &rhs.data_[0], size() * sizeof(T));
|
||
|
}
|
||
|
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
bool operator==(vector<T,N> &vec)
|
||
|
{
|
||
|
if (empty_ && vec.empty_) {
|
||
|
return true;
|
||
|
}
|
||
|
|
||
|
if (size() != vec.size()) {
|
||
|
return false;
|
||
|
}
|
||
|
|
||
|
return memcmp(&data_[0], &vec.data_[0], size() * sizeof(T)) == 0 ? true : false;
|
||
|
}
|
||
|
|
||
|
operator T* () { return data_; }
|
||
|
operator const T* () const { return data_; }
|
||
|
|
||
|
bool empty (void) const
|
||
|
{
|
||
|
return empty_;
|
||
|
}
|
||
|
|
||
|
unsigned int max_size (void) const
|
||
|
{
|
||
|
return N;
|
||
|
}
|
||
|
|
||
|
unsigned int capacity () const
|
||
|
{
|
||
|
return sizeof(T) * N;
|
||
|
}
|
||
|
|
||
|
T& operator[](int index)
|
||
|
{
|
||
|
return data_[index];
|
||
|
}
|
||
|
|
||
|
T operator[](int index) const
|
||
|
{
|
||
|
return data_[index];
|
||
|
}
|
||
|
|
||
|
template<class I>
|
||
|
void assign(I start, I end)
|
||
|
{
|
||
|
clear();
|
||
|
while(start < end) {
|
||
|
push_back(*start);
|
||
|
start++;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
/*! \class iterator
|
||
|
* \brief Iterator class for vectors
|
||
|
*/
|
||
|
class iterator
|
||
|
{
|
||
|
private:
|
||
|
vector<T,N> vec_;
|
||
|
int index_;
|
||
|
bool initialized_;
|
||
|
public:
|
||
|
iterator(void) :
|
||
|
index_(-1),
|
||
|
initialized_(false)
|
||
|
{
|
||
|
index_ = -1;
|
||
|
initialized_ = false;
|
||
|
}
|
||
|
|
||
|
~iterator(void) {}
|
||
|
|
||
|
static iterator begin(vector<T,N> &vec)
|
||
|
{
|
||
|
iterator i;
|
||
|
|
||
|
if (!vec.empty()) {
|
||
|
i.index_ = 0;
|
||
|
}
|
||
|
|
||
|
i.vec_ = vec;
|
||
|
i.initialized_ = true;
|
||
|
return i;
|
||
|
}
|
||
|
|
||
|
static iterator end(vector<T,N> &vec)
|
||
|
{
|
||
|
iterator i;
|
||
|
|
||
|
if (!vec.empty()) {
|
||
|
i.index_ = vec.size();
|
||
|
}
|
||
|
i.vec_ = vec;
|
||
|
i.initialized_ = true;
|
||
|
return i;
|
||
|
}
|
||
|
|
||
|
bool operator==(iterator i)
|
||
|
{
|
||
|
return ((vec_ == i.vec_) &&
|
||
|
(index_ == i.index_) &&
|
||
|
(initialized_ == i.initialized_));
|
||
|
}
|
||
|
|
||
|
bool operator!=(iterator i)
|
||
|
{
|
||
|
return (!(*this==i));
|
||
|
}
|
||
|
|
||
|
void operator++()
|
||
|
{
|
||
|
index_++;
|
||
|
}
|
||
|
|
||
|
void operator++(int x)
|
||
|
{
|
||
|
index_ += x;
|
||
|
}
|
||
|
|
||
|
void operator--()
|
||
|
{
|
||
|
index_--;
|
||
|
}
|
||
|
|
||
|
void operator--(int x)
|
||
|
{
|
||
|
index_ -= x;
|
||
|
}
|
||
|
|
||
|
T operator *()
|
||
|
{
|
||
|
return vec_[index_];
|
||
|
}
|
||
|
};
|
||
|
|
||
|
iterator begin(void)
|
||
|
{
|
||
|
return iterator::begin(*this);
|
||
|
}
|
||
|
|
||
|
iterator end(void)
|
||
|
{
|
||
|
return iterator::end(*this);
|
||
|
}
|
||
|
|
||
|
T& front(void)
|
||
|
{
|
||
|
return data_[0];
|
||
|
}
|
||
|
|
||
|
T& back(void)
|
||
|
{
|
||
|
return data_[size_];
|
||
|
}
|
||
|
|
||
|
const T& front(void) const
|
||
|
{
|
||
|
return data_[0];
|
||
|
}
|
||
|
|
||
|
const T& back(void) const
|
||
|
{
|
||
|
return data_[size_];
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*!
|
||
|
* \brief size_t class used to interface between C++ and
|
||
|
* OpenCL C calls that require arrays of size_t values, who's
|
||
|
* size is known statically.
|
||
|
*/
|
||
|
template <int N>
|
||
|
struct size_t : public cl::vector< ::size_t, N> { };
|
||
|
|
||
|
namespace detail {
|
||
|
|
||
|
// GetInfo help struct
|
||
|
template <typename Functor, typename T>
|
||
|
struct GetInfoHelper
|
||
|
{
|
||
|
static cl_int
|
||
|
get(Functor f, cl_uint name, T* param)
|
||
|
{
|
||
|
return f(name, sizeof(T), param, NULL);
|
||
|
}
|
||
|
};
|
||
|
|
||
|
// Specialized GetInfoHelper for VECTOR_CLASS params
|
||
|
template <typename Func, typename T>
|
||
|
struct GetInfoHelper<Func, VECTOR_CLASS<T> >
|
||
|
{
|
||
|
static cl_int get(Func f, cl_uint name, VECTOR_CLASS<T>* param)
|
||
|
{
|
||
|
::size_t required;
|
||
|
cl_int err = f(name, 0, NULL, &required);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return err;
|
||
|
}
|
||
|
|
||
|
T* value = (T*) alloca(required);
|
||
|
err = f(name, required, value, NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return err;
|
||
|
}
|
||
|
|
||
|
param->assign(&value[0], &value[required/sizeof(T)]);
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
// Specialized for getInfo<CL_PROGRAM_BINARIES>
|
||
|
template <typename Func>
|
||
|
struct GetInfoHelper<Func, VECTOR_CLASS<char *> >
|
||
|
{
|
||
|
static cl_int
|
||
|
get(Func f, cl_uint name, VECTOR_CLASS<char *>* param)
|
||
|
{
|
||
|
cl_uint err = f(name, param->size() * sizeof(char *), &(*param)[0], NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return err;
|
||
|
}
|
||
|
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
// Specialized GetInfoHelper for STRING_CLASS params
|
||
|
template <typename Func>
|
||
|
struct GetInfoHelper<Func, STRING_CLASS>
|
||
|
{
|
||
|
static cl_int get(Func f, cl_uint name, STRING_CLASS* param)
|
||
|
{
|
||
|
::size_t required;
|
||
|
cl_int err = f(name, 0, NULL, &required);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return err;
|
||
|
}
|
||
|
|
||
|
char* value = (char*) alloca(required);
|
||
|
err = f(name, required, value, NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return err;
|
||
|
}
|
||
|
|
||
|
*param = value;
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
#define __GET_INFO_HELPER_WITH_RETAIN(CPP_TYPE) \
|
||
|
namespace detail { \
|
||
|
template <typename Func> \
|
||
|
struct GetInfoHelper<Func, CPP_TYPE> \
|
||
|
{ \
|
||
|
static cl_int get(Func f, cl_uint name, CPP_TYPE* param) \
|
||
|
{ \
|
||
|
cl_uint err = f(name, sizeof(CPP_TYPE), param, NULL); \
|
||
|
if (err != CL_SUCCESS) { \
|
||
|
return err; \
|
||
|
} \
|
||
|
\
|
||
|
return ReferenceHandler<CPP_TYPE::cl_type>::retain((*param)()); \
|
||
|
} \
|
||
|
}; \
|
||
|
}
|
||
|
|
||
|
|
||
|
#define __PARAM_NAME_INFO_1_0(F) \
|
||
|
F(cl_platform_info, CL_PLATFORM_PROFILE, STRING_CLASS) \
|
||
|
F(cl_platform_info, CL_PLATFORM_VERSION, STRING_CLASS) \
|
||
|
F(cl_platform_info, CL_PLATFORM_NAME, STRING_CLASS) \
|
||
|
F(cl_platform_info, CL_PLATFORM_VENDOR, STRING_CLASS) \
|
||
|
F(cl_platform_info, CL_PLATFORM_EXTENSIONS, STRING_CLASS) \
|
||
|
\
|
||
|
F(cl_device_info, CL_DEVICE_TYPE, cl_device_type) \
|
||
|
F(cl_device_info, CL_DEVICE_VENDOR_ID, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_COMPUTE_UNITS, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_WORK_GROUP_SIZE, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_WORK_ITEM_SIZES, VECTOR_CLASS< ::size_t>) \
|
||
|
F(cl_device_info, CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_CLOCK_FREQUENCY, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_ADDRESS_BITS, cl_bitfield) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_READ_IMAGE_ARGS, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_WRITE_IMAGE_ARGS, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_MEM_ALLOC_SIZE, cl_ulong) \
|
||
|
F(cl_device_info, CL_DEVICE_IMAGE2D_MAX_WIDTH, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_IMAGE2D_MAX_HEIGHT, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_IMAGE3D_MAX_WIDTH, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_IMAGE3D_MAX_HEIGHT, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_IMAGE3D_MAX_DEPTH, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_IMAGE_SUPPORT, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_PARAMETER_SIZE, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_SAMPLERS, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MEM_BASE_ADDR_ALIGN, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_SINGLE_FP_CONFIG, cl_device_fp_config) \
|
||
|
F(cl_device_info, CL_DEVICE_GLOBAL_MEM_CACHE_TYPE, cl_device_mem_cache_type) \
|
||
|
F(cl_device_info, CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE, cl_uint)\
|
||
|
F(cl_device_info, CL_DEVICE_GLOBAL_MEM_CACHE_SIZE, cl_ulong) \
|
||
|
F(cl_device_info, CL_DEVICE_GLOBAL_MEM_SIZE, cl_ulong) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE, cl_ulong) \
|
||
|
F(cl_device_info, CL_DEVICE_MAX_CONSTANT_ARGS, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_LOCAL_MEM_TYPE, cl_device_local_mem_type) \
|
||
|
F(cl_device_info, CL_DEVICE_LOCAL_MEM_SIZE, cl_ulong) \
|
||
|
F(cl_device_info, CL_DEVICE_ERROR_CORRECTION_SUPPORT, cl_bool) \
|
||
|
F(cl_device_info, CL_DEVICE_PROFILING_TIMER_RESOLUTION, ::size_t) \
|
||
|
F(cl_device_info, CL_DEVICE_ENDIAN_LITTLE, cl_bool) \
|
||
|
F(cl_device_info, CL_DEVICE_AVAILABLE, cl_bool) \
|
||
|
F(cl_device_info, CL_DEVICE_COMPILER_AVAILABLE, cl_bool) \
|
||
|
F(cl_device_info, CL_DEVICE_EXECUTION_CAPABILITIES, cl_device_exec_capabilities) \
|
||
|
F(cl_device_info, CL_DEVICE_QUEUE_PROPERTIES, cl_command_queue_properties) \
|
||
|
F(cl_device_info, CL_DEVICE_PLATFORM, cl_platform_id) \
|
||
|
F(cl_device_info, CL_DEVICE_NAME, STRING_CLASS) \
|
||
|
F(cl_device_info, CL_DEVICE_VENDOR, STRING_CLASS) \
|
||
|
F(cl_device_info, CL_DRIVER_VERSION, STRING_CLASS) \
|
||
|
F(cl_device_info, CL_DEVICE_PROFILE, STRING_CLASS) \
|
||
|
F(cl_device_info, CL_DEVICE_VERSION, STRING_CLASS) \
|
||
|
F(cl_device_info, CL_DEVICE_EXTENSIONS, STRING_CLASS) \
|
||
|
\
|
||
|
F(cl_context_info, CL_CONTEXT_REFERENCE_COUNT, cl_uint) \
|
||
|
F(cl_context_info, CL_CONTEXT_DEVICES, VECTOR_CLASS<Device>) \
|
||
|
F(cl_context_info, CL_CONTEXT_PROPERTIES, VECTOR_CLASS<cl_context_properties>) \
|
||
|
\
|
||
|
F(cl_event_info, CL_EVENT_COMMAND_QUEUE, cl::CommandQueue) \
|
||
|
F(cl_event_info, CL_EVENT_COMMAND_TYPE, cl_command_type) \
|
||
|
F(cl_event_info, CL_EVENT_REFERENCE_COUNT, cl_uint) \
|
||
|
F(cl_event_info, CL_EVENT_COMMAND_EXECUTION_STATUS, cl_uint) \
|
||
|
\
|
||
|
F(cl_profiling_info, CL_PROFILING_COMMAND_QUEUED, cl_ulong) \
|
||
|
F(cl_profiling_info, CL_PROFILING_COMMAND_SUBMIT, cl_ulong) \
|
||
|
F(cl_profiling_info, CL_PROFILING_COMMAND_START, cl_ulong) \
|
||
|
F(cl_profiling_info, CL_PROFILING_COMMAND_END, cl_ulong) \
|
||
|
\
|
||
|
F(cl_mem_info, CL_MEM_TYPE, cl_mem_object_type) \
|
||
|
F(cl_mem_info, CL_MEM_FLAGS, cl_mem_flags) \
|
||
|
F(cl_mem_info, CL_MEM_SIZE, ::size_t) \
|
||
|
F(cl_mem_info, CL_MEM_HOST_PTR, void*) \
|
||
|
F(cl_mem_info, CL_MEM_MAP_COUNT, cl_uint) \
|
||
|
F(cl_mem_info, CL_MEM_REFERENCE_COUNT, cl_uint) \
|
||
|
F(cl_mem_info, CL_MEM_CONTEXT, cl::Context) \
|
||
|
\
|
||
|
F(cl_image_info, CL_IMAGE_FORMAT, cl_image_format) \
|
||
|
F(cl_image_info, CL_IMAGE_ELEMENT_SIZE, ::size_t) \
|
||
|
F(cl_image_info, CL_IMAGE_ROW_PITCH, ::size_t) \
|
||
|
F(cl_image_info, CL_IMAGE_SLICE_PITCH, ::size_t) \
|
||
|
F(cl_image_info, CL_IMAGE_WIDTH, ::size_t) \
|
||
|
F(cl_image_info, CL_IMAGE_HEIGHT, ::size_t) \
|
||
|
F(cl_image_info, CL_IMAGE_DEPTH, ::size_t) \
|
||
|
\
|
||
|
F(cl_sampler_info, CL_SAMPLER_REFERENCE_COUNT, cl_uint) \
|
||
|
F(cl_sampler_info, CL_SAMPLER_CONTEXT, cl::Context) \
|
||
|
F(cl_sampler_info, CL_SAMPLER_NORMALIZED_COORDS, cl_addressing_mode) \
|
||
|
F(cl_sampler_info, CL_SAMPLER_ADDRESSING_MODE, cl_filter_mode) \
|
||
|
F(cl_sampler_info, CL_SAMPLER_FILTER_MODE, cl_bool) \
|
||
|
\
|
||
|
F(cl_program_info, CL_PROGRAM_REFERENCE_COUNT, cl_uint) \
|
||
|
F(cl_program_info, CL_PROGRAM_CONTEXT, cl::Context) \
|
||
|
F(cl_program_info, CL_PROGRAM_NUM_DEVICES, cl_uint) \
|
||
|
F(cl_program_info, CL_PROGRAM_DEVICES, VECTOR_CLASS<cl_device_id>) \
|
||
|
F(cl_program_info, CL_PROGRAM_SOURCE, STRING_CLASS) \
|
||
|
F(cl_program_info, CL_PROGRAM_BINARY_SIZES, VECTOR_CLASS< ::size_t>) \
|
||
|
F(cl_program_info, CL_PROGRAM_BINARIES, VECTOR_CLASS<char *>) \
|
||
|
\
|
||
|
F(cl_program_build_info, CL_PROGRAM_BUILD_STATUS, cl_build_status) \
|
||
|
F(cl_program_build_info, CL_PROGRAM_BUILD_OPTIONS, STRING_CLASS) \
|
||
|
F(cl_program_build_info, CL_PROGRAM_BUILD_LOG, STRING_CLASS) \
|
||
|
\
|
||
|
F(cl_kernel_info, CL_KERNEL_FUNCTION_NAME, STRING_CLASS) \
|
||
|
F(cl_kernel_info, CL_KERNEL_NUM_ARGS, cl_uint) \
|
||
|
F(cl_kernel_info, CL_KERNEL_REFERENCE_COUNT, cl_uint) \
|
||
|
F(cl_kernel_info, CL_KERNEL_CONTEXT, cl::Context) \
|
||
|
F(cl_kernel_info, CL_KERNEL_PROGRAM, cl::Program) \
|
||
|
\
|
||
|
F(cl_kernel_work_group_info, CL_KERNEL_WORK_GROUP_SIZE, ::size_t) \
|
||
|
F(cl_kernel_work_group_info, CL_KERNEL_COMPILE_WORK_GROUP_SIZE, cl::size_t<3>) \
|
||
|
F(cl_kernel_work_group_info, CL_KERNEL_LOCAL_MEM_SIZE, cl_ulong) \
|
||
|
\
|
||
|
F(cl_command_queue_info, CL_QUEUE_CONTEXT, cl::Context) \
|
||
|
F(cl_command_queue_info, CL_QUEUE_DEVICE, cl::Device) \
|
||
|
F(cl_command_queue_info, CL_QUEUE_REFERENCE_COUNT, cl_uint) \
|
||
|
F(cl_command_queue_info, CL_QUEUE_PROPERTIES, cl_command_queue_properties)
|
||
|
|
||
|
#if defined(CL_VERSION_1_1)
|
||
|
#define __PARAM_NAME_INFO_1_1(F) \
|
||
|
F(cl_context_info, CL_CONTEXT_NUM_DEVICES, cl_uint)\
|
||
|
F(cl_device_info, CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_NATIVE_VECTOR_WIDTH_INT, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF, cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_DOUBLE_FP_CONFIG, cl_device_fp_config) \
|
||
|
F(cl_device_info, CL_DEVICE_HALF_FP_CONFIG, cl_device_fp_config) \
|
||
|
F(cl_device_info, CL_DEVICE_HOST_UNIFIED_MEMORY, cl_bool) \
|
||
|
\
|
||
|
F(cl_mem_info, CL_MEM_ASSOCIATED_MEMOBJECT, cl::Memory) \
|
||
|
F(cl_mem_info, CL_MEM_OFFSET, ::size_t) \
|
||
|
\
|
||
|
F(cl_kernel_work_group_info, CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE, ::size_t) \
|
||
|
F(cl_kernel_work_group_info, CL_KERNEL_PRIVATE_MEM_SIZE, cl_ulong) \
|
||
|
\
|
||
|
F(cl_event_info, CL_EVENT_CONTEXT, cl::Context)
|
||
|
#endif // CL_VERSION_1_1
|
||
|
|
||
|
#if defined(USE_CL_DEVICE_FISSION)
|
||
|
#define __PARAM_NAME_DEVICE_FISSION(F) \
|
||
|
F(cl_device_info, CL_DEVICE_PARENT_DEVICE_EXT, cl_device_id) \
|
||
|
F(cl_device_info, CL_DEVICE_PARTITION_TYPES_EXT, VECTOR_CLASS<cl_device_partition_property_ext>) \
|
||
|
F(cl_device_info, CL_DEVICE_AFFINITY_DOMAINS_EXT, VECTOR_CLASS<cl_device_partition_property_ext>) \
|
||
|
F(cl_device_info, CL_DEVICE_REFERENCE_COUNT_EXT , cl_uint) \
|
||
|
F(cl_device_info, CL_DEVICE_PARTITION_STYLE_EXT, VECTOR_CLASS<cl_device_partition_property_ext>)
|
||
|
#endif // USE_CL_DEVICE_FISSION
|
||
|
|
||
|
template <typename enum_type, cl_int Name>
|
||
|
struct param_traits {};
|
||
|
|
||
|
#define __DECLARE_PARAM_TRAITS(token, param_name, T) \
|
||
|
struct token; \
|
||
|
template<> \
|
||
|
struct param_traits<detail:: token,param_name> \
|
||
|
{ \
|
||
|
enum { value = param_name }; \
|
||
|
typedef T param_type; \
|
||
|
};
|
||
|
|
||
|
__PARAM_NAME_INFO_1_0(__DECLARE_PARAM_TRAITS);
|
||
|
#if defined(CL_VERSION_1_1)
|
||
|
__PARAM_NAME_INFO_1_1(__DECLARE_PARAM_TRAITS);
|
||
|
#endif // CL_VERSION_1_1
|
||
|
|
||
|
#if defined(USE_CL_DEVICE_FISSION)
|
||
|
__PARAM_NAME_DEVICE_FISSION(__DECLARE_PARAM_TRAITS);
|
||
|
#endif // USE_CL_DEVICE_FISSION
|
||
|
|
||
|
#undef __DECLARE_PARAM_TRAITS
|
||
|
|
||
|
// Convenience functions
|
||
|
|
||
|
template <typename Func, typename T>
|
||
|
inline cl_int
|
||
|
getInfo(Func f, cl_uint name, T* param)
|
||
|
{
|
||
|
return GetInfoHelper<Func, T>::get(f, name, param);
|
||
|
}
|
||
|
|
||
|
template <typename Func, typename Arg0>
|
||
|
struct GetInfoFunctor0
|
||
|
{
|
||
|
Func f_; const Arg0& arg0_;
|
||
|
cl_int operator ()(
|
||
|
cl_uint param, ::size_t size, void* value, ::size_t* size_ret)
|
||
|
{ return f_(arg0_, param, size, value, size_ret); }
|
||
|
};
|
||
|
|
||
|
template <typename Func, typename Arg0, typename Arg1>
|
||
|
struct GetInfoFunctor1
|
||
|
{
|
||
|
Func f_; const Arg0& arg0_; const Arg1& arg1_;
|
||
|
cl_int operator ()(
|
||
|
cl_uint param, ::size_t size, void* value, ::size_t* size_ret)
|
||
|
{ return f_(arg0_, arg1_, param, size, value, size_ret); }
|
||
|
};
|
||
|
|
||
|
template <typename Func, typename Arg0, typename T>
|
||
|
inline cl_int
|
||
|
getInfo(Func f, const Arg0& arg0, cl_uint name, T* param)
|
||
|
{
|
||
|
GetInfoFunctor0<Func, Arg0> f0 = { f, arg0 };
|
||
|
return GetInfoHelper<GetInfoFunctor0<Func, Arg0>, T>
|
||
|
::get(f0, name, param);
|
||
|
}
|
||
|
|
||
|
template <typename Func, typename Arg0, typename Arg1, typename T>
|
||
|
inline cl_int
|
||
|
getInfo(Func f, const Arg0& arg0, const Arg1& arg1, cl_uint name, T* param)
|
||
|
{
|
||
|
GetInfoFunctor1<Func, Arg0, Arg1> f0 = { f, arg0, arg1 };
|
||
|
return GetInfoHelper<GetInfoFunctor1<Func, Arg0, Arg1>, T>
|
||
|
::get(f0, name, param);
|
||
|
}
|
||
|
|
||
|
template<typename T>
|
||
|
struct ReferenceHandler
|
||
|
{ };
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_device_id>
|
||
|
{
|
||
|
// cl_device_id does not have retain().
|
||
|
static cl_int retain(cl_device_id)
|
||
|
{ return CL_INVALID_DEVICE; }
|
||
|
// cl_device_id does not have release().
|
||
|
static cl_int release(cl_device_id)
|
||
|
{ return CL_INVALID_DEVICE; }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_platform_id>
|
||
|
{
|
||
|
// cl_platform_id does not have retain().
|
||
|
static cl_int retain(cl_platform_id)
|
||
|
{ return CL_INVALID_PLATFORM; }
|
||
|
// cl_platform_id does not have release().
|
||
|
static cl_int release(cl_platform_id)
|
||
|
{ return CL_INVALID_PLATFORM; }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_context>
|
||
|
{
|
||
|
static cl_int retain(cl_context context)
|
||
|
{ return ::clRetainContext(context); }
|
||
|
static cl_int release(cl_context context)
|
||
|
{ return ::clReleaseContext(context); }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_command_queue>
|
||
|
{
|
||
|
static cl_int retain(cl_command_queue queue)
|
||
|
{ return ::clRetainCommandQueue(queue); }
|
||
|
static cl_int release(cl_command_queue queue)
|
||
|
{ return ::clReleaseCommandQueue(queue); }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_mem>
|
||
|
{
|
||
|
static cl_int retain(cl_mem memory)
|
||
|
{ return ::clRetainMemObject(memory); }
|
||
|
static cl_int release(cl_mem memory)
|
||
|
{ return ::clReleaseMemObject(memory); }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_sampler>
|
||
|
{
|
||
|
static cl_int retain(cl_sampler sampler)
|
||
|
{ return ::clRetainSampler(sampler); }
|
||
|
static cl_int release(cl_sampler sampler)
|
||
|
{ return ::clReleaseSampler(sampler); }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_program>
|
||
|
{
|
||
|
static cl_int retain(cl_program program)
|
||
|
{ return ::clRetainProgram(program); }
|
||
|
static cl_int release(cl_program program)
|
||
|
{ return ::clReleaseProgram(program); }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_kernel>
|
||
|
{
|
||
|
static cl_int retain(cl_kernel kernel)
|
||
|
{ return ::clRetainKernel(kernel); }
|
||
|
static cl_int release(cl_kernel kernel)
|
||
|
{ return ::clReleaseKernel(kernel); }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct ReferenceHandler<cl_event>
|
||
|
{
|
||
|
static cl_int retain(cl_event event)
|
||
|
{ return ::clRetainEvent(event); }
|
||
|
static cl_int release(cl_event event)
|
||
|
{ return ::clReleaseEvent(event); }
|
||
|
};
|
||
|
|
||
|
template <typename T>
|
||
|
class Wrapper
|
||
|
{
|
||
|
public:
|
||
|
typedef T cl_type;
|
||
|
|
||
|
protected:
|
||
|
cl_type object_;
|
||
|
|
||
|
public:
|
||
|
Wrapper() : object_(NULL) { }
|
||
|
|
||
|
~Wrapper()
|
||
|
{
|
||
|
if (object_ != NULL) { release(); }
|
||
|
}
|
||
|
|
||
|
Wrapper(const Wrapper<cl_type>& rhs)
|
||
|
{
|
||
|
object_ = rhs.object_;
|
||
|
if (object_ != NULL) { retain(); }
|
||
|
}
|
||
|
|
||
|
Wrapper<cl_type>& operator = (const Wrapper<cl_type>& rhs)
|
||
|
{
|
||
|
if (object_ != NULL) { release(); }
|
||
|
object_ = rhs.object_;
|
||
|
if (object_ != NULL) { retain(); }
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
cl_type operator ()() const { return object_; }
|
||
|
|
||
|
cl_type& operator ()() { return object_; }
|
||
|
|
||
|
protected:
|
||
|
|
||
|
cl_int retain() const
|
||
|
{
|
||
|
return ReferenceHandler<cl_type>::retain(object_);
|
||
|
}
|
||
|
|
||
|
cl_int release() const
|
||
|
{
|
||
|
return ReferenceHandler<cl_type>::release(object_);
|
||
|
}
|
||
|
};
|
||
|
|
||
|
#if defined(__CL_ENABLE_EXCEPTIONS)
|
||
|
static inline cl_int errHandler (
|
||
|
cl_int err,
|
||
|
const char * errStr = NULL) throw(Error)
|
||
|
{
|
||
|
if (err != CL_SUCCESS) {
|
||
|
throw Error(err, errStr);
|
||
|
}
|
||
|
return err;
|
||
|
}
|
||
|
#else
|
||
|
static inline cl_int errHandler (cl_int err, const char * errStr = NULL)
|
||
|
{
|
||
|
return err;
|
||
|
}
|
||
|
#endif // __CL_ENABLE_EXCEPTIONS
|
||
|
|
||
|
} // namespace detail
|
||
|
//! \endcond
|
||
|
|
||
|
/*! \stuct ImageFormat
|
||
|
* \brief ImageFormat interface fro cl_image_format.
|
||
|
*/
|
||
|
struct ImageFormat : public cl_image_format
|
||
|
{
|
||
|
ImageFormat(){}
|
||
|
|
||
|
ImageFormat(cl_channel_order order, cl_channel_type type)
|
||
|
{
|
||
|
image_channel_order = order;
|
||
|
image_channel_data_type = type;
|
||
|
}
|
||
|
|
||
|
ImageFormat& operator = (const ImageFormat& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
this->image_channel_data_type = rhs.image_channel_data_type;
|
||
|
this->image_channel_order = rhs.image_channel_order;
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class Device
|
||
|
* \brief Device interface for cl_device_id.
|
||
|
*/
|
||
|
class Device : public detail::Wrapper<cl_device_id>
|
||
|
{
|
||
|
public:
|
||
|
Device(cl_device_id device) { object_ = device; }
|
||
|
|
||
|
Device() : detail::Wrapper<cl_type>() { }
|
||
|
|
||
|
Device(const Device& device) : detail::Wrapper<cl_type>(device) { }
|
||
|
|
||
|
Device& operator = (const Device& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_device_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetDeviceInfo, object_, name, param),
|
||
|
__GET_DEVICE_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_device_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_device_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
#if defined(USE_CL_DEVICE_FISSION)
|
||
|
cl_int createSubDevices(
|
||
|
const cl_device_partition_property_ext * properties,
|
||
|
VECTOR_CLASS<Device>* devices)
|
||
|
{
|
||
|
typedef CL_API_ENTRY cl_int
|
||
|
( CL_API_CALL * PFN_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;
|
||
|
|
||
|
static PFN_clCreateSubDevicesEXT pfn_clCreateSubDevicesEXT = NULL;
|
||
|
__INIT_CL_EXT_FCN_PTR(clCreateSubDevicesEXT);
|
||
|
|
||
|
cl_uint n = 0;
|
||
|
cl_int err = pfn_clCreateSubDevicesEXT(object_, properties, 0, NULL, &n);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __CREATE_SUB_DEVICES);
|
||
|
}
|
||
|
|
||
|
cl_device_id* ids = (cl_device_id*) alloca(n * sizeof(cl_device_id));
|
||
|
err = pfn_clCreateSubDevicesEXT(object_, properties, n, ids, NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __CREATE_SUB_DEVICES);
|
||
|
}
|
||
|
|
||
|
devices->assign(&ids[0], &ids[n]);
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
#endif
|
||
|
};
|
||
|
|
||
|
/*! \class Platform
|
||
|
* \brief Platform interface.
|
||
|
*/
|
||
|
class Platform : public detail::Wrapper<cl_platform_id>
|
||
|
{
|
||
|
public:
|
||
|
static const Platform null();
|
||
|
|
||
|
Platform(cl_platform_id platform) { object_ = platform; }
|
||
|
|
||
|
Platform() : detail::Wrapper<cl_type>() { }
|
||
|
|
||
|
Platform(const Platform& platform) : detail::Wrapper<cl_type>(platform) { }
|
||
|
|
||
|
Platform& operator = (const Platform& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
cl_int getInfo(cl_platform_info name, STRING_CLASS* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetPlatformInfo, object_, name, param),
|
||
|
__GET_PLATFORM_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_platform_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_platform_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
cl_int getDevices(
|
||
|
cl_device_type type,
|
||
|
VECTOR_CLASS<Device>* devices) const
|
||
|
{
|
||
|
cl_uint n = 0;
|
||
|
cl_int err = ::clGetDeviceIDs(object_, type, 0, NULL, &n);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_DEVICE_IDS_ERR);
|
||
|
}
|
||
|
|
||
|
cl_device_id* ids = (cl_device_id*) alloca(n * sizeof(cl_device_id));
|
||
|
err = ::clGetDeviceIDs(object_, type, n, ids, NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_DEVICE_IDS_ERR);
|
||
|
}
|
||
|
|
||
|
devices->assign(&ids[0], &ids[n]);
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
|
||
|
#if defined(USE_DX_INTEROP)
|
||
|
/*! \brief Get the list of available D3D10 devices.
|
||
|
*
|
||
|
* \param d3d_device_source.
|
||
|
*
|
||
|
* \param d3d_object.
|
||
|
*
|
||
|
* \param d3d_device_set.
|
||
|
*
|
||
|
* \param devices returns a vector of OpenCL D3D10 devices found. The cl::Device
|
||
|
* values returned in devices can be used to identify a specific OpenCL
|
||
|
* device. If \a devices argument is NULL, this argument is ignored.
|
||
|
*
|
||
|
* \return One of the following values:
|
||
|
* - CL_SUCCESS if the function is executed successfully.
|
||
|
*
|
||
|
* The application can query specific capabilities of the OpenCL device(s)
|
||
|
* returned by cl::getDevices. This can be used by the application to
|
||
|
* determine which device(s) to use.
|
||
|
*
|
||
|
* \note In the case that exceptions are enabled and a return value
|
||
|
* other than CL_SUCCESS is generated, then cl::Error exception is
|
||
|
* generated.
|
||
|
*/
|
||
|
cl_int getDevices(
|
||
|
cl_d3d10_device_source_khr d3d_device_source,
|
||
|
void * d3d_object,
|
||
|
cl_d3d10_device_set_khr d3d_device_set,
|
||
|
VECTOR_CLASS<Device>* devices) const
|
||
|
{
|
||
|
typedef CL_API_ENTRY cl_int (CL_API_CALL *PFN_clGetDeviceIDsFromD3D10KHR)(
|
||
|
cl_platform_id platform,
|
||
|
cl_d3d10_device_source_khr d3d_device_source,
|
||
|
void * d3d_object,
|
||
|
cl_d3d10_device_set_khr d3d_device_set,
|
||
|
cl_uint num_entries,
|
||
|
cl_device_id * devices,
|
||
|
cl_uint* num_devices);
|
||
|
|
||
|
static PFN_clGetDeviceIDsFromD3D10KHR pfn_clGetDeviceIDsFromD3D10KHR = NULL;
|
||
|
__INIT_CL_EXT_FCN_PTR(clGetDeviceIDsFromD3D10KHR);
|
||
|
|
||
|
cl_uint n = 0;
|
||
|
cl_int err = pfn_clGetDeviceIDsFromD3D10KHR(
|
||
|
object_,
|
||
|
d3d_device_source,
|
||
|
d3d_object,
|
||
|
d3d_device_set,
|
||
|
0,
|
||
|
NULL,
|
||
|
&n);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_DEVICE_IDS_ERR);
|
||
|
}
|
||
|
|
||
|
cl_device_id* ids = (cl_device_id*) alloca(n * sizeof(cl_device_id));
|
||
|
err = pfn_clGetDeviceIDsFromD3D10KHR(
|
||
|
object_,
|
||
|
d3d_device_source,
|
||
|
d3d_object,
|
||
|
d3d_device_set,
|
||
|
n,
|
||
|
ids,
|
||
|
NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_DEVICE_IDS_ERR);
|
||
|
}
|
||
|
|
||
|
devices->assign(&ids[0], &ids[n]);
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
#endif
|
||
|
|
||
|
static cl_int get(
|
||
|
VECTOR_CLASS<Platform>* platforms)
|
||
|
{
|
||
|
cl_uint n = 0;
|
||
|
cl_int err = ::clGetPlatformIDs(0, NULL, &n);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_PLATFORM_IDS_ERR);
|
||
|
}
|
||
|
|
||
|
cl_platform_id* ids = (cl_platform_id*) alloca(
|
||
|
n * sizeof(cl_platform_id));
|
||
|
err = ::clGetPlatformIDs(n, ids, NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_PLATFORM_IDS_ERR);
|
||
|
}
|
||
|
|
||
|
platforms->assign(&ids[0], &ids[n]);
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
static inline cl_int
|
||
|
UnloadCompiler()
|
||
|
{
|
||
|
return ::clUnloadCompiler();
|
||
|
}
|
||
|
|
||
|
class Context : public detail::Wrapper<cl_context>
|
||
|
{
|
||
|
public:
|
||
|
Context(
|
||
|
const VECTOR_CLASS<Device>& devices,
|
||
|
cl_context_properties* properties = NULL,
|
||
|
void (CL_CALLBACK * notifyFptr)(
|
||
|
const char *,
|
||
|
const void *,
|
||
|
::size_t,
|
||
|
void *) = NULL,
|
||
|
void* data = NULL,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateContext(
|
||
|
properties, (cl_uint) devices.size(),
|
||
|
(cl_device_id*) &devices.front(),
|
||
|
notifyFptr, data, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_CONTEXT_FROM_TYPE_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Context(
|
||
|
cl_device_type type,
|
||
|
cl_context_properties* properties = NULL,
|
||
|
void (CL_CALLBACK * notifyFptr)(
|
||
|
const char *,
|
||
|
const void *,
|
||
|
::size_t,
|
||
|
void *) = NULL,
|
||
|
void* data = NULL,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateContextFromType(
|
||
|
properties, type, notifyFptr, data, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_CONTEXT_FROM_TYPE_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Context() : detail::Wrapper<cl_type>() { }
|
||
|
|
||
|
Context(const Context& context) : detail::Wrapper<cl_type>(context) { }
|
||
|
|
||
|
Context& operator = (const Context& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_context_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetContextInfo, object_, name, param),
|
||
|
__GET_CONTEXT_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_context_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_context_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
cl_int getSupportedImageFormats(
|
||
|
cl_mem_flags flags,
|
||
|
cl_mem_object_type type,
|
||
|
VECTOR_CLASS<ImageFormat>* formats) const
|
||
|
{
|
||
|
cl_uint numEntries;
|
||
|
cl_int err = ::clGetSupportedImageFormats(
|
||
|
object_,
|
||
|
flags,
|
||
|
type,
|
||
|
0,
|
||
|
NULL,
|
||
|
&numEntries);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_SUPPORTED_IMAGE_FORMATS_ERR);
|
||
|
}
|
||
|
|
||
|
ImageFormat* value = (ImageFormat*)
|
||
|
alloca(numEntries * sizeof(ImageFormat));
|
||
|
err = ::clGetSupportedImageFormats(
|
||
|
object_,
|
||
|
flags,
|
||
|
type,
|
||
|
numEntries,
|
||
|
(cl_image_format*) value,
|
||
|
NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __GET_SUPPORTED_IMAGE_FORMATS_ERR);
|
||
|
}
|
||
|
|
||
|
formats->assign(&value[0], &value[numEntries]);
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
__GET_INFO_HELPER_WITH_RETAIN(cl::Context)
|
||
|
|
||
|
/*! \class Event
|
||
|
* \brief Event interface for cl_event.
|
||
|
*/
|
||
|
class Event : public detail::Wrapper<cl_event>
|
||
|
{
|
||
|
public:
|
||
|
Event() : detail::Wrapper<cl_type>() { }
|
||
|
|
||
|
Event(const Event& event) : detail::Wrapper<cl_type>(event) { }
|
||
|
|
||
|
Event& operator = (const Event& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_event_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetEventInfo, object_, name, param),
|
||
|
__GET_EVENT_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_event_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_event_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getProfilingInfo(cl_profiling_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(detail::getInfo(
|
||
|
&::clGetEventProfilingInfo, object_, name, param),
|
||
|
__GET_EVENT_PROFILE_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_profiling_info, name>::param_type
|
||
|
getProfilingInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_profiling_info, name>::param_type param;
|
||
|
cl_int result = getProfilingInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
cl_int wait() const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clWaitForEvents(1, &object_),
|
||
|
__WAIT_FOR_EVENTS_ERR);
|
||
|
}
|
||
|
|
||
|
#if defined(CL_VERSION_1_1)
|
||
|
cl_int setCallback(
|
||
|
cl_int type,
|
||
|
void (CL_CALLBACK * pfn_notify)(cl_event, cl_int, void *),
|
||
|
void * user_data = NULL)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clSetEventCallback(
|
||
|
object_,
|
||
|
type,
|
||
|
pfn_notify,
|
||
|
user_data),
|
||
|
__SET_EVENT_CALLBACK_ERR);
|
||
|
}
|
||
|
#endif
|
||
|
|
||
|
static cl_int
|
||
|
waitForEvents(const VECTOR_CLASS<Event>& events)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clWaitForEvents(
|
||
|
(cl_uint) events.size(), (cl_event*)&events.front()),
|
||
|
__WAIT_FOR_EVENTS_ERR);
|
||
|
}
|
||
|
};
|
||
|
|
||
|
__GET_INFO_HELPER_WITH_RETAIN(cl::Event)
|
||
|
|
||
|
#if defined(CL_VERSION_1_1)
|
||
|
/*! \class UserEvent
|
||
|
* \brief User event interface for cl_event.
|
||
|
*/
|
||
|
class UserEvent : public Event
|
||
|
{
|
||
|
public:
|
||
|
UserEvent(
|
||
|
const Context& context,
|
||
|
cl_int * err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateUserEvent(
|
||
|
context(),
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_USER_EVENT_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
UserEvent() : Event() { }
|
||
|
|
||
|
UserEvent(const UserEvent& event) : Event(event) { }
|
||
|
|
||
|
UserEvent& operator = (const UserEvent& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Event::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
cl_int setStatus(cl_int status)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clSetUserEventStatus(object_,status),
|
||
|
__SET_USER_EVENT_STATUS_ERR);
|
||
|
}
|
||
|
};
|
||
|
#endif
|
||
|
|
||
|
inline static cl_int
|
||
|
WaitForEvents(const VECTOR_CLASS<Event>& events)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clWaitForEvents(
|
||
|
(cl_uint) events.size(), (cl_event*)&events.front()),
|
||
|
__WAIT_FOR_EVENTS_ERR);
|
||
|
}
|
||
|
|
||
|
/*! \class Memory
|
||
|
* \brief Memory interface for cl_mem.
|
||
|
*/
|
||
|
class Memory : public detail::Wrapper<cl_mem>
|
||
|
{
|
||
|
public:
|
||
|
Memory() : detail::Wrapper<cl_type>() { }
|
||
|
|
||
|
Memory(const Memory& memory) : detail::Wrapper<cl_type>(memory) { }
|
||
|
|
||
|
Memory& operator = (const Memory& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_mem_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetMemObjectInfo, object_, name, param),
|
||
|
__GET_MEM_OBJECT_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_mem_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_mem_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
#if defined(CL_VERSION_1_1)
|
||
|
cl_int setDestructorCallback(
|
||
|
void (CL_CALLBACK * pfn_notify)(cl_mem, void *),
|
||
|
void * user_data = NULL)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clSetMemObjectDestructorCallback(
|
||
|
object_,
|
||
|
pfn_notify,
|
||
|
user_data),
|
||
|
__SET_MEM_OBJECT_DESTRUCTOR_CALLBACK_ERR);
|
||
|
}
|
||
|
#endif
|
||
|
|
||
|
};
|
||
|
|
||
|
__GET_INFO_HELPER_WITH_RETAIN(cl::Memory)
|
||
|
|
||
|
/*! \class Buffer
|
||
|
* \brief Memory buffer interface.
|
||
|
*/
|
||
|
class Buffer : public Memory
|
||
|
{
|
||
|
public:
|
||
|
Buffer(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
::size_t size,
|
||
|
void* host_ptr = NULL,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateBuffer(context(), flags, size, host_ptr, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_BUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Buffer() : Memory() { }
|
||
|
|
||
|
Buffer(const Buffer& buffer) : Memory(buffer) { }
|
||
|
|
||
|
Buffer& operator = (const Buffer& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Memory::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
#if defined(CL_VERSION_1_1)
|
||
|
Buffer createSubBuffer(
|
||
|
cl_mem_flags flags,
|
||
|
cl_buffer_create_type buffer_create_type,
|
||
|
const void * buffer_create_info,
|
||
|
cl_int * err = NULL)
|
||
|
{
|
||
|
Buffer result;
|
||
|
cl_int error;
|
||
|
result.object_ = ::clCreateSubBuffer(
|
||
|
object_,
|
||
|
flags,
|
||
|
buffer_create_type,
|
||
|
buffer_create_info,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_SUBBUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
|
||
|
return result;
|
||
|
}
|
||
|
#endif
|
||
|
};
|
||
|
|
||
|
#if defined (USE_DX_INTEROP)
|
||
|
class BufferD3D10 : public Buffer
|
||
|
{
|
||
|
public:
|
||
|
typedef CL_API_ENTRY cl_mem (CL_API_CALL *PFN_clCreateFromD3D10BufferKHR)(
|
||
|
cl_context context, cl_mem_flags flags, ID3D10Buffer* buffer,
|
||
|
cl_int* errcode_ret);
|
||
|
|
||
|
BufferD3D10(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
ID3D10Buffer* bufobj,
|
||
|
cl_int * err = NULL)
|
||
|
{
|
||
|
static PFN_clCreateFromD3D10BufferKHR pfn_clCreateFromD3D10BufferKHR = NULL;
|
||
|
__INIT_CL_EXT_FCN_PTR(clCreateFromD3D10BufferKHR);
|
||
|
|
||
|
cl_int error;
|
||
|
object_ = pfn_clCreateFromD3D10BufferKHR(
|
||
|
context(),
|
||
|
flags,
|
||
|
bufobj,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_GL_BUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
BufferD3D10() : Buffer() { }
|
||
|
|
||
|
BufferD3D10(const BufferD3D10& buffer) : Buffer(buffer) { }
|
||
|
|
||
|
BufferD3D10& operator = (const BufferD3D10& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Buffer::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
};
|
||
|
#endif
|
||
|
|
||
|
/*! \class BufferGL
|
||
|
* \brief Memory buffer interface for GL interop.
|
||
|
*/
|
||
|
class BufferGL : public Buffer
|
||
|
{
|
||
|
public:
|
||
|
BufferGL(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
GLuint bufobj,
|
||
|
cl_int * err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateFromGLBuffer(
|
||
|
context(),
|
||
|
flags,
|
||
|
bufobj,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_GL_BUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
BufferGL() : Buffer() { }
|
||
|
|
||
|
BufferGL(const BufferGL& buffer) : Buffer(buffer) { }
|
||
|
|
||
|
BufferGL& operator = (const BufferGL& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Buffer::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
cl_int getObjectInfo(
|
||
|
cl_gl_object_type *type,
|
||
|
GLuint * gl_object_name)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clGetGLObjectInfo(object_,type,gl_object_name),
|
||
|
__GET_GL_OBJECT_INFO_ERR);
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class BufferRenderGL
|
||
|
* \brief Memory buffer interface for GL interop with renderbuffer.
|
||
|
*/
|
||
|
class BufferRenderGL : public Buffer
|
||
|
{
|
||
|
public:
|
||
|
BufferRenderGL(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
GLuint bufobj,
|
||
|
cl_int * err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateFromGLRenderbuffer(
|
||
|
context(),
|
||
|
flags,
|
||
|
bufobj,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_GL_BUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
BufferRenderGL() : Buffer() { }
|
||
|
|
||
|
BufferRenderGL(const BufferGL& buffer) : Buffer(buffer) { }
|
||
|
|
||
|
BufferRenderGL& operator = (const BufferRenderGL& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Buffer::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
cl_int getObjectInfo(
|
||
|
cl_gl_object_type *type,
|
||
|
GLuint * gl_object_name)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clGetGLObjectInfo(object_,type,gl_object_name),
|
||
|
__GET_GL_OBJECT_INFO_ERR);
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class Image
|
||
|
* \brief Base class interface for all images.
|
||
|
*/
|
||
|
class Image : public Memory
|
||
|
{
|
||
|
protected:
|
||
|
Image() : Memory() { }
|
||
|
|
||
|
Image(const Image& image) : Memory(image) { }
|
||
|
|
||
|
Image& operator = (const Image& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Memory::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
public:
|
||
|
template <typename T>
|
||
|
cl_int getImageInfo(cl_image_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetImageInfo, object_, name, param),
|
||
|
__GET_IMAGE_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_image_info, name>::param_type
|
||
|
getImageInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_image_info, name>::param_type param;
|
||
|
cl_int result = getImageInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class Image2D
|
||
|
* \brief Image interface for 2D images.
|
||
|
*/
|
||
|
class Image2D : public Image
|
||
|
{
|
||
|
public:
|
||
|
Image2D(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
ImageFormat format,
|
||
|
::size_t width,
|
||
|
::size_t height,
|
||
|
::size_t row_pitch = 0,
|
||
|
void* host_ptr = NULL,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateImage2D(
|
||
|
context(), flags,&format, width, height, row_pitch, host_ptr, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_IMAGE2D_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Image2D() { }
|
||
|
|
||
|
Image2D(const Image2D& image2D) : Image(image2D) { }
|
||
|
|
||
|
Image2D& operator = (const Image2D& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Image::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class Image2DGL
|
||
|
* \brief 2D image interface for GL interop.
|
||
|
*/
|
||
|
class Image2DGL : public Image2D
|
||
|
{
|
||
|
public:
|
||
|
Image2DGL(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
GLenum target,
|
||
|
GLint miplevel,
|
||
|
GLuint texobj,
|
||
|
cl_int * err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateFromGLTexture2D(
|
||
|
context(),
|
||
|
flags,
|
||
|
target,
|
||
|
miplevel,
|
||
|
texobj,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_GL_BUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Image2DGL() : Image2D() { }
|
||
|
|
||
|
Image2DGL(const Image2DGL& image) : Image2D(image) { }
|
||
|
|
||
|
Image2DGL& operator = (const Image2DGL& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Image2D::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class Image3D
|
||
|
* \brief Image interface for 3D images.
|
||
|
*/
|
||
|
class Image3D : public Image
|
||
|
{
|
||
|
public:
|
||
|
Image3D(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
ImageFormat format,
|
||
|
::size_t width,
|
||
|
::size_t height,
|
||
|
::size_t depth,
|
||
|
::size_t row_pitch = 0,
|
||
|
::size_t slice_pitch = 0,
|
||
|
void* host_ptr = NULL,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateImage3D(
|
||
|
context(), flags, &format, width, height, depth, row_pitch,
|
||
|
slice_pitch, host_ptr, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_IMAGE3D_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Image3D() { }
|
||
|
|
||
|
Image3D(const Image3D& image3D) : Image(image3D) { }
|
||
|
|
||
|
Image3D& operator = (const Image3D& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Image::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class Image2DGL
|
||
|
* \brief 2D image interface for GL interop.
|
||
|
*/
|
||
|
class Image3DGL : public Image3D
|
||
|
{
|
||
|
public:
|
||
|
Image3DGL(
|
||
|
const Context& context,
|
||
|
cl_mem_flags flags,
|
||
|
GLenum target,
|
||
|
GLint miplevel,
|
||
|
GLuint texobj,
|
||
|
cl_int * err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateFromGLTexture3D(
|
||
|
context(),
|
||
|
flags,
|
||
|
target,
|
||
|
miplevel,
|
||
|
texobj,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_GL_BUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Image3DGL() : Image3D() { }
|
||
|
|
||
|
Image3DGL(const Image3DGL& image) : Image3D(image) { }
|
||
|
|
||
|
Image3DGL& operator = (const Image3DGL& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
Image3D::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
/*! \class Sampler
|
||
|
* \brief Sampler interface for cl_sampler.
|
||
|
*/
|
||
|
class Sampler : public detail::Wrapper<cl_sampler>
|
||
|
{
|
||
|
public:
|
||
|
Sampler() { }
|
||
|
|
||
|
Sampler(
|
||
|
const Context& context,
|
||
|
cl_bool normalized_coords,
|
||
|
cl_addressing_mode addressing_mode,
|
||
|
cl_filter_mode filter_mode,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateSampler(
|
||
|
context(),
|
||
|
normalized_coords,
|
||
|
addressing_mode,
|
||
|
filter_mode,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_SAMPLER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Sampler(const Sampler& sampler) : detail::Wrapper<cl_type>(sampler) { }
|
||
|
|
||
|
Sampler& operator = (const Sampler& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_sampler_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetSamplerInfo, object_, name, param),
|
||
|
__GET_SAMPLER_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_sampler_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_sampler_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
__GET_INFO_HELPER_WITH_RETAIN(cl::Sampler)
|
||
|
|
||
|
class Program;
|
||
|
class CommandQueue;
|
||
|
class Kernel;
|
||
|
|
||
|
/*! \class NDRange
|
||
|
* \brief NDRange interface
|
||
|
*/
|
||
|
class NDRange
|
||
|
{
|
||
|
private:
|
||
|
size_t<3> sizes_;
|
||
|
cl_uint dimensions_;
|
||
|
|
||
|
public:
|
||
|
NDRange()
|
||
|
: dimensions_(0)
|
||
|
{ }
|
||
|
|
||
|
NDRange(::size_t size0)
|
||
|
: dimensions_(1)
|
||
|
{
|
||
|
sizes_.push_back(size0);
|
||
|
}
|
||
|
|
||
|
NDRange(::size_t size0, ::size_t size1)
|
||
|
: dimensions_(2)
|
||
|
{
|
||
|
sizes_.push_back(size0);
|
||
|
sizes_.push_back(size1);
|
||
|
}
|
||
|
|
||
|
NDRange(::size_t size0, ::size_t size1, ::size_t size2)
|
||
|
: dimensions_(3)
|
||
|
{
|
||
|
sizes_.push_back(size0);
|
||
|
sizes_.push_back(size1);
|
||
|
sizes_.push_back(size2);
|
||
|
}
|
||
|
|
||
|
operator const ::size_t*() const { return (const ::size_t*) sizes_; }
|
||
|
::size_t dimensions() const { return dimensions_; }
|
||
|
};
|
||
|
|
||
|
static const NDRange NullRange;
|
||
|
|
||
|
/*!
|
||
|
* \struct LocalSpaceArg
|
||
|
* \brief Local address raper for use with Kernel::setArg
|
||
|
*/
|
||
|
struct LocalSpaceArg
|
||
|
{
|
||
|
::size_t size_;
|
||
|
};
|
||
|
|
||
|
namespace detail {
|
||
|
|
||
|
template <typename T>
|
||
|
struct KernelArgumentHandler
|
||
|
{
|
||
|
static ::size_t size(const T&) { return sizeof(T); }
|
||
|
static T* ptr(T& value) { return &value; }
|
||
|
};
|
||
|
|
||
|
template <>
|
||
|
struct KernelArgumentHandler<LocalSpaceArg>
|
||
|
{
|
||
|
static ::size_t size(const LocalSpaceArg& value) { return value.size_; }
|
||
|
static void* ptr(LocalSpaceArg&) { return NULL; }
|
||
|
};
|
||
|
|
||
|
}
|
||
|
//! \endcond
|
||
|
|
||
|
inline LocalSpaceArg
|
||
|
__local(::size_t size)
|
||
|
{
|
||
|
LocalSpaceArg ret = { size };
|
||
|
return ret;
|
||
|
}
|
||
|
|
||
|
class KernelFunctor;
|
||
|
|
||
|
/*! \class Kernel
|
||
|
* \brief Kernel interface that implements cl_kernel
|
||
|
*/
|
||
|
class Kernel : public detail::Wrapper<cl_kernel>
|
||
|
{
|
||
|
public:
|
||
|
inline Kernel(const Program& program, const char* name, cl_int* err = NULL);
|
||
|
|
||
|
Kernel() { }
|
||
|
|
||
|
Kernel(const Kernel& kernel) : detail::Wrapper<cl_type>(kernel) { }
|
||
|
|
||
|
Kernel& operator = (const Kernel& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_kernel_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetKernelInfo, object_, name, param),
|
||
|
__GET_KERNEL_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_kernel_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_kernel_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getWorkGroupInfo(
|
||
|
const Device& device, cl_kernel_work_group_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(
|
||
|
&::clGetKernelWorkGroupInfo, object_, device(), name, param),
|
||
|
__GET_KERNEL_WORK_GROUP_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_kernel_work_group_info, name>::param_type
|
||
|
getWorkGroupInfo(const Device& device, cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_kernel_work_group_info, name>::param_type param;
|
||
|
cl_int result = getWorkGroupInfo(device, name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int setArg(cl_uint index, T value)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clSetKernelArg(
|
||
|
object_,
|
||
|
index,
|
||
|
detail::KernelArgumentHandler<T>::size(value),
|
||
|
detail::KernelArgumentHandler<T>::ptr(value)),
|
||
|
__SET_KERNEL_ARGS_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int setArg(cl_uint index, ::size_t size, void* argPtr)
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clSetKernelArg(object_, index, size, argPtr),
|
||
|
__SET_KERNEL_ARGS_ERR);
|
||
|
}
|
||
|
|
||
|
KernelFunctor bind(
|
||
|
const CommandQueue& queue,
|
||
|
const NDRange& offset,
|
||
|
const NDRange& global,
|
||
|
const NDRange& local);
|
||
|
|
||
|
KernelFunctor bind(
|
||
|
const CommandQueue& queue,
|
||
|
const NDRange& global,
|
||
|
const NDRange& local);
|
||
|
};
|
||
|
|
||
|
__GET_INFO_HELPER_WITH_RETAIN(cl::Kernel)
|
||
|
|
||
|
/*! \class Program
|
||
|
* \brief Program interface that implements cl_program.
|
||
|
*/
|
||
|
class Program : public detail::Wrapper<cl_program>
|
||
|
{
|
||
|
public:
|
||
|
typedef VECTOR_CLASS<std::pair<const void*, ::size_t> > Binaries;
|
||
|
typedef VECTOR_CLASS<std::pair<const char*, ::size_t> > Sources;
|
||
|
|
||
|
Program(
|
||
|
const Context& context,
|
||
|
const Sources& sources,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
|
||
|
const ::size_t n = (::size_t)sources.size();
|
||
|
::size_t* lengths = (::size_t*) alloca(n * sizeof(::size_t));
|
||
|
const char** strings = (const char**) alloca(n * sizeof(const char*));
|
||
|
|
||
|
for (::size_t i = 0; i < n; ++i) {
|
||
|
strings[i] = sources[(int)i].first;
|
||
|
lengths[i] = sources[(int)i].second;
|
||
|
}
|
||
|
|
||
|
object_ = ::clCreateProgramWithSource(
|
||
|
context(), (cl_uint)n, strings, lengths, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_PROGRAM_WITH_SOURCE_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Program(
|
||
|
const Context& context,
|
||
|
const VECTOR_CLASS<Device>& devices,
|
||
|
const Binaries& binaries,
|
||
|
VECTOR_CLASS<cl_int>* binaryStatus = NULL,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
const ::size_t n = binaries.size();
|
||
|
::size_t* lengths = (::size_t*) alloca(n * sizeof(::size_t));
|
||
|
const unsigned char** images = (const unsigned char**) alloca(n * sizeof(const void*));
|
||
|
|
||
|
for (::size_t i = 0; i < n; ++i) {
|
||
|
images[i] = (const unsigned char*)binaries[(int)i].first;
|
||
|
lengths[i] = binaries[(int)i].second;
|
||
|
}
|
||
|
|
||
|
object_ = ::clCreateProgramWithBinary(
|
||
|
context(), (cl_uint) devices.size(),
|
||
|
(cl_device_id*)&devices.front(),
|
||
|
lengths, images, binaryStatus != NULL
|
||
|
? (cl_int*) &binaryStatus->front()
|
||
|
: NULL, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_PROGRAM_WITH_BINARY_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
Program() { }
|
||
|
|
||
|
Program(const Program& program) : detail::Wrapper<cl_type>(program) { }
|
||
|
|
||
|
Program& operator = (const Program& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
cl_int build(
|
||
|
const VECTOR_CLASS<Device>& devices,
|
||
|
const char* options = NULL,
|
||
|
void (CL_CALLBACK * notifyFptr)(cl_program, void *) = NULL,
|
||
|
void* data = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clBuildProgram(
|
||
|
object_,
|
||
|
(cl_uint)
|
||
|
devices.size(),
|
||
|
(cl_device_id*)&devices.front(),
|
||
|
options,
|
||
|
notifyFptr,
|
||
|
data),
|
||
|
__BUILD_PROGRAM_ERR);
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_program_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(&::clGetProgramInfo, object_, name, param),
|
||
|
__GET_PROGRAM_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_program_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_program_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getBuildInfo(
|
||
|
const Device& device, cl_program_build_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(
|
||
|
&::clGetProgramBuildInfo, object_, device(), name, param),
|
||
|
__GET_PROGRAM_BUILD_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_program_build_info, name>::param_type
|
||
|
getBuildInfo(const Device& device, cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_program_build_info, name>::param_type param;
|
||
|
cl_int result = getBuildInfo(device, name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
cl_int createKernels(VECTOR_CLASS<Kernel>* kernels)
|
||
|
{
|
||
|
cl_uint numKernels;
|
||
|
cl_int err = ::clCreateKernelsInProgram(object_, 0, NULL, &numKernels);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __CREATE_KERNELS_IN_PROGRAM_ERR);
|
||
|
}
|
||
|
|
||
|
Kernel* value = (Kernel*) alloca(numKernels * sizeof(Kernel));
|
||
|
err = ::clCreateKernelsInProgram(
|
||
|
object_, numKernels, (cl_kernel*) value, NULL);
|
||
|
if (err != CL_SUCCESS) {
|
||
|
return detail::errHandler(err, __CREATE_KERNELS_IN_PROGRAM_ERR);
|
||
|
}
|
||
|
|
||
|
kernels->assign(&value[0], &value[numKernels]);
|
||
|
return CL_SUCCESS;
|
||
|
}
|
||
|
};
|
||
|
|
||
|
__GET_INFO_HELPER_WITH_RETAIN(cl::Program)
|
||
|
|
||
|
inline Kernel::Kernel(const Program& program, const char* name, cl_int* err)
|
||
|
{
|
||
|
cl_int error;
|
||
|
|
||
|
object_ = ::clCreateKernel(program(), name, &error);
|
||
|
detail::errHandler(error, __CREATE_KERNEL_ERR);
|
||
|
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
|
||
|
}
|
||
|
|
||
|
/*! \class CommandQueue
|
||
|
* \brief CommandQueue interface for cl_command_queue.
|
||
|
*/
|
||
|
class CommandQueue : public detail::Wrapper<cl_command_queue>
|
||
|
{
|
||
|
public:
|
||
|
CommandQueue(
|
||
|
const Context& context,
|
||
|
const Device& device,
|
||
|
cl_command_queue_properties properties = 0,
|
||
|
cl_int* err = NULL)
|
||
|
{
|
||
|
cl_int error;
|
||
|
object_ = ::clCreateCommandQueue(
|
||
|
context(), device(), properties, &error);
|
||
|
|
||
|
detail::errHandler(error, __CREATE_COMMAND_QUEUE_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
}
|
||
|
|
||
|
CommandQueue() { }
|
||
|
|
||
|
CommandQueue(const CommandQueue& commandQueue) : detail::Wrapper<cl_type>(commandQueue) { }
|
||
|
|
||
|
CommandQueue& operator = (const CommandQueue& rhs)
|
||
|
{
|
||
|
if (this != &rhs) {
|
||
|
detail::Wrapper<cl_type>::operator=(rhs);
|
||
|
}
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
template <typename T>
|
||
|
cl_int getInfo(cl_command_queue_info name, T* param) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
detail::getInfo(
|
||
|
&::clGetCommandQueueInfo, object_, name, param),
|
||
|
__GET_COMMAND_QUEUE_INFO_ERR);
|
||
|
}
|
||
|
|
||
|
template <cl_int name> typename
|
||
|
detail::param_traits<detail::cl_command_queue_info, name>::param_type
|
||
|
getInfo(cl_int* err = NULL) const
|
||
|
{
|
||
|
typename detail::param_traits<
|
||
|
detail::cl_command_queue_info, name>::param_type param;
|
||
|
cl_int result = getInfo(name, ¶m);
|
||
|
if (err != NULL) {
|
||
|
*err = result;
|
||
|
}
|
||
|
return param;
|
||
|
}
|
||
|
|
||
|
cl_int enqueueReadBuffer(
|
||
|
const Buffer& buffer,
|
||
|
cl_bool blocking,
|
||
|
::size_t offset,
|
||
|
::size_t size,
|
||
|
void* ptr,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueReadBuffer(
|
||
|
object_, buffer(), blocking, offset, size,
|
||
|
ptr,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_READ_BUFFER_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueWriteBuffer(
|
||
|
const Buffer& buffer,
|
||
|
cl_bool blocking,
|
||
|
::size_t offset,
|
||
|
::size_t size,
|
||
|
const void* ptr,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueWriteBuffer(
|
||
|
object_, buffer(), blocking, offset, size,
|
||
|
ptr,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_WRITE_BUFFER_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueCopyBuffer(
|
||
|
const Buffer& src,
|
||
|
const Buffer& dst,
|
||
|
::size_t src_offset,
|
||
|
::size_t dst_offset,
|
||
|
::size_t size,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueCopyBuffer(
|
||
|
object_, src(), dst(), src_offset, dst_offset, size,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQEUE_COPY_BUFFER_ERR);
|
||
|
}
|
||
|
|
||
|
#if defined(CL_VERSION_1_1)
|
||
|
cl_int enqueueReadBufferRect(
|
||
|
const Buffer& buffer,
|
||
|
cl_bool blocking,
|
||
|
const size_t<3>& buffer_offset,
|
||
|
const size_t<3>& host_offset,
|
||
|
const size_t<3>& region,
|
||
|
::size_t buffer_row_pitch,
|
||
|
::size_t buffer_slice_pitch,
|
||
|
::size_t host_row_pitch,
|
||
|
::size_t host_slice_pitch,
|
||
|
void *ptr,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueReadBufferRect(
|
||
|
object_,
|
||
|
buffer(),
|
||
|
blocking,
|
||
|
(const ::size_t *)buffer_offset,
|
||
|
(const ::size_t *)host_offset,
|
||
|
(const ::size_t *)region,
|
||
|
buffer_row_pitch,
|
||
|
buffer_slice_pitch,
|
||
|
host_row_pitch,
|
||
|
host_slice_pitch,
|
||
|
ptr,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_READ_BUFFER_RECT_ERR);
|
||
|
}
|
||
|
|
||
|
|
||
|
cl_int enqueueWriteBufferRect(
|
||
|
const Buffer& buffer,
|
||
|
cl_bool blocking,
|
||
|
const size_t<3>& buffer_offset,
|
||
|
const size_t<3>& host_offset,
|
||
|
const size_t<3>& region,
|
||
|
::size_t buffer_row_pitch,
|
||
|
::size_t buffer_slice_pitch,
|
||
|
::size_t host_row_pitch,
|
||
|
::size_t host_slice_pitch,
|
||
|
void *ptr,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueWriteBufferRect(
|
||
|
object_,
|
||
|
buffer(),
|
||
|
blocking,
|
||
|
(const ::size_t *)buffer_offset,
|
||
|
(const ::size_t *)host_offset,
|
||
|
(const ::size_t *)region,
|
||
|
buffer_row_pitch,
|
||
|
buffer_slice_pitch,
|
||
|
host_row_pitch,
|
||
|
host_slice_pitch,
|
||
|
ptr,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_WRITE_BUFFER_RECT_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueCopyBufferRect(
|
||
|
const Buffer& src,
|
||
|
const Buffer& dst,
|
||
|
const size_t<3>& src_origin,
|
||
|
const size_t<3>& dst_origin,
|
||
|
const size_t<3>& region,
|
||
|
::size_t src_row_pitch,
|
||
|
::size_t src_slice_pitch,
|
||
|
::size_t dst_row_pitch,
|
||
|
::size_t dst_slice_pitch,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueCopyBufferRect(
|
||
|
object_,
|
||
|
src(),
|
||
|
dst(),
|
||
|
(const ::size_t *)src_origin,
|
||
|
(const ::size_t *)dst_origin,
|
||
|
(const ::size_t *)region,
|
||
|
src_row_pitch,
|
||
|
src_slice_pitch,
|
||
|
dst_row_pitch,
|
||
|
dst_slice_pitch,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQEUE_COPY_BUFFER_RECT_ERR);
|
||
|
}
|
||
|
#endif
|
||
|
|
||
|
cl_int enqueueReadImage(
|
||
|
const Image& image,
|
||
|
cl_bool blocking,
|
||
|
const size_t<3>& origin,
|
||
|
const size_t<3>& region,
|
||
|
::size_t row_pitch,
|
||
|
::size_t slice_pitch,
|
||
|
void* ptr,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueReadImage(
|
||
|
object_, image(), blocking, (const ::size_t *) origin,
|
||
|
(const ::size_t *) region, row_pitch, slice_pitch, ptr,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_READ_IMAGE_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueWriteImage(
|
||
|
const Image& image,
|
||
|
cl_bool blocking,
|
||
|
const size_t<3>& origin,
|
||
|
const size_t<3>& region,
|
||
|
::size_t row_pitch,
|
||
|
::size_t slice_pitch,
|
||
|
void* ptr,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueWriteImage(
|
||
|
object_, image(), blocking, (const ::size_t *) origin,
|
||
|
(const ::size_t *) region, row_pitch, slice_pitch, ptr,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_WRITE_IMAGE_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueCopyImage(
|
||
|
const Image& src,
|
||
|
const Image& dst,
|
||
|
const size_t<3>& src_origin,
|
||
|
const size_t<3>& dst_origin,
|
||
|
const size_t<3>& region,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueCopyImage(
|
||
|
object_, src(), dst(), (const ::size_t *) src_origin,
|
||
|
(const ::size_t *)dst_origin, (const ::size_t *) region,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_COPY_IMAGE_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueCopyImageToBuffer(
|
||
|
const Image& src,
|
||
|
const Buffer& dst,
|
||
|
const size_t<3>& src_origin,
|
||
|
const size_t<3>& region,
|
||
|
::size_t dst_offset,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueCopyImageToBuffer(
|
||
|
object_, src(), dst(), (const ::size_t *) src_origin,
|
||
|
(const ::size_t *) region, dst_offset,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_COPY_IMAGE_TO_BUFFER_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueCopyBufferToImage(
|
||
|
const Buffer& src,
|
||
|
const Image& dst,
|
||
|
::size_t src_offset,
|
||
|
const size_t<3>& dst_origin,
|
||
|
const size_t<3>& region,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueCopyBufferToImage(
|
||
|
object_, src(), dst(), src_offset,
|
||
|
(const ::size_t *) dst_origin, (const ::size_t *) region,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_COPY_BUFFER_TO_IMAGE_ERR);
|
||
|
}
|
||
|
|
||
|
void* enqueueMapBuffer(
|
||
|
const Buffer& buffer,
|
||
|
cl_bool blocking,
|
||
|
cl_map_flags flags,
|
||
|
::size_t offset,
|
||
|
::size_t size,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL,
|
||
|
cl_int* err = NULL) const
|
||
|
{
|
||
|
cl_int error;
|
||
|
void * result = ::clEnqueueMapBuffer(
|
||
|
object_, buffer(), blocking, flags, offset, size,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __ENQUEUE_MAP_BUFFER_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
return result;
|
||
|
}
|
||
|
|
||
|
void* enqueueMapImage(
|
||
|
const Image& buffer,
|
||
|
cl_bool blocking,
|
||
|
cl_map_flags flags,
|
||
|
const size_t<3>& origin,
|
||
|
const size_t<3>& region,
|
||
|
::size_t * row_pitch,
|
||
|
::size_t * slice_pitch,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL,
|
||
|
cl_int* err = NULL) const
|
||
|
{
|
||
|
cl_int error;
|
||
|
void * result = ::clEnqueueMapImage(
|
||
|
object_, buffer(), blocking, flags,
|
||
|
(const ::size_t *) origin, (const ::size_t *) region,
|
||
|
row_pitch, slice_pitch,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event,
|
||
|
&error);
|
||
|
|
||
|
detail::errHandler(error, __ENQUEUE_MAP_IMAGE_ERR);
|
||
|
if (err != NULL) {
|
||
|
*err = error;
|
||
|
}
|
||
|
return result;
|
||
|
}
|
||
|
|
||
|
cl_int enqueueUnmapMemObject(
|
||
|
const Memory& memory,
|
||
|
void* mapped_ptr,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueUnmapMemObject(
|
||
|
object_, memory(), mapped_ptr,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_UNMAP_MEM_OBJECT_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueNDRangeKernel(
|
||
|
const Kernel& kernel,
|
||
|
const NDRange& offset,
|
||
|
const NDRange& global,
|
||
|
const NDRange& local,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueNDRangeKernel(
|
||
|
object_, kernel(), (cl_uint) global.dimensions(),
|
||
|
offset.dimensions() != 0 ? (const ::size_t*) offset : NULL,
|
||
|
(const ::size_t*) global,
|
||
|
local.dimensions() != 0 ? (const ::size_t*) local : NULL,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_NDRANGE_KERNEL_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueTask(
|
||
|
const Kernel& kernel,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueTask(
|
||
|
object_, kernel(),
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_TASK_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueNativeKernel(
|
||
|
void (*userFptr)(void *),
|
||
|
std::pair<void*, ::size_t> args,
|
||
|
const VECTOR_CLASS<Memory>* mem_objects = NULL,
|
||
|
const VECTOR_CLASS<const void*>* mem_locs = NULL,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
cl_mem * mems = (mem_objects != NULL && mem_objects->size() > 0)
|
||
|
? (cl_mem*) alloca(mem_objects->size() * sizeof(cl_mem))
|
||
|
: NULL;
|
||
|
|
||
|
if (mems != NULL) {
|
||
|
for (unsigned int i = 0; i < mem_objects->size(); i++) {
|
||
|
mems[i] = ((*mem_objects)[i])();
|
||
|
}
|
||
|
}
|
||
|
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueNativeKernel(
|
||
|
object_, userFptr, args.first, args.second,
|
||
|
(mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0,
|
||
|
mems,
|
||
|
(mem_locs != NULL) ? (const void **) &mem_locs->front() : NULL,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_NATIVE_KERNEL);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueMarker(Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueMarker(object_, (cl_event*) event),
|
||
|
__ENQUEUE_MARKER_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueWaitForEvents(const VECTOR_CLASS<Event>& events) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueWaitForEvents(
|
||
|
object_,
|
||
|
(cl_uint) events.size(),
|
||
|
(const cl_event*) &events.front()),
|
||
|
__ENQUEUE_WAIT_FOR_EVENTS_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueAcquireGLObjects(
|
||
|
const VECTOR_CLASS<Memory>* mem_objects = NULL,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueAcquireGLObjects(
|
||
|
object_,
|
||
|
(mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0,
|
||
|
(mem_objects != NULL) ? (const cl_mem *) &mem_objects->front(): NULL,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_ACQUIRE_GL_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueReleaseGLObjects(
|
||
|
const VECTOR_CLASS<Memory>* mem_objects = NULL,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueReleaseGLObjects(
|
||
|
object_,
|
||
|
(mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0,
|
||
|
(mem_objects != NULL) ? (const cl_mem *) &mem_objects->front(): NULL,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_RELEASE_GL_ERR);
|
||
|
}
|
||
|
|
||
|
#if defined (USE_DX_INTEROP)
|
||
|
typedef CL_API_ENTRY cl_int (CL_API_CALL *PFN_clEnqueueAcquireD3D10ObjectsKHR)(
|
||
|
cl_command_queue command_queue, cl_uint num_objects,
|
||
|
const cl_mem* mem_objects, cl_uint num_events_in_wait_list,
|
||
|
const cl_event* event_wait_list, cl_event* event);
|
||
|
typedef CL_API_ENTRY cl_int (CL_API_CALL *PFN_clEnqueueReleaseD3D10ObjectsKHR)(
|
||
|
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_int enqueueAcquireD3D10Objects(
|
||
|
const VECTOR_CLASS<Memory>* mem_objects = NULL,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
static PFN_clEnqueueAcquireD3D10ObjectsKHR pfn_clEnqueueAcquireD3D10ObjectsKHR = NULL;
|
||
|
__INIT_CL_EXT_FCN_PTR(clEnqueueAcquireD3D10ObjectsKHR);
|
||
|
|
||
|
return detail::errHandler(
|
||
|
pfn_clEnqueueAcquireD3D10ObjectsKHR(
|
||
|
object_,
|
||
|
(mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0,
|
||
|
(mem_objects != NULL) ? (const cl_mem *) &mem_objects->front(): NULL,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_ACQUIRE_GL_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int enqueueReleaseD3D10Objects(
|
||
|
const VECTOR_CLASS<Memory>* mem_objects = NULL,
|
||
|
const VECTOR_CLASS<Event>* events = NULL,
|
||
|
Event* event = NULL) const
|
||
|
{
|
||
|
static PFN_clEnqueueReleaseD3D10ObjectsKHR pfn_clEnqueueReleaseD3D10ObjectsKHR = NULL;
|
||
|
__INIT_CL_EXT_FCN_PTR(clEnqueueReleaseD3D10ObjectsKHR);
|
||
|
|
||
|
return detail::errHandler(
|
||
|
pfn_clEnqueueReleaseD3D10ObjectsKHR(
|
||
|
object_,
|
||
|
(mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0,
|
||
|
(mem_objects != NULL) ? (const cl_mem *) &mem_objects->front(): NULL,
|
||
|
(events != NULL) ? (cl_uint) events->size() : 0,
|
||
|
(events != NULL) ? (cl_event*) &events->front() : NULL,
|
||
|
(cl_event*) event),
|
||
|
__ENQUEUE_RELEASE_GL_ERR);
|
||
|
}
|
||
|
#endif
|
||
|
|
||
|
cl_int enqueueBarrier() const
|
||
|
{
|
||
|
return detail::errHandler(
|
||
|
::clEnqueueBarrier(object_),
|
||
|
__ENQUEUE_BARRIER_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int flush() const
|
||
|
{
|
||
|
return detail::errHandler(::clFlush(object_), __FLUSH_ERR);
|
||
|
}
|
||
|
|
||
|
cl_int finish() const
|
||
|
{
|
||
|
return detail::errHandler(::clFinish(object_), __FINISH_ERR);
|
||
|
}
|
||
|
};
|
||
|
|
||
|
__GET_INFO_HELPER_WITH_RETAIN(cl::CommandQueue)
|
||
|
|
||
|
/*! \class KernelFunctor
|
||
|
* \brief Kernel functor interface
|
||
|
*
|
||
|
* \note Currently only functors of zero to ten arguments are supported. It
|
||
|
* is straightforward to add more and a more general solution, similar to
|
||
|
* Boost.Lambda could be followed if required in the future.
|
||
|
*/
|
||
|
class KernelFunctor
|
||
|
{
|
||
|
private:
|
||
|
Kernel kernel_;
|
||
|
CommandQueue queue_;
|
||
|
NDRange offset_;
|
||
|
NDRange global_;
|
||
|
NDRange local_;
|
||
|
|
||
|
cl_int err_;
|
||
|
public:
|
||
|
KernelFunctor() { }
|
||
|
|
||
|
KernelFunctor(
|
||
|
const Kernel& kernel,
|
||
|
const CommandQueue& queue,
|
||
|
const NDRange& offset,
|
||
|
const NDRange& global,
|
||
|
const NDRange& local) :
|
||
|
kernel_(kernel),
|
||
|
queue_(queue),
|
||
|
offset_(offset),
|
||
|
global_(global),
|
||
|
local_(local),
|
||
|
err_(CL_SUCCESS)
|
||
|
{}
|
||
|
|
||
|
KernelFunctor& operator=(const KernelFunctor& rhs);
|
||
|
|
||
|
KernelFunctor(const KernelFunctor& rhs);
|
||
|
|
||
|
cl_int getError() { return err_; }
|
||
|
|
||
|
inline Event operator()(const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<typename A1>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5, class A6>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4,
|
||
|
class A5, class A6, class A7>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12, class A13>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const A13& a13,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12, class A13, class A14>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const A13& a13,
|
||
|
const A14& a14,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12, class A13, class A14, class A15>
|
||
|
inline Event operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const A13& a13,
|
||
|
const A14& a14,
|
||
|
const A15& a15,
|
||
|
const VECTOR_CLASS<Event>* events = NULL);
|
||
|
};
|
||
|
|
||
|
inline KernelFunctor Kernel::bind(
|
||
|
const CommandQueue& queue,
|
||
|
const NDRange& offset,
|
||
|
const NDRange& global,
|
||
|
const NDRange& local)
|
||
|
{
|
||
|
return KernelFunctor(*this,queue,offset,global,local);
|
||
|
}
|
||
|
|
||
|
inline KernelFunctor Kernel::bind(
|
||
|
const CommandQueue& queue,
|
||
|
const NDRange& global,
|
||
|
const NDRange& local)
|
||
|
{
|
||
|
return KernelFunctor(*this,queue,NullRange,global,local);
|
||
|
}
|
||
|
|
||
|
inline KernelFunctor& KernelFunctor::operator=(const KernelFunctor& rhs)
|
||
|
{
|
||
|
if (this == &rhs) {
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
kernel_ = rhs.kernel_;
|
||
|
queue_ = rhs.queue_;
|
||
|
offset_ = rhs.offset_;
|
||
|
global_ = rhs.global_;
|
||
|
local_ = rhs.local_;
|
||
|
|
||
|
return *this;
|
||
|
}
|
||
|
|
||
|
inline KernelFunctor::KernelFunctor(const KernelFunctor& rhs) :
|
||
|
kernel_(rhs.kernel_),
|
||
|
queue_(rhs.queue_),
|
||
|
offset_(rhs.offset_),
|
||
|
global_(rhs.global_),
|
||
|
local_(rhs.local_)
|
||
|
{
|
||
|
}
|
||
|
|
||
|
Event KernelFunctor::operator()(const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3, typename A4>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3, typename A4, typename A5>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3, typename A4, typename A5,
|
||
|
typename A6>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3, typename A4,
|
||
|
typename A5, typename A6, typename A7>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3, typename A4, typename A5,
|
||
|
typename A6, typename A7, typename A8>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3, typename A4, typename A5,
|
||
|
typename A6, typename A7, typename A8, typename A9>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
kernel_.setArg(8,a9);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<typename A1, typename A2, typename A3, typename A4, typename A5,
|
||
|
typename A6, typename A7, typename A8, typename A9, typename A10>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
kernel_.setArg(8,a9);
|
||
|
kernel_.setArg(9,a10);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
kernel_.setArg(8,a9);
|
||
|
kernel_.setArg(9,a10);
|
||
|
kernel_.setArg(10,a11);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
kernel_.setArg(8,a9);
|
||
|
kernel_.setArg(9,a10);
|
||
|
kernel_.setArg(10,a11);
|
||
|
kernel_.setArg(11,a12);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12, class A13>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const A13& a13,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
kernel_.setArg(8,a9);
|
||
|
kernel_.setArg(9,a10);
|
||
|
kernel_.setArg(10,a11);
|
||
|
kernel_.setArg(11,a12);
|
||
|
kernel_.setArg(12,a13);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12, class A13, class A14>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const A13& a13,
|
||
|
const A14& a14,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
kernel_.setArg(8,a9);
|
||
|
kernel_.setArg(9,a10);
|
||
|
kernel_.setArg(10,a11);
|
||
|
kernel_.setArg(11,a12);
|
||
|
kernel_.setArg(12,a13);
|
||
|
kernel_.setArg(13,a14);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
template<class A1, class A2, class A3, class A4, class A5,
|
||
|
class A6, class A7, class A8, class A9, class A10,
|
||
|
class A11, class A12, class A13, class A14, class A15>
|
||
|
Event KernelFunctor::operator()(
|
||
|
const A1& a1,
|
||
|
const A2& a2,
|
||
|
const A3& a3,
|
||
|
const A4& a4,
|
||
|
const A5& a5,
|
||
|
const A6& a6,
|
||
|
const A7& a7,
|
||
|
const A8& a8,
|
||
|
const A9& a9,
|
||
|
const A10& a10,
|
||
|
const A11& a11,
|
||
|
const A12& a12,
|
||
|
const A13& a13,
|
||
|
const A14& a14,
|
||
|
const A15& a15,
|
||
|
const VECTOR_CLASS<Event>* events)
|
||
|
{
|
||
|
Event event;
|
||
|
|
||
|
kernel_.setArg(0,a1);
|
||
|
kernel_.setArg(1,a2);
|
||
|
kernel_.setArg(2,a3);
|
||
|
kernel_.setArg(3,a4);
|
||
|
kernel_.setArg(4,a5);
|
||
|
kernel_.setArg(5,a6);
|
||
|
kernel_.setArg(6,a7);
|
||
|
kernel_.setArg(7,a8);
|
||
|
kernel_.setArg(8,a9);
|
||
|
kernel_.setArg(9,a10);
|
||
|
kernel_.setArg(10,a11);
|
||
|
kernel_.setArg(11,a12);
|
||
|
kernel_.setArg(12,a13);
|
||
|
kernel_.setArg(13,a14);
|
||
|
kernel_.setArg(14,a15);
|
||
|
|
||
|
err_ = queue_.enqueueNDRangeKernel(
|
||
|
kernel_,
|
||
|
offset_,
|
||
|
global_,
|
||
|
local_,
|
||
|
NULL, // bgaster_fixme - do we want to allow wait event lists?
|
||
|
&event);
|
||
|
|
||
|
return event;
|
||
|
}
|
||
|
|
||
|
#undef __ERR_STR
|
||
|
#if !defined(__CL_USER_OVERRIDE_ERROR_STRINGS)
|
||
|
#undef __GET_DEVICE_INFO_ERR
|
||
|
#undef __GET_PLATFORM_INFO_ERR
|
||
|
#undef __GET_DEVICE_IDS_ERR
|
||
|
#undef __GET_CONTEXT_INFO_ERR
|
||
|
#undef __GET_EVENT_INFO_ERR
|
||
|
#undef __GET_EVENT_PROFILE_INFO_ERR
|
||
|
#undef __GET_MEM_OBJECT_INFO_ERR
|
||
|
#undef __GET_IMAGE_INFO_ERR
|
||
|
#undef __GET_SAMPLER_INFO_ERR
|
||
|
#undef __GET_KERNEL_INFO_ERR
|
||
|
#undef __GET_KERNEL_WORK_GROUP_INFO_ERR
|
||
|
#undef __GET_PROGRAM_INFO_ERR
|
||
|
#undef __GET_PROGRAM_BUILD_INFO_ERR
|
||
|
#undef __GET_COMMAND_QUEUE_INFO_ERR
|
||
|
|
||
|
#undef __CREATE_CONTEXT_FROM_TYPE_ERR
|
||
|
#undef __GET_SUPPORTED_IMAGE_FORMATS_ERR
|
||
|
|
||
|
#undef __CREATE_BUFFER_ERR
|
||
|
#undef __CREATE_SUBBUFFER_ERR
|
||
|
#undef __CREATE_IMAGE2D_ERR
|
||
|
#undef __CREATE_IMAGE3D_ERR
|
||
|
#undef __CREATE_SAMPLER_ERR
|
||
|
#undef __SET_MEM_OBJECT_DESTRUCTOR_CALLBACK_ERR
|
||
|
|
||
|
#undef __CREATE_USER_EVENT_ERR
|
||
|
#undef __SET_USER_EVENT_STATUS_ERR
|
||
|
#undef __SET_EVENT_CALLBACK_ERR
|
||
|
|
||
|
#undef __WAIT_FOR_EVENTS_ERR
|
||
|
|
||
|
#undef __CREATE_KERNEL_ERR
|
||
|
#undef __SET_KERNEL_ARGS_ERR
|
||
|
#undef __CREATE_PROGRAM_WITH_SOURCE_ERR
|
||
|
#undef __CREATE_PROGRAM_WITH_BINARY_ERR
|
||
|
#undef __BUILD_PROGRAM_ERR
|
||
|
#undef __CREATE_KERNELS_IN_PROGRAM_ERR
|
||
|
|
||
|
#undef __CREATE_COMMAND_QUEUE_ERR
|
||
|
#undef __SET_COMMAND_QUEUE_PROPERTY_ERR
|
||
|
#undef __ENQUEUE_READ_BUFFER_ERR
|
||
|
#undef __ENQUEUE_WRITE_BUFFER_ERR
|
||
|
#undef __ENQUEUE_READ_BUFFER_RECT_ERR
|
||
|
#undef __ENQUEUE_WRITE_BUFFER_RECT_ERR
|
||
|
#undef __ENQEUE_COPY_BUFFER_ERR
|
||
|
#undef __ENQEUE_COPY_BUFFER_RECT_ERR
|
||
|
#undef __ENQUEUE_READ_IMAGE_ERR
|
||
|
#undef __ENQUEUE_WRITE_IMAGE_ERR
|
||
|
#undef __ENQUEUE_COPY_IMAGE_ERR
|
||
|
#undef __ENQUEUE_COPY_IMAGE_TO_BUFFER_ERR
|
||
|
#undef __ENQUEUE_COPY_BUFFER_TO_IMAGE_ERR
|
||
|
#undef __ENQUEUE_MAP_BUFFER_ERR
|
||
|
#undef __ENQUEUE_MAP_IMAGE_ERR
|
||
|
#undef __ENQUEUE_UNMAP_MEM_OBJECT_ERR
|
||
|
#undef __ENQUEUE_NDRANGE_KERNEL_ERR
|
||
|
#undef __ENQUEUE_TASK_ERR
|
||
|
#undef __ENQUEUE_NATIVE_KERNEL
|
||
|
|
||
|
#undef __UNLOAD_COMPILER_ERR
|
||
|
#endif //__CL_USER_OVERRIDE_ERROR_STRINGS
|
||
|
|
||
|
#undef __GET_INFO_HELPER_WITH_RETAIN
|
||
|
|
||
|
// Extensions
|
||
|
#undef __INIT_CL_EXT_FCN_PTR
|
||
|
#undef __CREATE_SUB_DEVICES
|
||
|
|
||
|
#if defined(USE_CL_DEVICE_FISSION)
|
||
|
#undef __PARAM_NAME_DEVICE_FISSION
|
||
|
#endif // USE_CL_DEVICE_FISSION
|
||
|
|
||
|
} // namespace cl
|
||
|
|
||
|
#endif // CL_HPP_
|