Cycles: svn merge -r41225:41232 ^/trunk/blender
[blender.git] / intern / cycles / kernel / kernel_compat_cuda.h
1 /*
2  * Copyright 2011, Blender Foundation.
3  *
4  * This program is free software; you can redistribute it and/or
5  * modify it under the terms of the GNU General Public License
6  * as published by the Free Software Foundation; either version 2
7  * of the License, or (at your option) any later version.
8  *
9  * This program is distributed in the hope that it will be useful,
10  * but WITHOUT ANY WARRANTY; without even the implied warranty of
11  * MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
12  * GNU General Public License for more details.
13  *
14  * You should have received a copy of the GNU General Public License
15  * along with this program; if not, write to the Free Software Foundation,
16  * Inc., 51 Franklin Street, Fifth Floor, Boston, MA 02110-1301, USA.
17  */
18
19 #ifndef __KERNEL_COMPAT_CUDA_H__
20 #define __KERNEL_COMPAT_CUDA_H__
21
22 #define __KERNEL_GPU__
23 #define __KERNEL_CUDA__
24 #define CCL_NAMESPACE_BEGIN
25 #define CCL_NAMESPACE_END
26
27 #include <cuda.h>
28 #include <float.h>
29
30 #include "util_types.h"
31
32 /* Qualifier wrappers for different names on different devices */
33
34 #define __device  __device__ __inline__
35 #define __device_inline  __device__ __inline__
36 #define __device_noinline  __device__ __noinline__
37 #define __global
38 #define __shared __shared__
39 #define __constant
40
41 /* No assert supported for CUDA */
42
43 #define kernel_assert(cond)
44
45 /* Textures */
46
47 typedef texture<float4, 1> texture_float4;
48 typedef texture<float, 1> texture_float;
49 typedef texture<uint, 1> texture_uint;
50 typedef texture<int, 1> texture_int;
51 typedef texture<uint4, 1> texture_uint4;
52 typedef texture<float4, 2> texture_image_float4;
53 typedef texture<uchar4, 2, cudaReadModeNormalizedFloat> texture_image_uchar4;
54
55 /* Macros to handle different memory storage on different devices */
56
57 #define kernel_tex_fetch(t, index) tex1Dfetch(t, index)
58 #define kernel_tex_interp(t, x) tex1D(t, x)
59 #define kernel_tex_image_interp(t, x, y) tex2D(t, x, y)
60
61 #define kernel_data __data
62
63 #endif /* __KERNEL_COMPAT_CUDA_H__ */
64