Direct Rendering Manager: differenze tra le versioni

Versione delle 01:29, 29 nov 2013

Versione attuale delle 13:03, 17 dic 2023

(9 versioni intermedie di 8 utenti non mostrate)

Riga 1:

Il '''Direct Rendering Manager''' ('''DRM''') è 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 [[Computer grafica 3D|3D]]) nei sistemi [[Unix-like]].

[[File:Linux Graphics Stack 2013.svg|thumb|300px|EL '''Direct Rendering Manager''' e componente in user space.]]

[[File:Linux graphics drivers DRI early.svg|thumb|300px|[[Direct Rendering Infrastructure]] versus "indirect rendering": el [[servidor de pantalla|X server]] es [[root]] porque él continua 2D driver.]]

[[File:Linux graphics drivers DRI current.svg|thumb|300px|Solo el '''Direct Rendering Manager''' accesos la GPU.]]

[[File:Linux graphics drivers DRI Wayland.svg|thumb|300px|In Linux kernel 3.12 ''render nodes'' were merged into the '''DRM'''. The [[Kernel mode-setting|KMS]] was split of. [[Wayland (protocolo)|Wayland]] implementa "direct rendering" para [[EGL (API)|EGL]].]]

Il '''Direct Rendering Manager''' ('''DRM''') è 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 [[Computer grafica 3D|3D]]) nei sistemi [[Unix-like]].

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

== Il driver generico del DRM ==

Line 14 ⟶ 10:

# 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 possibilità di una ''[[privilege escalation]]'')

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

Line 26 ⟶ 22:

==== 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).

*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 DRM utilizza in una modalità ottimizzata il DMA, Il migliore ''[[throughput]]'' è permesso dai seguenti fattori:

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

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

# Il client può riservare alcuni di questi ''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 buffer 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 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 DRM 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ò ottenere delle informazioni in tempo reale ed in seguito richiedere quali operazioni può eseguire sull'hardware presente nella macchina. Il server X si accorge di quale hardware è collegato e decide con quali modalità renderlo disponibile. Questo facilita l'utilizzo di eventuali nuovi devicedispositivi 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==

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

{{Freedesktop.org}}