blob: 4b91b2441999a58a4027e6932af2a98f759dd45d [file] [log] [blame]
//
// fragment_main
//
#include <metal_stdlib>
using namespace metal;
struct tint_module_vars_struct {
device uint2* prevent_dce;
};
uint2 subgroupExclusiveAdd_48acea() {
uint2 res = simd_prefix_exclusive_sum(uint2(1u));
return res;
}
fragment void fragment_main(device uint2* prevent_dce [[buffer(0)]]) {
tint_module_vars_struct const tint_module_vars = tint_module_vars_struct{.prevent_dce=prevent_dce};
(*tint_module_vars.prevent_dce) = subgroupExclusiveAdd_48acea();
}
//
// compute_main
//
#include <metal_stdlib>
using namespace metal;
struct tint_module_vars_struct {
device uint2* prevent_dce;
};
uint2 subgroupExclusiveAdd_48acea() {
uint2 res = simd_prefix_exclusive_sum(uint2(1u));
return res;
}
kernel void compute_main(device uint2* prevent_dce [[buffer(0)]]) {
tint_module_vars_struct const tint_module_vars = tint_module_vars_struct{.prevent_dce=prevent_dce};
(*tint_module_vars.prevent_dce) = subgroupExclusiveAdd_48acea();
}