3f8c995109
Updated Embree 4 library with GPU support is required for it to be compiled - compatiblity with Embree 3 and Embree 4 without GPU support is maintained. Enabling hardware raytracing is an opt-in user setting for now. Pull Request: https://projects.blender.org/blender/blender/pulls/106266
50 lines
1.4 KiB
C
50 lines
1.4 KiB
C
/* SPDX-License-Identifier: Apache-2.0
|
|
* Copyright 2021-2022 Intel Corporation */
|
|
|
|
#pragma once
|
|
|
|
#include "kernel/integrator/state.h"
|
|
#include "kernel/types.h"
|
|
#include "kernel/util/profiling.h"
|
|
|
|
CCL_NAMESPACE_BEGIN
|
|
|
|
/* NOTE(@nsirgien): With SYCL we can't declare __constant__ global variable, which will be
|
|
* accessible from device code, like it has been done for Cycles CUDA backend. So, the backend will
|
|
* allocate this "constant" memory regions and store pointers to them in oneAPI context class */
|
|
|
|
struct IntegratorStateGPU;
|
|
struct IntegratorQueueCounter;
|
|
|
|
typedef struct KernelGlobalsGPU {
|
|
|
|
#define KERNEL_DATA_ARRAY(type, name) const type *__##name = nullptr;
|
|
#include "kernel/data_arrays.h"
|
|
#undef KERNEL_DATA_ARRAY
|
|
IntegratorStateGPU *integrator_state;
|
|
const KernelData *__data;
|
|
|
|
#ifdef WITH_ONEAPI_SYCL_HOST_TASK
|
|
size_t nd_item_local_id_0;
|
|
size_t nd_item_local_range_0;
|
|
size_t nd_item_group_id_0;
|
|
size_t nd_item_group_range_0;
|
|
size_t nd_item_global_id_0;
|
|
size_t nd_item_global_range_0;
|
|
#else
|
|
sycl::kernel_handler kernel_handler;
|
|
#endif
|
|
} KernelGlobalsGPU;
|
|
|
|
typedef ccl_global KernelGlobalsGPU *ccl_restrict KernelGlobals;
|
|
|
|
#define kernel_data (*(__data))
|
|
#define kernel_integrator_state (*(integrator_state))
|
|
|
|
/* data lookup defines */
|
|
|
|
#define kernel_data_fetch(name, index) __##name[index]
|
|
#define kernel_data_array(name) __##name
|
|
|
|
CCL_NAMESPACE_END
|