Cycles:
authorThomas Dinges <blender@dingto.org>
Tue, 14 May 2013 21:18:20 +0000 (21:18 +0000)
committerThomas Dinges <blender@dingto.org>
Tue, 14 May 2013 21:18:20 +0000 (21:18 +0000)
* Code cleanup, remove unused "resolution" variable from the DeviceTask class, was never used.

14 files changed:
intern/cycles/device/device_cpu.cpp
intern/cycles/device/device_cuda.cpp
intern/cycles/device/device_network.h
intern/cycles/device/device_opencl.cpp
intern/cycles/device/device_task.cpp
intern/cycles/device/device_task.h
intern/cycles/kernel/kernel.cl
intern/cycles/kernel/kernel.cpp
intern/cycles/kernel/kernel.cu
intern/cycles/kernel/kernel.h
intern/cycles/kernel/kernel_film.h
intern/cycles/kernel/kernel_sse2.cpp
intern/cycles/kernel/kernel_sse3.cpp
intern/cycles/render/session.cpp

index 47f3273fdfaee8f5a0952e38a2f36f53a84438ed..95df2e216081e02e357cf69cd96f68e76f9f37d7 100644 (file)
@@ -246,13 +246,13 @@ public:
                        for(int y = task.y; y < task.y + task.h; y++)
                                for(int x = task.x; x < task.x + task.w; x++)
                                        kernel_cpu_sse3_tonemap(&kernel_globals, (uchar4*)task.rgba, (float*)task.buffer,
-                                               task.sample, task.resolution, x, y, task.offset, task.stride);
+                                               task.sample, x, y, task.offset, task.stride);
                }
                else if(system_cpu_support_sse2()) {
                        for(int y = task.y; y < task.y + task.h; y++)
                                for(int x = task.x; x < task.x + task.w; x++)
                                        kernel_cpu_sse2_tonemap(&kernel_globals, (uchar4*)task.rgba, (float*)task.buffer,
-                                               task.sample, task.resolution, x, y, task.offset, task.stride);
+                                               task.sample, x, y, task.offset, task.stride);
                }
                else
 #endif
@@ -260,7 +260,7 @@ public:
                        for(int y = task.y; y < task.y + task.h; y++)
                                for(int x = task.x; x < task.x + task.w; x++)
                                        kernel_cpu_tonemap(&kernel_globals, (uchar4*)task.rgba, (float*)task.buffer,
-                                               task.sample, task.resolution, x, y, task.offset, task.stride);
+                                               task.sample, x, y, task.offset, task.stride);
                }
        }
 
index ec7440c972cb2495bd91ff6d2ccb96a947515498..f32c6dde63958b7c5c2f6a63598250ff74b33e28 100644 (file)
@@ -611,9 +611,6 @@ public:
                cuda_assert(cuParamSeti(cuFilmConvert, offset, task.sample))
                offset += sizeof(task.sample);
 
-               cuda_assert(cuParamSeti(cuFilmConvert, offset, task.resolution))
-               offset += sizeof(task.resolution);
-
                cuda_assert(cuParamSeti(cuFilmConvert, offset, task.x))
                offset += sizeof(task.x);
 
index b74329888d309c5bb7e7682b03e733ded5313a04..10b8dadc35d486f8d28f19302796751bf38c5061 100644 (file)
@@ -97,7 +97,7 @@ public:
 
                archive & type & task.x & task.y & task.w & task.h;
                archive & task.rgba & task.buffer & task.sample & task.num_samples;
-               archive & task.resolution & task.offset & task.stride;
+               archive & task.offset & task.stride;
                archive & task.shader_input & task.shader_output & task.shader_eval_type;
                archive & task.shader_x & task.shader_w;
        }
@@ -106,7 +106,7 @@ public:
        {
                archive & tile.x & tile.y & tile.w & tile.h;
                archive & tile.start_sample & tile.num_samples & tile.sample;
-               archive & tile.resolution & tile.offset & tile.stride;
+               archive & tile.offset & tile.stride;
                archive & tile.buffer & tile.rng_state & tile.rgba;
        }
 
index 73d6ae47190cd4fb0c2aa47a53524a8b8dfd443c..4608c06c3d505c9cc3f1ef845e9d6f2838724185 100644 (file)
@@ -651,7 +651,6 @@ public:
                cl_int d_w = task.w;
                cl_int d_h = task.h;
                cl_int d_sample = task.sample;
-               cl_int d_resolution = task.resolution;
                cl_int d_offset = task.offset;
                cl_int d_stride = task.stride;
 
@@ -668,7 +667,6 @@ public:
 #include "kernel_textures.h"
 
                ciErr |= clSetKernelArg(ckFilmConvertKernel, narg++, sizeof(d_sample), (void*)&d_sample);
-               ciErr |= clSetKernelArg(ckFilmConvertKernel, narg++, sizeof(d_resolution), (void*)&d_resolution);
                ciErr |= clSetKernelArg(ckFilmConvertKernel, narg++, sizeof(d_x), (void*)&d_x);
                ciErr |= clSetKernelArg(ckFilmConvertKernel, narg++, sizeof(d_y), (void*)&d_y);
                ciErr |= clSetKernelArg(ckFilmConvertKernel, narg++, sizeof(d_w), (void*)&d_w);
index b3f02deaf6ff14bab5491547a785312dbe8177dd..ad5ff84196336e7f4e5a268995fbb801a29ef1f8 100644 (file)
@@ -30,7 +30,7 @@ CCL_NAMESPACE_BEGIN
 
 DeviceTask::DeviceTask(Type type_)
 : type(type_), x(0), y(0), w(0), h(0), rgba(0), buffer(0),
-  sample(0), num_samples(1), resolution(0),
+  sample(0), num_samples(1),
   shader_input(0), shader_output(0),
   shader_eval_type(0), shader_x(0), shader_w(0)
 {
index 8ca8b88ea49037b318efb231a58d37ee278ec372..cfeb2860d418c9bf98fd598ccc3a1f8798d33c50 100644 (file)
@@ -44,7 +44,6 @@ public:
        device_ptr buffer;
        int sample;
        int num_samples;
-       int resolution;
        int offset, stride;
 
        device_ptr shader_input;
index f98414d4f0221fe17205ebd9a74982f86701510b..22cb806b8e00db4577de976bfa88e3bfd44535bf 100644 (file)
@@ -62,7 +62,7 @@ __kernel void kernel_ocl_tonemap(
        __global type *name,
 #include "kernel_textures.h"
 
-       int sample, int resolution,
+       int sample,
        int sx, int sy, int sw, int sh, int offset, int stride)
 {
        KernelGlobals kglobals, *kg = &kglobals;
@@ -77,7 +77,7 @@ __kernel void kernel_ocl_tonemap(
        int y = sy + get_global_id(1);
 
        if(x < sx + sw && y < sy + sh)
-               kernel_film_tonemap(kg, rgba, buffer, sample, resolution, x, y, offset, stride);
+               kernel_film_tonemap(kg, rgba, buffer, sample, x, y, offset, stride);
 }
 
 /*__kernel void kernel_ocl_shader(__global uint4 *input, __global float *output, int type, int sx)
index d760e63a290688710d0f513f0615656713daeba5..69bc5d8ebb15d4c65e3524d871b4ac069327d3a5 100644 (file)
@@ -95,9 +95,9 @@ void kernel_cpu_path_trace(KernelGlobals *kg, float *buffer, unsigned int *rng_s
 
 /* Tonemapping */
 
-void kernel_cpu_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer, int sample, int resolution, int x, int y, int offset, int stride)
+void kernel_cpu_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer, int sample, int x, int y, int offset, int stride)
 {
-       kernel_film_tonemap(kg, rgba, buffer, sample, resolution, x, y, offset, stride);
+       kernel_film_tonemap(kg, rgba, buffer, sample, x, y, offset, stride);
 }
 
 /* Shader Evaluation */
index fc7992c87f0ab58a73ab6c0cd53e22a1dcea27ad..52e3fe01c0e3f65e47d2bf7fa628889d371343cc 100644 (file)
@@ -35,13 +35,13 @@ extern "C" __global__ void kernel_cuda_path_trace(float *buffer, uint *rng_state
                kernel_path_trace(NULL, buffer, rng_state, sample, x, y, offset, stride);
 }
 
-extern "C" __global__ void kernel_cuda_tonemap(uchar4 *rgba, float *buffer, int sample, int resolution, int sx, int sy, int sw, int sh, int offset, int stride)
+extern "C" __global__ void kernel_cuda_tonemap(uchar4 *rgba, float *buffer, int sample, int sx, int sy, int sw, int sh, int offset, int stride)
 {
        int x = sx + blockDim.x*blockIdx.x + threadIdx.x;
        int y = sy + blockDim.y*blockIdx.y + threadIdx.y;
 
        if(x < sx + sw && y < sy + sh)
-               kernel_film_tonemap(NULL, rgba, buffer, sample, resolution, x, y, offset, stride);
+               kernel_film_tonemap(NULL, rgba, buffer, sample, x, y, offset, stride);
 }
 
 extern "C" __global__ void kernel_cuda_shader(uint4 *input, float4 *output, int type, int sx)
index 20ea5a61906113297e7e29917b4d1b394b236a58..a87cfa395501da061344135b624149b91b367562 100644 (file)
@@ -39,7 +39,7 @@ void kernel_tex_copy(KernelGlobals *kg, const char *name, device_ptr mem, size_t
 void kernel_cpu_path_trace(KernelGlobals *kg, float *buffer, unsigned int *rng_state,
        int sample, int x, int y, int offset, int stride);
 void kernel_cpu_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer,
-       int sample, int resolution, int x, int y, int offset, int stride);
+       int sample, int x, int y, int offset, int stride);
 void kernel_cpu_shader(KernelGlobals *kg, uint4 *input, float4 *output,
        int type, int i);
 
@@ -47,14 +47,14 @@ void kernel_cpu_shader(KernelGlobals *kg, uint4 *input, float4 *output,
 void kernel_cpu_sse2_path_trace(KernelGlobals *kg, float *buffer, unsigned int *rng_state,
        int sample, int x, int y, int offset, int stride);
 void kernel_cpu_sse2_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer,
-       int sample, int resolution, int x, int y, int offset, int stride);
+       int sample, int x, int y, int offset, int stride);
 void kernel_cpu_sse2_shader(KernelGlobals *kg, uint4 *input, float4 *output,
        int type, int i);
 
 void kernel_cpu_sse3_path_trace(KernelGlobals *kg, float *buffer, unsigned int *rng_state,
        int sample, int x, int y, int offset, int stride);
 void kernel_cpu_sse3_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer,
-       int sample, int resolution, int x, int y, int offset, int stride);
+       int sample, int x, int y, int offset, int stride);
 void kernel_cpu_sse3_shader(KernelGlobals *kg, uint4 *input, float4 *output,
        int type, int i);
 #endif
index 232049fb6cb9ff76258b6d457425032e0817f7e9..293b557a38e7f0ddb74714f2d29110591cbfdb76 100644 (file)
@@ -50,7 +50,7 @@ __device uchar4 film_float_to_byte(float4 color)
 
 __device void kernel_film_tonemap(KernelGlobals *kg,
        __global uchar4 *rgba, __global float *buffer,
-       int sample, int resolution, int x, int y, int offset, int stride)
+       int sample, int x, int y, int offset, int stride)
 {
        /* buffer offset */
        int index = offset + x + y*stride;
index e9d482ae5cf00107eaec3dbf82d0163ab8a36004..b58e41f954f00df26f0dcb59cca6b46c583ae649 100644 (file)
@@ -42,9 +42,9 @@ void kernel_cpu_sse2_path_trace(KernelGlobals *kg, float *buffer, unsigned int *
 
 /* Tonemapping */
 
-void kernel_cpu_sse2_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer, int sample, int resolution, int x, int y, int offset, int stride)
+void kernel_cpu_sse2_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer, int sample, int x, int y, int offset, int stride)
 {
-       kernel_film_tonemap(kg, rgba, buffer, sample, resolution, x, y, offset, stride);
+       kernel_film_tonemap(kg, rgba, buffer, sample, x, y, offset, stride);
 }
 
 /* Shader Evaluate */
index 9a8b389cf68461b7d613be7184b1cb914369127d..6982570c59bd497145f8d367f8a6626812205733 100644 (file)
@@ -42,9 +42,9 @@ void kernel_cpu_sse3_path_trace(KernelGlobals *kg, float *buffer, unsigned int *
 
 /* Tonemapping */
 
-void kernel_cpu_sse3_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer, int sample, int resolution, int x, int y, int offset, int stride)
+void kernel_cpu_sse3_tonemap(KernelGlobals *kg, uchar4 *rgba, float *buffer, int sample, int x, int y, int offset, int stride)
 {
-       kernel_film_tonemap(kg, rgba, buffer, sample, resolution, x, y, offset, stride);
+       kernel_film_tonemap(kg, rgba, buffer, sample, x, y, offset, stride);
 }
 
 /* Shader Evaluate */
index 569c29e0b094e7ef08eba7f005acb4829f6d3668..bc847d5719c6f5c2d4d665c3e55770bfb077c7b6 100644 (file)
@@ -831,7 +831,6 @@ void Session::tonemap()
        task.rgba = display->rgba.device_pointer;
        task.buffer = buffers->buffer.device_pointer;
        task.sample = tile_manager.state.sample;
-       task.resolution = tile_manager.state.resolution_divider;
        tile_manager.state.buffer.get_offset_stride(task.offset, task.stride);
 
        if(task.w > 0 && task.h > 0) {