599be97fbe
Freeze Compute Governor v2 and asynchronous Vulkan Matcher execution. Governor now owns production task admission and live resource adaptation, with GPU-first AUTO selection for validated backends, CPU12 host capacity, desktop CPU/RAM reserves, UMA accounting, pressure throttling, hysteresis, and recovery. Validate and freeze the rolling Vulkan ORB Matcher path, host topology policy, task capability envelopes, runtime telemetry, restart/durability contracts, portable CPU fallback, and scientific equivalence. COMPUTE_GOVERNOR_V2=PASS/FROZEN ORB_VULKAN_ASYNC_EXECUTION=PASS/FROZEN MATCHER_GPU=EXISTING_BACKEND_VALIDATED_AND_PREFERRED
106 lines
3.9 KiB
C
106 lines
3.9 KiB
C
#ifndef LARDON3D_ORB_VULKAN_BACKEND_H
|
|
#define LARDON3D_ORB_VULKAN_BACKEND_H
|
|
|
|
#include <stdbool.h>
|
|
#include <stddef.h>
|
|
#include <stdint.h>
|
|
|
|
#ifdef __cplusplus
|
|
extern "C" {
|
|
#endif
|
|
|
|
typedef struct Lardon3DOrbVulkanBackend Lardon3DOrbVulkanBackend;
|
|
|
|
enum {
|
|
/* Stable minimum/depth-1 payload cost used by durable resource signatures:
|
|
* two 8192x32 descriptor buffers plus one 8192x4x32-bit top-2 buffer. The
|
|
* private rolling backend may own two such slots; backend_info reports the
|
|
* ORB request-slot payload actually retained at the observation instant
|
|
* without changing this public ABI. */
|
|
LARDON3D_ORB_VULKAN_PERMANENT_BUFFER_BYTES = 640 * 1024,
|
|
};
|
|
|
|
typedef struct {
|
|
uint32_t neighbor_count;
|
|
uint32_t best_index;
|
|
uint32_t best_distance;
|
|
uint32_t second_index;
|
|
uint32_t second_distance;
|
|
} Lardon3DOrbTop2;
|
|
|
|
#ifdef LARDON3D_SIFT_VULKAN_FEASIBILITY
|
|
typedef struct {
|
|
uint32_t neighbor_count;
|
|
uint32_t best_index;
|
|
float best_squared_distance;
|
|
uint32_t second_index;
|
|
float second_squared_distance;
|
|
} Lardon3DSiftTop2;
|
|
#endif
|
|
|
|
typedef enum {
|
|
LARDON3D_ORB_VULKAN_OK = 0,
|
|
LARDON3D_ORB_VULKAN_UNAVAILABLE,
|
|
LARDON3D_ORB_VULKAN_FAILED,
|
|
LARDON3D_ORB_VULKAN_INVALID_ARGUMENT
|
|
} Lardon3DOrbVulkanResult;
|
|
|
|
typedef struct {
|
|
bool available;
|
|
bool initialized;
|
|
bool dedicated_compute_queue;
|
|
char device_name[256];
|
|
uint32_t workgroup_size;
|
|
uint64_t permanent_payload_bytes;
|
|
uint64_t initialization_ns;
|
|
uint64_t dispatch_ns;
|
|
uint64_t gpu_ns;
|
|
} Lardon3DOrbVulkanInfo;
|
|
|
|
/* Create an uninitialized backend without probing Vulkan or changing process
|
|
* environment. The caller owns the returned object and must exclude every
|
|
* concurrent or future use before destroy; destroy accepts NULL. */
|
|
Lardon3DOrbVulkanBackend *lardon3d_orb_vulkan_backend_create(void);
|
|
void lardon3d_orb_vulkan_backend_destroy(Lardon3DOrbVulkanBackend *backend);
|
|
|
|
bool lardon3d_orb_vulkan_should_use(uint32_t feature_count_a,
|
|
uint32_t feature_count_b);
|
|
|
|
/* Compute deterministic ORB/Hamming top-2 results. Nonzero counts are bounded
|
|
* to 8192; output_capacity covers feature_count_a.
|
|
* Empty A succeeds without output, and empty B writes zero-neighbor rows.
|
|
*
|
|
* In a Vulkan-enabled build, the first nonempty request may initialize Mesa.
|
|
* Before any process thread is created, the process owner must establish
|
|
* MESA_SHADER_CACHE_DISABLE to exact "true" or "1". The backend never mutates
|
|
* that environment. An absent, false, or malformed value makes the first
|
|
* initializing request return UNAVAILABLE, caches that state for this backend,
|
|
* and leaves output untouched. Invalid arguments return INVALID_ARGUMENT;
|
|
* initialization absence/failure returns UNAVAILABLE, while an initialized
|
|
* request/session failure returns FAILED. */
|
|
Lardon3DOrbVulkanResult lardon3d_orb_vulkan_top2(
|
|
Lardon3DOrbVulkanBackend *backend, const unsigned char *descriptors_a,
|
|
uint32_t feature_count_a, const unsigned char *descriptors_b,
|
|
uint32_t feature_count_b, Lardon3DOrbTop2 *output, size_t output_capacity);
|
|
|
|
#ifdef LARDON3D_SIFT_VULKAN_FEASIBILITY
|
|
/* Feasibility-only SIFT top-2 obeys the same bounds, ownership, process-policy,
|
|
* UNAVAILABLE caching, and no-partial-output rules as ORB top-2. */
|
|
Lardon3DOrbVulkanResult lardon3d_sift_vulkan_top2(
|
|
Lardon3DOrbVulkanBackend *backend, const float *descriptors_a,
|
|
uint32_t feature_count_a, const float *descriptors_b,
|
|
uint32_t feature_count_b, Lardon3DSiftTop2 *output, size_t output_capacity);
|
|
#endif
|
|
|
|
/* Read current backend metadata without probing or initializing Vulkan and
|
|
* without requiring or changing MESA_SHADER_CACHE_DISABLE. Both pointers are
|
|
* required; the caller owns the output snapshot. A policy-rejected backend is
|
|
* initialized=true and available=false. */
|
|
bool lardon3d_orb_vulkan_backend_info(Lardon3DOrbVulkanBackend *backend,
|
|
Lardon3DOrbVulkanInfo *info);
|
|
|
|
#ifdef __cplusplus
|
|
}
|
|
#endif
|
|
|
|
#endif
|