Program Listing for File SyclUnifiedMemoryResourceFactory.cpp

↰ Return to documentation for file (umpire/resource/SyclUnifiedMemoryResourceFactory.cpp)

//////////////////////////////////////////////////////////////////////////////
// Copyright (c) 2016-20, Lawrence Livermore National Security, LLC and Umpire
// project contributors. See the COPYRIGHT file for details.
//
// SPDX-License-Identifier: (MIT)
//////////////////////////////////////////////////////////////////////////////
#include "umpire/resource/SyclUnifiedMemoryResourceFactory.hpp"

#include "umpire/alloc/SyclMallocManagedAllocator.hpp"
#include "umpire/resource/SyclDeviceMemoryResource.hpp"
#include "umpire/util/make_unique.hpp"

namespace umpire {
namespace resource {

bool SyclUnifiedMemoryResourceFactory::isValidMemoryResourceFor(
    const std::string& name) noexcept
{
  // can easily do it with host_unified_memory<>()
  if (name.find("UM") != std::string::npos) {
    return true;
  } else {
    return false;
  }
}

std::unique_ptr<resource::MemoryResource>
SyclUnifiedMemoryResourceFactory::create(const std::string& name, int id)
{
  return create(name, id, getDefaultTraits());
}

std::unique_ptr<resource::MemoryResource>
SyclUnifiedMemoryResourceFactory::create(const std::string& name, int id,
                                         MemoryResourceTraits traits)
{
  return util::make_unique<
      resource::SyclDeviceMemoryResource<alloc::SyclMallocManagedAllocator>>(
      Platform::sycl, name, id, traits);
}

MemoryResourceTraits SyclUnifiedMemoryResourceFactory::getDefaultTraits()
{
  MemoryResourceTraits traits;

  cl::sycl::gpu_selector gpuSelect;
  cl::sycl::device sycl_device(gpuSelect);
  const std::string deviceName =
      sycl_device.get_info<cl::sycl::info::device::name>();
  if (sycl_device.is_gpu() &&
      (deviceName.find("Intel(R) Gen9 HD Graphics NEO") != std::string::npos)) {
    traits.size =
        sycl_device
            .get_info<cl::sycl::info::device::global_mem_size>(); // in bytes
    traits.unified =
        sycl_device.get_info<cl::sycl::info::device::host_unified_memory>();

    traits.id = 0;

    traits.vendor = MemoryResourceTraits::vendor_type::INTEL;
    traits.kind = MemoryResourceTraits::memory_type::GDDR;
    traits.used_for = MemoryResourceTraits::optimized_for::any;
    traits.resource = MemoryResourceTraits::resource_type::UM;
  }

  return traits;
}

} // end of namespace resource
} // end of namespace umpire