2021-05-20 10:49:33 +00:00
|
|
|
// Copyright 2009-2021 Intel Corporation
|
2021-04-20 16:38:09 +00:00
|
|
|
// SPDX-License-Identifier: Apache-2.0
|
|
|
|
|
|
|
|
#pragma once
|
|
|
|
|
|
|
|
#include "platform.h"
|
|
|
|
#include <vector>
|
|
|
|
#include <set>
|
|
|
|
|
|
|
|
namespace embree
|
|
|
|
{
|
2024-02-24 11:40:55 +00:00
|
|
|
#if defined(EMBREE_SYCL_SUPPORT)
|
|
|
|
|
|
|
|
/* enables SYCL USM allocation */
|
|
|
|
void enableUSMAllocEmbree(sycl::context* context, sycl::device* device);
|
|
|
|
void enableUSMAllocTutorial(sycl::context* context, sycl::device* device);
|
|
|
|
|
|
|
|
/* disables SYCL USM allocation */
|
|
|
|
void disableUSMAllocEmbree();
|
|
|
|
void disableUSMAllocTutorial();
|
|
|
|
|
|
|
|
#endif
|
|
|
|
|
|
|
|
#define ALIGNED_STRUCT_(align) \
|
|
|
|
void* operator new(size_t size) { return alignedMalloc(size,align); } \
|
|
|
|
void operator delete(void* ptr) { alignedFree(ptr); } \
|
2021-04-20 16:38:09 +00:00
|
|
|
void* operator new[](size_t size) { return alignedMalloc(size,align); } \
|
|
|
|
void operator delete[](void* ptr) { alignedFree(ptr); }
|
2024-02-24 11:40:55 +00:00
|
|
|
|
|
|
|
#define ALIGNED_STRUCT_USM_(align) \
|
|
|
|
void* operator new(size_t size) { return alignedUSMMalloc(size,align); } \
|
|
|
|
void operator delete(void* ptr) { alignedUSMFree(ptr); } \
|
|
|
|
void* operator new[](size_t size) { return alignedUSMMalloc(size,align); } \
|
|
|
|
void operator delete[](void* ptr) { alignedUSMFree(ptr); }
|
|
|
|
|
|
|
|
#define ALIGNED_CLASS_(align) \
|
|
|
|
public: \
|
|
|
|
ALIGNED_STRUCT_(align) \
|
|
|
|
private:
|
2021-04-20 16:38:09 +00:00
|
|
|
|
2024-02-24 11:40:55 +00:00
|
|
|
#define ALIGNED_CLASS_USM_(align) \
|
2021-04-20 16:38:09 +00:00
|
|
|
public: \
|
2024-02-24 11:40:55 +00:00
|
|
|
ALIGNED_STRUCT_USM_(align) \
|
2021-04-20 16:38:09 +00:00
|
|
|
private:
|
2024-02-24 11:40:55 +00:00
|
|
|
|
|
|
|
enum EmbreeUSMMode {
|
|
|
|
EMBREE_USM_SHARED = 0,
|
|
|
|
EMBREE_USM_SHARED_DEVICE_READ_WRITE = 0,
|
|
|
|
EMBREE_USM_SHARED_DEVICE_READ_ONLY = 1
|
|
|
|
};
|
2021-04-20 16:38:09 +00:00
|
|
|
|
|
|
|
/*! aligned allocation */
|
|
|
|
void* alignedMalloc(size_t size, size_t align);
|
|
|
|
void alignedFree(void* ptr);
|
2024-02-24 11:40:55 +00:00
|
|
|
|
|
|
|
/*! aligned allocation using SYCL USM */
|
|
|
|
void* alignedUSMMalloc(size_t size, size_t align = 16, EmbreeUSMMode mode = EMBREE_USM_SHARED_DEVICE_READ_ONLY);
|
|
|
|
void alignedUSMFree(void* ptr);
|
|
|
|
|
|
|
|
#if defined(EMBREE_SYCL_SUPPORT)
|
|
|
|
|
|
|
|
/*! aligned allocation using SYCL USM */
|
|
|
|
void* alignedSYCLMalloc(sycl::context* context, sycl::device* device, size_t size, size_t align, EmbreeUSMMode mode);
|
|
|
|
void alignedSYCLFree(sycl::context* context, void* ptr);
|
|
|
|
|
|
|
|
// deleter functor to use as deleter in std unique or shared pointers that
|
|
|
|
// capture raw pointers created by sycl::malloc and it's variants
|
|
|
|
template<typename T>
|
|
|
|
struct sycl_deleter
|
|
|
|
{
|
|
|
|
void operator()(T const* ptr)
|
|
|
|
{
|
|
|
|
alignedUSMFree((void*)ptr);
|
|
|
|
}
|
|
|
|
};
|
|
|
|
|
|
|
|
#endif
|
2021-04-20 16:38:09 +00:00
|
|
|
|
|
|
|
/*! allocator that performs aligned allocations */
|
|
|
|
template<typename T, size_t alignment>
|
|
|
|
struct aligned_allocator
|
|
|
|
{
|
|
|
|
typedef T value_type;
|
|
|
|
typedef T* pointer;
|
|
|
|
typedef const T* const_pointer;
|
|
|
|
typedef T& reference;
|
|
|
|
typedef const T& const_reference;
|
|
|
|
typedef std::size_t size_type;
|
|
|
|
typedef std::ptrdiff_t difference_type;
|
|
|
|
|
|
|
|
__forceinline pointer allocate( size_type n ) {
|
|
|
|
return (pointer) alignedMalloc(n*sizeof(value_type),alignment);
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void deallocate( pointer p, size_type n ) {
|
|
|
|
return alignedFree(p);
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void construct( pointer p, const_reference val ) {
|
|
|
|
new (p) T(val);
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void destroy( pointer p ) {
|
|
|
|
p->~T();
|
|
|
|
}
|
|
|
|
};
|
|
|
|
|
|
|
|
/*! allocates pages directly from OS */
|
|
|
|
bool win_enable_selockmemoryprivilege(bool verbose);
|
|
|
|
bool os_init(bool hugepages, bool verbose);
|
|
|
|
void* os_malloc (size_t bytes, bool& hugepages);
|
|
|
|
size_t os_shrink (void* ptr, size_t bytesNew, size_t bytesOld, bool hugepages);
|
|
|
|
void os_free (void* ptr, size_t bytes, bool hugepages);
|
|
|
|
void os_advise (void* ptr, size_t bytes);
|
|
|
|
|
|
|
|
/*! allocator that performs OS allocations */
|
|
|
|
template<typename T>
|
|
|
|
struct os_allocator
|
|
|
|
{
|
|
|
|
typedef T value_type;
|
|
|
|
typedef T* pointer;
|
|
|
|
typedef const T* const_pointer;
|
|
|
|
typedef T& reference;
|
|
|
|
typedef const T& const_reference;
|
|
|
|
typedef std::size_t size_type;
|
|
|
|
typedef std::ptrdiff_t difference_type;
|
|
|
|
|
|
|
|
__forceinline os_allocator ()
|
|
|
|
: hugepages(false) {}
|
|
|
|
|
|
|
|
__forceinline pointer allocate( size_type n ) {
|
|
|
|
return (pointer) os_malloc(n*sizeof(value_type),hugepages);
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void deallocate( pointer p, size_type n ) {
|
|
|
|
return os_free(p,n*sizeof(value_type),hugepages);
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void construct( pointer p, const_reference val ) {
|
|
|
|
new (p) T(val);
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void destroy( pointer p ) {
|
|
|
|
p->~T();
|
|
|
|
}
|
|
|
|
|
|
|
|
bool hugepages;
|
|
|
|
};
|
|
|
|
|
2024-02-24 11:40:55 +00:00
|
|
|
/*! allocator that newer performs allocations */
|
|
|
|
template<typename T>
|
|
|
|
struct no_allocator
|
|
|
|
{
|
|
|
|
typedef T value_type;
|
|
|
|
typedef T* pointer;
|
|
|
|
typedef const T* const_pointer;
|
|
|
|
typedef T& reference;
|
|
|
|
typedef const T& const_reference;
|
|
|
|
typedef std::size_t size_type;
|
|
|
|
typedef std::ptrdiff_t difference_type;
|
|
|
|
|
|
|
|
__forceinline pointer allocate( size_type n ) {
|
|
|
|
// -- GODOT start --
|
|
|
|
// throw std::runtime_error("no allocation supported");
|
|
|
|
abort();
|
|
|
|
// -- GODOT end --
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void deallocate( pointer p, size_type n ) {
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void construct( pointer p, const_reference val ) {
|
|
|
|
new (p) T(val);
|
|
|
|
}
|
|
|
|
|
|
|
|
__forceinline void destroy( pointer p ) {
|
|
|
|
p->~T();
|
|
|
|
}
|
|
|
|
};
|
|
|
|
|
2021-04-20 16:38:09 +00:00
|
|
|
/*! allocator for IDs */
|
|
|
|
template<typename T, size_t max_id>
|
|
|
|
struct IDPool
|
|
|
|
{
|
|
|
|
typedef T value_type;
|
|
|
|
|
|
|
|
IDPool ()
|
|
|
|
: nextID(0) {}
|
|
|
|
|
|
|
|
T allocate()
|
|
|
|
{
|
|
|
|
/* return ID from list */
|
|
|
|
if (!IDs.empty())
|
|
|
|
{
|
|
|
|
T id = *IDs.begin();
|
|
|
|
IDs.erase(IDs.begin());
|
|
|
|
return id;
|
|
|
|
}
|
|
|
|
|
|
|
|
/* allocate new ID */
|
|
|
|
else
|
|
|
|
{
|
|
|
|
if (size_t(nextID)+1 > max_id)
|
|
|
|
return -1;
|
|
|
|
|
|
|
|
return nextID++;
|
|
|
|
}
|
|
|
|
}
|
|
|
|
|
|
|
|
/* adds an ID provided by the user */
|
|
|
|
bool add(T id)
|
|
|
|
{
|
|
|
|
if (id > max_id)
|
|
|
|
return false;
|
|
|
|
|
|
|
|
/* check if ID should be in IDs set */
|
|
|
|
if (id < nextID) {
|
|
|
|
auto p = IDs.find(id);
|
|
|
|
if (p == IDs.end()) return false;
|
|
|
|
IDs.erase(p);
|
|
|
|
return true;
|
|
|
|
}
|
|
|
|
|
|
|
|
/* otherwise increase ID set */
|
|
|
|
else
|
|
|
|
{
|
|
|
|
for (T i=nextID; i<id; i++) {
|
|
|
|
IDs.insert(i);
|
|
|
|
}
|
|
|
|
nextID = id+1;
|
|
|
|
return true;
|
|
|
|
}
|
|
|
|
}
|
|
|
|
|
|
|
|
void deallocate( T id )
|
|
|
|
{
|
|
|
|
assert(id < nextID);
|
|
|
|
MAYBE_UNUSED auto done = IDs.insert(id).second;
|
|
|
|
assert(done);
|
|
|
|
}
|
|
|
|
|
|
|
|
private:
|
|
|
|
std::set<T> IDs; //!< stores deallocated IDs to be reused
|
|
|
|
T nextID; //!< next ID to use when IDs vector is empty
|
|
|
|
};
|
|
|
|
}
|
|
|
|
|