Metal setup merge (#1616)
Signed-off-by: dependabot[bot] <support@github.com> Co-authored-by: Alex Cristici <alex.cristici@gmail.com> Co-authored-by: mwilsnd <mwilsnd@gmail.com> Co-authored-by: Stefan Karschti <stefan.karschti@gmail.com> Co-authored-by: Bart Louwers <bart@emeel.net> Co-authored-by: Alex Cristici <alex@skoon.energy> Co-authored-by: Bart Louwers <bart.louwers@gmail.com> Co-authored-by: Wei Chen <alanchenboy@gmail.com> Co-authored-by: Siarhei Fedartsou <siarhei.fedartsou@gmail.com> Co-authored-by: tdcosta100 <tdcosta100@gmail.com>
This commit is contained in:
Tim Sylvester
207
include/mbgl/shaders/mtl/common.hpp
Normal file
207
include/mbgl/shaders/mtl/common.hpp
Normal file
@@ -0,0 +1,207 @@
|
||||
#pragma once
|
||||
|
||||
#define MLN_MTL_UNIFORM_BLOCK(idx, vert, frag, struc) \
|
||||
{ idx, vert, frag, sizeof(struc), MLN_STRINGIZE(struc) }
|
||||
|
||||
namespace mbgl {
|
||||
namespace shaders {
|
||||
|
||||
constexpr auto prelude = R"(
|
||||
#include <metal_stdlib>
|
||||
using namespace metal;
|
||||
|
||||
template <typename T1, typename T2>
|
||||
inline auto mod(T1 x, T2 y) -> decltype(x - y * floor(x/y)) {
|
||||
return x - y * metal::floor(x/y);
|
||||
}
|
||||
|
||||
enum class AttributeSource : int32_t {
|
||||
Constant,
|
||||
PerVertex,
|
||||
Computed,
|
||||
};
|
||||
|
||||
struct Expression {};
|
||||
|
||||
struct Attribute {
|
||||
AttributeSource source;
|
||||
Expression expression;
|
||||
};
|
||||
|
||||
struct alignas(16) ExpressionInputsUBO {
|
||||
// These can use uint64_t in later versions of Metal
|
||||
/* 0 */ uint32_t time_lo; // Current scene time (nanoseconds)
|
||||
/* 4 */ uint32_t time_hi;
|
||||
/* 8 */ uint32_t frame_lo; // Current frame count
|
||||
/* 12 */ uint32_t frame_hi;
|
||||
/* 16 */ float zoom; // Current zoom level
|
||||
/* 20 */ float pad1, pad2, pad3;
|
||||
/* 32 */
|
||||
};
|
||||
|
||||
// Unpack a pair of values that have been packed into a single float.
|
||||
// The packed values are assumed to be 8-bit unsigned integers, and are
|
||||
// packed like so: packedValue = floor(input[0]) * 256 + input[1],
|
||||
float2 unpack_float(const float packedValue) {
|
||||
const int packedIntValue = int(packedValue);
|
||||
const int v0 = packedIntValue / 256;
|
||||
return float2(v0, packedIntValue - v0 * 256);
|
||||
}
|
||||
float2 unpack_opacity(const float packedOpacity) {
|
||||
return float2(float(int(packedOpacity) / 2) / 127.0, fmod(packedOpacity, 2.0));
|
||||
}
|
||||
// To minimize the number of attributes needed, we encode a 4-component
|
||||
// color into a pair of floats (i.e. a vec2) as follows:
|
||||
// [ floor(color.r * 255) * 256 + color.g * 255, floor(color.b * 255) * 256 + color.g * 255 ]
|
||||
float4 decode_color(const float2 encoded) {
|
||||
return float4(unpack_float(encoded[0]) / 255, unpack_float(encoded[1]) / 255);
|
||||
}
|
||||
// Unpack a pair of paint values and interpolate between them.
|
||||
float unpack_mix_float(const float2 packedValue, const float t) {
|
||||
return mix(packedValue[0], packedValue[1], t);
|
||||
}
|
||||
// Unpack a pair of paint values and interpolate between them.
|
||||
float4 unpack_mix_color(const float4 packedColors, const float t) {
|
||||
return mix(decode_color(float2(packedColors[0], packedColors[1])),
|
||||
decode_color(float2(packedColors[2], packedColors[3])), t);
|
||||
}
|
||||
|
||||
float valueFor(device const Attribute& attrib,
|
||||
device const float& constValue,
|
||||
thread const float2& vertexValue,
|
||||
device const float& t,
|
||||
device const ExpressionInputsUBO&) {
|
||||
switch (attrib.source) {
|
||||
case AttributeSource::PerVertex: return unpack_mix_float(vertexValue, t);
|
||||
case AttributeSource::Computed: // TODO
|
||||
default:
|
||||
case AttributeSource::Constant: return constValue;
|
||||
}
|
||||
}
|
||||
// single packed color
|
||||
float4 colorFor(device const Attribute& attrib,
|
||||
device const float4& constValue,
|
||||
thread const float2& vertexValue,
|
||||
device const ExpressionInputsUBO&) {
|
||||
switch (attrib.source) {
|
||||
case AttributeSource::PerVertex: return decode_color(float2(vertexValue[0], vertexValue[1]));
|
||||
case AttributeSource::Computed: // TODO
|
||||
default:
|
||||
case AttributeSource::Constant: return constValue;
|
||||
}
|
||||
}
|
||||
// interpolated packed colors
|
||||
float4 colorFor(device const Attribute& attrib,
|
||||
device const float4& constValue,
|
||||
thread const float4& vertexValue,
|
||||
device const float& t,
|
||||
device const ExpressionInputsUBO&) {
|
||||
switch (attrib.source) {
|
||||
case AttributeSource::PerVertex: return unpack_mix_color(vertexValue, t);
|
||||
case AttributeSource::Computed: // TODO
|
||||
default:
|
||||
case AttributeSource::Constant: return constValue;
|
||||
}
|
||||
}
|
||||
|
||||
// The maximum allowed miter limit is 2.0 at the moment. the extrude normal is stored
|
||||
// in a byte (-128..127). We scale regular normals up to length 63, but there are also
|
||||
// "special" normals that have a bigger length (of up to 126 in this case).
|
||||
constant float LINE_NORMAL_SCALE = 1.0 / (127 / 2);
|
||||
|
||||
// The attribute conveying progress along a line is scaled to [0, 2^15).
|
||||
constant float MAX_LINE_DISTANCE = 32767.0;
|
||||
|
||||
struct alignas(16) LineUBO {
|
||||
float4x4 matrix;
|
||||
float2 units_to_pixels;
|
||||
float ratio;
|
||||
float device_pixel_ratio;
|
||||
};
|
||||
|
||||
struct alignas(16) LineGradientUBO {
|
||||
float4x4 matrix;
|
||||
float2 units_to_pixels;
|
||||
float ratio;
|
||||
float device_pixel_ratio;
|
||||
};
|
||||
|
||||
struct alignas(16) LinePropertiesUBO {
|
||||
float4 color;
|
||||
float blur;
|
||||
float opacity;
|
||||
float gapwidth;
|
||||
float offset;
|
||||
float width;
|
||||
float pad1, pad2, pad3;
|
||||
};
|
||||
|
||||
struct alignas(16) LineGradientPropertiesUBO {
|
||||
float blur;
|
||||
float opacity;
|
||||
float gapwidth;
|
||||
float offset;
|
||||
float width;
|
||||
float pad1, pad2, pad3;
|
||||
};
|
||||
|
||||
struct alignas(16) LinePermutationUBO {
|
||||
Attribute color;
|
||||
Attribute blur;
|
||||
Attribute opacity;
|
||||
Attribute gapwidth;
|
||||
Attribute offset;
|
||||
Attribute width;
|
||||
Attribute floorwidth;
|
||||
Attribute pattern_from;
|
||||
Attribute pattern_to;
|
||||
bool overdrawInspector;
|
||||
uint8_t pad1, pad2, pad3;
|
||||
float pad4;
|
||||
};
|
||||
|
||||
struct alignas(16) LineInterpolationUBO {
|
||||
float color_t;
|
||||
float blur_t;
|
||||
float opacity_t;
|
||||
float gapwidth_t;
|
||||
float offset_t;
|
||||
float width_t;
|
||||
float pad1, pad2;
|
||||
};
|
||||
|
||||
struct alignas(16) LineGradientInterpolationUBO {
|
||||
float blur_t;
|
||||
float opacity_t;
|
||||
float gapwidth_t;
|
||||
float offset_t;
|
||||
float width_t;
|
||||
float pad1, pad2, pad3;
|
||||
};
|
||||
|
||||
// interpolated packed pattern
|
||||
float4 patternFor(device const Attribute& attrib,
|
||||
device const float4& constValue,
|
||||
thread const ushort4& vertexValue,
|
||||
device const float& ,
|
||||
device const ExpressionInputsUBO&) {
|
||||
switch (attrib.source) {
|
||||
case AttributeSource::PerVertex: return float4(vertexValue);
|
||||
case AttributeSource::Computed: // TODO
|
||||
default:
|
||||
case AttributeSource::Constant: return constValue;
|
||||
}
|
||||
}
|
||||
|
||||
// unpack pattern position
|
||||
inline float2 get_pattern_pos(const float2 pixel_coord_upper, const float2 pixel_coord_lower,
|
||||
const float2 pattern_size, const float tile_units_to_pixels, const float2 pos) {
|
||||
|
||||
float2 offset = mod(mod(mod(pixel_coord_upper, pattern_size) * 256.0, pattern_size) * 256.0 + pixel_coord_lower, pattern_size);
|
||||
return (tile_units_to_pixels * pos + offset) / pattern_size;
|
||||
}
|
||||
|
||||
)";
|
||||
|
||||
}
|
||||
} // namespace mbgl
|
||||
Reference in New Issue
Block a user