Debian Kernel Howto: differenze tra le versioni

Da Guide@Debianizzati.Org.
Vai alla navigazione Vai alla ricerca
(→‎Configurazione del kernel: aggiunti link sulla configurazione)
m (→‎Bisogna usare l'initrd oppure no?: commentati link obsoleti)
 
(100 versioni intermedie di 24 utenti non mostrate)
Riga 1: Riga 1:
==Caratteristiche==
{{Versioni compatibili|Wheezy|Jessie|Testing_2015|Unstable_2015}}
== Introduzione ==
In Debian, il [[kernel]] Linux può essere ricompilato con il metodo standard (valido con tutte le distribuzioni, e quindi anche con Debian) oppure nel cosiddetto [[Debian-way]] (traduzione: ''metodo Debian'' o ''alla Debian'').


* Intel Centrino 1.6 GHz
Questa guida illustrerà il metodo Debian di compilare il kernel Linux. Questo metodo consiste nel creare un [[pacchetto]] Debian del kernel compilato per una sua facile installazione/disinstallazione.
* 512 MB DDR-SDRAM
* 40 GB Matshita hd
* Mobility Radeon 9600 series
* Matshita DVD-RAM UJ-820s
* Schermo 15.4"


Tutti i passi descritti in questa guida non richiedono i permessi di [[root]]. Le uniche operazioni che richiedono l'intervento dell'amministratore della macchina sono l'installazione dei pacchetti necessari alla compilazione e l'installazione del pacchetto .deb creato alla fine del processo di compilazione.


'''INSTALLAZIONE di Gnu/Linux Debian Sarge (3.1r0a)'''
== Installazione dei pacchetti ==


==I==
Avremo innanzitutto bisogno di alcuni pacchetti di base per compilare e pacchettizzare un kernel:


Fate un backup dei vostri documenti, file, musica, video, etc...
<pre>
# apt-get install module-init-tools kernel-package libncurses5-dev fakeroot
</pre>


Fate una deframmentazione, meglio se da DOS, in modo da avere il sistema operativo su una parte precisa del disco (all'inizio).
A questo punto è necessario installare il pacchetto Debian contenente i sorgenti del kernel. Per prima cosa, cerchiamo questo pacchetto:


Se volete mantenere, come ho fatto io, il sistema op. della microsoft, create le partizioni (almeno 2) da Windows. Si possono creare, credo, anche con l'installer di Debian, ma � un po' complicato. Non fate come il sottoscritto, procuratevi un programma open source per partizionare. : )
<pre>
$ apt-cache search linux-source | grep ^linux-source
linux-source-3.16 - sorgenti del kernel Linux per la versione 3.16 con patch Debian
linux-source - sorgenti del kernel Linux (metapacchetto)
linux-source-3.19 - Linux kernel source for version 3.19 with Debian patches
</pre>


Io ne ho create 2:
{{Box|Nota|Ogni versione di Debian ([[unstable]], [[testing]], [[stable]]) utilizza in genere una certa versione del kernel e specifiche versioni di altri pacchetti ad esso correlati in modo tale che l'insieme sia il più possibile stabile. È quindi altamente consigliato usare la versione dei sorgenti del kernel che troveremo nei repository della nostra versione di Debian, a meno che non si sappia esattamente quello che si sta facendo.}}


1) Primaria da 14 GB per / [destinazione dell'intero sistema operativo]
Adesso installiamo il pacchetto dei sorgenti del kernel che intendiamo utilizzare. Notare che i sorgenti del kernel forniti con Debian sono leggermente differenti da quelli del [[kernel vanilla]] rilasciato dal team di Linus Torvalds ([http://kernel-handbook.alioth.debian.org/ch-source.html#s-changes maggiori informazioni qui]). Nel seguito prenderemo come esempio la versione 3.19 del kernel, sostituitela con qualsiasi altra versione vogliate usare.


2) Logica da 1 GB per lo swap ["memoria virtuale"]
<pre>
# apt-get install linux-source-3.19
</pre>


La partizione di swap non � obbligatoria, ma consigliata.
Alla fine dell'installazione verrà creato un file compresso con estensione .tar.xz nella directory <code>/usr/src</code> .


==II==
{{Box|Nota|Prima della versione 2.6.12 del kernel Linux, i pacchetti sorgenti e binari Debian si chiamavano rispettivamente <code>kernel-source-x.x.x</code> e <code>kernel-image-x.x.x</code> (invece dell'attuale denominazione <code>linux-source-x.x.x</code> e
<code>linux-image.x.x.x</code>). Questo perché è previsto l'inserimento di nuovi kernel (come GNU HURD e FreeBSD) all'interno di Debian. }}


Se fate partire l'installazione della Sarge su questo modello Toshiba si blocca sul rilevamento dei controller PCMCIA, in particolare su:
== Configurazione del kernel ==
=== Passi preliminari ===
<pre>Rilevamento dell'hardware in corso alla ricerca di lettori CD-ROM --> Avvio dei servizi "PC-CARD" in corso</pre>
Per prima cosa è opportuno creare una directory in cui inserire i file da compilare. In questo caso si chiamerà "sorgenti" all'interno della nostra home directory, cambiatela a vostro piacimento:
Ma non disperate, al boot basta scrivere, per far partire l'installer correttamente:
<pre>
 
$ mkdir ~/sorgenti
<pre>hw-detect/start_pcmcia=false</pre>
 
Siccome, io credo, non viene riconosciuto correttamente nemmeno l'adattatore grafico, bisogna aggiungere:
 
<pre>vga=771</pre>
 
se no vi troverete davanti ad una schermata nera. Il comando completo diventa quindi:
 
<pre>linux26 acpi=yes vga=771 hw-detect/start_pcmcia=false</pre>
 
Prima del processo di partizionamento dell'installer, vi verr� chiesto di formattare tutto l'hd o di modificare la tabella delle partizioni manualmente: se volete tenervi Windows, scegliete la seconda opzione.
Vi apparir� il men� di partizionamento con visualizzate le tre partizioni:
 
<pre>- (numero partizione) (tipo) (dimensione) (file system) (uso)
-
-
</pre>
</pre>
 
Spostiamoci nella directory appena creata e decomprimiamo al suo interno l'archivio compresso contenente i sorgenti del kernel:
 
<pre>
Quella dell'altro SO non va toccata, assicuratevi che sia impostata su "non usare la partizione".
$ tar -xvf /usr/src/linux-source-3.19.tar.xz -C .
Quella principale (per /) va configurata cos�:
 
<pre>usato come (cio� il file system): reiserFS
mount point: /
opzioni: default
etichetta: /
flag "avviabile": attivato
</pre>
</pre>
 
{{Box|Nota|Fino alla versione 3.9 i sorgenti del kernel sono contenuti in un file compresso con estensione .tar.bz2, per cui il comando cambierà così:<pre>$ tar -xjvf /usr/src/linux-source-3.9.tar.bz2 -C .</pre>o equivalente in base al nome del file compresso.}}
Quella di swap cos�:
A fine operazione verrà creata una nuova directory:
 
<pre>usato come: area di swap</pre>
 
Proseguite con il partizionamento guidato e il resto dell'installazione. PRIMA di confermare il partizionamento, VERIFICATE nel riepilogo che le partizioni di altri OS non vengano modificate.
 
Scegliete di installare il boot loader GRUB nel master boot record.
 
==III==
 
Finita la prima parte dell'installazione, il sistema verr� riavviato, cos� che vi troverete davanti al men� di GRUB (scelta del sistema operativo). Selezionate, con la tastiera:
 
Debian GNU/LINUX, kernel 2.6.8-2-686    (o simile)
 
e premete "e" per editarlo, quindi selezionate:
 
kernel /boot/vwlinuz-2.6.8-2-686 root=/dev/hda2 ro acpi=yes vga=771    (o simile)
 
e premete di nuovo "e" , aggiungete in fondo alla riga, senza virgolette: "1" (credo si possa aggiungere anche "single"), ora premete INVIO e poi "b". Il sistema comincia la seconda parte di installazione; ad un certo punto vi troverete al prompt di manutenzione, digitate (senza #):
 
<pre>
<pre>
# cd /etc/rc2.d/
$ ls
# rm *pcmcia*
linux-source-3.19
# init2
</pre>
</pre>
spostiamoci al suo interno e procediamo con i passi successivi.


Abbiamo rimosso i riferimenti ai controller PCMCIA. L'installazione parte come previsto. Se non avessimo eseguito quest'ultima operazione, si sarebbe verficato un blocco del sistema a:
Puliamo i sorgenti del kernel:


<pre>
<pre>
Starting PCMCIA services: cardmgr[2808]: watching 1 socket
$ make-kpkg clean
cs: IO port probe 0x0100-0x04ff: clean
cs: IO port probe 0x0800-0x08ff: _ |
</pre>
</pre>


==IV==
Questo passaggio è inutile se è la prima volta che compilate il kernel, ma dalla seconda volta in poi diviene necessario per eliminare i file generati dalle precedenti compilazioni che potrebbero creare conflitti.
 
Scegliete "ambiente desktop". Beh...io ho fatto cos�... ; )
 
Vi verr� in seguito chiesto di scegliere i driver per la vostra scheda video. Io ho proceduto cos�:
non sapendo quale scegliere ho seguito i consigli dell'installer, il quale dice di selezionare il driver con il nome del modello o della casa costruttrice. Cos� ho scelto ATI, visto che Radeon non c'� (o non l'ho visto...se c'� scegliete Radeon!). Ma mi dava dei problemi quando, a sistema installato, andavo a cambiare la risoluzione.
In particolare non potevo aumentare la risoluzione (massimo 800x600). Se lo facevo, c'erano dei problemi gravi di visualizzazione del desktop.
 
Quindi scegliete "Radeon". Quando avete finito l'installazione (finalmente! ), la risoluzione sar� 800x600. Se non avete altri casini, dovete, con i diritti di amministratore, modificare il file:
 
/etc/X11/XF86Config-4
 
se non ce l'avete allora:
 
/etc/X11/Xorg.conf    oppure    /etc/X11/Xfree86.conf
 
nella sezione "Screen", appare:


Ora, se avete installato un kernel precompilato che abbia la stessa versione del kernel che volete ricompilare potreste usare il suo file di configurazione come base di partenza per configurare il vostro kernel. A tal scopo basta copiare il file di configurazione che si trova in <code>/boot</code> (i file di configurazione dei kernel installati hanno come nome <code>config</code> seguito dalla versione del kernel) nella directory dei sorgenti.<br/>
Il nome del file da creare deve essere sempre ".config".
<pre>
<pre>
Subsection "Display"
$ cp /boot/config-3.19.1-amd64 .config
    Deph          24
    Modes        "800x600" "640x480"
</pre>
</pre>


aggiungete, prima di "800x600":
C'è chi arriva anche a scaricare il pacchetto contenente il kernel semplicemente per il suo file di configurazione. Se avete banda da sprecare è possibile farlo. Tuttavia si può benissimo partire da zero senza copiare nessun file di configurazione.


<pre>"1280x800" "1024x768"</pre>
=== Configurazione: <code>make menuconfig</code> ===


con le virgolette e separati da uno spazio tra loro. Se mettete "1152x768" al posto di "1280x800" avrete un effetto tipo antialias veramente fastidioso, soprattutto per i carratteri piccoli; infatti questa risoluzione non � specifica a questo video. Non so se le risoluzioni vanno aggiunte anche per le altre profondit� di colore, almeno in "Deph 16" credo.
A questo punto, per configurare il nostro kernel, non ci resta che lanciare il comando:


Nota: Nel Toshiba M30X-159, per vedere bene le risoluzioni da 1024x768 in su.. ho dovuto modificare nella sezione "Monitor" la sincronizzazione orizzontale e verticale nel seguente modo :
<pre>
<pre>
Section "Monitor"
$ make menuconfig
Identifier "LPL:0000"
HorizSync 30-61
VertRefresh 56-75
Option "DPMS"
EndSection
</pre>
</pre>


Se come driver non avete scelto Radeon, dovete cambiarlo nello stesso file, scrivendo "radeon" al posto di "vesa" o "Ati".
Vi apparirà un'interfaccia testuale dalla quale sarà possibile configurare le opzioni del kernel. ''Questo è il passaggio più delicato, nonché il più lungo e difficile''.  
Riavviate il portatile e modificate la risoluzione.


Se dovete configurare un kernel per la prima volta prendetevi almeno un'ora di tempo ed iniziate con calma, leggendo tutte le pagine dell'help in linea. Uno dei vantaggi di un kernel ricompilato è la possibilità di ottenere un kernel estremamente piccolo e leggero proprio perché viene compilato il supporto per le sole periferiche e i soli filesystem effettivamente usati. In questo modo si ha un kernel piccolo e pochi moduli. Un kernel di questo tipo impiega anche molto meno tempo ad essere compilato. Per fare un esempio potrebbe impiegare sui 10 minuti su in athlon 1000, quando un kernel Debian ufficiale impiegherebbe sicuramente più di un'ora sulla stessa macchina. In definitiva, compilando un kernel snello, sarà possibile anche fare più prove ed ottimizzarlo quindi al meglio.


==LAN==
Per trovare quali moduli sono richiesti dal vostro hardware potete usare il comando <code>'''lspci'''</code> o meglio <code>'''lspci -v'''</code>. Inoltre risulta utilissimo consultare il database dei driver di Linux a [http://kmuto.jp/debian/hcl/ questo indirizzo]: inserendo semplicemente l'output di <code>lspci -n</code>, otterrete l'elenco dei moduli da compilare


Sono riuscito a configurare anche la connessione a internet tramite router. La procedura � ben descritta in [[Condividere la connessione a internet]].
Per approfondire la configurazione del kernel:


==WIRELESS==
* [[esempio configurazione kernel]] nel nostro Wiki, per un semplice esempio;
* [http://a2.pluto.it/a2/a219.htm#almltitle285 elementi della configurazione] per una descrizione più dettagliata delle varie voci. Questo è un capitolo della monumentale opera [http://a2.pluto.it/a2/ Appunti di Informatica Libera], per la quale tutti noi siamo grati all'autore '''Daniele Giacomini''';
* [http://kernel.xc.net/ Linux Kernel Configuration Archive]: potrete cercare le varie opzioni di configurazione di ogni versione del kernel.


Be'.. mi permetto di aggiungere questa mini guida per far funzionare il WireLess.. compresa la chiave WEP !
In bocca al lupo con la configurazione ;-).
(Prove fatte su Versione Stable)


=== Dedian Way ===
Una volta finita la configurazione, uscite e salvate i cambiamenti. A questo punto il file <code>~/sorgenti/linux-source-3.19/.config</code> conterrà la nostra configurazione del kernel.
''(by ckale)''


Per evitare di fare il passaggio 1 e 2 in parte, installate attraverso apt-get il "module-assistant". Questo vi consentir� di recuperare, pachettizzare ed installare il modulo per il ipw2200. Una volta installato con apt-get install module assistant modifichiamo anche il source.list di apt che si trova /etc/apt/source.list aggiungendo "non-free" e "contrib" sia per il repo "deb" che deb-src come in esempio :
{{Box|Nota|Se avete già ricompilato il vostro kernel e volete passare ad una versione più aggiornata, ma non troppo diversa (ad esempio: 2.6.30 --> 2.6.32), non conviene rifare tutta la configurazione da capo. D'altro canto non è neanche possibile usare il vecchio file di configurazione dato che nel nuovo kernel ci saranno voci in più e o in meno e sarebbe improponibile cercarle ad una ad una.


deb http://debian.fastweb.it/debian/ stable main non-free contrib
Basta allora copiare il vecchio file di configurazione nella directory dei sorgenti del nuovo kernel e lanciare il comando:
deb-src http://debian.fastweb.it/debian/ stable main non-free contrib


Un volta fatto ci� aggiorniamo apt-get update e lanciamo module-assistant.
<pre>$ make oldconfig</pre>
Ricordiamoci pero' di copiare i file firmware nella cartella /usr/lib/hotplug/firmware/
A questo punto proviamo a caricare il modulo con modprobe ipw2200


Una volta caricato il modulo procediamo con l'installazione delle utility wireless, apt-get install wireless-utility. Con il comando iwconfig possiamo vedere le interfacce di rete wifi.
in questo modo verranno fatte delle domande su come configurare ''le sole nuove voci'' presenti nel kernel. Se i due kernel sono troppo diversi questo metodo non conviene più dato che bisogna rispondere ad uno ad uno a tutte le domande sulle voci diverse. Sicuramente non conviene usarlo per il passaggio 2.4 --> 2.6.<br>
Un file "config" del vostro attuale kernel può essere trovato in <code>/boot</code> sotto il nome di <code>config-2.x.x</code>.<br/>
Se non sapete bene ciò che state facendo oppure avete dei dubbi, scegliete la risposta di default.
Notare che è possibile ricorrere ai comandi:
<pre>
$ make olddefconfig
</pre>
per accettare automaticamente le risposte di default, oppure:
<pre>
$ make oldnoconfig
</pre>
per rispondere negativamente a tutte le domande (default "n") }}


{{Warningbox|Se non funziona controllate il log del modprobe e verificate che il modulo cerchi il driver corretto, mi � capitato che lui cercasse un file con un nome diverso, naturalmente mi � bastato rinominare i firmware ;)}}
=== Alternative a <code>make menuconfig</code> ===


=== Old Style ===
Per completezza si segnalano le altre interfacce grafiche che è possibile usare per configurare il kernel al posto di <code>make menuconfig</code>.
''(by jockerfox)''


1) Dal sito Sourceforge.net
;<code>make xconfig</code>: per usare una interfaccia grafica '''QT''' per la configurazione (serviranno i [[pacchetto|pacchetti]] <code>libqt4-dev</code> e <code>pkg-config</code>);
scaricate i seguenti pacchetti :
;<code>make gconfig</code>: per usare una interfaccia grafica '''GTK''' per la configurazione.


http://ipw2200.sourceforge.net/#downloads il driver "ipw2200-1.0.4.tgz"
Questi frontend non aggiungono niente di nuovo e sono pertanto funzionalmente equivalenti tra di loro. Per usarli sono però necessarie le librerie di sviluppo, rispettivamente, di ''QT'' e ''GTK''.
http://ipw2200.sourceforge.net/firmware.php il firmware "v1.0.4-current firmware"


Con Synaptic scaricare i seguenti pacchetti:
== Compilazione del kernel ==
:1: kernel-headers-2.6.8-2-686 (in automatico scaricher� anche kernel-headers-2.6.8-2 e kernel-kbuild-2.6-3)
:2: net-tools


2) Fatto cio':
Ora è venuto il momento di cominciare la compilazione, a tal scopo useremo <code>make-kpkg</code>. Vediamo come utilizzare velocemente questo tool per compilare il nostro kernel personalizzato:
:* scompattare "ipw2200-1.0.4.tgz" in una directory qualsiasi e da SU (#) fate un "make", poi "make install"
:* scompattare in una diversa directory "v1.0.4-current firmware" e copiare tutto in /usr/lib/hotplug/firmware/
 
'''P.S.''': non occorre copiare i file tipo "LICENZE" e varie... che non servono a nulla.
 
3) aprite una Konsole e da SU scrivete "nano /etc/network/interfaces" e aggiungete prima di eth0:


<pre>
<pre>
auto eth1
$ fakeroot make-kpkg --append-to-version -nomepersonalizzato --revision=1 kernel_image
iface eth1 inet dhcp
</pre>
</pre>
{{Box|Nota|Dopo la versione 3.0 del kernel make-kpkg è  considerato  deprecato il supporto è stato mantenuto per  retrocompatibilità il comando da dare ora è il seguente:
<pre>$ make KDEB_PKGVERSION=1.0 deb-pkg
</pre> Per il nomepersonalizzato si deve modificare il valore di CONFIG_LOCALVERSION del file .config (il file di configurazione che si trova nella cartella del sorgente) con il valore -nomepersonalizzato.
}}
Questo comando compilerà il nostro kernel e lo inserirà in un pacchetto Debian nella directory <code>~/sorgenti</code>.
Diamo uno sguardo alle opzioni usate:


4) reboot ... e funziona !!
; <code>--append-to-version</code> : serve ad aggiungere un nome personalizzato al pacchetto che verrà aggiunto dopo il numero di versione, che in questo caso diventerà <code>''2.6.32-nomepersonalizzato''</code>;


{{Warningbox|Ricordate di mettere il router senza chiave WEP (o varie cifrature) per essere sicuru che tutto funzioni come da dovere... dopo di che' abilitate allora la Key WEP nel router (vedi sotto per Debian)}}
; <code>--revision</code> : permette di impostare il numero di revisione del pacchetto, normalmente viene indicato con un numero intero;


; <code>kernel_image</code> : dice a make-kpkg di compilare l'immagine del kernel creare il pacchetto Debian.


=== Il WEP ===
Se ad esempio compileremo per la seconda volta lo stesso kernel, per fare solo delle modifiche minori, può essere utile usare lo stesso nome per <code>--append-to-version</code> ed usare un numero di revisione maggiore. In questo modo quando installerete il pacchetto del kernel ricompilato questo sostituirà il pacchetto precedente. Al contrario se ricompilate un secondo kernel cambiando la stringa da appendere alla versione, il pacchetto del nuovo kernel conviverà tranquillamente col precedente.


No problem !
In realtà il comando <code>'''make-kpkg'''</code> accetta molti ulteriori parametri (elencherò solo i più importanti per gli altri leggete l'amichevole pagina di manuale aka read the friendly manual):


A.S.: Il KWiFIManager e' utile, ma non per configurare la chiave WEP!!!
; <code>--initrd</code> : da usare se state compilando un kernel che utilizza le immagini <code>initrd.img</code> (''vedi [[Debian_Kernel_Howto#Bisogna_usare_l.27initrd_oppure_no.3F|FAQ: Bisogna usare l'initrd_oppure no?]]'');
; <code>--added-modules foo</code> : compila dei sorgenti esterni (presenti in <code>/usr/src/modules</code>) insieme al kernel, potete mettere più nomi separati da virgole;
; <code>--added-patches foo</code> : aggiunge delle patch al kernel, le patch possono essere molteplici separate da virgole;
; <code>--config</code> : sceglie quale frontend usare per configurare il kernel (config, menuconfig, xconfig, gconfig);
; <code>--zimage</code> : crea una zImage per il kernel;
; <code>--bzImage</code> : crea una bzImage per il kernel;
; <code>--mkimage</code> : qui potete passare dei parametri a <code>mkinitrd</code>, ad esempio se volete creare una immagine rom: <code>genromfs -d %s -f %s</code>;
; <code>--rootcmd foo</code> : per passare un comando a make-kpkg ad esempio fakeroot o sudo;
; <code>CONCURRENCY_LEVEL</code> : questa variabile è l'omonimo di <code>-j</code> per make, per usarla vi basta mettere il numero intero che desiderate usare (''$ CONCURRENCY_LEVEL=4 make-kpkg --blabla ecc.ecc...'' ).


;Importante: In primis, abilitate la chiave WEP nel router (esempio io la ho abilitata in 128 bit)
Come ultimo parametro dovremo mettere un'azione da compiere, vediamo le principali:
e '''scrivetevi il codice esadecimale''' in un foglio senza sbagliare !!
# Da Konsole digitate : network-admin (lo trovate anche nel menu' K) e vi chiedera' la password di amministratore.. inseritela !
# Una volta "entrati dentro", cliccate sull'icona del Wireless, e poi cliccate sull'icona "modifica" (e' un'icona con una chiave inglese) e inserite la chiave WEP in esadecimale (ex:ABF0D3...); non occorre aggiungere "0x" avanti alla chiave, (0xABFoD3...NO!!) digitatela direttamente in esadecimale (ABF0D3...SI!)
# selezionate la casellina "questo dispositivo e' configurato"
# le altre opzioni se volete... tipo ESSID Dopo premete OK (due volte) e reboot !!!


Sperando di non essermi dimenticato qualcosa... ciao!
; <code>clean</code> : pulisce i sorgenti;
; <code>kernel_headers</code> : questo genera un pacchetto con gli header del kernel;
; <code>binary</code> : questo genera un nuovo pacchetto deb con i sorgenti, uno con gli header, uno con la documentazione e uno con l'immagine del kernel;
; <code>buildpackage</code> : pulisce i sorgenti e avvia "binary" (vedere sopra);
; <code>build</code> : compila solo l'immagine del kernel;
; <code>modules</code> : compila tutti moduli esterni sotto <code>/usr/src/modules</code> e genera un file <code>.diff</code> e un pacchetto sorgente;
; <code>modules_config</code> : permette di configurare i moduli esterni residenti in <code>/usr/src/modules</code> prima di compilarli;
; <code>modules_image</code> : crea i pacchetti deb dei moduli esterni residenti in <code>/usr/src/modules</code> senza il file .diff e senza creare un altro pacchetto sorgente;
; <code>modules_clean</code>: pulisce i sorgenti dei moduli esterni presenti in <code>/usr/src/modules</code>;
; <code>debian</code> : questo crea la directory <code>./debian</code> utile per compilare i kernel vanilla e patcharli alla maniera Debian.


Fine .
Nel caso di sistemi multiprocessore è possibile velocizzare la compilazione aggiungendo <code>CONCURRENCY_LEVEL=n</code> dove n corrisponde al numero di processi che il compilatore usa in parallelo (normalmente si usa un processo in più rispetto al numero di processori presenti).
(by jockerfox)
Per esempio se vogliamo compilare kernel su un PC dotato di un processore quadcore su può usare:


==GRAFICA==
<pre>
La guida per la Ati Mobility Radeon 9700 SE potrbbe esservi utile:
$ fakeroot CONCURRENCY_LEVEL=5 make-kpkg --append-to-version -nomepersonalizzato --revision=1 kernel_image --initrd kernel_headers
</pre>
{{Box|Nota|Data la deprecazione di make-kpkg ora per fare la stessa cosa si usa -jn dove n è il numero di processori il comando da dare ora è il seguente per una macchina a 4 core:
<pre>$ make KDEB_PKGVERSION=1 deb-pkg -j4
</pre>
}}


[http://guide.debianizzati.org/index.php/Installazione_Driver_ATI_per_schede_ATI_RADEON_MOBILITY_9700_SE guide.debianizzati.org]
== Installazione nuovo kernel ==
Una volta finito torneremo alla riga di comando e ci sposteremo nella directory precedente (<code>~/sorgenti</code>) dove troveremo il pacchetto .deb del kernel appena compilato:


Comunque per abilitare l'accelerazione hardware 3D, bisogna scaricare gli ultimi driver proprietari della ATI (al 13/11/2005 gli 8.19.10 , circa 60 MB) dal sito Ati e seguire le istruzioni.
<pre>
$ cd ..
$ ls
...
linux-image-3.19.1_nomepersonalizzato_1_amd64.deb
...
</pre>


Niente di complicato.
Adesso possiamo installare il pacchetto con il nostro nuovo kernel ricompilato. Diventiamo quindi root con '''su''', e digitiamo:
Prima di far partire l'installer salvate una copia di /etc/X11/XF86config-4 , che in caso di problemi andra' sostituita a quella nuova (creata dall'istallazione).
<pre>
# dpkg -i linux-image-3.19.1_nomepersonalizzato_1_amd64.deb
</pre>


Dopo il riavvio della macchina, se tutto va bene, tornate nel nuovo file di configurazione (/etc/X11/XF86config-4) e aggiungete le risoluzioni come descritto sopra.
Se abbiamo LILO dovremo configurare <code>lilo.conf</code> aggiungendo le righe relative al kernel. Ricordatevi che, con LILO, per rendere effettive le modifiche bisogna aggiornare il [[MBR]] (Master Boot Record) con il comando:


Questo e' il mio XF86config-4 senza i commenti:
<pre>
<pre># File: XF86Config-4
# lilo -v
# File generated by fglrxconfig (C) ATI Technologies, a substitute for xf86config.
</pre>


Section "dri"
Se abbiamo Grub, invece, non ci resta altro che riavviare :D. Tuttavia per approfondire le personalizzazioni che è possibile fare su Grub, potete leggere l'apposita sezione della [[Guida a Grub]]:


    Mode 0666
* [[Guida_a_Grub#Usare_update-grub|Guida a Grub: Usare update-grub]]


EndSection
== Installare e gestire i moduli ==


Per compilare e creare automaticamente pacchetti .deb per moduli non presenti nei sorgenti del kernel, Debian fornisce un comodo strumento: [[Pagina di manuale di module-assistant|module-assistant]]. Per un uso interattivo basterà lanciarlo da root per installare i pacchetti, scaricare i sorgenti del modulo che interessa, compilarlo e creare un pacchetto Debian.


Section "Module"
Per scegliere invece quali moduli fare partire all'avvio ci sono diverse strade.


    Load        "dbe"  # Double buffer extension
# Se si usa l'hotplug, questi dovrebbe caricare automaticamente al boot tutti i moduli necessari. Per evitare il caricamento di certi moduli che possono creare conflitti basta inserirli in <code>'''/etc/hotplug/blacklist'''</code>.
# Se non si usa l'hotplug bisogna specificare manualmente quali moduli caricare all'avvio. Per far ciò basterà inserire i nomi dei moduli da caricare in <code>'''/etc/modules'''</code>, uno per riga. Se non vi va di editare un file di testo (o non ricordate esattamente i nomi dei moduli) potrete usare <code>'''modconf'''</code> che permette di scegliere interattivamente quali moduli caricare all'avvio.


    SubSection  "extmod"
== FAQ ==
      Option    "omit xfree86-dga"  # don't initialise the DGA extension
=== Per aggiungere un modulo devo ricompilare tutto il kernel? ===
    EndSubSection
Dipende.


    Load        "type1"
Se il modulo fa parte del kernel Debian (cioè il suo sorgente è contenuto nel pacchetto <code>kernel-source</code> del kernel) allora bisogna ricompilare il kernel. Tenete presente, tuttavia, che i kernel binari Debian includono già la maggior parte dei moduli presenti nei sorgenti del kernel. Per caricarli basta usare:
    Load        "freetype"
<pre>
    Load        "glx"   # libglx.a
   # modprobe ''nomemodulo''
    Load        "dri"   # libdri.a
</pre>
Se il sorgente del modulo è invece pacchettizzato singolarmente (il nome di questi pacchetti comincia per <code>module-source</code>) '''non è necessario''' ricompilare il kernel.
Debian ci fornisce la comoda utility '''module-assistant''' che permette di scaricare, compilare e pacchettizzare un modulo del kernel. Basta lanciare il comando
<pre>
   # m-a
</pre>
e una interfaccia ''dialog'' ci guiderà passo passo.


EndSection
Si può usare il comando <code>module-assistant list-avaible</code> (o il diminutivo <code>m-a la</code>) per ottenere la lista completa dei moduli installabili con module-assistant. Per le altre innumerevoli opzioni potete leggere la pagina di manuale tradotta in italiano:


* [[Pagina di manuale di module-assistant]]


Section "Files"
===Bisogna usare l'initrd oppure no?===
La risposta breve è: no non usatelo.


    RgbPath "/usr/X11R6/lib/X11/rgb"
Di seguito la risposta lunga:
    FontPath  "/usr/X11R6/lib/X11/fonts/misc/"
    FontPath  "/usr/X11R6/lib/X11/fonts/75dpi/:unscaled"
    FontPath  "/usr/X11R6/lib/X11/fonts/100dpi/:unscaled"
    FontPath  "/usr/X11R6/lib/X11/fonts/Type1/"
    FontPath  "/usr/X11R6/lib/X11/fonts/Speedo/"
    FontPath  "/usr/X11R6/lib/X11/fonts/75dpi/"
    FontPath  "/usr/X11R6/lib/X11/fonts/100dpi/"


EndSection
L'immagine initrd (ramdisk iniziale) serve per caricare dei moduli nel kernel prima che questo abbia l'accesso alla partizione di root. Quindi basta compilare questi moduli staticamente e non avremo mai bisogno di un ramdisk. Ma quali sono questi moduli che servono nelle prime fasi di avvio? Semplicemente i moduli che permettono di leggere la partizione di root, ovvero:


* il modulo del controller del proprio harddisk
* il modulo del filesystem della partizione di root


Section "ServerFlags"
Completato questo passaggio si può procedere alla modifica del file: <pre>/etc/default/grub</pre><br/>
{{Warningbox|Si consiglia di eseguire questa modifica prima di installare il kernel privo di initrd per evitare di ritrovarsi con una macchina non avviabile.}}


EndSection
Il suddetto file va modificato poiché, senza l'initrd, il nostro sistema non sarà in grado, in fase di avvio, di riconoscere i dischi attraverso gli UUID, ma solo per mezzo degli indirizzi <pre>/dev/sda</pre>
Con un editor di testo è necessario decommentare l'opzione <pre>#GRUB_DISABLE_LINUX_UUID=true</pre> rimuovendo il simbolo "#". Il passaggio conclusivo consiste nell'eseguire <pre># update-grub</pre> per aggiornare la configurazione di grub.<br/>


Per un kernel ricompilato, l'initrd è generalmente inutile e rende l'avvio leggermente più lento. È anche facile sbagliare se non attivate le giuste opzioni nel kernel (vedi [[#Ma se io devo usare l'initrd assolutamente?|FAQ successiva]]), in tal caso otterreste un <code>kernel panic</code> all'avvio. L'initrd serve soprattutto per i kernel ufficiali delle distribuzioni che devono supportare tutti i controller esistenti e una gran varietà di filesystem. Sarebbe assurdo compilare tutti questi supporti staticamente e quindi vengono inseriti come moduli nel ram disk. <--


Section "InputDevice"
*** ATTENZIONE *** PARTE COMMENTATA *** ATTENZIONE ***


    Identifier "Keyboard1"
L'initrd è necessario anche se si vuole usare un bootsplash, ma questa è un'altra storia:
    Driver "Keyboard"
    Option "AutoRepeat" "500 30"
    Option "XkbRules" "xfree86"
    Option "XkbModel" "pc101"
    Option "XkbLayout" "it"


EndSection
* [[Old:Compilazione Kernel 2.6.11 con Bootsplash]]
* [[Old:Kernel2.6.10 - Framebuffer - Gensplash Patch]]


*** FINE PARTE COMMENTATA *** -->


Section "InputDevice"
La risposta lunga è quindi no, non usate l'initrd quando questo non sia strettamente necessario.


    Identifier "Mouse1"
=== Ma il kernel non fa il boot senza initrd! ===
    Driver "mouse"
Vedi FAQ precedente. L'initrd non è necessario per fare il boot. Se il sistema non parte ciò dipende da una non corretta configurazione del kernel.
    Option "Protocol"  "ImPS/2"
    Option "ZAxisMapping"  "4 5"
    Option "Device"    "/dev/input/mice"
    Option "Emulate3Buttons"


EndSection
Questo è quasi sempre vero, ma ci sono delle eccezioni. In alcuni casi, quali ad esempio l'avvio da una memoria USB con filesystem di root nella stessa, può essere necessario fare uso di initrd affinché vengano generati correttamente i device (vedi sda1, sda2 ecc.). Questo pur avendo compilato tutti i moduli staticamente all'interno del kernel.


===Ma se io devo usare l'initrd assolutamente?===
Per usare l'intrd '''si deve''' compilare staticamente il supporto per l'initrd impostando le seguenti voci:


Section "Monitor"
<pre>
Device Drivers  --->
  Block devices  --->
    <*> RAM disk support
    (16)  Default number of RAM disks
    (8192) Default RAM disk size (kbytes)
    [*]  Initial RAM disk (initrd) support
</pre>


    Identifier  "Monitor0"
A partire dal kernel 2.6.13 si usano di default immagini del filesystem in formato '''cpio''' per cui non è più necessario aggiungere il supporto al '''cramfs'''.
    HorizSync  30-70
    VertRefresh 50-100
    Option "DPMS"


EndSection
Con tale configurazione è possibile compilare il kernel con initrd aggiungendo semplicemente l'opzione <code>--initrd</code> al comando <code>make-kpkg</code>. Il pacchetto risultante conterrà degli script che creeranno l'immagine initrd in fase di installazione del pacchetto.


Attualmente (Squeeze) lo strumento in Debian che permette di creare l'immagine initrd è <code>update-initramfs</code> (fornito dal pacchetto <code>initramfs-tools</code>) e utilizzabile con kernel 2.6.13 o più recenti. Questo strumento aggiunge tutti i controller del disco e i supporti che potrebbero servire per il boot che sono stati compilati come moduli;


Section "Monitor"
Per ulteriori informazioni sui kernel Debian e le immagini initrd:


    Identifier  "Monitor1"
* [http://kernel-handbook.alioth.debian.org/ch-initramfs.html Debian Linux Kernel Handbook: Managing the initial ramfs (initramfs) archive]
    HorizSync  30-70
    VertRefresh 50-100
    Option "DPMS"


EndSection
=== Posso usare make-kpkg con un kernel vanilla ===
Certamente, <code>make-kpkg</code> può essere usato indifferentemente sia con i sorgenti Debian del kernel di Linux che con i sorgenti del [[kernel vanilla]].


I sorgenti Debian sono contenuti nei pacchetti <code>kernel-source-*</code> (o <code>linux-source-*</code> per i kernel dal 2.6.12 in poi) e sono installabili come usuali pacchetti con [[APT]].


Section "Device"
I sorgenti vanilla devono essere scaricati manualmente da [http://www.kernel.org www.kernel.org]. Devono essere scompattati in <code>/usr/src</code>, e per il resto la procedura di compilazione è assolutamente identica al caso di sorgenti Debian.


    Identifier  "Standard VGA"
Nel caso di sorgenti vanilla, può essere interessante vedere l'opzione <code>debian</code> nella sezione [[Debian_Kernel_Howto#Compilazione_del_kernel|Compilazione del kernel]], tuttavia l'uso di tale parametro è del tutto opzionale.
    VendorName  "Unknown"
    BoardName  "Unknown"
    Driver      "vga"


EndSection
===Errore con l'opzione <code>--revision</code> ===
Può capitare che, ricompilando il kernel variando il valore dell'opzione <code>--revision</code> venga rilevato un errore simile al seguente:
<pre>
I note that you are using the --revision flag with the value
  2.
However, the ./debian/changelog file exists, and has a different value
  1.
I am confused by this discrepancy, and am halting.</pre>


Questo problema è semplicemente dovuto al fatto che non si è pulito il tree dei sorgenti dopo la prima compilazione. Per ovviare basta dunque:


# === ATI device section ===
<pre>$ make-kpkg clean</pre>


Section "Device"
e rilanciare la compilazione.
    Identifier                          "ATI Graphics Adapter"
    Driver                              "fglrx"
# ### generic DRI settings ###
# === disable PnP Monitor  ===
    #Option                              "NoDDC"
# === disable/enable XAA/DRI ===
    Option "no_accel"                  "no"
    Option "no_dri"                    "no"
# === misc DRI settings ===
    Option "mtrr"                      "off" # disable DRI mtrr mapper, driver has its own code for mtrr
# ### FireGL DDX driver module specific settings ###
# === Screen Management ===
    Option "DesktopSetup"              "Clone"
    Option "HSync2"                    "30-70"
    Option "VRefresh2"                  "50-100"
    Option "ScreenOverlap"              "0"
# === TV-out Management ===
    Option "TVFormat"                  "PAL-B"   
    Option "TVStandard"                "NTSC-M"
    Option "TVHSizeAdj"                "0"   
    Option "TVVSizeAdj"                "0"   
    Option "TVHPosAdj"                  "0"   
    Option "TVVPosAdj"                  "0"   
    Option "TVHStartAdj"                "0"   
    Option "TVColorAdj"                "0"   
    Option "GammaCorrectionI"          "0x06419064"
    Option "GammaCorrectionII"          "0x06419064"
# === OpenGL specific profiles/settings ===
    Option "Capabilities"              "0x00000000"
    Option "CapabilitiesEx"            "0x00000000"
# === Video Overlay for the Xv extension ===
    Option "VideoOverlay"              "on"
# === OpenGL Overlay ===
# Note: When OpenGL Overlay is enabled, Video Overlay
#      will be disabled automatically
    Option "OpenGLOverlay"              "off"
# === Center Mode (Laptops only) ===
    Option "CenterMode"                "off"
# === Pseudo Color Visuals (8-bit visuals) ===
    Option "PseudoColorVisuals"        "off"
# === QBS Management ===
    Option "Stereo"                    "off"
    Option "StereoSyncEnable"          "1"
# === FSAA Management ===
    Option "FSAAEnable"                "no"
    Option "FSAAScale"                  "1"
    Option "FSAADisableGamma"          "no"
    Option "FSAACustomizeMSPos"        "no"
    Option "FSAAMSPosX0"                "0.000000"
    Option "FSAAMSPosY0"                "0.000000"
    Option "FSAAMSPosX1"                "0.000000"
    Option "FSAAMSPosY1"                "0.000000"
    Option "FSAAMSPosX2"                "0.000000"
    Option "FSAAMSPosY2"                "0.000000"
    Option "FSAAMSPosX3"                "0.000000"
    Option "FSAAMSPosY3"                "0.000000"
    Option "FSAAMSPosX4"                "0.000000"
    Option "FSAAMSPosY4"                "0.000000"
    Option "FSAAMSPosX5"                "0.000000"
    Option "FSAAMSPosY5"                "0.000000"
# === Misc Options ===
    Option "UseFastTLS"                "0"
    Option "BlockSignalsOnLock"        "on"
    Option "UseInternalAGPGART"        "yes"
    Option "ForceGenericCPU"            "no"
    BusID "PCI:1:0:0"    # vendor=1002, device=4e50
    Screen 0
EndSection


# **********************************************************************
===You are attempting to install a kernel image (version ''version-revision'') However, the directory /lib/modules/''version-revision'' still exists.===
# Screen sections
Se si aggiorna il kernel ad una [[revisione]] successiva, durante l'installazione del pacchetto verrà fatta la seguente domanda:
# **********************************************************************
 
<pre>
# Any number of screen sections may be presentEach describes
You are attempting to install a kernel image (version 2.6.15.4-swsusp) However, the directory /lib/modules/2.6.15.4-swsusp still existsIf this directory
# the configuration of a single screenA single specific screen section
belongs to a previous linux-image-2.6.15.4-swsusp package, and if you have deselected some modules, or installed standalone modules packages, this could be
# may be specified from the X server command line with the "-screen"
bad. However, if this directory exists because you are also installing some stand alone modules right now, and they got unpacked before I did, then this is
# option.
pretty benignUnfortunately, I can not tell the difference.


Section "Screen"
If /lib/modules/2.6.15.4-swsusp belongs to a old install of linux-image-2.6.15.4-swsusp, then this is your last chance to abort the installation of this
    Identifier  "Screen0"
kernel image (nothing has been changed yet).
    Device      "ATI Graphics Adapter"
    Monitor    "Monitor0"
    DefaultDepth 24
    #Option "backingstore"


    Subsection "Display"
If this directory is because of stand alone modules being installed right now, or if it does belong to an older linux-image-2.6.15.4-swsusp package but you
        Depth      24
know what you are doing, and if you feel that this image should be installed despite this anomaly, Please answer n to the question.
        Modes      "1280x800" "1024x768" "800x600" "640x480"
        ViewPort    0 0  # initial origin if mode is smaller than desktop
#        Virtual    1280 1024
    EndSubsection
EndSection


Otherwise, I suggest you move /lib/modules/2.6.15.4-swsusp out of the way, perhaps to /lib/modules/2.6.15.4-swsusp.old or something, and then try
re-installing this image. 


Section "ServerLayout"
Stop install since the kernel-image is already installed? 
 
    Identifier  "Server Layout"
    Screen "Screen0"
    InputDevice "Mouse1" "CorePointer"
    InputDevice "Keyboard1" "CoreKeyboard"
 
EndSection
 
### EOF ###
</pre>
</pre>
Se volete provare l'accelerazione:
<pre># fgl_glxgears</pre>
dovrebbe apparire una finestra con un cubo rotante e, sul terminale, le statistiche della prova con risultati degli FPS di circa 400 o piu':
<pre>Using GLX_SGIX_pbuffer
1685 frames in 5.0 seconds = 337.000 FPS
2096 frames in 5.0 seconds = 419.200 FPS
2095 frames in 5.0 seconds = 419.000 FPS
</pre>
Adesso provatevi Tuxracer (ppracer) e Armagetron. Have fun!
==AUDIO==
Bisogna installare i paccheti ALSA:
<pre># apt-get install alsa-base alsa-utils</pre>
Poi fare un bel:
<pre># alsaconf</pre>
seguire le istruzioni e poi:
<pre># alsamixer</pre>
per settare i volumi.
Ho scoperto piu' tardi che il mio sistema ha il server sonoro un po' incasinato. Se viene disabilitato, i suoni si sentono lo stesso, in pi impossibile sentire i suoni di sistema. Il comando:
<pre>lsof|grep dsp</pre>
non d risultati.
Cerchero' di risolvere.
==PCMCIA==
Su internet ho trovato che l'adattatore PCMCIA, su questo modello, riconosciuto con il modulo "yenta_socket".
==Gestione energetica==
Per quanto riguarda il risparmio energetico, il centro di controllo di KDE dice che:
'''Il computer ha l'installazione ACPI parziale, bisogna abilitare "AC adaptor" e "Control method battery". Quindi ricompilare il kernel.'''
Io ho risolto installando da zero la Debian testing (Etch).
==Note==
Il mio mouse (Logitech Optical USB) riconosciuto subito; il touchpad va cofigurato in /etc/X11/XF86config-4 .
Totem d un messaggio di errore quando si cerca di riprodurre un file audio o video. Dopo la (re)installazione dei pacchetti ALSA funziona. Le altre applicazioni multimediali vanno bene, tranne XMMS che va solo se non sono in esecuzione altre applicazioni multimediali e il demone "artsd" (?).
Una buona guida all'installazione a Debian Sarge qui:
[http://fabrizio.ciacchi.it/guide.php?pagina=sarge Guida veloce]
==Note su Debian Etch==
La testing al 13/11/2005 ha il kernel 2.6.12, gnome 2.10, e xorg 6.8.2
Il comando di boot resta quasi lo stesso:
<pre>install acpi=yes vga=771 hw-detect/start_pcmcia=false</pre>
Installando da zero la testing ho risolto alcuni problemi, tra cui la gestione energetica e il controllo della batteria.
Durante il processo di installazione ho scelto: ambiente desktop, sistema base e portatile.


'''Gestione energetica'''  
La risposta da dare è '''<code>No</code>'''! L'avvertimento ci ricorda che i moduli del vecchio kernel (quello con la stessa versione ma numero di revisione diverso) verranno cancellati e sostituiti dai moduli del nuovo kernel.


Finita l'installazione, con modconf (da installare) ho attivato i seguenti moduli:
Questo è il comportamento normale, infatti, nel caso non si voglia sostituire un vecchio kernel ma semplicemente installarne parallelamente uno nuovo (con la stessa identica versione) si sarebbe dovuta modificare la stringa dopo <code>--append-to-version</code> invece che quella dopo <code>--revision</code> (vedi sez. [[Debian_Kernel_Howto#Compilazione_del_kernel|Compilazione kernel]]).
<pre>acpi-cpufreq
ac
battery
button
fan
processor
thermal
cpufreq_userspace
freq_table</pre>
Comunque molti sono gia' attivati.
Inoltre va installato:
<pre>powernowd</pre>
e facoltativamente, credo:
<pre>cpufrequtils</pre>
Aggiungete le applet (se avete Gnome) "Variazione frequenza CPU" e "Carica batteria" e siete a posto.


Con il comando:
Se il kernel che si sta sostituendo è quello in esecuzione ''è necessario riavviare la macchina il prima possibile!''
<pre>cpufreq-set</pre>
potete cambiare la frequenza del processore. Esempio:
<pre>cpufreq-set -f 1.2GHz</pre>
oppure ottenere info con:
<pre>cpufreq-info</pre>


== Link ==


----
* [http://www.debian.org/doc/manuals/reference/ch-kernel.it.html Manuale di Riferimento Debian: Capitolo 7 - Il kernel Linux su Debian]
* [http://kernel-handbook.alioth.debian.org/index.html Debian Linux Kernel Handbook ]: ottimo documento sulla gestione dei kernel Debian delle relative patch (''in inglese'').
* [http://a2.pluto.it/a2/a219.htm#almltitle282 Appunti di informatica Libera: Kernel Linux]: Il capitolo dedicato al kernel della monumentale opera di ''Daniele Giacomini'' contiene sia istruzioni generiche che istruzioni per Debian. Inoltre c'è una descrizione dettagliata della configurazione delle varie voci del kernel!
* [http://kernel.xc.net/ Linux Kernel Configuration Archive]: database che permette di ricercare tra le voci di configurazione (e le loro descrizioni) per varie versioni di kernel.


Chiunque volesse contribuire a questa guida � benvenuto (soprattutto e a maggior ragione se ho detto cose '''poco esatte''').
Buon divertimento con Debian GNU/Linux!


----
{{Autori
|Autore=[[Utente:Abortigeno|Abortigeno]]
|Verificata_da=
:[[Utente:TheNoise|~ The Noise]]
: [[Utente:Lorenzoz|Lorenzoz]] 09:57, 11 ott 2014 (CEST)
:[[Utente:Oscarandrea|Oscarandrea]]  14:50, 8 giu 2015 (CEST)
|Estesa_da=
:[[Utente:TheNoise|~ The Noise]]
:[[Utente:fw_crocodile| fw_crocodile]]
:[[Utente:Lorenzoz|Lorenzoz]] 09:57, 11 ott 2014 (CEST)
|Numero_revisori=3
}}


Autore: [[Utente:Superflieriam|Superflieriam]]
[[Categoria:Linux]]

Versione attuale delle 11:40, 15 mag 2016

Edit-clear-history.png Attenzione. Questa guida è da considerarsi abbandonata, per via del tempo trascorso dall'ultima verifica.

Potrà essere resa obsoleta, previa segnalazione sul forum, se nessuno si propone per l'adozione.


Debian-swirl.png Versioni Compatibili

Debian 7 "wheezy"
Debian 8 "jessie"

Introduzione

In Debian, il kernel Linux può essere ricompilato con il metodo standard (valido con tutte le distribuzioni, e quindi anche con Debian) oppure nel cosiddetto Debian-way (traduzione: metodo Debian o alla Debian).

Questa guida illustrerà il metodo Debian di compilare il kernel Linux. Questo metodo consiste nel creare un pacchetto Debian del kernel compilato per una sua facile installazione/disinstallazione.

Tutti i passi descritti in questa guida non richiedono i permessi di root. Le uniche operazioni che richiedono l'intervento dell'amministratore della macchina sono l'installazione dei pacchetti necessari alla compilazione e l'installazione del pacchetto .deb creato alla fine del processo di compilazione.

Installazione dei pacchetti

Avremo innanzitutto bisogno di alcuni pacchetti di base per compilare e pacchettizzare un kernel:

# apt-get install module-init-tools kernel-package libncurses5-dev fakeroot

A questo punto è necessario installare il pacchetto Debian contenente i sorgenti del kernel. Per prima cosa, cerchiamo questo pacchetto:

$ apt-cache search linux-source | grep ^linux-source
linux-source-3.16 - sorgenti del kernel Linux per la versione 3.16 con patch Debian
linux-source - sorgenti del kernel Linux (metapacchetto)
linux-source-3.19 - Linux kernel source for version 3.19 with Debian patches
Info.png Nota
Ogni versione di Debian (unstable, testing, stable) utilizza in genere una certa versione del kernel e specifiche versioni di altri pacchetti ad esso correlati in modo tale che l'insieme sia il più possibile stabile. È quindi altamente consigliato usare la versione dei sorgenti del kernel che troveremo nei repository della nostra versione di Debian, a meno che non si sappia esattamente quello che si sta facendo.


Adesso installiamo il pacchetto dei sorgenti del kernel che intendiamo utilizzare. Notare che i sorgenti del kernel forniti con Debian sono leggermente differenti da quelli del kernel vanilla rilasciato dal team di Linus Torvalds (maggiori informazioni qui). Nel seguito prenderemo come esempio la versione 3.19 del kernel, sostituitela con qualsiasi altra versione vogliate usare.

# apt-get install linux-source-3.19

Alla fine dell'installazione verrà creato un file compresso con estensione .tar.xz nella directory /usr/src .

Info.png Nota
Prima della versione 2.6.12 del kernel Linux, i pacchetti sorgenti e binari Debian si chiamavano rispettivamente kernel-source-x.x.x e kernel-image-x.x.x (invece dell'attuale denominazione linux-source-x.x.x e

linux-image.x.x.x). Questo perché è previsto l'inserimento di nuovi kernel (come GNU HURD e FreeBSD) all'interno di Debian.


Configurazione del kernel

Passi preliminari

Per prima cosa è opportuno creare una directory in cui inserire i file da compilare. In questo caso si chiamerà "sorgenti" all'interno della nostra home directory, cambiatela a vostro piacimento:

$ mkdir ~/sorgenti

Spostiamoci nella directory appena creata e decomprimiamo al suo interno l'archivio compresso contenente i sorgenti del kernel:

$ tar -xvf /usr/src/linux-source-3.19.tar.xz -C .
Info.png Nota
Fino alla versione 3.9 i sorgenti del kernel sono contenuti in un file compresso con estensione .tar.bz2, per cui il comando cambierà così:
$ tar -xjvf /usr/src/linux-source-3.9.tar.bz2 -C .
o equivalente in base al nome del file compresso.

A fine operazione verrà creata una nuova directory:

$ ls
linux-source-3.19

spostiamoci al suo interno e procediamo con i passi successivi.

Puliamo i sorgenti del kernel:

$ make-kpkg clean

Questo passaggio è inutile se è la prima volta che compilate il kernel, ma dalla seconda volta in poi diviene necessario per eliminare i file generati dalle precedenti compilazioni che potrebbero creare conflitti.

Ora, se avete installato un kernel precompilato che abbia la stessa versione del kernel che volete ricompilare potreste usare il suo file di configurazione come base di partenza per configurare il vostro kernel. A tal scopo basta copiare il file di configurazione che si trova in /boot (i file di configurazione dei kernel installati hanno come nome config seguito dalla versione del kernel) nella directory dei sorgenti.
Il nome del file da creare deve essere sempre ".config".

$ cp /boot/config-3.19.1-amd64 .config 

C'è chi arriva anche a scaricare il pacchetto contenente il kernel semplicemente per il suo file di configurazione. Se avete banda da sprecare è possibile farlo. Tuttavia si può benissimo partire da zero senza copiare nessun file di configurazione.

Configurazione: make menuconfig

A questo punto, per configurare il nostro kernel, non ci resta che lanciare il comando:

$ make menuconfig

Vi apparirà un'interfaccia testuale dalla quale sarà possibile configurare le opzioni del kernel. Questo è il passaggio più delicato, nonché il più lungo e difficile.

Se dovete configurare un kernel per la prima volta prendetevi almeno un'ora di tempo ed iniziate con calma, leggendo tutte le pagine dell'help in linea. Uno dei vantaggi di un kernel ricompilato è la possibilità di ottenere un kernel estremamente piccolo e leggero proprio perché viene compilato il supporto per le sole periferiche e i soli filesystem effettivamente usati. In questo modo si ha un kernel piccolo e pochi moduli. Un kernel di questo tipo impiega anche molto meno tempo ad essere compilato. Per fare un esempio potrebbe impiegare sui 10 minuti su in athlon 1000, quando un kernel Debian ufficiale impiegherebbe sicuramente più di un'ora sulla stessa macchina. In definitiva, compilando un kernel snello, sarà possibile anche fare più prove ed ottimizzarlo quindi al meglio.

Per trovare quali moduli sono richiesti dal vostro hardware potete usare il comando lspci o meglio lspci -v. Inoltre risulta utilissimo consultare il database dei driver di Linux a questo indirizzo: inserendo semplicemente l'output di lspci -n, otterrete l'elenco dei moduli da compilare

Per approfondire la configurazione del kernel:

In bocca al lupo con la configurazione ;-).

Una volta finita la configurazione, uscite e salvate i cambiamenti. A questo punto il file ~/sorgenti/linux-source-3.19/.config conterrà la nostra configurazione del kernel.

Info.png Nota
Se avete già ricompilato il vostro kernel e volete passare ad una versione più aggiornata, ma non troppo diversa (ad esempio: 2.6.30 --> 2.6.32), non conviene rifare tutta la configurazione da capo. D'altro canto non è neanche possibile usare il vecchio file di configurazione dato che nel nuovo kernel ci saranno voci in più e o in meno e sarebbe improponibile cercarle ad una ad una.

Basta allora copiare il vecchio file di configurazione nella directory dei sorgenti del nuovo kernel e lanciare il comando:

$ make oldconfig

in questo modo verranno fatte delle domande su come configurare le sole nuove voci presenti nel kernel. Se i due kernel sono troppo diversi questo metodo non conviene più dato che bisogna rispondere ad uno ad uno a tutte le domande sulle voci diverse. Sicuramente non conviene usarlo per il passaggio 2.4 --> 2.6.
Un file "config" del vostro attuale kernel può essere trovato in /boot sotto il nome di config-2.x.x.
Se non sapete bene ciò che state facendo oppure avete dei dubbi, scegliete la risposta di default. Notare che è possibile ricorrere ai comandi:

$ make olddefconfig

per accettare automaticamente le risposte di default, oppure:

$ make oldnoconfig

per rispondere negativamente a tutte le domande (default "n")


Alternative a make menuconfig

Per completezza si segnalano le altre interfacce grafiche che è possibile usare per configurare il kernel al posto di make menuconfig.

make xconfig
per usare una interfaccia grafica QT per la configurazione (serviranno i pacchetti libqt4-dev e pkg-config);
make gconfig
per usare una interfaccia grafica GTK per la configurazione.

Questi frontend non aggiungono niente di nuovo e sono pertanto funzionalmente equivalenti tra di loro. Per usarli sono però necessarie le librerie di sviluppo, rispettivamente, di QT e GTK.

Compilazione del kernel

Ora è venuto il momento di cominciare la compilazione, a tal scopo useremo make-kpkg. Vediamo come utilizzare velocemente questo tool per compilare il nostro kernel personalizzato:

$ fakeroot make-kpkg --append-to-version -nomepersonalizzato --revision=1 kernel_image
Info.png Nota
Dopo la versione 3.0 del kernel make-kpkg è considerato deprecato il supporto è stato mantenuto per retrocompatibilità il comando da dare ora è il seguente:
$ make KDEB_PKGVERSION=1.0 deb-pkg
Per il nomepersonalizzato si deve modificare il valore di CONFIG_LOCALVERSION del file .config (il file di configurazione che si trova nella cartella del sorgente) con il valore -nomepersonalizzato.

Questo comando compilerà il nostro kernel e lo inserirà in un pacchetto Debian nella directory ~/sorgenti. Diamo uno sguardo alle opzioni usate:

--append-to-version
serve ad aggiungere un nome personalizzato al pacchetto che verrà aggiunto dopo il numero di versione, che in questo caso diventerà 2.6.32-nomepersonalizzato;
--revision
permette di impostare il numero di revisione del pacchetto, normalmente viene indicato con un numero intero;
kernel_image
dice a make-kpkg di compilare l'immagine del kernel creare il pacchetto Debian.

Se ad esempio compileremo per la seconda volta lo stesso kernel, per fare solo delle modifiche minori, può essere utile usare lo stesso nome per --append-to-version ed usare un numero di revisione maggiore. In questo modo quando installerete il pacchetto del kernel ricompilato questo sostituirà il pacchetto precedente. Al contrario se ricompilate un secondo kernel cambiando la stringa da appendere alla versione, il pacchetto del nuovo kernel conviverà tranquillamente col precedente.

In realtà il comando make-kpkg accetta molti ulteriori parametri (elencherò solo i più importanti per gli altri leggete l'amichevole pagina di manuale aka read the friendly manual):

--initrd
da usare se state compilando un kernel che utilizza le immagini initrd.img (vedi FAQ: Bisogna usare l'initrd_oppure no?);
--added-modules foo
compila dei sorgenti esterni (presenti in /usr/src/modules) insieme al kernel, potete mettere più nomi separati da virgole;
--added-patches foo
aggiunge delle patch al kernel, le patch possono essere molteplici separate da virgole;
--config
sceglie quale frontend usare per configurare il kernel (config, menuconfig, xconfig, gconfig);
--zimage
crea una zImage per il kernel;
--bzImage
crea una bzImage per il kernel;
--mkimage
qui potete passare dei parametri a mkinitrd, ad esempio se volete creare una immagine rom: genromfs -d %s -f %s;
--rootcmd foo
per passare un comando a make-kpkg ad esempio fakeroot o sudo;
CONCURRENCY_LEVEL
questa variabile è l'omonimo di -j per make, per usarla vi basta mettere il numero intero che desiderate usare ($ CONCURRENCY_LEVEL=4 make-kpkg --blabla ecc.ecc... ).

Come ultimo parametro dovremo mettere un'azione da compiere, vediamo le principali:

clean
pulisce i sorgenti;
kernel_headers
questo genera un pacchetto con gli header del kernel;
binary
questo genera un nuovo pacchetto deb con i sorgenti, uno con gli header, uno con la documentazione e uno con l'immagine del kernel;
buildpackage
pulisce i sorgenti e avvia "binary" (vedere sopra);
build
compila solo l'immagine del kernel;
modules
compila tutti moduli esterni sotto /usr/src/modules e genera un file .diff e un pacchetto sorgente;
modules_config
permette di configurare i moduli esterni residenti in /usr/src/modules prima di compilarli;
modules_image
crea i pacchetti deb dei moduli esterni residenti in /usr/src/modules senza il file .diff e senza creare un altro pacchetto sorgente;
modules_clean
pulisce i sorgenti dei moduli esterni presenti in /usr/src/modules;
debian
questo crea la directory ./debian utile per compilare i kernel vanilla e patcharli alla maniera Debian.

Nel caso di sistemi multiprocessore è possibile velocizzare la compilazione aggiungendo CONCURRENCY_LEVEL=n dove n corrisponde al numero di processi che il compilatore usa in parallelo (normalmente si usa un processo in più rispetto al numero di processori presenti). Per esempio se vogliamo compilare kernel su un PC dotato di un processore quadcore su può usare:

$ fakeroot CONCURRENCY_LEVEL=5 make-kpkg --append-to-version -nomepersonalizzato --revision=1 kernel_image --initrd kernel_headers
Info.png Nota
Data la deprecazione di make-kpkg ora per fare la stessa cosa si usa -jn dove n è il numero di processori il comando da dare ora è il seguente per una macchina a 4 core:
$ make KDEB_PKGVERSION=1 deb-pkg -j4


Installazione nuovo kernel

Una volta finito torneremo alla riga di comando e ci sposteremo nella directory precedente (~/sorgenti) dove troveremo il pacchetto .deb del kernel appena compilato:

$ cd ..
$ ls
...
linux-image-3.19.1_nomepersonalizzato_1_amd64.deb
...

Adesso possiamo installare il pacchetto con il nostro nuovo kernel ricompilato. Diventiamo quindi root con su, e digitiamo:

# dpkg -i linux-image-3.19.1_nomepersonalizzato_1_amd64.deb

Se abbiamo LILO dovremo configurare lilo.conf aggiungendo le righe relative al kernel. Ricordatevi che, con LILO, per rendere effettive le modifiche bisogna aggiornare il MBR (Master Boot Record) con il comando:

# lilo -v

Se abbiamo Grub, invece, non ci resta altro che riavviare :D. Tuttavia per approfondire le personalizzazioni che è possibile fare su Grub, potete leggere l'apposita sezione della Guida a Grub:

Installare e gestire i moduli

Per compilare e creare automaticamente pacchetti .deb per moduli non presenti nei sorgenti del kernel, Debian fornisce un comodo strumento: module-assistant. Per un uso interattivo basterà lanciarlo da root per installare i pacchetti, scaricare i sorgenti del modulo che interessa, compilarlo e creare un pacchetto Debian.

Per scegliere invece quali moduli fare partire all'avvio ci sono diverse strade.

  1. Se si usa l'hotplug, questi dovrebbe caricare automaticamente al boot tutti i moduli necessari. Per evitare il caricamento di certi moduli che possono creare conflitti basta inserirli in /etc/hotplug/blacklist.
  2. Se non si usa l'hotplug bisogna specificare manualmente quali moduli caricare all'avvio. Per far ciò basterà inserire i nomi dei moduli da caricare in /etc/modules, uno per riga. Se non vi va di editare un file di testo (o non ricordate esattamente i nomi dei moduli) potrete usare modconf che permette di scegliere interattivamente quali moduli caricare all'avvio.

FAQ

Per aggiungere un modulo devo ricompilare tutto il kernel?

Dipende.

Se il modulo fa parte del kernel Debian (cioè il suo sorgente è contenuto nel pacchetto kernel-source del kernel) allora bisogna ricompilare il kernel. Tenete presente, tuttavia, che i kernel binari Debian includono già la maggior parte dei moduli presenti nei sorgenti del kernel. Per caricarli basta usare:

  # modprobe ''nomemodulo''

Se il sorgente del modulo è invece pacchettizzato singolarmente (il nome di questi pacchetti comincia per module-source) non è necessario ricompilare il kernel. Debian ci fornisce la comoda utility module-assistant che permette di scaricare, compilare e pacchettizzare un modulo del kernel. Basta lanciare il comando

  # m-a

e una interfaccia dialog ci guiderà passo passo.

Si può usare il comando module-assistant list-avaible (o il diminutivo m-a la) per ottenere la lista completa dei moduli installabili con module-assistant. Per le altre innumerevoli opzioni potete leggere la pagina di manuale tradotta in italiano:

Bisogna usare l'initrd oppure no?

La risposta breve è: no non usatelo.

Di seguito la risposta lunga:

L'immagine initrd (ramdisk iniziale) serve per caricare dei moduli nel kernel prima che questo abbia l'accesso alla partizione di root. Quindi basta compilare questi moduli staticamente e non avremo mai bisogno di un ramdisk. Ma quali sono questi moduli che servono nelle prime fasi di avvio? Semplicemente i moduli che permettono di leggere la partizione di root, ovvero:

  • il modulo del controller del proprio harddisk
  • il modulo del filesystem della partizione di root

Completato questo passaggio si può procedere alla modifica del file:

/etc/default/grub


Warning.png ATTENZIONE
Si consiglia di eseguire questa modifica prima di installare il kernel privo di initrd per evitare di ritrovarsi con una macchina non avviabile.


Il suddetto file va modificato poiché, senza l'initrd, il nostro sistema non sarà in grado, in fase di avvio, di riconoscere i dischi attraverso gli UUID, ma solo per mezzo degli indirizzi

/dev/sda

Con un editor di testo è necessario decommentare l'opzione

#GRUB_DISABLE_LINUX_UUID=true

rimuovendo il simbolo "#". Il passaggio conclusivo consiste nell'eseguire

# update-grub

per aggiornare la configurazione di grub.

Per un kernel ricompilato, l'initrd è generalmente inutile e rende l'avvio leggermente più lento. È anche facile sbagliare se non attivate le giuste opzioni nel kernel (vedi FAQ successiva), in tal caso otterreste un kernel panic all'avvio. L'initrd serve soprattutto per i kernel ufficiali delle distribuzioni che devono supportare tutti i controller esistenti e una gran varietà di filesystem. Sarebbe assurdo compilare tutti questi supporti staticamente e quindi vengono inseriti come moduli nel ram disk. <--

      • ATTENZIONE *** PARTE COMMENTATA *** ATTENZIONE ***

L'initrd è necessario anche se si vuole usare un bootsplash, ma questa è un'altra storia:

      • FINE PARTE COMMENTATA *** -->

La risposta lunga è quindi no, non usate l'initrd quando questo non sia strettamente necessario.

Ma il kernel non fa il boot senza initrd!

Vedi FAQ precedente. L'initrd non è necessario per fare il boot. Se il sistema non parte ciò dipende da una non corretta configurazione del kernel.

Questo è quasi sempre vero, ma ci sono delle eccezioni. In alcuni casi, quali ad esempio l'avvio da una memoria USB con filesystem di root nella stessa, può essere necessario fare uso di initrd affinché vengano generati correttamente i device (vedi sda1, sda2 ecc.). Questo pur avendo compilato tutti i moduli staticamente all'interno del kernel.

Ma se io devo usare l'initrd assolutamente?

Per usare l'intrd si deve compilare staticamente il supporto per l'initrd impostando le seguenti voci:

Device Drivers  --->
  Block devices  --->
    <*> RAM disk support
    (16)  Default number of RAM disks
    (8192) Default RAM disk size (kbytes)
    [*]   Initial RAM disk (initrd) support 

A partire dal kernel 2.6.13 si usano di default immagini del filesystem in formato cpio per cui non è più necessario aggiungere il supporto al cramfs.

Con tale configurazione è possibile compilare il kernel con initrd aggiungendo semplicemente l'opzione --initrd al comando make-kpkg. Il pacchetto risultante conterrà degli script che creeranno l'immagine initrd in fase di installazione del pacchetto.

Attualmente (Squeeze) lo strumento in Debian che permette di creare l'immagine initrd è update-initramfs (fornito dal pacchetto initramfs-tools) e utilizzabile con kernel 2.6.13 o più recenti. Questo strumento aggiunge tutti i controller del disco e i supporti che potrebbero servire per il boot che sono stati compilati come moduli;

Per ulteriori informazioni sui kernel Debian e le immagini initrd:

Posso usare make-kpkg con un kernel vanilla

Certamente, make-kpkg può essere usato indifferentemente sia con i sorgenti Debian del kernel di Linux che con i sorgenti del kernel vanilla.

I sorgenti Debian sono contenuti nei pacchetti kernel-source-* (o linux-source-* per i kernel dal 2.6.12 in poi) e sono installabili come usuali pacchetti con APT.

I sorgenti vanilla devono essere scaricati manualmente da www.kernel.org. Devono essere scompattati in /usr/src, e per il resto la procedura di compilazione è assolutamente identica al caso di sorgenti Debian.

Nel caso di sorgenti vanilla, può essere interessante vedere l'opzione debian nella sezione Compilazione del kernel, tuttavia l'uso di tale parametro è del tutto opzionale.

Errore con l'opzione --revision

Può capitare che, ricompilando il kernel variando il valore dell'opzione --revision venga rilevato un errore simile al seguente:

I note that you are using the --revision flag with the value
   2.
However, the ./debian/changelog file exists, and has a different value
   1.
I am confused by this discrepancy, and am halting.

Questo problema è semplicemente dovuto al fatto che non si è pulito il tree dei sorgenti dopo la prima compilazione. Per ovviare basta dunque:

$ make-kpkg clean

e rilanciare la compilazione.

You are attempting to install a kernel image (version version-revision) However, the directory /lib/modules/version-revision still exists.

Se si aggiorna il kernel ad una revisione successiva, durante l'installazione del pacchetto verrà fatta la seguente domanda:

You are attempting to install a kernel image (version 2.6.15.4-swsusp) However, the directory /lib/modules/2.6.15.4-swsusp still exists.  If this directory
belongs to a previous linux-image-2.6.15.4-swsusp package, and if you have deselected some modules, or installed standalone modules packages, this could be
bad. However, if this directory exists because you are also installing some stand alone modules right now, and they got unpacked before I did, then this is
pretty benign.  Unfortunately, I can not tell the difference.

If /lib/modules/2.6.15.4-swsusp belongs to a old install of linux-image-2.6.15.4-swsusp, then this is your last chance to abort the installation of this
kernel image (nothing has been changed yet). 

If this directory is because of stand alone modules being installed right now, or if it does belong to an older linux-image-2.6.15.4-swsusp package but you
know what you are doing, and if you feel that this image should be installed despite this anomaly, Please answer n to the question.

Otherwise, I suggest you move /lib/modules/2.6.15.4-swsusp out of the way, perhaps to /lib/modules/2.6.15.4-swsusp.old or something, and then try
re-installing this image.  

Stop install since the kernel-image is already installed?   

La risposta da dare è No! L'avvertimento ci ricorda che i moduli del vecchio kernel (quello con la stessa versione ma numero di revisione diverso) verranno cancellati e sostituiti dai moduli del nuovo kernel.

Questo è il comportamento normale, infatti, nel caso non si voglia sostituire un vecchio kernel ma semplicemente installarne parallelamente uno nuovo (con la stessa identica versione) si sarebbe dovuta modificare la stringa dopo --append-to-version invece che quella dopo --revision (vedi sez. Compilazione kernel).

Se il kernel che si sta sostituendo è quello in esecuzione è necessario riavviare la macchina il prima possibile!

Link

Buon divertimento con Debian GNU/Linux!




Guida scritta da: Abortigeno Swirl-auth80.png Debianized 80%
Estesa da:
~ The Noise
fw_crocodile
Lorenzoz 09:57, 11 ott 2014 (CEST)
Verificata da:
~ The Noise
Lorenzoz 09:57, 11 ott 2014 (CEST)
Oscarandrea 14:50, 8 giu 2015 (CEST)

Verificare ed estendere la guida | Cos'è una guida Debianized