concinnity-device 0.19.119

//! Per-frame submission bookkeeping: the transient buffer rings and the pass
//! timing diagnostics.

use std::sync::atomic::AtomicU32;
use std::sync::{Arc, Mutex};

use concinnity_core::profile::RenderStats;

use super::InitGpu;
use crate::metal::context::{Diagnostics, FrameRings};
use crate::metal::frame_rings::{JointRing, TransientRing};
use crate::metal::material_params::MaterialParamRing;
use crate::metal::pass_timing::PassTimingResources;

// The bindless buffers an async reflection-probe bake reads across frames
// (object, draw-args, and the skinned joint palettes) get one EXTRA ring
// slot; its faces sample the frame's own bindless-texture-args instead.
// The frame only ever uses slots
// `frame_ring_index % frames_in_flight` -- i.e. `[0, frames_in_flight)`
// -- so slot `frames_in_flight` is reserved for the bake: a slot the
// frame never overwrites, keeping the bake's CPU-written buffers valid
// across its asynchronous (no `waitUntilCompleted`) GPU capture. See
// metal/probe.rs `bake_ring_slot`.
pub(super) fn build_rings(
    gpu: &InitGpu<'_>,
    material_params: Vec<concinnity_core::gfx::render_types::GpuMaterialParams>,
) -> FrameRings {
    let frames_in_flight = gpu.frames_in_flight;
    FrameRings {
        object: TransientRing::new(frames_in_flight.max(1) + 1),
        draw_args: TransientRing::new(frames_in_flight.max(1) + 1),
        model_history: TransientRing::new(frames_in_flight),
        bindless_tex: TransientRing::new(frames_in_flight.max(1)),
        probe_records: TransientRing::new(frames_in_flight.max(1) + 1),
        joint: JointRing::new(frames_in_flight.max(1) + 1),
        object_scratch: Vec::new(),
        draw_args_scratch: Vec::new(),
        material_params: MaterialParamRing::new(material_params, frames_in_flight.max(1) + 1),
    }
}

pub(super) fn build_diagnostics(gpu: &InitGpu<'_>) -> Diagnostics {
    // `None` when the device does not expose the timestamp counter set; the
    // per-pass GPU timer then stays at zero for every pass.
    let pass_timing = PassTimingResources::new(&gpu.hw.device);
    tracing::info!(
        "pass-timing: per-pass GPU sample buffers {}",
        if pass_timing.is_some() {
            "ready"
        } else {
            "unavailable (no MTLCommonCounterSetTimestamp)"
        }
    );
    Diagnostics {
        frame_stats: RenderStats::default(),
        gpu_time_us: Arc::new(AtomicU32::new(0)),
        device_error: Arc::new(Mutex::new(None)),
        pass_timing,
        pass_times_us: Arc::new(std::array::from_fn(|_| AtomicU32::new(0))),
        draw_calls_accum: AtomicU32::new(0),
    }
}