summaryrefslogtreecommitdiffstatshomepage
path: root/3rdparty/bgfx/3rdparty/spirv-cross/reference/shaders-msl/comp/barriers.comp
diff options
context:
space:
mode:
Diffstat (limited to '3rdparty/bgfx/3rdparty/spirv-cross/reference/shaders-msl/comp/barriers.comp')
-rw-r--r--3rdparty/bgfx/3rdparty/spirv-cross/reference/shaders-msl/comp/barriers.comp33
1 files changed, 22 insertions, 11 deletions
diff --git a/3rdparty/bgfx/3rdparty/spirv-cross/reference/shaders-msl/comp/barriers.comp b/3rdparty/bgfx/3rdparty/spirv-cross/reference/shaders-msl/comp/barriers.comp
index 8c9cfb5d129..82813906f68 100644
--- a/3rdparty/bgfx/3rdparty/spirv-cross/reference/shaders-msl/comp/barriers.comp
+++ b/3rdparty/bgfx/3rdparty/spirv-cross/reference/shaders-msl/comp/barriers.comp
@@ -7,57 +7,68 @@ using namespace metal;
constant uint3 gl_WorkGroupSize [[maybe_unused]] = uint3(4u, 1u, 1u);
-inline void barrier_shared()
+static inline __attribute__((always_inline))
+void barrier_shared()
{
threadgroup_barrier(mem_flags::mem_threadgroup);
}
-inline void full_barrier()
+static inline __attribute__((always_inline))
+void full_barrier()
{
threadgroup_barrier(mem_flags::mem_device | mem_flags::mem_threadgroup | mem_flags::mem_texture);
}
-inline void image_barrier()
+static inline __attribute__((always_inline))
+void image_barrier()
{
threadgroup_barrier(mem_flags::mem_texture);
}
-inline void buffer_barrier()
+static inline __attribute__((always_inline))
+void buffer_barrier()
{
threadgroup_barrier(mem_flags::mem_device);
}
-inline void group_barrier()
+static inline __attribute__((always_inline))
+void group_barrier()
{
threadgroup_barrier(mem_flags::mem_device | mem_flags::mem_threadgroup | mem_flags::mem_texture);
}
-inline void barrier_shared_exec()
+static inline __attribute__((always_inline))
+void barrier_shared_exec()
{
threadgroup_barrier(mem_flags::mem_threadgroup);
}
-inline void full_barrier_exec()
+static inline __attribute__((always_inline))
+void full_barrier_exec()
{
threadgroup_barrier(mem_flags::mem_device | mem_flags::mem_threadgroup | mem_flags::mem_texture);
}
-inline void image_barrier_exec()
+static inline __attribute__((always_inline))
+void image_barrier_exec()
{
threadgroup_barrier(mem_flags::mem_texture);
}
-inline void buffer_barrier_exec()
+static inline __attribute__((always_inline))
+void buffer_barrier_exec()
{
threadgroup_barrier(mem_flags::mem_device);
}
-inline void group_barrier_exec()
+static inline __attribute__((always_inline))
+void group_barrier_exec()
{
threadgroup_barrier(mem_flags::mem_device | mem_flags::mem_threadgroup | mem_flags::mem_texture);
}
-inline void exec_barrier()
+static inline __attribute__((always_inline))
+void exec_barrier()
{
threadgroup_barrier(mem_flags::mem_threadgroup);
}