blob: 4b4a8b807d4b8f0109eb151e51a460805d312374 [file] [log] [blame]
Anthony Barbier6ff3b192017-09-04 18:44:23 +01001/*
Gian Marco85e6f512018-02-01 16:57:48 +00002 * Copyright (c) 2016-2018 ARM Limited.
Anthony Barbier6ff3b192017-09-04 18:44:23 +01003 *
4 * SPDX-License-Identifier: MIT
5 *
6 * Permission is hereby granted, free of charge, to any person obtaining a copy
7 * of this software and associated documentation files (the "Software"), to
8 * deal in the Software without restriction, including without limitation the
9 * rights to use, copy, modify, merge, publish, distribute, sublicense, and/or
10 * sell copies of the Software, and to permit persons to whom the Software is
11 * furnished to do so, subject to the following conditions:
12 *
13 * The above copyright notice and this permission notice shall be included in all
14 * copies or substantial portions of the Software.
15 *
16 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
17 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
18 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
19 * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
20 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
21 * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN THE
22 * SOFTWARE.
23 */
24#ifndef __ARM_COMPUTE_OPENCL_H__
25#define __ARM_COMPUTE_OPENCL_H__
26
Moritz Pflanzer725788e2017-07-07 15:35:56 +010027#include <string>
28#include <utility>
29
Anthony Barbier6ff3b192017-09-04 18:44:23 +010030/* Configure the Khronos C++ wrapper to target OpenCL 1.2: */
Anthony Barbier340a2722018-01-03 16:21:54 +000031#ifndef ARM_COMPUTE_NO_EXCEPTIONS
Anthony Barbier6ff3b192017-09-04 18:44:23 +010032#define CL_HPP_ENABLE_EXCEPTIONS
Anthony Barbier340a2722018-01-03 16:21:54 +000033#endif // ARM_COMPUTE_NO_EXCEPTIONS
Anthony Barbier6ff3b192017-09-04 18:44:23 +010034#define CL_HPP_CL_1_2_DEFAULT_BUILD
35#define CL_HPP_TARGET_OPENCL_VERSION 110
36#define CL_HPP_MINIMUM_OPENCL_VERSION 110
37#include <CL/cl2.hpp>
38
39namespace cl
40{
41static const NDRange Range_128_1 = NDRange(128, 1);
Moritz Pflanzer725788e2017-07-07 15:35:56 +010042} // namespace cl
Anthony Barbier6ff3b192017-09-04 18:44:23 +010043
44namespace arm_compute
45{
Alex Gildayc357c472018-03-21 13:54:09 +000046/** Check if OpenCL is available.
47 *
48 * @return True if OpenCL is available.
49 */
Anthony Barbier6ff3b192017-09-04 18:44:23 +010050bool opencl_is_available();
Moritz Pflanzer725788e2017-07-07 15:35:56 +010051
Alex Gildayc357c472018-03-21 13:54:09 +000052/** Class for loading OpenCL symbols. */
Moritz Pflanzer725788e2017-07-07 15:35:56 +010053class CLSymbols final
54{
55private:
56 CLSymbols() = default;
57 void load_symbols(void *handle);
58
59public:
Alex Gildayc357c472018-03-21 13:54:09 +000060 /** Get the static instance of CLSymbols.
61 *
62 * @return The static instance of CLSymbols.
63 */
Moritz Pflanzer725788e2017-07-07 15:35:56 +010064 static CLSymbols &get();
Alex Gildayc357c472018-03-21 13:54:09 +000065 /** Load symbols from the given OpenCL library path.
66 *
67 * @param[in] library Path to the OpenCL library.
68 *
69 * @return True if loading the library is successful.
70 */
Moritz Pflanzer725788e2017-07-07 15:35:56 +010071 bool load(const std::string &library);
Alex Gildayc357c472018-03-21 13:54:09 +000072 /** Load symbols from any of the default OpenCL library names.
73 *
74 * @return True if loading any library is successful.
75 */
Moritz Pflanzer725788e2017-07-07 15:35:56 +010076 bool load_default();
77
Anthony Barbier58c4ff12017-11-09 09:15:32 +000078#define DECLARE_FUNCTION_PTR(func_name) \
79 std::function<decltype(func_name)> func_name##_ptr = nullptr
Moritz Pflanzer725788e2017-07-07 15:35:56 +010080
Anthony Barbiera9e15332017-12-22 16:37:30 +000081 DECLARE_FUNCTION_PTR(clCreateContextFromType);
82 DECLARE_FUNCTION_PTR(clCreateCommandQueue);
83 DECLARE_FUNCTION_PTR(clGetContextInfo);
Anthony Barbier58c4ff12017-11-09 09:15:32 +000084 DECLARE_FUNCTION_PTR(clBuildProgram);
85 DECLARE_FUNCTION_PTR(clEnqueueNDRangeKernel);
86 DECLARE_FUNCTION_PTR(clSetKernelArg);
87 DECLARE_FUNCTION_PTR(clReleaseKernel);
88 DECLARE_FUNCTION_PTR(clCreateProgramWithSource);
89 DECLARE_FUNCTION_PTR(clCreateBuffer);
90 DECLARE_FUNCTION_PTR(clRetainKernel);
91 DECLARE_FUNCTION_PTR(clCreateKernel);
92 DECLARE_FUNCTION_PTR(clGetProgramInfo);
93 DECLARE_FUNCTION_PTR(clFlush);
94 DECLARE_FUNCTION_PTR(clFinish);
95 DECLARE_FUNCTION_PTR(clReleaseProgram);
96 DECLARE_FUNCTION_PTR(clRetainContext);
97 DECLARE_FUNCTION_PTR(clCreateProgramWithBinary);
98 DECLARE_FUNCTION_PTR(clReleaseCommandQueue);
99 DECLARE_FUNCTION_PTR(clEnqueueMapBuffer);
100 DECLARE_FUNCTION_PTR(clRetainProgram);
101 DECLARE_FUNCTION_PTR(clGetProgramBuildInfo);
102 DECLARE_FUNCTION_PTR(clEnqueueReadBuffer);
103 DECLARE_FUNCTION_PTR(clEnqueueWriteBuffer);
104 DECLARE_FUNCTION_PTR(clReleaseEvent);
105 DECLARE_FUNCTION_PTR(clReleaseContext);
106 DECLARE_FUNCTION_PTR(clRetainCommandQueue);
107 DECLARE_FUNCTION_PTR(clEnqueueUnmapMemObject);
108 DECLARE_FUNCTION_PTR(clRetainMemObject);
109 DECLARE_FUNCTION_PTR(clReleaseMemObject);
110 DECLARE_FUNCTION_PTR(clGetDeviceInfo);
111 DECLARE_FUNCTION_PTR(clGetDeviceIDs);
112 DECLARE_FUNCTION_PTR(clRetainEvent);
113 DECLARE_FUNCTION_PTR(clGetPlatformIDs);
114 DECLARE_FUNCTION_PTR(clGetKernelWorkGroupInfo);
Gian Marco85e6f512018-02-01 16:57:48 +0000115 DECLARE_FUNCTION_PTR(clGetCommandQueueInfo);
116 DECLARE_FUNCTION_PTR(clGetKernelInfo);
117 DECLARE_FUNCTION_PTR(clGetEventProfilingInfo);
Anthony Barbier58c4ff12017-11-09 09:15:32 +0000118
119#undef DECLARE_FUNCTION_PTR
Moritz Pflanzer725788e2017-07-07 15:35:56 +0100120
121private:
122 std::pair<bool, bool> _loaded{ false, false };
123};
124} // namespace arm_compute
Anthony Barbier6ff3b192017-09-04 18:44:23 +0100125#endif /* __ARM_COMPUTE_OPENCL_H__ */