Cycles: OpenCL tweaks
[blender.git] / intern / cycles / kernel / kernel.cl
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 /* OpenCL kernel entry points - unfinished */
20
21 #include "kernel_compat_opencl.h"
22 #include "kernel_math.h"
23 #include "kernel_types.h"
24 #include "kernel_globals.h"
25
26 #include "kernel_film.h"
27 #include "kernel_path.h"
28 //#include "kernel_displace.h"
29
30 __kernel void kernel_ocl_path_trace(
31         __constant KernelData *data,
32         __global float4 *buffer,
33         __global uint *rng_state,
34
35 #define KERNEL_TEX(type, ttype, name) \
36         __global type *name,
37 #include "kernel_textures.h"
38
39         int sample,
40         int sx, int sy, int sw, int sh)
41 {
42         KernelGlobals kglobals, *kg = &kglobals;
43
44         kg->data = data;
45
46 #define KERNEL_TEX(type, ttype, name) \
47         kg->name = name;
48 #include "kernel_textures.h"
49
50         int x = sx + get_global_id(0);
51         int y = sy + get_global_id(1);
52
53         if(x < sx + sw && y < sy + sh)
54                 kernel_path_trace(kg, buffer, rng_state, sample, x, y);
55 }
56
57 __kernel void kernel_ocl_tonemap(
58         __constant KernelData *data,
59         __global uchar4 *rgba,
60         __global float4 *buffer,
61
62 #define KERNEL_TEX(type, ttype, name) \
63         __global type *name,
64 #include "kernel_textures.h"
65
66         int sample, int resolution,
67         int sx, int sy, int sw, int sh)
68 {
69         KernelGlobals kglobals, *kg = &kglobals;
70
71         kg->data = data;
72
73 #define KERNEL_TEX(type, ttype, name) \
74         kg->name = name;
75 #include "kernel_textures.h"
76
77         int x = sx + get_global_id(0);
78         int y = sy + get_global_id(1);
79
80         if(x < sx + sw && y < sy + sh)
81                 kernel_film_tonemap(kg, rgba, buffer, sample, resolution, x, y);
82 }
83
84 /*__kernel void kernel_ocl_displace(__global uint4 *input, __global float3 *offset, int sx)
85 {
86         int x = sx + get_global_id(0);
87
88         kernel_displace(input, offset, x);
89 }*/
90