Struct BufferRange 

pub struct BufferRange {
    pub buf_id: usize,
    pub p0: u64,
    pub p1: u64,
    pub role: MemRangeRole,
}

A buffer region recorded for dataflow tracking.

Mirrors struct ggml_mem_range in ggml-metal-common.cpp:10-17.

Fields

buf_id: usize

Backing metal::Buffer pointer cast to usize. Stable across the encoder lifetime as long as the MlxBuffer’s ARC clone outlives the CB (see CommandEncoder::new_with_residency caller contract).

p0: u64

Start byte address (contents_ptr() + byte_offset for MlxBuffer). Used for overlap arithmetic.

p1: u64

End byte address (start + element-extent). llama.cpp uses tensor->data + ggml_backend_buft_get_alloc_size(tensor) — for mlx-native we use the buffer’s byte_len() minus byte_offset(), which equals the slice extent.

role: MemRangeRole

Whether this range is read or written by the recording dispatch.

Implementations

impl BufferRange

pub fn from_buffer(buf: &MlxBuffer, role: MemRangeRole) -> Self

Build a BufferRange from an MlxBuffer and a role.

Uses metal_buffer().as_ptr() as usize as the buffer-id (so two slice_views of the same parent share a buf_id, which is the intended behavior — a slice write must barrier against a sibling-slice read of the same parent).

The (p0, p1) range covers the addressable extent the kernel can reach: [contents_ptr + byte_offset, contents_ptr + byte_offset + (byte_len - byte_offset)). For non-slice buffers byte_offset == 0 and the range covers the full allocation. For slices the range covers only the slice region — matching llama.cpp’s tensor->data .. tensor->data + alloc_size.

pub fn conflicts_with(&self, other: &BufferRange) -> bool

Whether self and other overlap by the same arithmetic llama.cpp uses at ggml-metal-common.cpp:138.

Returns false for cross-buffer pairs (different buf_id) and for src-vs-src pairs (read-read is always concurrent-safe).

Trait Implementations

impl Clone for BufferRange

fn clone(&self) -> BufferRange

Returns a duplicate of the value.

fn clone_from(&mut self, source: &Self)

Performs copy-assignment from source.

impl Debug for BufferRange

fn fmt(&self, f: &mut Formatter<'_>) -> Result

Formats the value using the given formatter.

impl Copy for BufferRange