---
title: FreeBSD Architecture Handbook
authors: 
  - author: The FreeBSD Documentation Project
copyright: Copyright © 2000-2006, 2012-2013 The FreeBSD Documentation Project
releaseinfo: "$FreeBSD$" 
trademarks: ["freebsd", "apple", "microsoft", "unix", "general"] 
---

= FreeBSD Architecture Handbook
:doctype: book
:toc: macro
:toclevels: 2
:icons: font
:xrefstyle: basic
:relfileprefix: ../
:outfilesuffix:
:sectnums:
:sectnumlevels: 6
:partnums:
:chapter-signifier: Chapter
:part-signifier: Part
:source-highlighter: rouge
:experimental:
:skip-front-matter:
:book: true
:pdf: false

ifeval::["{backend}" == "html5"]
include::shared/mirrors.adoc[]
include::shared/authors.adoc[]
include::shared/releases.adoc[]
include::shared/en/mailing-lists.adoc[]
include::shared/en/teams.adoc[]
include::shared/en/urls.adoc[]
:chapters-path: content/en/books/arch-handbook/
endif::[]

ifeval::["{backend}" == "pdf"]
include::../../../../shared/mirrors.adoc[]
include::../../../../shared/authors.adoc[]
include::../../../../shared/releases.adoc[]
include::../../../../shared/en/mailing-lists.adoc[]
include::../../../../shared/en/teams.adoc[]
include::../../../../shared/en/urls.adoc[]
:chapters-path:
endif::[]

ifeval::["{backend}" == "epub3"]
include::../../../../shared/mirrors.adoc[]
include::../../../../shared/authors.adoc[]
include::../../../../shared/releases.adoc[]
include::../../../../shared/en/mailing-lists.adoc[]
include::../../../../shared/en/teams.adoc[]
include::../../../../shared/en/urls.adoc[]
:chapters-path:
endif::[]

[.abstract-title]
Abstract

Welcome to the FreeBSD Architecture Handbook. This manual is a _work in progress_ and is the work of many individuals. Many sections do not yet exist and some of those that do exist need to be updated. If you are interested in helping with this project, send email to the {freebsd-doc}.

The latest version of this document is always available from the link:https://www.FreeBSD.org/[FreeBSD World Wide Web server]. It may also be downloaded in a variety of formats and compression options from the https://download.freebsd.org/ftp/doc/[FreeBSD FTP server] or one of the numerous link:{handbook}#mirrors-ftp/[mirror sites].

'''

toc::[]

// Section one
[[kernel]]
= Kernel

include::{chapters-path}boot/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}locking/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}kobj/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}jail/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}sysinit/chapter.adoc[leveloffset=+1], lines=7..21;32..-1]
include::{chapters-path}mac/chapter.adoc[leveloffset=+1, lines=12..26;37..-1]
include::{chapters-path}vm/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}smp/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]

// Section two
[[devicedrivers]]
= Device Drivers

include::{chapters-path}driverbasics/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}isa/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}pci/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}scsi/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}usb/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}newbus/chapter.adoc[leveloffset=+1, lines=12..26;37..-1]
include::{chapters-path}sound/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]
include::{chapters-path}pccard/chapter.adoc[leveloffset=+1, lines=7..21;32..-1]

// Section three
[[appendices]]
= Appendices

include::{chapters-path}bibliography/chapter.adoc[leveloffset=+1, lines=6..19;28..-1]