[Bf-blender-cvs] [0759f671ce1] blender-v3.3-release: Fix T100824: Cycles GPU render broken on macOS 13 Beta and Apple silicon

[Brecht Van Lommel]

Commit: 0759f671ce1ff687c4e3518ee518717c577ed22c
Author: Brecht Van Lommel
Date:   Tue Sep 6 17:27:55 2022 +0200
Branches: blender-v3.3-release
https://developer.blender.org/rB0759f671ce1ff687c4e3518ee518717c577ed22c

Fix T100824: Cycles GPU render broken on macOS 13 Beta and Apple silicon

The recent revert of Apple silicon inlining changes to avoid long compile times
worked on macOS 12, but in macOS 13 Beta it results in render errors. This may
be a compiler bug and perhaps get fixed in time, but try to be on the safe side
and ensure Blender 3.3.0 works regardless.

This brings part of the inlining back, which brings improved performance but
also longer compiler times again. Compile time is around 2min now, where the
previous full inlining was about 5-7min.

Patch by Michael Jones.

Differential Revision: https://developer.blender.org/D15897

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

M	intern/cycles/kernel/device/metal/compat.h

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

diff --git a/intern/cycles/kernel/device/metal/compat.h b/intern/cycles/kernel/device/metal/compat.h
index 674de554f61..b86d1f64307 100644
--- a/intern/cycles/kernel/device/metal/compat.h
+++ b/intern/cycles/kernel/device/metal/compat.h
@@ -46,8 +46,11 @@ using namespace metal::raytracing;
 #  define ccl_device
 #  define ccl_device_inline ccl_device
 #  define ccl_device_forceinline ccl_device
-#  define ccl_device_noinline ccl_device __attribute__((noinline))
-
+#  if defined(__KERNEL_METAL_APPLE__)
+#    define ccl_device_noinline ccl_device
+#  else
+#    define ccl_device_noinline ccl_device __attribute__((noinline))
+#  endif
 #endif
 
 #define ccl_device_noinline_cpu ccl_device