test/tint/builtins/gen/var/quadSwapX/9bea80.wgsl.expected.msl

//
// fragment_main
//
#include <metal_stdlib>

using namespace metal;
struct tint_private_vars_struct {
  uint tint_msl_thread_index_in_quadgroup;
};


float tint_msl_quadSwapX(float e, thread tint_private_vars_struct* const tint_private_vars) {
  return quad_shuffle(e,((*(tint_private_vars)).tint_msl_thread_index_in_quadgroup ^ 1u));
}

float quadSwapX_9bea80(thread tint_private_vars_struct* const tint_private_vars) {
  float arg_0 = 1.0f;
  float res = tint_msl_quadSwapX(arg_0, tint_private_vars);
  return res;
}

fragment void fragment_main(device float* 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_9bea80(&(tint_private_vars));
  return;
}

//
// compute_main
//
#include <metal_stdlib>

using namespace metal;
struct tint_private_vars_struct {
  uint tint_msl_thread_index_in_quadgroup;
};


float tint_msl_quadSwapX(float e, thread tint_private_vars_struct* const tint_private_vars) {
  return quad_shuffle(e,((*(tint_private_vars)).tint_msl_thread_index_in_quadgroup ^ 1u));
}

float quadSwapX_9bea80(thread tint_private_vars_struct* const tint_private_vars) {
  float arg_0 = 1.0f;
  float res = tint_msl_quadSwapX(arg_0, tint_private_vars);
  return res;
}

kernel void compute_main(device float* 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_9bea80(&(tint_private_vars));
  return;
}