Adding upstream version 124.0.1.upstream/124.0.1

Signed-off-by: Daniel Baumann <daniel.baumann@progress-linux.org>

1 files changed, 322 insertions, 0 deletions

diff --git a/third_party/rust/wgpu-hal/src/metal/conv.rs b/third_party/rust/wgpu-hal/src/metal/conv.rs
new file mode 100644
index 0000000000..8f6439b50b
--- /dev/null
+++ b/third_party/rust/wgpu-hal/src/metal/conv.rs
@@ -0,0 +1,322 @@
+pub fn map_texture_usage(
+    format: wgt::TextureFormat,
+    usage: crate::TextureUses,
+) -> metal::MTLTextureUsage {
+    use crate::TextureUses as Tu;
+
+    let mut mtl_usage = metal::MTLTextureUsage::Unknown;
+
+    mtl_usage.set(
+        metal::MTLTextureUsage::RenderTarget,
+        usage.intersects(Tu::COLOR_TARGET | Tu::DEPTH_STENCIL_READ | Tu::DEPTH_STENCIL_WRITE),
+    );
+    mtl_usage.set(
+        metal::MTLTextureUsage::ShaderRead,
+        usage.intersects(
+            Tu::RESOURCE | Tu::DEPTH_STENCIL_READ | Tu::STORAGE_READ | Tu::STORAGE_READ_WRITE,
+        ),
+    );
+    mtl_usage.set(
+        metal::MTLTextureUsage::ShaderWrite,
+        usage.intersects(Tu::STORAGE_READ_WRITE),
+    );
+    // needed for combined depth/stencil formats since we might
+    // create a stencil-only view from them
+    mtl_usage.set(
+        metal::MTLTextureUsage::PixelFormatView,
+        format.is_combined_depth_stencil_format(),
+    );
+
+    mtl_usage
+}
+
+pub fn map_texture_view_dimension(dim: wgt::TextureViewDimension) -> metal::MTLTextureType {
+    use metal::MTLTextureType::*;
+    use wgt::TextureViewDimension as Tvd;
+    match dim {
+        Tvd::D1 => D1,
+        Tvd::D2 => D2,
+        Tvd::D2Array => D2Array,
+        Tvd::D3 => D3,
+        Tvd::Cube => Cube,
+        Tvd::CubeArray => CubeArray,
+    }
+}
+
+pub fn map_compare_function(fun: wgt::CompareFunction) -> metal::MTLCompareFunction {
+    use metal::MTLCompareFunction::*;
+    use wgt::CompareFunction as Cf;
+    match fun {
+        Cf::Never => Never,
+        Cf::Less => Less,
+        Cf::LessEqual => LessEqual,
+        Cf::Equal => Equal,
+        Cf::GreaterEqual => GreaterEqual,
+        Cf::Greater => Greater,
+        Cf::NotEqual => NotEqual,
+        Cf::Always => Always,
+    }
+}
+
+pub fn map_filter_mode(filter: wgt::FilterMode) -> metal::MTLSamplerMinMagFilter {
+    use metal::MTLSamplerMinMagFilter::*;
+    match filter {
+        wgt::FilterMode::Nearest => Nearest,
+        wgt::FilterMode::Linear => Linear,
+    }
+}
+
+pub fn map_address_mode(address: wgt::AddressMode) -> metal::MTLSamplerAddressMode {
+    use metal::MTLSamplerAddressMode::*;
+    use wgt::AddressMode as Fm;
+    match address {
+        Fm::Repeat => Repeat,
+        Fm::MirrorRepeat => MirrorRepeat,
+        Fm::ClampToEdge => ClampToEdge,
+        Fm::ClampToBorder => ClampToBorderColor,
+        //Fm::MirrorClamp => MirrorClampToEdge,
+    }
+}
+
+pub fn map_border_color(border_color: wgt::SamplerBorderColor) -> metal::MTLSamplerBorderColor {
+    use metal::MTLSamplerBorderColor::*;
+    match border_color {
+        wgt::SamplerBorderColor::TransparentBlack => TransparentBlack,
+        wgt::SamplerBorderColor::OpaqueBlack => OpaqueBlack,
+        wgt::SamplerBorderColor::OpaqueWhite => OpaqueWhite,
+        wgt::SamplerBorderColor::Zero => unreachable!(),
+    }
+}
+
+pub fn map_primitive_topology(
+    topology: wgt::PrimitiveTopology,
+) -> (metal::MTLPrimitiveTopologyClass, metal::MTLPrimitiveType) {
+    use wgt::PrimitiveTopology as Pt;
+    match topology {
+        Pt::PointList => (
+            metal::MTLPrimitiveTopologyClass::Point,
+            metal::MTLPrimitiveType::Point,
+        ),
+        Pt::LineList => (
+            metal::MTLPrimitiveTopologyClass::Line,
+            metal::MTLPrimitiveType::Line,
+        ),
+        Pt::LineStrip => (
+            metal::MTLPrimitiveTopologyClass::Line,
+            metal::MTLPrimitiveType::LineStrip,
+        ),
+        Pt::TriangleList => (
+            metal::MTLPrimitiveTopologyClass::Triangle,
+            metal::MTLPrimitiveType::Triangle,
+        ),
+        Pt::TriangleStrip => (
+            metal::MTLPrimitiveTopologyClass::Triangle,
+            metal::MTLPrimitiveType::TriangleStrip,
+        ),
+    }
+}
+
+pub fn map_color_write(mask: wgt::ColorWrites) -> metal::MTLColorWriteMask {
+    let mut raw_mask = metal::MTLColorWriteMask::empty();
+
+    if mask.contains(wgt::ColorWrites::RED) {
+        raw_mask |= metal::MTLColorWriteMask::Red;
+    }
+    if mask.contains(wgt::ColorWrites::GREEN) {
+        raw_mask |= metal::MTLColorWriteMask::Green;
+    }
+    if mask.contains(wgt::ColorWrites::BLUE) {
+        raw_mask |= metal::MTLColorWriteMask::Blue;
+    }
+    if mask.contains(wgt::ColorWrites::ALPHA) {
+        raw_mask |= metal::MTLColorWriteMask::Alpha;
+    }
+
+    raw_mask
+}
+
+pub fn map_blend_factor(factor: wgt::BlendFactor) -> metal::MTLBlendFactor {
+    use metal::MTLBlendFactor::*;
+    use wgt::BlendFactor as Bf;
+
+    match factor {
+        Bf::Zero => Zero,
+        Bf::One => One,
+        Bf::Src => SourceColor,
+        Bf::OneMinusSrc => OneMinusSourceColor,
+        Bf::Dst => DestinationColor,
+        Bf::OneMinusDst => OneMinusDestinationColor,
+        Bf::SrcAlpha => SourceAlpha,
+        Bf::OneMinusSrcAlpha => OneMinusSourceAlpha,
+        Bf::DstAlpha => DestinationAlpha,
+        Bf::OneMinusDstAlpha => OneMinusDestinationAlpha,
+        Bf::Constant => BlendColor,
+        Bf::OneMinusConstant => OneMinusBlendColor,
+        Bf::SrcAlphaSaturated => SourceAlphaSaturated,
+        Bf::Src1 => Source1Color,
+        Bf::OneMinusSrc1 => OneMinusSource1Color,
+        Bf::Src1Alpha => Source1Alpha,
+        Bf::OneMinusSrc1Alpha => OneMinusSource1Alpha,
+    }
+}
+
+pub fn map_blend_op(operation: wgt::BlendOperation) -> metal::MTLBlendOperation {
+    use metal::MTLBlendOperation::*;
+    use wgt::BlendOperation as Bo;
+
+    match operation {
+        Bo::Add => Add,
+        Bo::Subtract => Subtract,
+        Bo::ReverseSubtract => ReverseSubtract,
+        Bo::Min => Min,
+        Bo::Max => Max,
+    }
+}
+
+pub fn map_blend_component(
+    component: &wgt::BlendComponent,
+) -> (
+    metal::MTLBlendOperation,
+    metal::MTLBlendFactor,
+    metal::MTLBlendFactor,
+) {
+    (
+        map_blend_op(component.operation),
+        map_blend_factor(component.src_factor),
+        map_blend_factor(component.dst_factor),
+    )
+}
+
+pub fn map_vertex_format(format: wgt::VertexFormat) -> metal::MTLVertexFormat {
+    use metal::MTLVertexFormat::*;
+    use wgt::VertexFormat as Vf;
+
+    match format {
+        Vf::Unorm8x2 => UChar2Normalized,
+        Vf::Snorm8x2 => Char2Normalized,
+        Vf::Uint8x2 => UChar2,
+        Vf::Sint8x2 => Char2,
+        Vf::Unorm8x4 => UChar4Normalized,
+        Vf::Snorm8x4 => Char4Normalized,
+        Vf::Uint8x4 => UChar4,
+        Vf::Sint8x4 => Char4,
+        Vf::Unorm16x2 => UShort2Normalized,
+        Vf::Snorm16x2 => Short2Normalized,
+        Vf::Uint16x2 => UShort2,
+        Vf::Sint16x2 => Short2,
+        Vf::Float16x2 => Half2,
+        Vf::Unorm16x4 => UShort4Normalized,
+        Vf::Snorm16x4 => Short4Normalized,
+        Vf::Uint16x4 => UShort4,
+        Vf::Sint16x4 => Short4,
+        Vf::Float16x4 => Half4,
+        Vf::Uint32 => UInt,
+        Vf::Sint32 => Int,
+        Vf::Float32 => Float,
+        Vf::Uint32x2 => UInt2,
+        Vf::Sint32x2 => Int2,
+        Vf::Float32x2 => Float2,
+        Vf::Uint32x3 => UInt3,
+        Vf::Sint32x3 => Int3,
+        Vf::Float32x3 => Float3,
+        Vf::Uint32x4 => UInt4,
+        Vf::Sint32x4 => Int4,
+        Vf::Float32x4 => Float4,
+        Vf::Float64 | Vf::Float64x2 | Vf::Float64x3 | Vf::Float64x4 => unimplemented!(),
+    }
+}
+
+pub fn map_step_mode(mode: wgt::VertexStepMode) -> metal::MTLVertexStepFunction {
+    match mode {
+        wgt::VertexStepMode::Vertex => metal::MTLVertexStepFunction::PerVertex,
+        wgt::VertexStepMode::Instance => metal::MTLVertexStepFunction::PerInstance,
+    }
+}
+
+pub fn map_stencil_op(op: wgt::StencilOperation) -> metal::MTLStencilOperation {
+    use metal::MTLStencilOperation::*;
+    use wgt::StencilOperation as So;
+
+    match op {
+        So::Keep => Keep,
+        So::Zero => Zero,
+        So::Replace => Replace,
+        So::IncrementClamp => IncrementClamp,
+        So::IncrementWrap => IncrementWrap,
+        So::DecrementClamp => DecrementClamp,
+        So::DecrementWrap => DecrementWrap,
+        So::Invert => Invert,
+    }
+}
+
+pub fn map_winding(winding: wgt::FrontFace) -> metal::MTLWinding {
+    match winding {
+        wgt::FrontFace::Cw => metal::MTLWinding::Clockwise,
+        wgt::FrontFace::Ccw => metal::MTLWinding::CounterClockwise,
+    }
+}
+
+pub fn map_cull_mode(face: Option<wgt::Face>) -> metal::MTLCullMode {
+    match face {
+        None => metal::MTLCullMode::None,
+        Some(wgt::Face::Front) => metal::MTLCullMode::Front,
+        Some(wgt::Face::Back) => metal::MTLCullMode::Back,
+    }
+}
+
+pub fn map_range(range: &crate::MemoryRange) -> metal::NSRange {
+    metal::NSRange {
+        location: range.start,
+        length: range.end - range.start,
+    }
+}
+
+pub fn map_copy_extent(extent: &crate::CopyExtent) -> metal::MTLSize {
+    metal::MTLSize {
+        width: extent.width as u64,
+        height: extent.height as u64,
+        depth: extent.depth as u64,
+    }
+}
+
+pub fn map_origin(origin: &wgt::Origin3d) -> metal::MTLOrigin {
+    metal::MTLOrigin {
+        x: origin.x as u64,
+        y: origin.y as u64,
+        z: origin.z as u64,
+    }
+}
+
+pub fn map_store_action(store: bool, resolve: bool) -> metal::MTLStoreAction {
+    use metal::MTLStoreAction::*;
+    match (store, resolve) {
+        (true, true) => StoreAndMultisampleResolve,
+        (false, true) => MultisampleResolve,
+        (true, false) => Store,
+        (false, false) => DontCare,
+    }
+}
+
+pub fn map_clear_color(color: &wgt::Color) -> metal::MTLClearColor {
+    metal::MTLClearColor {
+        red: color.r,
+        green: color.g,
+        blue: color.b,
+        alpha: color.a,
+    }
+}
+
+pub fn get_blit_option(
+    format: wgt::TextureFormat,
+    aspect: crate::FormatAspects,
+) -> metal::MTLBlitOption {
+    if format.is_combined_depth_stencil_format() {
+        match aspect {
+            crate::FormatAspects::DEPTH => metal::MTLBlitOption::DepthFromDepthStencil,
+            crate::FormatAspects::STENCIL => metal::MTLBlitOption::StencilFromDepthStencil,
+            _ => unreachable!(),
+        }
+    } else {
+        metal::MTLBlitOption::None
+    }
+}