concinnity-device 0.19.119

GPU backends (Metal, Vulkan, DirectX) behind a device facade for Concinnity
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42

//! The GPU-driven shadow views, cascades and spot slices alike: the
//! frustum-only decision kernel and the depth-only bindless shadow pipeline.

use concinnity_core::render::error::RenderResult;
use objc2::rc::Retained;
use objc2::runtime::ProtocolObject;
use objc2_metal::{MTLComputePipelineState, MTLRenderPipelineState, MTLVertexDescriptor};

use super::bindless::BindlessPass;
use crate::metal::cull::build_shadow_cull_pipeline;
use crate::metal::init::InitGpu;
use crate::metal::init::pipelines::build_shadow_bindless_pipeline;

pub(super) struct ShadowCull {
    pub(super) pipeline: Option<Retained<ProtocolObject<dyn MTLComputePipelineState>>>,
    pub(super) bindless_pipeline: Option<Retained<ProtocolObject<dyn MTLRenderPipelineState>>>,
}

// Built only for a scene world with shadows enabled; a UI-only or shadowless
// world leaves both `None` and renders no shadow views. The cascade and spot
// ICBs + their argument buffers are allocated lazily by
// `ensure_shadow_icb_capacity`, one region per view times `cull_count` once
// geometry is known.
pub(super) fn build_shadow_cull(
    gpu: &InitGpu<'_>,
    bindless: &BindlessPass,
    vert_desc: &MTLVertexDescriptor,
    shadow_enabled: bool,
) -> RenderResult<ShadowCull> {
    let device = &*gpu.hw.device;
    let (pipeline, bindless_pipeline) = if shadow_enabled && bindless.active {
        let sc = build_shadow_cull_pipeline(device, gpu.hot_reload)?;
        let sb = build_shadow_bindless_pipeline(device, vert_desc, gpu.hot_reload)?;
        (Some(sc), Some(sb))
    } else {
        (None, None)
    };
    Ok(ShadowCull {
        pipeline,
        bindless_pipeline,
    })
}