[Bf-blender-cvs] [4789c5ca6d] cycles_split_kernel: Cycles: Fix building of CUDA split kernel

Mai Lavelle noreply at git.blender.org
Tue Mar 7 11:34:59 CET 2017


Commit: 4789c5ca6d0317a4d1745bec454319ead99f20b1
Author: Mai Lavelle
Date:   Tue Mar 7 05:22:44 2017 -0500
Branches: cycles_split_kernel
https://developer.blender.org/rB4789c5ca6d0317a4d1745bec454319ead99f20b1

Cycles: Fix building of CUDA split kernel

===================================================================

M	intern/cycles/kernel/kernels/cuda/kernel_split.cu

===================================================================

diff --git a/intern/cycles/kernel/kernels/cuda/kernel_split.cu b/intern/cycles/kernel/kernels/cuda/kernel_split.cu
index 3445573550..250d957673 100644
--- a/intern/cycles/kernel/kernels/cuda/kernel_split.cu
+++ b/intern/cycles/kernel/kernels/cuda/kernel_split.cu
@@ -25,6 +25,7 @@
 
 #include "../../split/kernel_split_common.h"
 #include "../../split/kernel_data_init.h"
+#include "../../split/kernel_path_init.h"
 #include "../../split/kernel_scene_intersect.h"
 #include "../../split/kernel_lamp_emission.h"
 #include "../../split/kernel_queue_enqueue.h"
@@ -34,12 +35,10 @@
 #include "../../split/kernel_direct_lighting.h"
 #include "../../split/kernel_shadow_blocked.h"
 #include "../../split/kernel_next_iteration_setup.h"
-#include "../../split/kernel_sum_all_radiance.h"
 
 #include "../../kernel_film.h"
 
 /* kernels */
-
 extern "C" __global__ void
 CUDA_LAUNCH_BOUNDS(CUDA_THREADS_BLOCK_WIDTH, CUDA_KERNEL_MAX_REGISTERS)
 kernel_cuda_state_buffer_size(uint num_threads, uint *size)
@@ -49,6 +48,13 @@ kernel_cuda_state_buffer_size(uint num_threads, uint *size)
 
 extern "C" __global__ void
 CUDA_LAUNCH_BOUNDS(CUDA_THREADS_BLOCK_WIDTH, CUDA_KERNEL_MAX_REGISTERS)
+kernel_cuda_path_init()
+{
+	kernel_path_init(NULL);
+}
+
+extern "C" __global__ void
+CUDA_LAUNCH_BOUNDS(CUDA_THREADS_BLOCK_WIDTH, CUDA_KERNEL_MAX_REGISTERS)
 kernel_cuda_path_trace_data_init(
         ccl_global void *split_data_buffer,
         int num_elements,
@@ -57,17 +63,11 @@ kernel_cuda_path_trace_data_init(
         int start_sample,
         int end_sample,
         int sx, int sy, int sw, int sh, int offset, int stride,
-        int rng_state_offset_x,
-        int rng_state_offset_y,
-        int rng_state_stride,
         ccl_global int *Queue_index,
         int queuesize,
         ccl_global char *use_queues_flag,
         ccl_global unsigned int *work_pool_wgs,
         unsigned int num_samples,
-        int buffer_offset_x,
-        int buffer_offset_y,
-        int buffer_stride,
         ccl_global float *buffer)
 {
 	kernel_data_init(NULL,
@@ -79,17 +79,11 @@ kernel_cuda_path_trace_data_init(
 	                 start_sample,
 	                 end_sample,
 	                 sx, sy, sw, sh, offset, stride,
-	                 rng_state_offset_x,
-	                 rng_state_offset_y,
-	                 rng_state_stride,
 	                 Queue_index,
 	                 queuesize,
 	                 use_queues_flag,
 	                 work_pool_wgs,
 	                 num_samples,
-	                 buffer_offset_x,
-	                 buffer_offset_y,
-	                 buffer_stride,
 	                 buffer);
 }




More information about the Bf-blender-cvs mailing list