Cycles: Fix compilation error of AVX2 kernels with SSE optimization disabled
authorSergey Sharybin <sergey.vfx@gmail.com>
Mon, 10 Apr 2017 11:37:19 +0000 (13:37 +0200)
committerSergey Sharybin <sergey.vfx@gmail.com>
Mon, 10 Apr 2017 12:44:04 +0000 (14:44 +0200)
intern/cycles/kernel/geom/geom_curve.h
intern/cycles/kernel/geom/geom_motion_curve.h

index bb33b91847eb0e29ab900e2d669e0e941e5c1919..8888000f0e65740d5af83f7b9ef31f4f826024a0 100644 (file)
@@ -270,7 +270,7 @@ ccl_device_curveintersect bool bvh_cardinal_curve_intersect(KernelGlobals *kg, I
                int ka = max(k0 - 1, v00.x);
                int kb = min(k1 + 1, v00.x + v00.y - 1);
 
-#if defined(__KERNEL_AVX2__) && (!defined(_MSC_VER) || _MSC_VER > 1800)
+#if defined(__KERNEL_AVX2__) && defined(__KERNEL_SSE__) && (!defined(_MSC_VER) || _MSC_VER > 1800)
                avxf P_curve_0_1, P_curve_2_3;
                if(is_curve_primitive) {
                        P_curve_0_1 = _mm256_loadu2_m128(&kg->__curve_keys.data[k0].x, &kg->__curve_keys.data[ka].x);
@@ -305,7 +305,7 @@ ccl_device_curveintersect bool bvh_cardinal_curve_intersect(KernelGlobals *kg, I
                ssef htfm1 = shuffle<1, 0, 1, 3>(load1f_first(extract<0>(d_ss)), vdir0);
                ssef htfm2 = shuffle<1, 3, 2, 3>(mul_shuf, vdir0);
 
-#if defined(__KERNEL_AVX2__) && (!defined(_MSC_VER) || _MSC_VER > 1800)
+#if defined(__KERNEL_AVX2__) && defined(__KERNEL_SSE__) && (!defined(_MSC_VER) || _MSC_VER > 1800)
                const avxf vPP = _mm256_broadcast_ps(&P.m128);
                const avxf htfm00 = avxf(htfm0.m128, htfm0.m128);
                const avxf htfm11 = avxf(htfm1.m128, htfm1.m128);
index dc1388b66439357b0aa865e35fee5a02d0392f40..119bdb2f15c2e5e1ad7289b7f869e4a7d7fd7de2 100644 (file)
@@ -152,7 +152,7 @@ ccl_device_inline void motion_cardinal_curve_keys(KernelGlobals *kg,
        keys[3] = (1.0f - t)*keys[3] + t*next_keys[3];
 }
 
-#ifdef __KERNEL_AVX2__
+#if defined(__KERNEL_AVX2__) && defined(__KERNEL_SSE__)
 /* Similar to above, but returns keys as pair of two AVX registers with each
  * holding two float4.
  */