Cr8-xyz/blender
1
0
Fork 0
Code Issues Pull Requests Actions 1 Packages Projects Releases Wiki Activity

Cycles: Disable bake OpenCL kernel for NVidia devices prior to sm_30

Browse Source 
Driver fails to compile kernel in reasonable time for those devices here,
so for easier testing of the OpenCL split kernel work disabling bake kernel
for now.
This commit is contained in:
Sergey Sharybin
2015-05-15 12:30:04 +05:00
parent 960d7df56f
commit c9e8888f87
1 changed files with 12 additions and 1 deletions
Download Patch File Download Diff File Expand all files Collapse all files

13
intern/cycles/kernel/kernel.cl
View File

@@ -102,8 +102,19 @@ __kernel void kernel_ocl_bake(
int x = sx + get_global_id(0); int x = sx + get_global_id(0);
if(x < sx + sw) if(x < sx + sw) {
#if defined(__KERNEL_OPENCL_NVIDIA__) && __COMPUTE_CAPABILITY__ < 300
/* NVidia compiler is spending infinite amount of time trying
* to deal with kernel_bake_evaluate() on architectures prior
* to sm_30.
* For now we disable baking kernel for those devices, so at
* least rendering with split kernel could be compiled.
*/
output[x] = make_float4(0.0f, 0.0f, 0.0f, 0.0f);
#else
kernel_bake_evaluate(kg, input, output, (ShaderEvalType)type, x, offset, sample); kernel_bake_evaluate(kg, input, output, (ShaderEvalType)type, x, offset, sample);
#endif
}
} }
__kernel void kernel_ocl_convert_to_byte( __kernel void kernel_ocl_convert_to_byte(