Lines Matching +full:opencl +full:- +full:clhpp
2 // Copyright (c) 2008-2020 The Khronos Group Inc.
8 // http://www.apache.org/licenses/LICENSE-2.0
19 * \brief C++ bindings for OpenCL 1.0, OpenCL 1.1, OpenCL 1.2,
20 * OpenCL 2.0, OpenCL 2.1, OpenCL 2.2, and OpenCL 3.0.
23 * Derived from the OpenCL 1.x C++ bindings written by
29 * Tom Deakin and Simon McIntosh-Smith, July 2013
30 * James Price, 2015-
32 * \date 2019-09-18
47 * http://khronosgroup.github.io/OpenCL-CLHPP/
51 * https://github.com/KhronosGroup/OpenCL-CLHPP/releases
55 * https://github.com/KhronosGroup/OpenCL-CLHPP
61 * reasonable to define C++ bindings for OpenCL.
63 * The interface is contained with a single C++ header file \em opencl.hpp and all
66 * bindings; it is enough to simply include \em opencl.hpp.
73 * fixes in the new header as well as additional OpenCL 2.0 features.
75 * reason we release it as opencl.hpp rather than a new version of cl.hpp.
79 * Due to the evolution of the underlying OpenCL API the 2.0 C++ bindings
81 * and the range of valid underlying OpenCL runtime versions supported.
85 * decimal values representing OpenCL runime versions. The default for
86 * the target is 200, representing OpenCL 2.0 and the minimum is also
91 * Note that this is a compile-time setting, and so affects linking against
107 * custom interface-compatible versions using the CL_HPP_NO_STD_ARRAY,
111 * The OpenCL 1.x versions of the C++ bindings included a size_t wrapper
114 * In the 2.0 version we have replaced this with a std::array-based interface.
118 * Finally, the program construction interface used a clumsy vector-of-pairs
120 * vector-of-vectors and vector-of-strings design. However, for backward
124 * In OpenCL 2.0 OpenCL C is not entirely backward compatibility with
125 * earlier versions. As a result a flag must be passed to the OpenCL C
126 * compiled to request OpenCL 2.0 compilation of kernels with 1.2 as
129 * For those cases the compilation defaults to OpenCL C 2.0.
132 * If more fine-grained decisions on a per-kernel bases are required
139 * - CL_HPP_TARGET_OPENCL_VERSION
141 * Defines the target OpenCL runtime version to build the header
142 * against. Defaults to 200, representing OpenCL 2.0.
144 * - CL_HPP_NO_STD_STRING
147 * defined and may be defined by the user before opencl.hpp is
150 * - CL_HPP_NO_STD_VECTOR
153 * defined and may be defined by the user before opencl.hpp is
156 * - CL_HPP_NO_STD_ARRAY
159 * defined and may be defined by the user before opencl.hpp is
162 * - CL_HPP_NO_STD_UNIQUE_PTR
166 * defined by the user before opencl.hpp is included.
168 * - CL_HPP_ENABLE_EXCEPTIONS
173 * - CL_HPP_ENABLE_SIZE_T_COMPATIBILITY
175 * Backward compatibility option to support cl.hpp-style size_t
182 * - CL_HPP_ENABLE_PROGRAM_CONSTRUCTION_FROM_ARRAY_COMPATIBILITY
187 * - CL_HPP_CL_1_2_DEFAULT_BUILD
189 * Default to OpenCL C 1.2 compilation rather than OpenCL C 2.0
193 * - CL_HPP_USE_CL_DEVICE_FISSION
197 * - CL_HPP_USE_CL_IMAGE2D_FROM_BUFFER_KHR
201 * - CL_HPP_USE_CL_SUB_GROUPS_KHR
205 * - CL_HPP_USE_DX_INTEROP
209 * - CL_HPP_USE_IL_KHR
222 * compiled using special command-line options (such as "-pthread") on some
229 #include <CL/opencl.hpp>
245 if (platver.find("OpenCL 2.") != std::string::npos ||
246 platver.find("OpenCL 3.") != std::string::npos) {
247 // Note: an OpenCL 3.x platform may not support all required features!
252 std::cout << "No OpenCL 2.0 or newer platform found.\n";
253 return -1;
259 return -1;
277 …utput[get_global_id(0)] = inputA[get_global_id(0)] + inputB[get_global_id(0)] + val + *(aNum->bar);
304 vectorAddProgram.build("-cl-std=CL2.0");
319 // Get and run kernel that initializes the program-scope global
334 fooPointer->bar = anSVMInt.get();
404 # pragma message("opencl.hpp: USE_DX_INTEROP is deprecated. Define CL_HPP_USE_DX_INTEROP instead")
408 # pragma message("opencl.hpp: USE_CL_DEVICE_FISSION is deprecated. Define CL_HPP_USE_CL_DEVICE_FISS…
412 # pragma message("opencl.hpp: __CL_ENABLE_EXCEPTIONS is deprecated. Define CL_HPP_ENABLE_EXCEPTIONS…
416 # pragma message("opencl.hpp: __NO_STD_VECTOR is deprecated. Define CL_HPP_NO_STD_VECTOR instead")
420 # pragma message("opencl.hpp: __NO_STD_STRING is deprecated. Define CL_HPP_NO_STD_STRING instead")
424 # pragma message("opencl.hpp: VECTOR_CLASS is deprecated. Alias cl::vector instead")
427 # pragma message("opencl.hpp: STRING_CLASS is deprecated. Alias cl::string instead.")
430 # pragma message("opencl.hpp: __CL_USER_OVERRIDE_ERROR_STRINGS is deprecated. Define CL_HPP_USER_OV…
437 # pragma message("opencl.hpp: __USE_DEV_VECTOR is no longer supported. Expect compilation errors")
440 # pragma message("opencl.hpp: __USE_DEV_STRING is no longer supported. Expect compilation errors")
445 # pragma message("opencl.hpp: CL_HPP_TARGET_OPENCL_VERSION is not defined. It will default to 300 (…
455 …a message("opencl.hpp: CL_HPP_TARGET_OPENCL_VERSION is not a valid value (100, 110, 120, 200, 210,…
460 /* Forward target OpenCL version to C headers if necessary */
481 # pragma message("opencl.hpp: CL_HPP_MINIMUM_OPENCL_VERSION is not a valid value (100, 110, 120, 20…
527 #error Visual studio 2013 or another C++11-supporting compiler required
536 #include <OpenCL/opencl.h>
538 #include <CL/opencl.h>
558 // in case they are not pre-defined
643 // Define size_type appropriately to allow backward-compatibility
649 * OpenCL C calls that require arrays of size_t values, whose
717 * \brief The OpenCL C++ bindings are defined within this namespace.
1013 size_type numBinaries = param->size(); in getInfoHelper()
1056 /* Specialization for reference-counted types. This depends on the
1082 param->resize(elements); in getInfoHelper()
1112 param->assign(begin(value), prev(end(value))); in getInfoHelper()
1116 param->assign(""); in getInfoHelper()
1153 /* Specialization for reference-counted types. This depends on the
1170 err = param->retain(); in getInfoHelper()
1492 // Flags deprecated in OpenCL 2.0
1691 * OpenCL 1.2 devices do have retain/release.
1721 * OpenCL 1.1 devices do not have retain/release.
1819 highVersion += versionInfo[index]-'0'; in getVersion()
1825 lowVersion += versionInfo[index]-'0'; in getVersion()
2112 //! \brief Default constructor - performs no initialization.
2129 this->image_channel_data_type = rhs.image_channel_data_type; in operator =()
2130 this->image_channel_order = rhs.image_channel_order; in operator =()
2179 //! \brief Default constructor - initializes to NULL.
2291 clGetHostTimer(this->get(), &retVal); in getHostTimer()
2315 clGetDeviceAndHostTimer(this->get(), &(retVal.first), &(retVal.second)); in getDeviceAndHostTimer()
2350 devices->resize(ids.size()); in createSubDevices()
2397 devices->resize(ids.size()); in createSubDevices()
2541 //! \brief Default constructor - initializes to NULL.
2640 // API-owned objects. in getDevices()
2642 devices->resize(ids.size()); in getDevices()
2662 * \param devices returns a vector of OpenCL D3D10 devices found. The cl::Device
2663 * values returned in devices can be used to identify a specific OpenCL
2667 * - CL_SUCCESS if the function is executed successfully.
2669 * The application can query specific capabilities of the OpenCL device(s)
2728 // API-owned objects. in getDevices()
2730 devices->resize(ids.size()); in getDevices()
2767 platforms->resize(ids.size()); in get()
2831 * Unload the OpenCL compiler.
2832 * \note Deprecated for OpenCL 1.2. Use Platform::unloadCompiler instead.
3128 //! \brief Default constructor - initializes to NULL.
3131 /*! \brief Constructor from cl_context - takes ownership.
3139 /*! \brief Assignment operator from cl_context - takes ownership.
3212 formats->assign(begin(value), end(value)); in getSupportedImageFormats()
3216 formats->clear(); in getSupportedImageFormats()
3267 //! \brief Default constructor - initializes to NULL.
3270 /*! \brief Constructor from cl_event - takes ownership.
3281 /*! \brief Assignment operator from cl_event - takes ownership.
3410 //! \brief Default constructor - initializes to NULL.
3450 //! \brief Default constructor - initializes to NULL.
3453 /*! \brief Constructor from cl_mem - takes ownership.
3467 /*! \brief Assignment operator from cl_mem - takes ownership.
3542 * value - not the Memory class instance.
3559 // Pre-declare copy functions
3651 // Pre-declare SVM map function
3662 * STL-like allocator class for managing SVM objects provided for convenience.
3666 …* The allocator should not be used to construct a unique_ptr if we are using coarse-grained SVM mo…
3667 …* the coarse-grained management behaviour would behave incorrectly with respect to reference count…
3734 * If the allocator is coarse-grained, this will take ownership to allow
3757 // If allocation was coarse-grained then map it in allocate()
3801 p->~U(); in destroy()
3910 /*! \brief Vector alias to simplify contruction of coarse-grained SVM containers.
3916 /*! \brief Vector alias to simplify contruction of fine-grained SVM containers.
3922 /*! \brief Vector alias to simplify contruction of fine-grained SVM containers that support platfor…
4018 size_type size = sizeof(DataType)*(endIterator - startIterator); in Buffer()
4059 //! \brief Default constructor - initializes to NULL.
4062 /*! \brief Constructor from cl_mem - takes ownership.
4072 /*! \brief Assignment from cl_mem - performs shallow copy.
4141 /*! \brief Class interface for creating OpenCL buffers from ID3D10Buffer's.
4171 cl_platform platform = -1; in BufferD3D10()
4195 //! \brief Default constructor - initializes to NULL.
4198 /*! \brief Constructor from cl_mem - takes ownership.
4208 /*! \brief Assignment from cl_mem - performs shallow copy.
4284 //! \brief Default constructor - initializes to NULL.
4287 /*! \brief Constructor from cl_mem - takes ownership.
4297 /*! \brief Assignment from cl_mem - performs shallow copy.
4381 //! \brief Default constructor - initializes to NULL.
4384 /*! \brief Constructor from cl_mem - takes ownership.
4394 /*! \brief Assignment from cl_mem - performs shallow copy.
4452 //! \brief Default constructor - initializes to NULL.
4455 /*! \brief Constructor from cl_mem - takes ownership.
4465 /*! \brief Assignment from cl_mem - performs shallow copy.
4571 //! \brief Default constructor - initializes to NULL.
4574 /*! \brief Constructor from cl_mem - takes ownership.
4584 /*! \brief Assignment from cl_mem - performs shallow copy.
4661 /*! \brief Constructor from cl_mem - takes ownership.
4747 /*! \brief Constructor from cl_mem - takes ownership.
4823 // Run-time decision based on the actual platform in Image2D()
4826 useCreateImage = (version >= 0x10002); // OpenCL 1.2 or above in Image2D()
4918 * The channel order may differ as described in the OpenCL
4973 //! \brief Default constructor - initializes to NULL.
4976 /*! \brief Constructor from cl_mem - takes ownership.
4986 /*! \brief Assignment from cl_mem - performs shallow copy.
5035 * \note Deprecated for OpenCL 1.2. Please use ImageGL instead.
5069 //! \brief Default constructor - initializes to NULL.
5072 /*! \brief Constructor from cl_mem - takes ownership.
5082 /*! \brief Assignment from cl_mem - performs shallow copy.
5168 /*! \brief Constructor from cl_mem - takes ownership.
5242 // Run-time decision based on the actual platform in Image3D()
5245 useCreateImage = (version >= 0x10002); // OpenCL 1.2 or above in Image3D()
5293 //! \brief Default constructor - initializes to NULL.
5296 /*! \brief Constructor from cl_mem - takes ownership.
5306 /*! \brief Assignment from cl_mem - performs shallow copy.
5385 //! \brief Default constructor - initializes to NULL.
5388 /*! \brief Constructor from cl_mem - takes ownership.
5398 /*! \brief Assignment from cl_mem - performs shallow copy.
5443 * was performed by OpenCL anyway.
5473 /*! \brief Constructor from cl_mem - takes ownership.
5584 //! \brief Default constructor - initializes to NULL.
5587 /*! \brief Constructor from cl_mem - takes ownership.
5597 /*! \brief Assignment from cl_mem - performs shallow copy.
5672 //! \brief Default constructor - initializes to NULL.
5718 /*! \brief Constructor from cl_sampler - takes ownership.
5729 /*! \brief Assignment operator from cl_sampler - takes ownership.
5805 //! \brief Default constructor - resulting range has zero dimensions.
5814 //! \brief Constructs one-dimensional range.
5823 //! \brief Constructs two-dimensional range.
5832 //! \brief Constructs three-dimensional range.
5873 //! \brief A zero-dimensional range.
5940 //! \brief Default constructor - initializes to NULL.
5943 /*! \brief Constructor from cl_kernel - takes ownership.
5954 /*! \brief Assignment operator from cl_kernel - takes ownership.
6179 /*! \brief Enable fine-grained system SVM.
6181 * \note It is only possible to enable fine-grained system SVM if all devices
6184 * \param svmEnabled True if fine-grained system SVM is requested. False otherwise.
6186 * if no devices in the context support fine-grained system SVM.
6273 Kernel retValue(clCloneKernel(this->get(), &error)); in clone()
6319 "-cl-std=CL2.0", in Program()
6356 "-cl-std=CL2.0", in Program()
6444 * Program constructor to allow construction of program from SPIR-V or another IL.
6445 * Valid for either OpenCL >= 2.1 or when CL_HPP_USE_IL_KHR is defined.
6481 "-cl-std=CL2.0", in Program()
6497 * Program constructor to allow construction of program from SPIR-V or another IL
6499 * Valid for either OpenCL >= 2.1 or when CL_HPP_USE_IL_KHR is defined.
6533 "-cl-std=CL2.0", in Program()
6550 * Construct a program object from a list of devices and a per-device list of binaries.
6551 * \param context A valid OpenCL context in which to construct the program.
6552 * \param devices A vector of OpenCL device objects for which the program will be created.
6560 …* \param err if non-NULL will be set to CL_SUCCESS on successful operation or one of the following…
6564 …* CL_INVALID_DEVICE if OpenCL devices listed in devices are not in the list of devices associate…
6566 …* CL_OUT_OF_HOST_MEMORY if there is a failure to allocate resources required by the OpenCL imple…
6610 binaryStatus->resize(numDevices); in Program()
6617 ? &binaryStatus->front() in Program()
6630 * \param kernelNames Semi-colon separated list of builtin kernel names
6664 /*! \brief Constructor from cl_program - takes ownership.
6894 kernels->resize(value.size()); in createKernels()
6932 /*! \brief Sets a SPIR-V specialization constant.
6949 /*! \brief Sets a SPIR-V specialization constant.
7060 param->resize(numBinaries); in getInfo()
7219 // Run-time decision based on the actual platform in CommandQueue()
7222 useWithProperties = (version >= 0x20000); // OpenCL 2.0 or above in CommandQueue()
7285 // Run-time decision based on the actual platform in CommandQueue()
7288 useWithProperties = (version >= 0x20000); // OpenCL 2.0 or above in CommandQueue()
7350 // Run-time decision based on the actual platform in CommandQueue()
7353 useWithProperties = (version >= 0x20000); // OpenCL 2.0 or above in CommandQueue()
7417 // Run-time decision based on the actual platform in CommandQueue()
7420 useWithProperties = (version >= 0x20000); // OpenCL 2.0 or above in CommandQueue()
7468 // Run-time decision based on the actual platform in CommandQueue()
7471 useWithProperties = (version >= 0x20000); // OpenCL 2.0 or above in CommandQueue()
7519 // Run-time decision based on the actual platform in CommandQueue()
7522 useWithProperties = (version >= 0x20000); // OpenCL 2.0 or above in CommandQueue()
7587 /*! \brief Constructor from cl_command_queue - takes ownership.
7666 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueReadBuffer()
7667 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueReadBuffer()
7691 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueWriteBuffer()
7692 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueWriteBuffer()
7715 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueCopyBuffer()
7716 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueCopyBuffer()
7754 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueReadBufferRect()
7755 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueReadBufferRect()
7793 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueWriteBufferRect()
7794 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueWriteBufferRect()
7830 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueCopyBufferRect()
7831 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueCopyBufferRect()
7846 * The pattern type must be an accepted OpenCL data type.
7871 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueFillBuffer()
7872 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueFillBuffer()
7905 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueReadImage()
7906 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueReadImage()
7938 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueWriteImage()
7939 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueWriteImage()
7967 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueCopyImage()
7968 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueCopyImage()
7982 * This is a four component RGBA floating-point color value if
8002 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueFillImage()
8003 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueFillImage()
8036 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueFillImage()
8037 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueFillImage()
8070 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueFillImage()
8071 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueFillImage()
8100 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueCopyImageToBuffer()
8101 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueCopyImageToBuffer()
8129 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueCopyBufferToImage()
8130 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueCopyBufferToImage()
8154 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueMapBuffer()
8155 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueMapBuffer()
8188 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueMapImage()
8189 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueMapImage()
8204 … * Enqueues a command that will allow the host to update a region of a coarse-grained SVM buffer.
8219 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueMapSVM()
8220 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueMapSVM()
8232 … * Enqueues a command that will allow the host to update a region of a coarse-grained SVM buffer.
8247 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueMapSVM()
8248 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueMapSVM()
8259 … * Enqueues a command that will allow the host to update a region of a coarse-grained SVM buffer.
8273 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueMapSVM()
8274 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueMapSVM()
8295 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueUnmapMemObject()
8296 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueUnmapMemObject()
8309 * Enqueues a command that will release a coarse-grained SVM buffer back to the OpenCL runtime.
8322 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueUnmapSVM()
8323 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueUnmapSVM()
8334 * Enqueues a command that will release a coarse-grained SVM buffer back to the OpenCL runtime.
8347 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueUnmapSVM()
8348 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueUnmapSVM()
8359 * Enqueues a command that will release a coarse-grained SVM buffer back to the OpenCL runtime.
8372 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueUnmapSVM()
8373 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueUnmapSVM()
8404 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueMarkerWithWaitList()
8405 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueMarkerWithWaitList()
8434 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueBarrierWithWaitList()
8435 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueBarrierWithWaitList()
8470 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueMigrateMemObjects()
8471 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueMigrateMemObjects()
8487 * @param sizes - The length from each pointer to migrate.
8503 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueMigrateSVM()
8504 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueMigrateSVM()
8532 * @param sizes - The length from each pointer to migrate.
8569 * @param sizes - The length from the beginning of each container to migrate.
8619 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueNDRangeKernel()
8620 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueNDRangeKernel()
8640 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueTask()
8641 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueTask()
8662 elements = mem_objects->size(); in enqueueNativeKernel()
8673 (mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0, in enqueueNativeKernel()
8675 … (mem_locs != NULL && mem_locs->size() > 0) ? (const void **) &mem_locs->front() : NULL, in enqueueNativeKernel()
8676 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueNativeKernel()
8677 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueNativeKernel()
8728 (mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0, in enqueueAcquireGLObjects()
8729 … (mem_objects != NULL && mem_objects->size() > 0) ? (const cl_mem *) &mem_objects->front(): NULL, in enqueueAcquireGLObjects()
8730 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueAcquireGLObjects()
8731 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueAcquireGLObjects()
8750 (mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0, in enqueueReleaseGLObjects()
8751 … (mem_objects != NULL && mem_objects->size() > 0) ? (const cl_mem *) &mem_objects->front(): NULL, in enqueueReleaseGLObjects()
8752 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueReleaseGLObjects()
8753 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueReleaseGLObjects()
8793 (mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0, in enqueueAcquireD3D10Objects()
8794 … (mem_objects != NULL && mem_objects->size() > 0) ? (const cl_mem *) &mem_objects->front(): NULL, in enqueueAcquireD3D10Objects()
8795 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueAcquireD3D10Objects()
8796 (events != NULL) ? (cl_event*) &events->front() : NULL, in enqueueAcquireD3D10Objects()
8826 (mem_objects != NULL) ? (cl_uint) mem_objects->size() : 0, in enqueueReleaseD3D10Objects()
8827 … (mem_objects != NULL && mem_objects->size() > 0) ? (const cl_mem *) &mem_objects->front(): NULL, in enqueueReleaseD3D10Objects()
8828 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueReleaseD3D10Objects()
8829 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueReleaseD3D10Objects()
8967 /*! \brief Constructor from cl_command_queue - takes ownership.
9036 * function will return the pre-existing queue.
9066 * function will return the pre-existing queue.
9094 * function will return the pre-existing queue.
9188 size_type size = sizeof(DataType)*(endIterator - startIterator); in Buffer()
9239 size_type size = sizeof(DataType)*(endIterator - startIterator); in Buffer()
9321 (events != NULL) ? (cl_uint) events->size() : 0, in enqueueMapBuffer()
9322 (events != NULL && events->size() > 0) ? (cl_event*) &events->front() : NULL, in enqueueMapBuffer()
9337 * update a region of a coarse-grained SVM buffer.
9361 * update a region of a coarse-grained SVM buffer.
9385 * update a region of a coarse-grained SVM buffer.
9425 (events != NULL) ? (cl_uint)events->size() : 0, in enqueueUnmapMemObject()
9426 (events != NULL && events->size() > 0) ? (cl_event*)&events->front() : NULL, in enqueueUnmapMemObject()
9438 * Enqueues to the default queue a command that will release a coarse-grained
9439 * SVM buffer back to the OpenCL runtime.
9460 * Enqueues to the default queue a command that will release a coarse-grained
9461 * SVM buffer back to the OpenCL runtime.
9481 * Enqueues to the default queue a command that will release a coarse-grained
9482 * SVM buffer back to the OpenCL runtime.
9565 size_type length = endIterator-startIterator; in copy()
9604 size_type length = endIterator-startIterator; in copy()
9627 * Blocking SVM map operation - performs a blocking map underneath.
9636 * Blocking SVM map operation - performs a blocking map underneath.
10101 //----------------------------------------------------------------------------------------------
10216 * Backward compatibility class to ensure that cl.hpp code works with opencl.hpp.
10257 //-------------------------------------------------------------------------------------------------…