expose SUBGROUP, SUBGROUP_VERTEX, SUBGROUP_BARRIER native features

[zackgomez]

Simply pass these constants thru

Test Plan

use the following shader

@compute
@workgroup_size(32)
fn main(
    @builtin(global_invocation_id) global_id: vec3<u32>,
    @builtin(subgroup_size) subgroup_size: u32,
    @builtin(subgroup_invocation_id) subgroup_invocation_id: u32,
    ) {
    let x = subgroup_size;
    let id = subgroup_invocation_id;

    // requires SUBGROUP
    subgroupAny(true);
    subgroupBallot(true);
    subgroupMax(5);
    
    // requires SUBGROUP_BARRIER
    subgroupBarrier();
}


@vertex
fn vertex_main() -> @builtin(position) vec4<f32> {
    // requires SUBGROUP_VERTEX
    subgroupAny(true);
    
    // Not allowed even with SubgroupBarrier & SubgroupVertex
    // subgroupBarrier();
    
    return vec4<f32>(0.0, 0.0, 0.0, 0.0);
}

use a main.c that compiles requires all the SUBGROUP features and loads this shader. Verify that removing various features causes expected shader complication errors