Fix cycles aliasing warnings caused by motion blur transforms.
[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 #define __may_alias
41
42 /* No assert supported for CUDA */
43
44 #define kernel_assert(cond)
45
46 /* Textures */
47
48 typedef texture<float4, 1> texture_float4;
49 typedef texture<float2, 1> texture_float2;
50 typedef texture<float, 1> texture_float;
51 typedef texture<uint, 1> texture_uint;
52 typedef texture<int, 1> texture_int;
53 typedef texture<uint4, 1> texture_uint4;
54 typedef texture<uchar4, 1> texture_uchar4;
55 typedef texture<float4, 2> texture_image_float4;
56 typedef texture<uchar4, 2, cudaReadModeNormalizedFloat> texture_image_uchar4;
57
58 /* Macros to handle different memory storage on different devices */
59
60 #define kernel_tex_fetch(t, index) tex1Dfetch(t, index)
61 #define kernel_tex_interp(t, x, size) tex1D(t, x)
62 #define kernel_tex_image_interp(t, x, y) tex2D(t, x, y)
63
64 #define kernel_data __data
65
66 /* Use fast math functions */
67
68 #define cosf(x) __cosf(((float)x))
69 #define sinf(x) __sinf(((float)x))
70 #define powf(x, y) __powf(((float)x), ((float)y))
71 #define tanf(x) __tanf(((float)x))
72 #define logf(x) __logf(((float)x))
73 #define expf(x) __expf(((float)x))
74
75 #endif /* __KERNEL_COMPAT_CUDA_H__ */
76