Changeset View
Changeset View
Standalone View
Standalone View
intern/cycles/kernel/device/cuda/globals.h
| Show All 21 Lines | |||||
| #include "kernel/kernel_types.h" | #include "kernel/kernel_types.h" | ||||
| #include "kernel/integrator/integrator_state.h" | #include "kernel/integrator/integrator_state.h" | ||||
| CCL_NAMESPACE_BEGIN | CCL_NAMESPACE_BEGIN | ||||
| /* Not actually used, just a NULL pointer that gets passed everywhere, which we | /* Not actually used, just a NULL pointer that gets passed everywhere, which we | ||||
| * hope gets optimized out by the compiler. */ | * hope gets optimized out by the compiler. */ | ||||
| struct KernelGlobals { | struct KernelGlobalsGPU { | ||||
| int unused[1]; | int unused[1]; | ||||
| }; | }; | ||||
| typedef ccl_global const KernelGlobalsGPU *ccl_restrict KernelGlobals; | |||||
| /* Global scene data and textures */ | /* Global scene data and textures */ | ||||
| __constant__ KernelData __data; | __constant__ KernelData __data; | ||||
| #define KERNEL_TEX(type, name) const __constant__ __device__ type *name; | #define KERNEL_TEX(type, name) const __constant__ __device__ type *name; | ||||
| #include "kernel/kernel_textures.h" | #include "kernel/kernel_textures.h" | ||||
| /* Integrator state */ | /* Integrator state */ | ||||
| __constant__ IntegratorStateGPU __integrator_state; | __constant__ IntegratorStateGPU __integrator_state; | ||||
| /* Abstraction macros */ | /* Abstraction macros */ | ||||
| #define kernel_data __data | #define kernel_data __data | ||||
| #define kernel_tex_fetch(t, index) t[(index)] | #define kernel_tex_fetch(t, index) t[(index)] | ||||
| #define kernel_tex_array(t) (t) | #define kernel_tex_array(t) (t) | ||||
| #define kernel_integrator_state __integrator_state | #define kernel_integrator_state __integrator_state | ||||
| CCL_NAMESPACE_END | CCL_NAMESPACE_END | ||||