Cleanup: Cycles: remove unused ccl_loop_no_unroll

Was added in 6121c28501eff722717fb8b777f6004fb6d4e152 to ensure compiling
on OpenCL, now the definition is empty on all platforms

Pull Request: https://projects.blender.org/blender/blender/pulls/131100

Author: Weizhen Huang

src/kernel/device/cuda/compat.h

@@ -52,7 +52,6 @@ typedef unsigned long long uint64_t;
 #define ccl_ray_data ccl_private
 #define ccl_may_alias
 #define ccl_restrict __restrict__
-#define ccl_loop_no_unroll
 #define ccl_align(n) __align__(n)
 #define ccl_optional_struct_init
 

src/kernel/device/hip/compat.h

@@ -45,7 +45,6 @@ typedef unsigned long long uint64_t;
 #define ccl_ray_data ccl_private
 #define ccl_may_alias
 #define ccl_restrict __restrict__
-#define ccl_loop_no_unroll
 #define ccl_align(n) __align__(n)
 #define ccl_optional_struct_init
 

src/kernel/device/metal/compat.h

@@ -58,7 +58,6 @@ using namespace metal::raytracing;
 #endif
 #define ccl_may_alias
 #define ccl_restrict __restrict
-#define ccl_loop_no_unroll
 #define ccl_align(n) alignas(n)
 #define ccl_optional_struct_init
 

src/kernel/device/oneapi/compat.h

@@ -47,7 +47,6 @@
 #define ccl_device_noinline_cpu ccl_device
 #define ccl_device_inline_method ccl_device
 #define ccl_restrict __restrict__
-#define ccl_loop_no_unroll
 #define ccl_optional_struct_init
 #define ccl_private
 #define ccl_ray_data ccl_private

src/kernel/device/optix/compat.h

@@ -52,7 +52,6 @@ typedef unsigned long long uint64_t;
 #define ccl_ray_data ccl_private
 #define ccl_may_alias
 #define ccl_restrict __restrict__
-#define ccl_loop_no_unroll
 #define ccl_align(n) __align__(n)
 
 /* Zero initialize structs to help the compiler figure out scoping */

src/kernel/svm/voronoi.h

@@ -660,8 +660,7 @@ ccl_device VoronoiOutput voronoi_f1(ccl_private const VoronoiParams &params, con
   float4 targetPosition = zero_float4();
   for (int u = -1; u <= 1; u++) {
     for (int k = -1; k <= 1; k++) {
-      ccl_loop_no_unroll for (int j = -1; j <= 1; j++)
-      {
+      for (int j = -1; j <= 1; j++) {
         for (int i = -1; i <= 1; i++) {
           float4 cellOffset = make_float4(i, j, k, u);
           float4 pointPosition = cellOffset + hash_float4_to_float4(cellPosition + cellOffset) *
@@ -696,8 +695,7 @@ ccl_device VoronoiOutput voronoi_smooth_f1(ccl_private const VoronoiParams &para
   float h = -1.0f;
   for (int u = -2; u <= 2; u++) {
     for (int k = -2; k <= 2; k++) {
-      ccl_loop_no_unroll for (int j = -2; j <= 2; j++)
-      {
+      for (int j = -2; j <= 2; j++) {
         for (int i = -2; i <= 2; i++) {
           float4 cellOffset = make_float4(i, j, k, u);
           float4 pointPosition = cellOffset + hash_float4_to_float4(cellPosition + cellOffset) *
@@ -739,8 +737,7 @@ ccl_device VoronoiOutput voronoi_f2(ccl_private const VoronoiParams &params, con
   float4 positionF2 = zero_float4();
   for (int u = -1; u <= 1; u++) {
     for (int k = -1; k <= 1; k++) {
-      ccl_loop_no_unroll for (int j = -1; j <= 1; j++)
-      {
+      for (int j = -1; j <= 1; j++) {
         for (int i = -1; i <= 1; i++) {
           float4 cellOffset = make_float4(i, j, k, u);
           float4 pointPosition = cellOffset + hash_float4_to_float4(cellPosition + cellOffset) *
@@ -781,8 +778,7 @@ ccl_device float voronoi_distance_to_edge(ccl_private const VoronoiParams &param
   float minDistance = FLT_MAX;
   for (int u = -1; u <= 1; u++) {
     for (int k = -1; k <= 1; k++) {
-      ccl_loop_no_unroll for (int j = -1; j <= 1; j++)
-      {
+      for (int j = -1; j <= 1; j++) {
         for (int i = -1; i <= 1; i++) {
           float4 cellOffset = make_float4(i, j, k, u);
           float4 vectorToPoint = cellOffset +
@@ -802,8 +798,7 @@ ccl_device float voronoi_distance_to_edge(ccl_private const VoronoiParams &param
   minDistance = FLT_MAX;
   for (int u = -1; u <= 1; u++) {
     for (int k = -1; k <= 1; k++) {
-      ccl_loop_no_unroll for (int j = -1; j <= 1; j++)
-      {
+      for (int j = -1; j <= 1; j++) {
         for (int i = -1; i <= 1; i++) {
           float4 cellOffset = make_float4(i, j, k, u);
           float4 vectorToPoint = cellOffset +
@@ -835,8 +830,7 @@ ccl_device float voronoi_n_sphere_radius(ccl_private const VoronoiParams &params
   float minDistance = FLT_MAX;
   for (int u = -1; u <= 1; u++) {
     for (int k = -1; k <= 1; k++) {
-      ccl_loop_no_unroll for (int j = -1; j <= 1; j++)
-      {
+      for (int j = -1; j <= 1; j++) {
         for (int i = -1; i <= 1; i++) {
           float4 cellOffset = make_float4(i, j, k, u);
           float4 pointPosition = cellOffset + hash_float4_to_float4(cellPosition + cellOffset) *
@@ -856,8 +850,7 @@ ccl_device float voronoi_n_sphere_radius(ccl_private const VoronoiParams &params
   float4 closestPointToClosestPoint = zero_float4();
   for (int u = -1; u <= 1; u++) {
     for (int k = -1; k <= 1; k++) {
-      ccl_loop_no_unroll for (int j = -1; j <= 1; j++)
-      {
+      for (int j = -1; j <= 1; j++) {
         for (int i = -1; i <= 1; i++) {
           if (i == 0 && j == 0 && k == 0 && u == 0) {
             continue;

src/util/defines.h

@@ -68,7 +68,6 @@
 
 #  define ccl_restrict __restrict
 #  define ccl_optional_struct_init
-#  define ccl_loop_no_unroll
 #  define ccl_attr_maybe_unused [[maybe_unused]]
 #  define __KERNEL_WITH_SSE_ALIGN__