Direct Rendering Manager: differenze tra le versioni

Versione delle 05:02, 3 gen 2010

Versione attuale delle 13:03, 17 dic 2023

(26 versioni intermedie di 17 utenti non mostrate)

Riga 1:

Il '''Gestore delDirect Rendering DirettoManager''' ('''DRM - Direct Rendering Manager''') è una componente dell''''Infrastrutturainfrastruttura del Renderingrendering Diretto'''diretto (DRI - ''[[Direct Rendering Infrastructure]]''), un sistema che permette di utilizzare efficientemente l'accelerazione video (soprattutto quella legata al [[Computer grafica 3D|3D]]) nei sistemi [[Unix-like]].

= Direct Rendering Manager =

Il '''Gestore del Rendering Diretto''' (DRM - Direct Rendering Manager) è una componente dell''''Infrastruttura del Rendering Diretto''' (DRI - [[Direct Rendering Infrastructure]]), un sistema che permette di utilizzare efficientemente l'accelerazione video (soprattutto quella legata al 3D) nei sistemi Unix-like.

Consiste di due moduli all'interno del [[kernel]] che fungono da drivers''[[driver]]'', un driver generico DRM ed un driver specifico per la [[scheda video]]. Questi driversdriver permettono ad un'applicazione in ''userspace'' di accedere direttamente all'hardware video.

== Il driver generico del DRM ==

Spesso quando si parla di DRM, si intende il driver del DRM, in questa seconda parte ci si riferirà al driver DRM usando semplicemente la sigla DRM.

=== DRM ed integrazione nel sistema ===

Il DRM è strettamente legato alle seguenti componenti che si possono trovare all'interno del sistema:

# Il DMA ([[Direct Memory Access]]) o accesso diretto alla memoria.

# Il [[gestore della memoria]] dell'AGP ([[Accelerated Graphics Port]]).

# Il blocco delle risorse.

# L'accesso sicuro all'hardware.

Le prime due componenti vengono utilizzate per la comunicazione con l'hardware.

La terza viene utilizzata per condividere il devicedispositivo video, infatti ci sono numerosi processi che potrebbero voler accedere all'hardware che gestisce la grafica, questo significa che il sistema deve poter bloccare l'accesso ad una determinata risorsa quando questa è in uso, cioè garantire la [[mutua esclusione]].

L'ultima serve a proteggere l'hardware da un eventuale codice malevolo, visto che teoricamente qualsiasi processo in ''userspace'' può usufruire del devicedispositivo come preferisce (c'è la possilibilitàpossibilità di una ''[[Privilegeprivilege escalation]]'')

===Il ruolo del DRM nel DRI===

Il DRM occupandosi della gestione, supporta il DRI in molti modi, la maggior parte dei quali usando le componenti citate sopra.

==== La mutua esclusione ====

Il DRM si occupa di far entrare in modalità sequenziale tutti quei processi che potrebbero voler accedere all'hardware grafico. Tuttavia il DRM non evita soltanto che due processi tentino di scrivere dati nel devicedispositivo in contemporanea, ma anche che un processo possa leggere dei dati inconsistentiincoerenti da esso.

È da notare che non tutti i programmi richiedono un accesso diretto, ad esempio molti programmi 2D passano per un gestore intermediario.

=== Politiche di sicurezza ===

Il DRM gestisce anche le politiche di sicurezza quando un determinato processo non ha i privilegi necessari per mappare le regioni di memoria dell'hardware grafico su /dev/mem.

Il DRM permette ad un processo [[client]] di mappare delle zone di memoria del devicedispositivo video con alcune restrizioni:

*Il client può mappare solo le regioni di memoria che gli appartengono, questo forza il client ad obbedire alle politiche di sicurezza che gli vengono imposte dal server X (come xauth un'applicazione che si occupa delle [[Autorizzazioni X Window]]).

*Il client può solo mappare le regioni se riesce ad accedere a /dev/drm, quindi l'amministratore può decidere se permettere ad un certo utente di accedere alle funzioni di rendering diretto. Per fare ciò un utente deve far parte di un gruppo specificato nel file di configurazioni XF86Config.

*Il client può solo mappare le regioni che il server X gli permette di mappare, infatti oltre a bloccare le zone che non gli appartengono direttamente, il server può decidere di restringere l'accesso a certe zone di memoria, ad esempio rendendole di sola lettura, in modo da poterci inserire dei [[dati sensibili]] (come ad esempio i dati relativi all'avvio del DMA).

==== Accesso ai dati ====

*Il client può solo mappare le regioni che il server X gli permette di mappare, infatti oltre a bloccare le zone che non gli appartengono direttamente, il server può decidere di restringere l'accesso a certe zone di memoria, ad esempio rendendole di sola lettura, in modo da poterci inserire dei dati sensibili (come ad esempio i dati relativi all'avvio del DMA).

Il DRM utilizza in una modalità ottimizzata il DMA, Il migliore ''[[throughput]]'' è permesso dai seguenti fattori:

=== Accesso ai dati ===

# Il server X può specificare un insieme di '''diverse dimensioni del ''buffer''''' che desidera allocare ed in seguito bloccare.

Il DRM utilizza in una modalità ottimizzata il DMA, Il migliore [[throughput]] è permesso dai seguenti fattori:

# Il client può mappare questi buffers''buffer'' usando un '''indirizzamento virtuale''' (tramite le [[Application programming interface|API]] DRM).

# Il client può riservare alcuni di questi buffers''buffer'' all'uso tramite DRM, ad esempio per riempirlo con dei dati e chiedere al DRM di inviare tali dati all'hardware grafico. (Di solito i buffersbuffer più piccoli vengono usati per assicurarsi che il server X possa ottenere il blocco durante i trasferimenti consecutivi tra ''buffer'' ed il devicedispositivo grafico, in tal modo il server diviene maggiormente reattivo).

# Il server X può specificare un insieme di diverse dimensioni del buffer che desidera allocare ed in seguito bloccare.

# Il DRM gestisce una coda di '''buffer del DMA''' per ogni contesto GLXContext dell'OpenGL, e si accorge quando è necessario uno switch. Quando risulta necessario cambiare contesto, si tenta di usare un driver specifico (in kernel-space), se questo non è disponibile si ritorna al server X che possiede un metodo generico per il GLXContext switching. Infine il DMRDRM si occupa anche di schedulare le richieste ai vari buffer per evitare di eseguire cambi di contesto inutili.

# Il client può mappare questi buffers usando un indirizzamento virtuale (tramite le [[API]] DRM).

# Il sistema DMA è generico nel senso che un server X può ottenreottenere delle informazioni in tempo reale eed in seguito richiederichiedere quali operazioni può eseguire sull'hardware presente nella macchina. Il server X si accorge di quale hardware e'è collegato e decide con quali modalità renderlo disponibile. Questo permette un facilefacilita l'utilizzo di eventuali nuovi devicedispositivi grafici tramite DRI, permettendo successivamente di usare un driver specifico che possa migliorarne le prestazioni.

# Il client può riservare alcuni di questi buffers all'uso tramite DRM, ad esempio per riempirlo con dei dati e chiedere al DRM di inviare tali dati all'hardware grafico. (Di solito i buffers più piccoli vengono usati per assicurarsi che il server X possa ottenere il blocco durante i trasferimenti consecutivi tra buffer ed il device grafico, in tal modo il server diviene maggiormente reattivo).

# Il DRM gestisce una coda di '''buffer del DMA''' per ogni contesto GLXContext dell'OpenGL, e si accorge quando è necessario uno switch. Quando risulta necessario cambiare contesto, si tenta di usare un driver specifico (in kernel-space), se questo non è disponibile si ritorna al server X che possiede un metodo generico per il GLXContext switching.Infine il DMR si occupa anche di schedulare le richieste ai vari buffer per evitare di eseguire cambi di contesto inutili.

# Il sistema DMA è generico nel senso che un server X può ottenre delle informazioni in tempo reale e richiede quali operazioni può eseguire sull'hardware presente nella macchina. Il server X si accorge di quale hardware e' collegato e decide con quali modalità renderlo disponibile. Questo permette un facile utilizzo di eventuali nuovi device grafici tramite DRI, permettendo successivamente di usare un driver specifico che possa migliorarne le prestazioni.

== Voci correlate ==

* [[Direct Rendering Infrastructure|DRI]]

* [[Direct Memory Access|DMA]]

==Collegamenti esterni==

* [http{{cita web|https://dri.freedesktop.org/wiki la wiki|Wiki su DRI e DRM]|lingua=en}}

{{Freedesktop.org}}

{{portale|software libero}}

[[Categoria:X Window System]]

[[Categoria:Freedesktop.org]]

[[Categoria:Progetti di software libero ad alta priorità]]

[[Categoria:Linux]]