backend_traits_opencl.hpp

Go to the documentation of this file.

//===---- backend_traits_opencl.hpp - Backend traits for OpenCL --*- C++-*-===//
//
// Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
// See https://llvm.org/LICENSE.txt for license information.
// SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
//
//===----------------------------------------------------------------------===//
//
// This file defines the specializations of the sycl::detail::interop,
// sycl::detail::BackendInput, sycl::detail::BackendReturn and
// sycl::detail::InteropFeatureSupportMap class templates for the OpenCL
// backend.
//
//===----------------------------------------------------------------------===//
 
#pragma once
 
#include <sycl/backend_types.hpp>         // for backend
#include <sycl/context.hpp>               // for context
#include <sycl/detail/backend_traits.hpp> // for BackendInput, BackendReturn
#include <sycl/detail/cl.h>               // for _cl_event, cl_event, cl_de...
#include <sycl/detail/ur.hpp>             // for assertion and ur handles
#include <sycl/device.hpp>                // for device
#include <sycl/event.hpp>                 // for event
#include <sycl/handler.hpp>               // for buffer
#include <sycl/kernel.hpp>                // for kernel
#include <sycl/kernel_bundle.hpp>         // for kernel_bundle
#include <sycl/kernel_bundle_enums.hpp>   // for bundle_state
#include <sycl/platform.hpp>              // for platform
#include <sycl/queue.hpp>                 // for queue
 
#include <vector> // for vector
 
namespace sycl {
inline namespace _V1 {
namespace detail {
 
// TODO the interops for context, device, event, platform and program
// may be removed after removing the deprecated 'get_native()' methods
// from the corresponding classes.
template <> struct interop<backend::opencl, context> {
  using type = cl_context;
};
 
template <> struct interop<backend::opencl, device> {
  using type = cl_device_id;
};
 
template <> struct interop<backend::opencl, queue> {
  using type = cl_command_queue;
};
 
template <> struct interop<backend::opencl, platform> {
  using type = cl_platform_id;
};
 
template <typename DataT, int Dimensions, typename AllocatorT>
struct BackendInput<backend::opencl, buffer<DataT, Dimensions, AllocatorT>> {
  using type = cl_mem;
};
 
template <typename DataT, int Dimensions, typename AllocatorT>
struct BackendReturn<backend::opencl, buffer<DataT, Dimensions, AllocatorT>> {
  using type = std::vector<cl_mem>;
};
 
template <> struct BackendInput<backend::opencl, context> {
  using type = cl_context;
};
 
template <> struct BackendReturn<backend::opencl, context> {
  using type = cl_context;
};
 
template <> struct BackendInput<backend::opencl, device> {
  using type = cl_device_id;
};
 
template <> struct BackendReturn<backend::opencl, device> {
  using type = cl_device_id;
};
 
template <> struct interop<backend::opencl, event> {
  using type = std::vector<cl_event>;
  using value_type = cl_event;
};
template <> struct BackendInput<backend::opencl, event> {
  using type = std::vector<cl_event>;
  using value_type = cl_event;
};
template <> struct BackendReturn<backend::opencl, event> {
  using type = std::vector<cl_event>;
  using value_type = cl_event;
};
 
template <> struct BackendInput<backend::opencl, queue> {
  using type = cl_command_queue;
};
 
template <> struct BackendReturn<backend::opencl, queue> {
  using type = cl_command_queue;
};
 
template <> struct BackendInput<backend::opencl, platform> {
  using type = cl_platform_id;
};
 
template <> struct BackendReturn<backend::opencl, platform> {
  using type = cl_platform_id;
};
 
template <bundle_state State>
struct BackendInput<backend::opencl, kernel_bundle<State>> {
  using type = cl_program;
};
 
template <bundle_state State>
struct BackendReturn<backend::opencl, kernel_bundle<State>> {
  using type = std::vector<cl_program>;
};
 
template <> struct BackendInput<backend::opencl, kernel> {
  using type = cl_kernel;
};
 
template <> struct BackendReturn<backend::opencl, kernel> {
  using type = cl_kernel;
};
 
template <> struct InteropFeatureSupportMap<backend::opencl> {
  static constexpr bool MakePlatform = true;
  static constexpr bool MakeDevice = true;
  static constexpr bool MakeContext = true;
  static constexpr bool MakeQueue = true;
  static constexpr bool MakeEvent = true;
  static constexpr bool MakeBuffer = true;
  static constexpr bool MakeKernel = true;
  static constexpr bool MakeKernelBundle = true;
  static constexpr bool MakeImage = false;
};
 
namespace ur {
// Cast for std::vector<cl_event>, according to the spec, make_event
// should create one(?) event from a vector of cl_event
template <class To> inline To cast(std::vector<cl_event> value) {
  assert(value.size() == 1 &&
         "Temporary workaround requires that the "
         "size of the input vector for make_event be equal to one.");
  return cast<To>(value[0]);
}
 
// These conversions should use UR interop API.
template <>
inline ur_program_handle_t
    cast(cl_program) = delete; // Use urProgramCreateWithNativeHandle
 
template <>
inline ur_device_handle_t
    cast(cl_device_id) = delete; // Use urDeviceCreateWithNativeHandle
} // namespace ur
} // namespace detail
} // namespace _V1
} // namespace sycl