helpers.cpp

Go to the documentation of this file.

//==---------------- helpers.cpp - SYCL helpers ---------------------------==//
//
// 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
//
//===----------------------------------------------------------------------===//
 
#include <CL/sycl/detail/helpers.hpp>
 
#include <CL/sycl/event.hpp>
#include <detail/context_impl.hpp>
#include <detail/event_impl.hpp>
 
#include <memory>
 
__SYCL_INLINE_NAMESPACE(cl) {
namespace sycl {
using ContextImplPtr = std::shared_ptr<cl::sycl::detail::context_impl>;
namespace detail {
std::vector<RT::PiEvent> getOrWaitEvents(std::vector<cl::sycl::event> DepEvents,
                                         ContextImplPtr Context) {
  std::vector<RT::PiEvent> Events;
  for (auto SyclEvent : DepEvents) {
    auto SyclEventImplPtr = detail::getSyclObjImpl(SyclEvent);
    // throwaway events created with default constructor will not have a context
    // (which is set lazily) calling is_host(), getContextImpl() would set that
    // context, which we wish to avoid as it is expensive.
    if (SyclEventImplPtr->MIsContextInitialized == false) {
      continue;
    }
    if (SyclEventImplPtr->is_host() ||
        SyclEventImplPtr->getContextImpl() != Context) {
      SyclEventImplPtr->waitInternal();
    } else {
      Events.push_back(SyclEventImplPtr->getHandleRef());
    }
  }
  return Events;
}
 
void waitEvents(std::vector<cl::sycl::event> DepEvents) {
  for (auto SyclEvent : DepEvents) {
    detail::getSyclObjImpl(SyclEvent)->waitInternal();
  }
}
 
} // namespace detail
} // namespace sycl
} // __SYCL_INLINE_NAMESPACE(cl)