2021-07-23 16:44:52 +00:00
|
|
|
#include <metal_stdlib>
|
|
|
|
|
|
|
|
using namespace metal;
|
|
|
|
struct UBO {
|
|
|
|
/* 0x0000 */ int dynamic_idx;
|
|
|
|
};
|
2022-02-09 23:55:51 +00:00
|
|
|
|
2021-07-23 16:44:52 +00:00
|
|
|
struct tint_array_wrapper {
|
|
|
|
int arr[64];
|
|
|
|
};
|
2022-02-09 23:55:51 +00:00
|
|
|
|
2021-07-23 16:44:52 +00:00
|
|
|
struct S {
|
|
|
|
tint_array_wrapper data;
|
|
|
|
};
|
2022-02-09 23:55:51 +00:00
|
|
|
|
2021-07-23 16:44:52 +00:00
|
|
|
struct Result {
|
|
|
|
/* 0x0000 */ int out;
|
|
|
|
};
|
|
|
|
|
2021-10-28 15:00:39 +00:00
|
|
|
void f_inner(uint local_invocation_index, threadgroup S* const tint_symbol, const constant UBO* const tint_symbol_1, device Result* const tint_symbol_2) {
|
2021-07-30 14:08:06 +00:00
|
|
|
for(uint idx = local_invocation_index; (idx < 64u); idx = (idx + 1u)) {
|
|
|
|
uint const i = idx;
|
2021-08-04 22:15:28 +00:00
|
|
|
(*(tint_symbol)).data.arr[i] = int();
|
2021-07-23 16:44:52 +00:00
|
|
|
}
|
|
|
|
threadgroup_barrier(mem_flags::mem_threadgroup);
|
2021-10-28 15:00:39 +00:00
|
|
|
(*(tint_symbol)).data.arr[(*(tint_symbol_1)).dynamic_idx] = 1;
|
|
|
|
(*(tint_symbol_2)).out = (*(tint_symbol)).data.arr[3];
|
2021-08-04 22:15:28 +00:00
|
|
|
}
|
|
|
|
|
2021-10-28 15:00:39 +00:00
|
|
|
kernel void f(const constant UBO* tint_symbol_4 [[buffer(0)]], device Result* tint_symbol_5 [[buffer(1)]], uint local_invocation_index [[thread_index_in_threadgroup]]) {
|
|
|
|
threadgroup S tint_symbol_3;
|
|
|
|
f_inner(local_invocation_index, &(tint_symbol_3), tint_symbol_4, tint_symbol_5);
|
2021-07-23 16:44:52 +00:00
|
|
|
return;
|
|
|
|
}
|
|
|
|
|