blob: 6a654fff16396d23ecc72ab389910a40637e42ae [file] [log] [blame]
#include <metal_stdlib>
using namespace metal;
struct tint_private_vars_struct {
uint tint_msl_thread_index_in_quadgroup;
};
uint4 tint_msl_quadSwapX(uint4 e, thread tint_private_vars_struct* const tint_private_vars) {
return quad_shuffle(e,((*(tint_private_vars)).tint_msl_thread_index_in_quadgroup ^ 1u));
}
uint4 quadSwapX_07f1fc(thread tint_private_vars_struct* const tint_private_vars) {
uint4 arg_0 = uint4(1u);
uint4 res = tint_msl_quadSwapX(arg_0, tint_private_vars);
return res;
}
fragment void fragment_main(device uint4* tint_symbol [[buffer(0)]], uint tint_thread_index_in_quadgroup [[thread_index_in_quadgroup]]) {
thread tint_private_vars_struct tint_private_vars = {};
{
tint_private_vars.tint_msl_thread_index_in_quadgroup = tint_thread_index_in_quadgroup;
}
*(tint_symbol) = quadSwapX_07f1fc(&(tint_private_vars));
return;
}
kernel void compute_main(device uint4* tint_symbol_1 [[buffer(0)]], uint tint_thread_index_in_quadgroup_1 [[thread_index_in_quadgroup]]) {
thread tint_private_vars_struct tint_private_vars = {};
{
tint_private_vars.tint_msl_thread_index_in_quadgroup = tint_thread_index_in_quadgroup_1;
}
*(tint_symbol_1) = quadSwapX_07f1fc(&(tint_private_vars));
return;
}