niansa-misc/linux
1
0
Fork 0
mirror of synced 2025-03-06 20:59:54 +01:00
Code Issues Projects Releases Packages Wiki Activity

docs: arm: convert docs to ReST and rename to *.rst

Browse source 
Converts ARM the text files to ReST, preparing them to be an
architecture book.

The conversion is actually:
  - add blank lines and identation in order to identify paragraphs;
  - fix tables markups;
  - add some lists markups;
  - mark literal blocks;
  - adjust title markups.

At its new index.rst, let's add a :orphan: while this is not linked to
the main index.rst file, in order to avoid build warnings.

Signed-off-by: Mauro Carvalho Chehab <mchehab+samsung@kernel.org>
Reviewed-by Corentin Labbe <clabbe.montjoie@gmail.com> # For sun4i-ss
This commit is contained in:
Mauro Carvalho Chehab 2019-04-14 15:51:10 -03:00
parent 0d07cf5e53
commit dc7a12bdfc
115 changed files with 1985 additions and 1420 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

395
Documentation/arm/Marvell/README
View file

@ -1,395 +0,0 @@
ARM Marvell SoCs
================
This document lists all the ARM Marvell SoCs that are currently
supported in mainline by the Linux kernel. As the Marvell families of
SoCs are large and complex, it is hard to understand where the support
for a particular SoC is available in the Linux kernel. This document
tries to help in understanding where those SoCs are supported, and to
match them with their corresponding public datasheet, when available.
Orion family
------------
Flavors:
88F5082
88F5181
88F5181L
88F5182
Datasheet : http://www.embeddedarm.com/documentation/third-party/MV88F5182-datasheet.pdf
Programmer's User Guide : http://www.embeddedarm.com/documentation/third-party/MV88F5182-opensource-manual.pdf
User Manual : http://www.embeddedarm.com/documentation/third-party/MV88F5182-usermanual.pdf
88F5281
Datasheet : http://www.ocmodshop.com/images/reviews/networking/qnap_ts409u/marvel_88f5281_data_sheet.pdf
88F6183
Core: Feroceon 88fr331 (88f51xx) or 88fr531-vd (88f52xx) ARMv5 compatible
Linux kernel mach directory: arch/arm/mach-orion5x
Linux kernel plat directory: arch/arm/plat-orion
Kirkwood family
---------------
Flavors:
88F6282 a.k.a Armada 300
Product Brief : http://www.marvell.com/embedded-processors/armada-300/assets/armada_310.pdf
88F6283 a.k.a Armada 310
Product Brief : http://www.marvell.com/embedded-processors/armada-300/assets/armada_310.pdf
88F6190
Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6190-003_WEB.pdf
Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F619x_OpenSource.pdf
Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
88F6192
Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6192-003_ver1.pdf
Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F619x_OpenSource.pdf
Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
88F6182
88F6180
Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6180-003_ver1.pdf
Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F6180_OpenSource.pdf
Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
88F6281
Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6281-004_ver1.pdf
Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F6281_OpenSource.pdf
Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
Homepage: http://www.marvell.com/embedded-processors/kirkwood/
Core: Feroceon 88fr131 ARMv5 compatible
Linux kernel mach directory: arch/arm/mach-mvebu
Linux kernel plat directory: none
Discovery family
----------------
Flavors:
MV78100
Product Brief : http://www.marvell.com/embedded-processors/discovery-innovation/assets/MV78100-003_WEB.pdf
Hardware Spec : http://www.marvell.com/embedded-processors/discovery-innovation/assets/HW_MV78100_OpenSource.pdf
Functional Spec: http://www.marvell.com/embedded-processors/discovery-innovation/assets/FS_MV76100_78100_78200_OpenSource.pdf
MV78200
Product Brief : http://www.marvell.com/embedded-processors/discovery-innovation/assets/MV78200-002_WEB.pdf
Hardware Spec : http://www.marvell.com/embedded-processors/discovery-innovation/assets/HW_MV78200_OpenSource.pdf
Functional Spec: http://www.marvell.com/embedded-processors/discovery-innovation/assets/FS_MV76100_78100_78200_OpenSource.pdf
MV76100
Not supported by the Linux kernel.
Core: Feroceon 88fr571-vd ARMv5 compatible
Linux kernel mach directory: arch/arm/mach-mv78xx0
Linux kernel plat directory: arch/arm/plat-orion
EBU Armada family
-----------------
Armada 370 Flavors:
88F6710
88F6707
88F6W11
Product Brief: http://www.marvell.com/embedded-processors/armada-300/assets/Marvell_ARMADA_370_SoC.pdf
Hardware Spec: http://www.marvell.com/embedded-processors/armada-300/assets/ARMADA370-datasheet.pdf
Functional Spec: http://www.marvell.com/embedded-processors/armada-300/assets/ARMADA370-FunctionalSpec-datasheet.pdf
Core: Sheeva ARMv7 compatible PJ4B
Armada 375 Flavors:
88F6720
Product Brief: http://www.marvell.com/embedded-processors/armada-300/assets/ARMADA_375_SoC-01_product_brief.pdf
Core: ARM Cortex-A9
Armada 38x Flavors:
88F6810 Armada 380
88F6820 Armada 385
88F6828 Armada 388
Product infos: http://www.marvell.com/embedded-processors/armada-38x/
Functional Spec: https://marvellcorp.wufoo.com/forms/marvell-armada-38x-functional-specifications/
Core: ARM Cortex-A9
Armada 39x Flavors:
88F6920 Armada 390
88F6928 Armada 398
Product infos: http://www.marvell.com/embedded-processors/armada-39x/
Core: ARM Cortex-A9
Armada XP Flavors:
MV78230
MV78260
MV78460
NOTE: not to be confused with the non-SMP 78xx0 SoCs
Product Brief: http://www.marvell.com/embedded-processors/armada-xp/assets/Marvell-ArmadaXP-SoC-product%20brief.pdf
Functional Spec: http://www.marvell.com/embedded-processors/armada-xp/assets/ARMADA-XP-Functional-SpecDatasheet.pdf
Hardware Specs:
http://www.marvell.com/embedded-processors/armada-xp/assets/HW_MV78230_OS.PDF
http://www.marvell.com/embedded-processors/armada-xp/assets/HW_MV78260_OS.PDF
http://www.marvell.com/embedded-processors/armada-xp/assets/HW_MV78460_OS.PDF
Core: Sheeva ARMv7 compatible Dual-core or Quad-core PJ4B-MP
Linux kernel mach directory: arch/arm/mach-mvebu
Linux kernel plat directory: none
EBU Armada family ARMv8
-----------------------
Armada 3710/3720 Flavors:
88F3710
88F3720
Core: ARM Cortex A53 (ARMv8)
Homepage: http://www.marvell.com/embedded-processors/armada-3700/
Product Brief: http://www.marvell.com/embedded-processors/assets/PB-88F3700-FNL.pdf
Device tree files: arch/arm64/boot/dts/marvell/armada-37*
Armada 7K Flavors:
88F7020 (AP806 Dual + one CP110)
88F7040 (AP806 Quad + one CP110)
Core: ARM Cortex A72
Homepage: http://www.marvell.com/embedded-processors/armada-70xx/
Product Brief: http://www.marvell.com/embedded-processors/assets/Armada7020PB-Jan2016.pdf
http://www.marvell.com/embedded-processors/assets/Armada7040PB-Jan2016.pdf
Device tree files: arch/arm64/boot/dts/marvell/armada-70*
Armada 8K Flavors:
88F8020 (AP806 Dual + two CP110)
88F8040 (AP806 Quad + two CP110)
Core: ARM Cortex A72
Homepage: http://www.marvell.com/embedded-processors/armada-80xx/
Product Brief: http://www.marvell.com/embedded-processors/assets/Armada8020PB-Jan2016.pdf
http://www.marvell.com/embedded-processors/assets/Armada8040PB-Jan2016.pdf
Device tree files: arch/arm64/boot/dts/marvell/armada-80*
Avanta family
-------------
Flavors:
88F6510
88F6530P
88F6550
88F6560
Homepage : http://www.marvell.com/broadband/
Product Brief: http://www.marvell.com/broadband/assets/Marvell_Avanta_88F6510_305_060-001_product_brief.pdf
No public datasheet available.
Core: ARMv5 compatible
Linux kernel mach directory: no code in mainline yet, planned for the future
Linux kernel plat directory: no code in mainline yet, planned for the future
Storage family
--------------
Armada SP:
88RC1580
Product infos: http://www.marvell.com/storage/armada-sp/
Core: Sheeva ARMv7 comatible Quad-core PJ4C
(not supported in upstream Linux kernel)
Dove family (application processor)
-----------------------------------
Flavors:
88AP510 a.k.a Armada 510
Product Brief : http://www.marvell.com/application-processors/armada-500/assets/Marvell_Armada510_SoC.pdf
Hardware Spec : http://www.marvell.com/application-processors/armada-500/assets/Armada-510-Hardware-Spec.pdf
Functional Spec : http://www.marvell.com/application-processors/armada-500/assets/Armada-510-Functional-Spec.pdf
Homepage: http://www.marvell.com/application-processors/armada-500/
Core: ARMv7 compatible
Directory: arch/arm/mach-mvebu (DT enabled platforms)
arch/arm/mach-dove (non-DT enabled platforms)
PXA 2xx/3xx/93x/95x family
--------------------------
Flavors:
PXA21x, PXA25x, PXA26x
Application processor only
Core: ARMv5 XScale1 core
PXA270, PXA271, PXA272
Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_pb.pdf
Design guide : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_design_guide.pdf
Developers manual : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_dev_man.pdf
Specification : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_emts.pdf
Specification update : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_spec_update.pdf
Application processor only
Core: ARMv5 XScale2 core
PXA300, PXA310, PXA320
PXA 300 Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/PXA300_PB_R4.pdf
PXA 310 Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/PXA310_PB_R4.pdf
PXA 320 Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/PXA320_PB_R4.pdf
Design guide : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_Design_Guide.pdf
Developers manual : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_Developers_Manual.zip
Specifications : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_EMTS.pdf
Specification Update : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_Spec_Update.zip
Reference Manual : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_TavorP_BootROM_Ref_Manual.pdf
Application processor only
Core: ARMv5 XScale3 core
PXA930, PXA935
Application processor with Communication processor
Core: ARMv5 XScale3 core
PXA955
Application processor with Communication processor
Core: ARMv7 compatible Sheeva PJ4 core
Comments:
* This line of SoCs originates from the XScale family developed by
Intel and acquired by Marvell in ~2006. The PXA21x, PXA25x,
PXA26x, PXA27x, PXA3xx and PXA93x were developed by Intel, while
the later PXA95x were developed by Marvell.
* Due to their XScale origin, these SoCs have virtually nothing in
common with the other (Kirkwood, Dove, etc.) families of Marvell
SoCs, except with the MMP/MMP2 family of SoCs.
Linux kernel mach directory: arch/arm/mach-pxa
Linux kernel plat directory: arch/arm/plat-pxa
MMP/MMP2/MMP3 family (communication processor)
-----------------------------------------
Flavors:
PXA168, a.k.a Armada 168
Homepage : http://www.marvell.com/application-processors/armada-100/armada-168.jsp
Product brief : http://www.marvell.com/application-processors/armada-100/assets/pxa_168_pb.pdf
Hardware manual : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_datasheet.pdf
Software manual : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_software_manual.pdf
Specification update : http://www.marvell.com/application-processors/armada-100/assets/ARMADA16x_Spec_update.pdf
Boot ROM manual : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_ref_manual.pdf
App node package : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_app_note_package.pdf
Application processor only
Core: ARMv5 compatible Marvell PJ1 88sv331 (Mohawk)
PXA910/PXA920
Homepage : http://www.marvell.com/communication-processors/pxa910/
Product Brief : http://www.marvell.com/communication-processors/pxa910/assets/Marvell_PXA910_Platform-001_PB_final.pdf
Application processor with Communication processor
Core: ARMv5 compatible Marvell PJ1 88sv331 (Mohawk)
PXA688, a.k.a. MMP2, a.k.a Armada 610
Product Brief : http://www.marvell.com/application-processors/armada-600/assets/armada610_pb.pdf
Application processor only
Core: ARMv7 compatible Sheeva PJ4 88sv581x core
PXA2128, a.k.a. MMP3 (OLPC XO4, Linux support not upstream)
Product Brief : http://www.marvell.com/application-processors/armada/pxa2128/assets/Marvell-ARMADA-PXA2128-SoC-PB.pdf
Application processor only
Core: Dual-core ARMv7 compatible Sheeva PJ4C core
PXA960/PXA968/PXA978 (Linux support not upstream)
Application processor with Communication Processor
Core: ARMv7 compatible Sheeva PJ4 core
PXA986/PXA988 (Linux support not upstream)
Application processor with Communication Processor
Core: Dual-core ARMv7 compatible Sheeva PJ4B-MP core
PXA1088/PXA1920 (Linux support not upstream)
Application processor with Communication Processor
Core: quad-core ARMv7 Cortex-A7
PXA1908/PXA1928/PXA1936
Application processor with Communication Processor
Core: multi-core ARMv8 Cortex-A53
Comments:
* This line of SoCs originates from the XScale family developed by
Intel and acquired by Marvell in ~2006. All the processors of
this MMP/MMP2 family were developed by Marvell.
* Due to their XScale origin, these SoCs have virtually nothing in
common with the other (Kirkwood, Dove, etc.) families of Marvell
SoCs, except with the PXA family of SoCs listed above.
Linux kernel mach directory: arch/arm/mach-mmp
Linux kernel plat directory: arch/arm/plat-pxa
Berlin family (Multimedia Solutions)
-------------------------------------
Flavors:
88DE3010, Armada 1000 (no Linux support)
Core: Marvell PJ1 (ARMv5TE), Dual-core
Product Brief: http://www.marvell.com.cn/digital-entertainment/assets/armada_1000_pb.pdf
88DE3005, Armada 1500 Mini
Design name: BG2CD
Core: ARM Cortex-A9, PL310 L2CC
88DE3006, Armada 1500 Mini Plus
Design name: BG2CDP
Core: Dual Core ARM Cortex-A7
88DE3100, Armada 1500
Design name: BG2
Core: Marvell PJ4B-MP (ARMv7), Tauros3 L2CC
88DE3114, Armada 1500 Pro
Design name: BG2Q
Core: Quad Core ARM Cortex-A9, PL310 L2CC
88DE3214, Armada 1500 Pro 4K
Design name: BG3
Core: ARM Cortex-A15, CA15 integrated L2CC
88DE3218, ARMADA 1500 Ultra
Core: ARM Cortex-A53
Homepage: https://www.synaptics.com/products/multimedia-solutions
Directory: arch/arm/mach-berlin
Comments:
* This line of SoCs is based on Marvell Sheeva or ARM Cortex CPUs
with Synopsys DesignWare (IRQ, GPIO, Timers, ...) and PXA IP (SDHCI, USB, ETH, ...).
* The Berlin family was acquired by Synaptics from Marvell in 2017.
CPU Cores
---------
The XScale cores were designed by Intel, and shipped by Marvell in the older
PXA processors. Feroceon is a Marvell designed core that developed in-house,
and that evolved into Sheeva. The XScale and Feroceon cores were phased out
over time and replaced with Sheeva cores in later products, which subsequently
got replaced with licensed ARM Cortex-A cores.
XScale 1
CPUID 0x69052xxx
ARMv5, iWMMXt
XScale 2
CPUID 0x69054xxx
ARMv5, iWMMXt
XScale 3
CPUID 0x69056xxx or 0x69056xxx
ARMv5, iWMMXt
Feroceon-1850 88fr331 "Mohawk"
CPUID 0x5615331x or 0x41xx926x
ARMv5TE, single issue
Feroceon-2850 88fr531-vd "Jolteon"
CPUID 0x5605531x or 0x41xx926x
ARMv5TE, VFP, dual-issue
Feroceon 88fr571-vd "Jolteon"
CPUID 0x5615571x
ARMv5TE, VFP, dual-issue
Feroceon 88fr131 "Mohawk-D"
CPUID 0x5625131x
ARMv5TE, single-issue in-order
Sheeva PJ1 88sv331 "Mohawk"
CPUID 0x561584xx
ARMv5, single-issue iWMMXt v2
Sheeva PJ4 88sv581x "Flareon"
CPUID 0x560f581x
ARMv7, idivt, optional iWMMXt v2
Sheeva PJ4B 88sv581x
CPUID 0x561f581x
ARMv7, idivt, optional iWMMXt v2
Sheeva PJ4B-MP / PJ4C
CPUID 0x562f584x
ARMv7, idivt/idiva, LPAE, optional iWMMXt v2 and/or NEON
Long-term plans
---------------
* Unify the mach-dove/, mach-mv78xx0/, mach-orion5x/ into the
mach-mvebu/ to support all SoCs from the Marvell EBU (Engineering
Business Unit) in a single mach-<foo> directory. The plat-orion/
would therefore disappear.
* Unify the mach-mmp/ and mach-pxa/ into the same mach-pxa
directory. The plat-pxa/ would therefore disappear.
Credits
-------
Maen Suleiman <maen@marvell.com>
Lior Amsalem <alior@marvell.com>
Thomas Petazzoni <thomas.petazzoni@free-electrons.com>
Andrew Lunn <andrew@lunn.ch>
Nicolas Pitre <nico@fluxnic.net>
Eric Miao <eric.y.miao@gmail.com>

78
Documentation/arm/Netwinder
View file

@ -1,78 +0,0 @@
NetWinder specific documentation
================================
The NetWinder is a small low-power computer, primarily designed
to run Linux. It is based around the StrongARM RISC processor,
DC21285 PCI bridge, with PC-type hardware glued around it.
Port usage
==========
Min - Max Description
---------------------------
0x0000 - 0x000f DMA1
0x0020 - 0x0021 PIC1
0x0060 - 0x006f Keyboard
0x0070 - 0x007f RTC
0x0080 - 0x0087 DMA1
0x0088 - 0x008f DMA2
0x00a0 - 0x00a3 PIC2
0x00c0 - 0x00df DMA2
0x0180 - 0x0187 IRDA
0x01f0 - 0x01f6 ide0
0x0201 Game port
0x0203 RWA010 configuration read
0x0220 - ? SoundBlaster
0x0250 - ? WaveArtist
0x0279 RWA010 configuration index
0x02f8 - 0x02ff Serial ttyS1
0x0300 - 0x031f Ether10
0x0338 GPIO1
0x033a GPIO2
0x0370 - 0x0371 W83977F configuration registers
0x0388 - ? AdLib
0x03c0 - 0x03df VGA
0x03f6 ide0
0x03f8 - 0x03ff Serial ttyS0
0x0400 - 0x0408 DC21143
0x0480 - 0x0487 DMA1
0x0488 - 0x048f DMA2
0x0a79 RWA010 configuration write
0xe800 - 0xe80f ide0/ide1 BM DMA
Interrupt usage
===============
IRQ type Description
---------------------------
0 ISA 100Hz timer
1 ISA Keyboard
2 ISA cascade
3 ISA Serial ttyS1
4 ISA Serial ttyS0
5 ISA PS/2 mouse
6 ISA IRDA
7 ISA Printer
8 ISA RTC alarm
9 ISA
10 ISA GP10 (Orange reset button)
11 ISA
12 ISA WaveArtist
13 ISA
14 ISA hda1
15 ISA
DMA usage
=========
DMA type Description
---------------------------
0 ISA IRDA
1 ISA
2 ISA cascade
3 ISA WaveArtist
4 ISA
5 ISA
6 ISA
7 ISA WaveArtist

21
Documentation/arm/SA1100/FreeBird
View file

@ -1,21 +0,0 @@
Freebird-1.1 is produced by Legend(C), Inc.
http://web.archive.org/web/*/http://www.legend.com.cn
and software/linux maintained by Coventive(C), Inc.
(http://www.coventive.com)
Based on the Nicolas's strongarm kernel tree.
===============================================================
Maintainer:
Chester Kuo <chester@coventive.com>
<chester@linux.org.tw>
Author :
Tim wu <timwu@coventive.com>
CIH <cih@coventive.com>
Eric Peng <ericpeng@coventive.com>
Jeff Lee <jeff_lee@coventive.com>
Allen Cheng
Tony Liu <tonyliu@coventive.com>

2
Documentation/arm/SA1100/empeg
View file

@ -1,2 +0,0 @@
See ../empeg/README

47
Documentation/arm/SA1100/serial_UART
View file

@ -1,47 +0,0 @@
The SA1100 serial port had its major/minor numbers officially assigned:
> Date: Sun, 24 Sep 2000 21:40:27 -0700
> From: H. Peter Anvin <hpa@transmeta.com>
> To: Nicolas Pitre <nico@CAM.ORG>
> Cc: Device List Maintainer <device@lanana.org>
> Subject: Re: device
>
> Okay. Note that device numbers 204 and 205 are used for "low density
> serial devices", so you will have a range of minors on those majors (the
> tty device layer handles this just fine, so you don't have to worry about
> doing anything special.)
>
> So your assignments are:
>
> 204 char Low-density serial ports
> 5 = /dev/ttySA0 SA1100 builtin serial port 0
> 6 = /dev/ttySA1 SA1100 builtin serial port 1
> 7 = /dev/ttySA2 SA1100 builtin serial port 2
>
> 205 char Low-density serial ports (alternate device)
> 5 = /dev/cusa0 Callout device for ttySA0
> 6 = /dev/cusa1 Callout device for ttySA1
> 7 = /dev/cusa2 Callout device for ttySA2
>
You must create those inodes in /dev on the root filesystem used
by your SA1100-based device:
mknod ttySA0 c 204 5
mknod ttySA1 c 204 6
mknod ttySA2 c 204 7
mknod cusa0 c 205 5
mknod cusa1 c 205 6
mknod cusa2 c 205 7
In addition to the creation of the appropriate device nodes above, you
must ensure your user space applications make use of the correct device
name. The classic example is the content of the /etc/inittab file where
you might have a getty process started on ttyS0. In this case:
- replace occurrences of ttyS0 with ttySA0, ttyS1 with ttySA1, etc.
- don't forget to add 'ttySA0', 'console', or the appropriate tty name
in /etc/securetty for root to be allowed to login as well.

44
Documentation/arm/README → Documentation/arm/arm.rst
View file

@ -1,5 +1,6 @@
ARM Linux 2.6 =======================
============= ARM Linux 2.6 and upper
=======================
Please check <ftp://ftp.arm.linux.org.uk/pub/armlinux> for Please check <ftp://ftp.arm.linux.org.uk/pub/armlinux> for
updates. updates.
@ -18,18 +19,24 @@ Compilation of kernel
line as detailed below. line as detailed below.
If you wish to cross-compile, then alter the following lines in the top If you wish to cross-compile, then alter the following lines in the top
level make file: level make file::
ARCH = <whatever> ARCH = <whatever>
with
with::
ARCH = arm ARCH = arm
and and::
CROSS_COMPILE= CROSS_COMPILE=
to
to::
CROSS_COMPILE=<your-path-to-your-compiler-without-gcc> CROSS_COMPILE=<your-path-to-your-compiler-without-gcc>
eg.
eg.::
CROSS_COMPILE=arm-linux- CROSS_COMPILE=arm-linux-
Do a 'make config', followed by 'make Image' to build the kernel Do a 'make config', followed by 'make Image' to build the kernel
@ -60,11 +67,13 @@ Include files
which are there to reduce the clutter in the top-level directory. These which are there to reduce the clutter in the top-level directory. These
directories, and their purpose is listed below: directories, and their purpose is listed below:
arch-* machine/platform specific header files ============= ==========================================================
hardware driver-internal ARM specific data structures/definitions `arch-*` machine/platform specific header files
mach descriptions of generic ARM to specific machine interfaces `hardware` driver-internal ARM specific data structures/definitions
proc-* processor dependent header files (currently only two `mach` descriptions of generic ARM to specific machine interfaces
`proc-*` processor dependent header files (currently only two
categories) categories)
============= ==========================================================
Machine/Platform support Machine/Platform support
@ -129,7 +138,7 @@ ST506 hard drives
HDC base to the source. HDC base to the source.
As of 31/3/96 it works with two drives (you should get the ADFS As of 31/3/96 it works with two drives (you should get the ADFS
*configure harddrive set to 2). I've got an internal 20MB and a great `*configure` harddrive set to 2). I've got an internal 20MB and a great
big external 5.25" FH 64MB drive (who could ever want more :-) ). big external 5.25" FH 64MB drive (who could ever want more :-) ).
I've just got 240K/s off it (a dd with bs=128k); thats about half of what I've just got 240K/s off it (a dd with bs=128k); thats about half of what
@ -149,13 +158,13 @@ ST506 hard drives
are welcome. are welcome.
CONFIG_MACH_ and CONFIG_ARCH_ `CONFIG_MACH_` and `CONFIG_ARCH_`
----------------------------- ---------------------------------
A change was made in 2003 to the macro names for new machines. A change was made in 2003 to the macro names for new machines.
Historically, CONFIG_ARCH_ was used for the bonafide architecture, Historically, `CONFIG_ARCH_` was used for the bonafide architecture,
e.g. SA1100, as well as implementations of the architecture, e.g. SA1100, as well as implementations of the architecture,
e.g. Assabet. It was decided to change the implementation macros e.g. Assabet. It was decided to change the implementation macros
to read CONFIG_MACH_ for clarity. Moreover, a retroactive fixup has to read `CONFIG_MACH_` for clarity. Moreover, a retroactive fixup has
not been made because it would complicate patching. not been made because it would complicate patching.
Previous registrations may be found online. Previous registrations may be found online.
@ -163,7 +172,7 @@ CONFIG_MACH_ and CONFIG_ARCH_
<http://www.arm.linux.org.uk/developer/machines/> <http://www.arm.linux.org.uk/developer/machines/>
Kernel entry (head.S) Kernel entry (head.S)
-------------------------- ---------------------
The initial entry into the kernel is via head.S, which uses machine The initial entry into the kernel is via head.S, which uses machine
independent code. The machine is selected by the value of 'r1' on independent code. The machine is selected by the value of 'r1' on
entry, which must be kept unique. entry, which must be kept unique.
@ -201,4 +210,5 @@ Kernel entry (head.S)
platform is DT-only, you do not need a registered machine type. platform is DT-only, you do not need a registered machine type.
--- ---
Russell King (15/03/2004) Russell King (15/03/2004)

51
Documentation/arm/Booting → Documentation/arm/booting.rst
View file

@ -1,7 +1,9 @@
=================
Booting ARM Linux Booting ARM Linux
================= =================
Author: Russell King Author: Russell King
Date : 18 May 2002 Date : 18 May 2002
The following documentation is relevant to 2.4.18-rmk6 and beyond. The following documentation is relevant to 2.4.18-rmk6 and beyond.
@ -25,8 +27,10 @@ following:
1. Setup and initialise RAM 1. Setup and initialise RAM
--------------------------- ---------------------------
Existing boot loaders: MANDATORY Existing boot loaders:
New boot loaders: MANDATORY MANDATORY
New boot loaders:
MANDATORY
The boot loader is expected to find and initialise all RAM that the The boot loader is expected to find and initialise all RAM that the
kernel will use for volatile data storage in the system. It performs kernel will use for volatile data storage in the system. It performs
@ -39,8 +43,10 @@ sees fit.)
2. Initialise one serial port 2. Initialise one serial port
----------------------------- -----------------------------
Existing boot loaders: OPTIONAL, RECOMMENDED Existing boot loaders:
New boot loaders: OPTIONAL, RECOMMENDED OPTIONAL, RECOMMENDED
New boot loaders:
OPTIONAL, RECOMMENDED
The boot loader should initialise and enable one serial port on the The boot loader should initialise and enable one serial port on the
target. This allows the kernel serial driver to automatically detect target. This allows the kernel serial driver to automatically detect
@ -57,8 +63,10 @@ serial format options as described in
3. Detect the machine type 3. Detect the machine type
-------------------------- --------------------------
Existing boot loaders: OPTIONAL Existing boot loaders:
New boot loaders: MANDATORY except for DT-only platforms OPTIONAL
New boot loaders:
MANDATORY except for DT-only platforms
The boot loader should detect the machine type its running on by some The boot loader should detect the machine type its running on by some
method. Whether this is a hard coded value or some algorithm that method. Whether this is a hard coded value or some algorithm that
@ -74,8 +82,10 @@ necessary, but assures that it will not match any existing types.
4. Setup boot data 4. Setup boot data
------------------ ------------------
Existing boot loaders: OPTIONAL, HIGHLY RECOMMENDED Existing boot loaders:
New boot loaders: MANDATORY OPTIONAL, HIGHLY RECOMMENDED
New boot loaders:
MANDATORY
The boot loader must provide either a tagged list or a dtb image for The boot loader must provide either a tagged list or a dtb image for
passing configuration data to the kernel. The physical address of the passing configuration data to the kernel. The physical address of the
@ -97,7 +107,7 @@ entirety; some tags behave as the former, others the latter.
The boot loader must pass at a minimum the size and location of The boot loader must pass at a minimum the size and location of
the system memory, and root filesystem location. Therefore, the the system memory, and root filesystem location. Therefore, the
minimum tagged list should look: minimum tagged list should look::
+-----------+ +-----------+
base -> | ATAG_CORE | | base -> | ATAG_CORE | |
@ -134,8 +144,10 @@ A safe location is just above the 128MiB boundary from start of RAM.
5. Load initramfs. 5. Load initramfs.
------------------ ------------------
Existing boot loaders: OPTIONAL Existing boot loaders:
New boot loaders: OPTIONAL OPTIONAL
New boot loaders:
OPTIONAL
If an initramfs is in use then, as with the dtb, it must be placed in If an initramfs is in use then, as with the dtb, it must be placed in
a region of memory where the kernel decompressor will not overwrite it a region of memory where the kernel decompressor will not overwrite it
@ -149,8 +161,10 @@ recommended above.
6. Calling the kernel image 6. Calling the kernel image
--------------------------- ---------------------------
Existing boot loaders: MANDATORY Existing boot loaders:
New boot loaders: MANDATORY MANDATORY
New boot loaders:
MANDATORY
There are two options for calling the kernel zImage. If the zImage There are two options for calling the kernel zImage. If the zImage
is stored in flash, and is linked correctly to be run from flash, is stored in flash, and is linked correctly to be run from flash,
@ -174,12 +188,14 @@ In any case, the following conditions must be met:
you many hours of debug. you many hours of debug.
- CPU register settings - CPU register settings
r0 = 0,
r1 = machine type number discovered in (3) above. - r0 = 0,
r2 = physical address of tagged list in system RAM, or - r1 = machine type number discovered in (3) above.
- r2 = physical address of tagged list in system RAM, or
physical address of device tree block (dtb) in system RAM physical address of device tree block (dtb) in system RAM
- CPU mode - CPU mode
All forms of interrupts must be disabled (IRQs and FIQs) All forms of interrupts must be disabled (IRQs and FIQs)
For CPUs which do not include the ARM virtualization extensions, the For CPUs which do not include the ARM virtualization extensions, the
@ -195,8 +211,11 @@ In any case, the following conditions must be met:
entered in SVC mode. entered in SVC mode.
- Caches, MMUs - Caches, MMUs
The MMU must be off. The MMU must be off.
Instruction cache may be on or off. Instruction cache may be on or off.
Data cache must be off. Data cache must be off.
If the kernel is entered in HYP mode, the above requirements apply to If the kernel is entered in HYP mode, the above requirements apply to

145
Documentation/arm/cluster-pm-race-avoidance.txt → Documentation/arm/cluster-pm-race-avoidance.rst
View file

@ -1,3 +1,4 @@
=========================================================
Cluster-wide Power-up/power-down race avoidance algorithm Cluster-wide Power-up/power-down race avoidance algorithm
========================================================= =========================================================
@ -46,10 +47,12 @@ Basic model
Each cluster and CPU is assigned a state, as follows: Each cluster and CPU is assigned a state, as follows:
DOWN - DOWN
COMING_UP - COMING_UP
UP - UP
GOING_DOWN - GOING_DOWN
::
+---------> UP ----------+ +---------> UP ----------+
| v | v
@ -60,18 +63,22 @@ Each cluster and CPU is assigned a state, as follows:
+--------- DOWN <--------+ +--------- DOWN <--------+
DOWN: The CPU or cluster is not coherent, and is either powered off or DOWN:
The CPU or cluster is not coherent, and is either powered off or
suspended, or is ready to be powered off or suspended. suspended, or is ready to be powered off or suspended.
COMING_UP: The CPU or cluster has committed to moving to the UP state. COMING_UP:
The CPU or cluster has committed to moving to the UP state.
It may be part way through the process of initialisation and It may be part way through the process of initialisation and
enabling coherency. enabling coherency.
UP: The CPU or cluster is active and coherent at the hardware UP:
The CPU or cluster is active and coherent at the hardware
level. A CPU in this state is not necessarily being used level. A CPU in this state is not necessarily being used
actively by the kernel. actively by the kernel.
GOING_DOWN: The CPU or cluster has committed to moving to the DOWN GOING_DOWN:
The CPU or cluster has committed to moving to the DOWN
state. It may be part way through the process of teardown and state. It may be part way through the process of teardown and
coherency exit. coherency exit.
@ -86,8 +93,8 @@ CPUs in the cluster simultaneously modifying the state. The cluster-
level states are described in the "Cluster state" section. level states are described in the "Cluster state" section.
To help distinguish the CPU states from cluster states in this To help distinguish the CPU states from cluster states in this
discussion, the state names are given a CPU_ prefix for the CPU states, discussion, the state names are given a `CPU_` prefix for the CPU states,
and a CLUSTER_ or INBOUND_ prefix for the cluster states. and a `CLUSTER_` or `INBOUND_` prefix for the cluster states.
CPU state CPU state
@ -101,10 +108,12 @@ This means that CPUs fit the basic model closely.
The algorithm defines the following states for each CPU in the system: The algorithm defines the following states for each CPU in the system:
CPU_DOWN - CPU_DOWN
CPU_COMING_UP - CPU_COMING_UP
CPU_UP - CPU_UP
CPU_GOING_DOWN - CPU_GOING_DOWN
::
cluster setup and cluster setup and
CPU setup complete policy decision CPU setup complete policy decision
@ -130,17 +139,17 @@ requirement for any external event to happen.
CPU_DOWN: CPU_DOWN:
A CPU reaches the CPU_DOWN state when it is ready for A CPU reaches the CPU_DOWN state when it is ready for
power-down. On reaching this state, the CPU will typically power-down. On reaching this state, the CPU will typically
power itself down or suspend itself, via a WFI instruction or a power itself down or suspend itself, via a WFI instruction or a
firmware call. firmware call.
Next state: CPU_COMING_UP Next state:
Conditions: none CPU_COMING_UP
Conditions:
none
Trigger events: Trigger events:
a) an explicit hardware power-up operation, resulting a) an explicit hardware power-up operation, resulting
from a policy decision on another CPU; from a policy decision on another CPU;
@ -148,15 +157,17 @@ CPU_DOWN:
CPU_COMING_UP: CPU_COMING_UP:
A CPU cannot start participating in hardware coherency until the A CPU cannot start participating in hardware coherency until the
cluster is set up and coherent. If the cluster is not ready, cluster is set up and coherent. If the cluster is not ready,
then the CPU will wait in the CPU_COMING_UP state until the then the CPU will wait in the CPU_COMING_UP state until the
cluster has been set up. cluster has been set up.
Next state: CPU_UP Next state:
Conditions: The CPU's parent cluster must be in CLUSTER_UP. CPU_UP
Trigger events: Transition of the parent cluster to CLUSTER_UP. Conditions:
The CPU's parent cluster must be in CLUSTER_UP.
Trigger events:
Transition of the parent cluster to CLUSTER_UP.
Refer to the "Cluster state" section for a description of the Refer to the "Cluster state" section for a description of the
CLUSTER_UP state. CLUSTER_UP state.
@ -178,20 +189,25 @@ CPU_UP:
The CPU remains in this state until an explicit policy decision The CPU remains in this state until an explicit policy decision
is made to shut down or suspend the CPU. is made to shut down or suspend the CPU.
Next state: CPU_GOING_DOWN Next state:
Conditions: none CPU_GOING_DOWN
Trigger events: explicit policy decision Conditions:
none
Trigger events:
explicit policy decision
CPU_GOING_DOWN: CPU_GOING_DOWN:
While in this state, the CPU exits coherency, including any While in this state, the CPU exits coherency, including any
operations required to achieve this (such as cleaning data operations required to achieve this (such as cleaning data
caches). caches).
Next state: CPU_DOWN Next state:
Conditions: local CPU teardown complete CPU_DOWN
Trigger events: (spontaneous) Conditions:
local CPU teardown complete
Trigger events:
(spontaneous)
Cluster state Cluster state
@ -214,18 +230,18 @@ reason, the cluster state is split into two parts:
"cluster" state: The global state of the cluster; or the state "cluster" state: The global state of the cluster; or the state
on the outbound side: on the outbound side:
CLUSTER_DOWN - CLUSTER_DOWN
CLUSTER_UP - CLUSTER_UP
CLUSTER_GOING_DOWN - CLUSTER_GOING_DOWN
"inbound" state: The state of the cluster on the inbound side. "inbound" state: The state of the cluster on the inbound side.
INBOUND_NOT_COMING_UP - INBOUND_NOT_COMING_UP
INBOUND_COMING_UP - INBOUND_COMING_UP
The different pairings of these states results in six possible The different pairings of these states results in six possible
states for the cluster as a whole: states for the cluster as a whole::
CLUSTER_UP CLUSTER_UP
+==========> INBOUND_NOT_COMING_UP -------------+ +==========> INBOUND_NOT_COMING_UP -------------+
@ -284,11 +300,12 @@ reason, the cluster state is split into two parts:
CLUSTER_DOWN/INBOUND_NOT_COMING_UP: CLUSTER_DOWN/INBOUND_NOT_COMING_UP:
Next state:
CLUSTER_DOWN/INBOUND_COMING_UP (inbound)
Conditions:
none
Next state: CLUSTER_DOWN/INBOUND_COMING_UP (inbound)
Conditions: none
Trigger events: Trigger events:
a) an explicit hardware power-up operation, resulting a) an explicit hardware power-up operation, resulting
from a policy decision on another CPU; from a policy decision on another CPU;
@ -306,9 +323,12 @@ CLUSTER_DOWN/INBOUND_COMING_UP:
setup to enable other CPUs in the cluster to enter coherency setup to enable other CPUs in the cluster to enter coherency
safely. safely.
Next state: CLUSTER_UP/INBOUND_COMING_UP (inbound) Next state:
Conditions: cluster-level setup and hardware coherency complete CLUSTER_UP/INBOUND_COMING_UP (inbound)
Trigger events: (spontaneous) Conditions:
cluster-level setup and hardware coherency complete
Trigger events:
(spontaneous)
CLUSTER_UP/INBOUND_COMING_UP: CLUSTER_UP/INBOUND_COMING_UP:
@ -321,9 +341,12 @@ CLUSTER_UP/INBOUND_COMING_UP:
CLUSTER_UP/INBOUND_NOT_COMING_UP. All other CPUs on the cluster CLUSTER_UP/INBOUND_NOT_COMING_UP. All other CPUs on the cluster
should consider treat these two states as equivalent. should consider treat these two states as equivalent.
Next state: CLUSTER_UP/INBOUND_NOT_COMING_UP (inbound) Next state:
Conditions: none CLUSTER_UP/INBOUND_NOT_COMING_UP (inbound)
Trigger events: (spontaneous) Conditions:
none
Trigger events:
(spontaneous)
CLUSTER_UP/INBOUND_NOT_COMING_UP: CLUSTER_UP/INBOUND_NOT_COMING_UP:
@ -335,9 +358,12 @@ CLUSTER_UP/INBOUND_NOT_COMING_UP:
The cluster will remain in this state until a policy decision is The cluster will remain in this state until a policy decision is
made to power the cluster down. made to power the cluster down.
Next state: CLUSTER_GOING_DOWN/INBOUND_NOT_COMING_UP (outbound) Next state:
Conditions: none CLUSTER_GOING_DOWN/INBOUND_NOT_COMING_UP (outbound)
Trigger events: policy decision to power down the cluster Conditions:
none
Trigger events:
policy decision to power down the cluster
CLUSTER_GOING_DOWN/INBOUND_NOT_COMING_UP: CLUSTER_GOING_DOWN/INBOUND_NOT_COMING_UP:
@ -359,13 +385,16 @@ CLUSTER_GOING_DOWN/INBOUND_NOT_COMING_UP:
Next states: Next states:
CLUSTER_DOWN/INBOUND_NOT_COMING_UP (outbound) CLUSTER_DOWN/INBOUND_NOT_COMING_UP (outbound)
Conditions: cluster torn down and ready to power off Conditions:
Trigger events: (spontaneous) cluster torn down and ready to power off
Trigger events:
(spontaneous)
CLUSTER_GOING_DOWN/INBOUND_COMING_UP (inbound) CLUSTER_GOING_DOWN/INBOUND_COMING_UP (inbound)
Conditions: none Conditions:
Trigger events: none
Trigger events:
a) an explicit hardware power-up operation, a) an explicit hardware power-up operation,
resulting from a policy decision on another resulting from a policy decision on another
CPU; CPU;
@ -396,13 +425,19 @@ CLUSTER_GOING_DOWN/INBOUND_COMING_UP:
Next states: Next states:
CLUSTER_UP/INBOUND_COMING_UP (outbound) CLUSTER_UP/INBOUND_COMING_UP (outbound)
Conditions: cluster-level setup and hardware Conditions:
cluster-level setup and hardware
coherency complete coherency complete
Trigger events: (spontaneous)
Trigger events:
(spontaneous)
CLUSTER_DOWN/INBOUND_COMING_UP (outbound) CLUSTER_DOWN/INBOUND_COMING_UP (outbound)
Conditions: cluster torn down and ready to power off Conditions:
Trigger events: (spontaneous) cluster torn down and ready to power off
Trigger events:
(spontaneous)
Last man and First man selection Last man and First man selection

14
Documentation/arm/firmware.txt → Documentation/arm/firmware.rst
View file

@ -1,5 +1,7 @@
Interface for registering and calling firmware-specific operations for ARM. ==========================================================================
---- Interface for registering and calling firmware-specific operations for ARM
==========================================================================
Written by Tomasz Figa <t.figa@samsung.com> Written by Tomasz Figa <t.figa@samsung.com>
Some boards are running with secure firmware running in TrustZone secure Some boards are running with secure firmware running in TrustZone secure
@ -9,7 +11,7 @@ operations and call them when needed.
Firmware operations can be specified by filling in a struct firmware_ops Firmware operations can be specified by filling in a struct firmware_ops
with appropriate callbacks and then registering it with register_firmware_ops() with appropriate callbacks and then registering it with register_firmware_ops()
function. function::
void register_firmware_ops(const struct firmware_ops *ops) void register_firmware_ops(const struct firmware_ops *ops)
@ -19,7 +21,7 @@ and its members can be found in arch/arm/include/asm/firmware.h header.
There is a default, empty set of operations provided, so there is no need to There is a default, empty set of operations provided, so there is no need to
set anything if platform does not require firmware operations. set anything if platform does not require firmware operations.
To call a firmware operation, a helper macro is provided To call a firmware operation, a helper macro is provided::
#define call_firmware_op(op, ...) \ #define call_firmware_op(op, ...) \
((firmware_ops->op) ? firmware_ops->op(__VA_ARGS__) : (-ENOSYS)) ((firmware_ops->op) ? firmware_ops->op(__VA_ARGS__) : (-ENOSYS))
@ -28,7 +30,7 @@ the macro checks if the operation is provided and calls it or otherwise returns
-ENOSYS to signal that given operation is not available (for example, to allow -ENOSYS to signal that given operation is not available (for example, to allow
fallback to legacy operation). fallback to legacy operation).
Example of registering firmware operations: Example of registering firmware operations::
/* board file */ /* board file */
@ -56,7 +58,7 @@ Example of registering firmware operations:
register_firmware_ops(&platformX_firmware_ops); register_firmware_ops(&platformX_firmware_ops);
} }
Example of using a firmware operation: Example of using a firmware operation::
/* some platform code, e.g. SMP initialization */ /* some platform code, e.g. SMP initialization */

80
Documentation/arm/index.rst Normal file
View file

@ -0,0 +1,80 @@
:orphan:
================
ARM Architecture
================
.. toctree::
:maxdepth: 1
arm
booting
cluster-pm-race-avoidance
firmware
interrupts
kernel_mode_neon
kernel_user_helpers
memory
mem_alignment
tcm
setup
swp_emulation
uefi
vlocks
porting
SoC-specific documents
======================
.. toctree::
:maxdepth: 1
ixp4xx
marvel
microchip
netwinder
nwfpe/index
keystone/overview
keystone/knav-qmss
omap/index
pxa/mfp
sa1100/index
stm32/stm32f746-overview
stm32/overview
stm32/stm32h743-overview
stm32/stm32f769-overview
stm32/stm32f429-overview
stm32/stm32mp157-overview
sunxi
samsung/index
samsung-s3c24xx/index
sunxi/clocks
spear/overview
sti/stih416-overview
sti/stih407-overview
sti/stih418-overview
sti/overview
sti/stih415-overview
vfp/release-notes
.. only:: subproject and html
Indices
=======
* :ref:`genindex`

34
Documentation/arm/Interrupts → Documentation/arm/interrupts.rst
View file

@ -1,6 +1,8 @@
2.5.2-rmk5 ==========
---------- Interrupts
==========
2.5.2-rmk5:
This is the first kernel that contains a major shake up of some of the This is the first kernel that contains a major shake up of some of the
major architecture-specific subsystems. major architecture-specific subsystems.
@ -18,7 +20,7 @@ Unfortunately, this means that machine types that touch the irq_desc[]
array (basically all machine types) will break, and this means every array (basically all machine types) will break, and this means every
machine type that we currently have. machine type that we currently have.
Lets take an example. On the Assabet with Neponset, we have: Lets take an example. On the Assabet with Neponset, we have::
GPIO25 IRR:2 GPIO25 IRR:2
SA1100 ------------> Neponset -----------> SA1111 SA1100 ------------> Neponset -----------> SA1111
@ -48,7 +50,7 @@ the irqdesc array). This doesn't have to be a real "IC"; indeed the
SA11x0 IRQs are handled by two separate "chip" structures, one for SA11x0 IRQs are handled by two separate "chip" structures, one for
GPIO0-10, and another for all the rest. It is just a container for GPIO0-10, and another for all the rest. It is just a container for
the various operations (maybe this'll change to a better name). the various operations (maybe this'll change to a better name).
This structure has the following operations: This structure has the following operations::
struct irqchip { struct irqchip {
/* /*
@ -75,15 +77,20 @@ struct irqchip {
int (*type)(unsigned int irq, unsigned int, type); int (*type)(unsigned int irq, unsigned int, type);
}; };
ack - required. May be the same function as mask for IRQs ack
- required. May be the same function as mask for IRQs
handled by do_level_IRQ. handled by do_level_IRQ.
mask - required. mask
unmask - required. - required.
rerun - optional. Not required if you're using do_level_IRQ for all unmask
- required.
rerun
- optional. Not required if you're using do_level_IRQ for all
IRQs that use this 'irqchip'. Generally expected to re-trigger IRQs that use this 'irqchip'. Generally expected to re-trigger
the hardware IRQ if possible. If not, may call the handler the hardware IRQ if possible. If not, may call the handler
directly. directly.
type - optional. If you don't support changing the type of an IRQ, type
- optional. If you don't support changing the type of an IRQ,
it should be null so people can detect if they are unable to it should be null so people can detect if they are unable to
set the IRQ type. set the IRQ type.
@ -109,6 +116,7 @@ manipulation, nor state tracking. This is useful for things like the
SMC9196 and USAR above. SMC9196 and USAR above.
So, what's changed? So, what's changed?
===================
1. Machine implementations must not write to the irqdesc array. 1. Machine implementations must not write to the irqdesc array.
@ -118,24 +126,19 @@ So, what's changed?
absolutely necessary. absolutely necessary.
set_irq_chip(irq,chip) set_irq_chip(irq,chip)
Set the mask/unmask methods for handling this IRQ Set the mask/unmask methods for handling this IRQ
set_irq_handler(irq,handler) set_irq_handler(irq,handler)
Set the handler for this IRQ (level, edge, simple) Set the handler for this IRQ (level, edge, simple)
set_irq_chained_handler(irq,handler) set_irq_chained_handler(irq,handler)
Set a "chained" handler for this IRQ - automatically Set a "chained" handler for this IRQ - automatically
enables this IRQ (eg, Neponset and SA1111 handlers). enables this IRQ (eg, Neponset and SA1111 handlers).
set_irq_flags(irq,flags) set_irq_flags(irq,flags)
Set the valid/probe/noautoenable flags. Set the valid/probe/noautoenable flags.
set_irq_type(irq,type) set_irq_type(irq,type)
Set active the IRQ edge(s)/level. This replaces the Set active the IRQ edge(s)/level. This replaces the
SA1111 INTPOL manipulation, and the set_GPIO_IRQ_edge() SA1111 INTPOL manipulation, and the set_GPIO_IRQ_edge()
function. Type should be one of IRQ_TYPE_xxx defined in function. Type should be one of IRQ_TYPE_xxx defined in
@ -158,10 +161,9 @@ So, what's changed?
be re-checked for pending events. (see the Neponset IRQ handler for be re-checked for pending events. (see the Neponset IRQ handler for
details). details).
7. fixup_irq() is gone, as is arch/arm/mach-*/include/mach/irq.h 7. fixup_irq() is gone, as is `arch/arm/mach-*/include/mach/irq.h`
Please note that this will not solve all problems - some of them are Please note that this will not solve all problems - some of them are
hardware based. Mixing level-based and edge-based IRQs on the same hardware based. Mixing level-based and edge-based IRQs on the same
parent signal (eg neponset) is one such area where a software based parent signal (eg neponset) is one such area where a software based
solution can't provide the full answer to low IRQ latency. solution can't provide the full answer to low IRQ latency.

19
Documentation/arm/IXP4xx → Documentation/arm/ixp4xx.rst
View file

@ -1,6 +1,6 @@
===========================================================
-------------------------------------------------------------------------
Release Notes for Linux on Intel's IXP4xx Network Processor Release Notes for Linux on Intel's IXP4xx Network Processor
===========================================================
Maintained by Deepak Saxena <dsaxena@plexity.net> Maintained by Deepak Saxena <dsaxena@plexity.net>
------------------------------------------------------------------------- -------------------------------------------------------------------------
@ -53,13 +53,13 @@ SOFTWARE.
There are several websites that provide directions/pointers on using There are several websites that provide directions/pointers on using
Intel's software: Intel's software:
http://sourceforge.net/projects/ixp4xx-osdg/ - http://sourceforge.net/projects/ixp4xx-osdg/
Open Source Developer's Guide for using uClinux and the Intel libraries Open Source Developer's Guide for using uClinux and the Intel libraries
http://gatewaymaker.sourceforge.net/ - http://gatewaymaker.sourceforge.net/
Simple one page summary of building a gateway using an IXP425 and Linux Simple one page summary of building a gateway using an IXP425 and Linux
http://ixp425.sourceforge.net/ - http://ixp425.sourceforge.net/
ATM device driver for IXP425 that relies on Intel's libraries ATM device driver for IXP425 that relies on Intel's libraries
3. Known Issues/Limitations 3. Known Issues/Limitations
@ -161,10 +161,11 @@ The IXP4xx work has been funded by Intel Corp. and MontaVista Software, Inc.
The following people have contributed patches/comments/etc: The following people have contributed patches/comments/etc:
Lennerty Buytenhek - Lennerty Buytenhek
Lutz Jaenicke - Lutz Jaenicke
Justin Mayfield - Justin Mayfield
Robert E. Ranslam - Robert E. Ranslam
[I know I've forgotten others, please email me to be added] [I know I've forgotten others, please email me to be added]
------------------------------------------------------------------------- -------------------------------------------------------------------------

3
Documentation/arm/kernel_mode_neon.txt → Documentation/arm/kernel_mode_neon.rst
View file

@ -1,3 +1,4 @@
================
Kernel mode NEON Kernel mode NEON
================ ================
@ -86,6 +87,7 @@ instructions appearing in unexpected places if no special care is taken.
Therefore, the recommended and only supported way of using NEON/VFP in the Therefore, the recommended and only supported way of using NEON/VFP in the
kernel is by adhering to the following rules: kernel is by adhering to the following rules:
* isolate the NEON code in a separate compilation unit and compile it with * isolate the NEON code in a separate compilation unit and compile it with
'-march=armv7-a -mfpu=neon -mfloat-abi=softfp'; '-march=armv7-a -mfpu=neon -mfloat-abi=softfp';
* issue the calls to kernel_neon_begin(), kernel_neon_end() as well as the calls * issue the calls to kernel_neon_begin(), kernel_neon_end() as well as the calls
@ -115,6 +117,7 @@ NEON intrinsics
NEON intrinsics are also supported. However, as code using NEON intrinsics NEON intrinsics are also supported. However, as code using NEON intrinsics
relies on the GCC header <arm_neon.h>, (which #includes <stdint.h>), you should relies on the GCC header <arm_neon.h>, (which #includes <stdint.h>), you should
observe the following in addition to the rules above: observe the following in addition to the rules above:
* Compile the unit containing the NEON intrinsics with '-ffreestanding' so GCC * Compile the unit containing the NEON intrinsics with '-ffreestanding' so GCC
uses its builtin version of <stdint.h> (this is a C99 header which the kernel uses its builtin version of <stdint.h> (this is a C99 header which the kernel
does not supply); does not supply);

33
Documentation/arm/kernel_user_helpers.txt → Documentation/arm/kernel_user_helpers.rst
View file

@ -1,3 +1,4 @@
============================
Kernel-provided User Helpers Kernel-provided User Helpers
============================ ============================
@ -43,7 +44,7 @@ kuser_helper_version
Location: 0xffff0ffc Location: 0xffff0ffc
Reference declaration: Reference declaration::
extern int32_t __kuser_helper_version; extern int32_t __kuser_helper_version;
@ -53,7 +54,7 @@ Definition:
running kernel. User space may read this to determine the availability running kernel. User space may read this to determine the availability
of a particular helper. of a particular helper.
Usage example: Usage example::
#define __kuser_helper_version (*(int32_t *)0xffff0ffc) #define __kuser_helper_version (*(int32_t *)0xffff0ffc)
@ -77,7 +78,7 @@ kuser_get_tls
Location: 0xffff0fe0 Location: 0xffff0fe0
Reference prototype: Reference prototype::
void * __kuser_get_tls(void); void * __kuser_get_tls(void);
@ -97,7 +98,7 @@ Definition:
Get the TLS value as previously set via the __ARM_NR_set_tls syscall. Get the TLS value as previously set via the __ARM_NR_set_tls syscall.
Usage example: Usage example::
typedef void * (__kuser_get_tls_t)(void); typedef void * (__kuser_get_tls_t)(void);
#define __kuser_get_tls (*(__kuser_get_tls_t *)0xffff0fe0) #define __kuser_get_tls (*(__kuser_get_tls_t *)0xffff0fe0)
@ -117,7 +118,7 @@ kuser_cmpxchg
Location: 0xffff0fc0 Location: 0xffff0fc0
Reference prototype: Reference prototype::
int __kuser_cmpxchg(int32_t oldval, int32_t newval, volatile int32_t *ptr); int __kuser_cmpxchg(int32_t oldval, int32_t newval, volatile int32_t *ptr);
@ -139,12 +140,12 @@ Clobbered registers:
Definition: Definition:
Atomically store newval in *ptr only if *ptr is equal to oldval. Atomically store newval in `*ptr` only if `*ptr` is equal to oldval.
Return zero if *ptr was changed or non-zero if no exchange happened. Return zero if `*ptr` was changed or non-zero if no exchange happened.
The C flag is also set if *ptr was changed to allow for assembly The C flag is also set if `*ptr` was changed to allow for assembly
optimization in the calling code. optimization in the calling code.
Usage example: Usage example::
typedef int (__kuser_cmpxchg_t)(int oldval, int newval, volatile int *ptr); typedef int (__kuser_cmpxchg_t)(int oldval, int newval, volatile int *ptr);
#define __kuser_cmpxchg (*(__kuser_cmpxchg_t *)0xffff0fc0) #define __kuser_cmpxchg (*(__kuser_cmpxchg_t *)0xffff0fc0)
@ -172,7 +173,7 @@ kuser_memory_barrier
Location: 0xffff0fa0 Location: 0xffff0fa0
Reference prototype: Reference prototype::
void __kuser_memory_barrier(void); void __kuser_memory_barrier(void);
@ -193,7 +194,7 @@ Definition:
Apply any needed memory barrier to preserve consistency with data modified Apply any needed memory barrier to preserve consistency with data modified
manually and __kuser_cmpxchg usage. manually and __kuser_cmpxchg usage.
Usage example: Usage example::
typedef void (__kuser_dmb_t)(void); typedef void (__kuser_dmb_t)(void);
#define __kuser_dmb (*(__kuser_dmb_t *)0xffff0fa0) #define __kuser_dmb (*(__kuser_dmb_t *)0xffff0fa0)
@ -207,7 +208,7 @@ kuser_cmpxchg64
Location: 0xffff0f60 Location: 0xffff0f60
Reference prototype: Reference prototype::
int __kuser_cmpxchg64(const int64_t *oldval, int __kuser_cmpxchg64(const int64_t *oldval,
const int64_t *newval, const int64_t *newval,
@ -231,14 +232,14 @@ Clobbered registers:
Definition: Definition:
Atomically store the 64-bit value pointed by *newval in *ptr only if *ptr Atomically store the 64-bit value pointed by `*newval` in `*ptr` only if `*ptr`
is equal to the 64-bit value pointed by *oldval. Return zero if *ptr was is equal to the 64-bit value pointed by `*oldval`. Return zero if `*ptr` was
changed or non-zero if no exchange happened. changed or non-zero if no exchange happened.
The C flag is also set if *ptr was changed to allow for assembly The C flag is also set if `*ptr` was changed to allow for assembly
optimization in the calling code. optimization in the calling code.
Usage example: Usage example::
typedef int (__kuser_cmpxchg64_t)(const int64_t *oldval, typedef int (__kuser_cmpxchg64_t)(const int64_t *oldval,
const int64_t *newval, const int64_t *newval,

6
Documentation/arm/keystone/knav-qmss.txt → Documentation/arm/keystone/knav-qmss.rst
View file

@ -1,4 +1,6 @@
* Texas Instruments Keystone Navigator Queue Management SubSystem driver ======================================================================
Texas Instruments Keystone Navigator Queue Management SubSystem driver
======================================================================
Driver source code path Driver source code path
drivers/soc/ti/knav_qmss.c drivers/soc/ti/knav_qmss.c
@ -34,11 +36,13 @@ driver that interface with the accumulator PDSP. This configures
accumulator channels defined in DTS (example in DT documentation) to monitor accumulator channels defined in DTS (example in DT documentation) to monitor
1 or 32 queues per channel. More description on the firmware is available in 1 or 32 queues per channel. More description on the firmware is available in
CPPI/QMSS Low Level Driver document (docs/CPPI_QMSS_LLD_SDS.pdf) at CPPI/QMSS Low Level Driver document (docs/CPPI_QMSS_LLD_SDS.pdf) at
git://git.ti.com/keystone-rtos/qmss-lld.git git://git.ti.com/keystone-rtos/qmss-lld.git
k2_qmss_pdsp_acc48_k2_le_1_0_0_9.bin firmware supports upto 48 accumulator k2_qmss_pdsp_acc48_k2_le_1_0_0_9.bin firmware supports upto 48 accumulator
channels. This firmware is available under ti-keystone folder of channels. This firmware is available under ti-keystone folder of
firmware.git at firmware.git at
git://git.kernel.org/pub/scm/linux/kernel/git/firmware/linux-firmware.git git://git.kernel.org/pub/scm/linux/kernel/git/firmware/linux-firmware.git
To use copy the firmware image to lib/firmware folder of the initramfs or To use copy the firmware image to lib/firmware folder of the initramfs or

39
Documentation/arm/keystone/Overview.txt → Documentation/arm/keystone/overview.rst
View file

@ -1,5 +1,6 @@
==========================
TI Keystone Linux Overview TI Keystone Linux Overview
-------------------------- ==========================
Introduction Introduction
------------ ------------
@ -9,30 +10,42 @@ for users to run Linux on Keystone based EVMs from Texas Instruments.
Following SoCs & EVMs are currently supported:- Following SoCs & EVMs are currently supported:-
------------ K2HK SoC and EVM -------------------------------------------------- K2HK SoC and EVM
=================
a.k.a Keystone 2 Hawking/Kepler SoC a.k.a Keystone 2 Hawking/Kepler SoC
TCI6636K2H & TCI6636K2K: See documentation at TCI6636K2H & TCI6636K2K: See documentation at
http://www.ti.com/product/tci6638k2k http://www.ti.com/product/tci6638k2k
http://www.ti.com/product/tci6638k2h http://www.ti.com/product/tci6638k2h
EVM: EVM:
http://www.advantech.com/Support/TI-EVM/EVMK2HX_sd.aspx http://www.advantech.com/Support/TI-EVM/EVMK2HX_sd.aspx
------------ K2E SoC and EVM --------------------------------------------------- K2E SoC and EVM
===============
a.k.a Keystone 2 Edison SoC a.k.a Keystone 2 Edison SoC
K2E - 66AK2E05: See documentation at
K2E - 66AK2E05:
See documentation at
http://www.ti.com/product/66AK2E05/technicaldocuments http://www.ti.com/product/66AK2E05/technicaldocuments
EVM: EVM:
https://www.einfochips.com/index.php/partnerships/texas-instruments/k2e-evm.html https://www.einfochips.com/index.php/partnerships/texas-instruments/k2e-evm.html
------------ K2L SoC and EVM --------------------------------------------------- K2L SoC and EVM
===============
a.k.a Keystone 2 Lamarr SoC a.k.a Keystone 2 Lamarr SoC
K2L - TCI6630K2L: See documentation at
K2L - TCI6630K2L:
See documentation at
http://www.ti.com/product/TCI6630K2L/technicaldocuments http://www.ti.com/product/TCI6630K2L/technicaldocuments
EVM: EVM:
https://www.einfochips.com/index.php/partnerships/texas-instruments/k2l-evm.html https://www.einfochips.com/index.php/partnerships/texas-instruments/k2l-evm.html
@ -41,15 +54,21 @@ Configuration
All of the K2 SoCs/EVMs share a common defconfig, keystone_defconfig and same All of the K2 SoCs/EVMs share a common defconfig, keystone_defconfig and same
image is used to boot on individual EVMs. The platform configuration is image is used to boot on individual EVMs. The platform configuration is
specified through DTS. Following are the DTS used:- specified through DTS. Following are the DTS used:
K2HK EVM : k2hk-evm.dts
K2E EVM : k2e-evm.dts K2HK EVM:
K2L EVM : k2l-evm.dts k2hk-evm.dts
K2E EVM:
k2e-evm.dts
K2L EVM:
k2l-evm.dts
The device tree documentation for the keystone machines are located at The device tree documentation for the keystone machines are located at
Documentation/devicetree/bindings/arm/keystone/keystone.txt Documentation/devicetree/bindings/arm/keystone/keystone.txt
Document Author Document Author
--------------- ---------------
Murali Karicheri <m-karicheri2@ti.com> Murali Karicheri <m-karicheri2@ti.com>
Copyright 2015 Texas Instruments Copyright 2015 Texas Instruments

488
Documentation/arm/marvel.rst Normal file
View file

@ -0,0 +1,488 @@
================
ARM Marvell SoCs
================
This document lists all the ARM Marvell SoCs that are currently
supported in mainline by the Linux kernel. As the Marvell families of
SoCs are large and complex, it is hard to understand where the support
for a particular SoC is available in the Linux kernel. This document
tries to help in understanding where those SoCs are supported, and to
match them with their corresponding public datasheet, when available.
Orion family
------------
Flavors:
- 88F5082
- 88F5181
- 88F5181L
- 88F5182
- Datasheet: http://www.embeddedarm.com/documentation/third-party/MV88F5182-datasheet.pdf
- Programmer's User Guide: http://www.embeddedarm.com/documentation/third-party/MV88F5182-opensource-manual.pdf
- User Manual: http://www.embeddedarm.com/documentation/third-party/MV88F5182-usermanual.pdf
- 88F5281
- Datasheet: http://www.ocmodshop.com/images/reviews/networking/qnap_ts409u/marvel_88f5281_data_sheet.pdf
- 88F6183
Core:
Feroceon 88fr331 (88f51xx) or 88fr531-vd (88f52xx) ARMv5 compatible
Linux kernel mach directory:
arch/arm/mach-orion5x
Linux kernel plat directory:
arch/arm/plat-orion
Kirkwood family
---------------
Flavors:
- 88F6282 a.k.a Armada 300
- Product Brief : http://www.marvell.com/embedded-processors/armada-300/assets/armada_310.pdf
- 88F6283 a.k.a Armada 310
- Product Brief : http://www.marvell.com/embedded-processors/armada-300/assets/armada_310.pdf
- 88F6190
- Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6190-003_WEB.pdf
- Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F619x_OpenSource.pdf
- Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
- 88F6192
- Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6192-003_ver1.pdf
- Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F619x_OpenSource.pdf
- Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
- 88F6182
- 88F6180
- Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6180-003_ver1.pdf
- Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F6180_OpenSource.pdf
- Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
- 88F6281
- Product Brief : http://www.marvell.com/embedded-processors/kirkwood/assets/88F6281-004_ver1.pdf
- Hardware Spec : http://www.marvell.com/embedded-processors/kirkwood/assets/HW_88F6281_OpenSource.pdf
- Functional Spec: http://www.marvell.com/embedded-processors/kirkwood/assets/FS_88F6180_9x_6281_OpenSource.pdf
Homepage:
http://www.marvell.com/embedded-processors/kirkwood/
Core:
Feroceon 88fr131 ARMv5 compatible
Linux kernel mach directory:
arch/arm/mach-mvebu
Linux kernel plat directory:
none
Discovery family
----------------
Flavors:
- MV78100
- Product Brief : http://www.marvell.com/embedded-processors/discovery-innovation/assets/MV78100-003_WEB.pdf
- Hardware Spec : http://www.marvell.com/embedded-processors/discovery-innovation/assets/HW_MV78100_OpenSource.pdf
- Functional Spec: http://www.marvell.com/embedded-processors/discovery-innovation/assets/FS_MV76100_78100_78200_OpenSource.pdf
- MV78200
- Product Brief : http://www.marvell.com/embedded-processors/discovery-innovation/assets/MV78200-002_WEB.pdf
- Hardware Spec : http://www.marvell.com/embedded-processors/discovery-innovation/assets/HW_MV78200_OpenSource.pdf
- Functional Spec: http://www.marvell.com/embedded-processors/discovery-innovation/assets/FS_MV76100_78100_78200_OpenSource.pdf
- MV76100
Not supported by the Linux kernel.
Core:
Feroceon 88fr571-vd ARMv5 compatible
Linux kernel mach directory:
arch/arm/mach-mv78xx0
Linux kernel plat directory:
arch/arm/plat-orion
EBU Armada family
-----------------
Armada 370 Flavors:
- 88F6710
- 88F6707
- 88F6W11
- Product Brief: http://www.marvell.com/embedded-processors/armada-300/assets/Marvell_ARMADA_370_SoC.pdf
- Hardware Spec: http://www.marvell.com/embedded-processors/armada-300/assets/ARMADA370-datasheet.pdf
- Functional Spec: http://www.marvell.com/embedded-processors/armada-300/assets/ARMADA370-FunctionalSpec-datasheet.pdf
Core:
Sheeva ARMv7 compatible PJ4B
Armada 375 Flavors:
- 88F6720
- Product Brief: http://www.marvell.com/embedded-processors/armada-300/assets/ARMADA_375_SoC-01_product_brief.pdf
Core:
ARM Cortex-A9
Armada 38x Flavors:
- 88F6810 Armada 380
- 88F6820 Armada 385
- 88F6828 Armada 388
- Product infos: http://www.marvell.com/embedded-processors/armada-38x/
- Functional Spec: https://marvellcorp.wufoo.com/forms/marvell-armada-38x-functional-specifications/
Core:
ARM Cortex-A9
Armada 39x Flavors:
- 88F6920 Armada 390
- 88F6928 Armada 398
- Product infos: http://www.marvell.com/embedded-processors/armada-39x/
Core:
ARM Cortex-A9
Armada XP Flavors:
- MV78230
- MV78260
- MV78460
NOTE:
not to be confused with the non-SMP 78xx0 SoCs
Product Brief:
http://www.marvell.com/embedded-processors/armada-xp/assets/Marvell-ArmadaXP-SoC-product%20brief.pdf
Functional Spec:
http://www.marvell.com/embedded-processors/armada-xp/assets/ARMADA-XP-Functional-SpecDatasheet.pdf
- Hardware Specs:
- http://www.marvell.com/embedded-processors/armada-xp/assets/HW_MV78230_OS.PDF
- http://www.marvell.com/embedded-processors/armada-xp/assets/HW_MV78260_OS.PDF
- http://www.marvell.com/embedded-processors/armada-xp/assets/HW_MV78460_OS.PDF
Core:
Sheeva ARMv7 compatible Dual-core or Quad-core PJ4B-MP
Linux kernel mach directory:
arch/arm/mach-mvebu
Linux kernel plat directory:
none
EBU Armada family ARMv8
-----------------------
Armada 3710/3720 Flavors:
- 88F3710
- 88F3720
Core:
ARM Cortex A53 (ARMv8)
Homepage:
http://www.marvell.com/embedded-processors/armada-3700/
Product Brief:
http://www.marvell.com/embedded-processors/assets/PB-88F3700-FNL.pdf
Device tree files:
arch/arm64/boot/dts/marvell/armada-37*
Armada 7K Flavors:
- 88F7020 (AP806 Dual + one CP110)
- 88F7040 (AP806 Quad + one CP110)
Core: ARM Cortex A72
Homepage:
http://www.marvell.com/embedded-processors/armada-70xx/
Product Brief:
- http://www.marvell.com/embedded-processors/assets/Armada7020PB-Jan2016.pdf
- http://www.marvell.com/embedded-processors/assets/Armada7040PB-Jan2016.pdf
Device tree files:
arch/arm64/boot/dts/marvell/armada-70*
Armada 8K Flavors:
- 88F8020 (AP806 Dual + two CP110)
- 88F8040 (AP806 Quad + two CP110)
Core:
ARM Cortex A72
Homepage:
http://www.marvell.com/embedded-processors/armada-80xx/
Product Brief:
- http://www.marvell.com/embedded-processors/assets/Armada8020PB-Jan2016.pdf
- http://www.marvell.com/embedded-processors/assets/Armada8040PB-Jan2016.pdf
Device tree files:
arch/arm64/boot/dts/marvell/armada-80*
Avanta family
-------------
Flavors:
- 88F6510
- 88F6530P
- 88F6550
- 88F6560
Homepage:
http://www.marvell.com/broadband/
Product Brief:
http://www.marvell.com/broadband/assets/Marvell_Avanta_88F6510_305_060-001_product_brief.pdf
No public datasheet available.
Core:
ARMv5 compatible
Linux kernel mach directory:
no code in mainline yet, planned for the future
Linux kernel plat directory:
no code in mainline yet, planned for the future
Storage family
--------------
Armada SP:
- 88RC1580
Product infos:
http://www.marvell.com/storage/armada-sp/
Core:
Sheeva ARMv7 comatible Quad-core PJ4C
(not supported in upstream Linux kernel)
Dove family (application processor)
-----------------------------------
Flavors:
- 88AP510 a.k.a Armada 510
Product Brief:
http://www.marvell.com/application-processors/armada-500/assets/Marvell_Armada510_SoC.pdf
Hardware Spec:
http://www.marvell.com/application-processors/armada-500/assets/Armada-510-Hardware-Spec.pdf
Functional Spec:
http://www.marvell.com/application-processors/armada-500/assets/Armada-510-Functional-Spec.pdf
Homepage:
http://www.marvell.com/application-processors/armada-500/
Core:
ARMv7 compatible
Directory:
- arch/arm/mach-mvebu (DT enabled platforms)
- arch/arm/mach-dove (non-DT enabled platforms)
PXA 2xx/3xx/93x/95x family
--------------------------
Flavors:
- PXA21x, PXA25x, PXA26x
- Application processor only
- Core: ARMv5 XScale1 core
- PXA270, PXA271, PXA272
- Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_pb.pdf
- Design guide : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_design_guide.pdf
- Developers manual : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_dev_man.pdf
- Specification : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_emts.pdf
- Specification update : http://www.marvell.com/application-processors/pxa-family/assets/pxa_27x_spec_update.pdf
- Application processor only
- Core: ARMv5 XScale2 core
- PXA300, PXA310, PXA320
- PXA 300 Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/PXA300_PB_R4.pdf
- PXA 310 Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/PXA310_PB_R4.pdf
- PXA 320 Product Brief : http://www.marvell.com/application-processors/pxa-family/assets/PXA320_PB_R4.pdf
- Design guide : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_Design_Guide.pdf
- Developers manual : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_Developers_Manual.zip
- Specifications : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_EMTS.pdf
- Specification Update : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_Spec_Update.zip
- Reference Manual : http://www.marvell.com/application-processors/pxa-family/assets/PXA3xx_TavorP_BootROM_Ref_Manual.pdf
- Application processor only
- Core: ARMv5 XScale3 core
- PXA930, PXA935
- Application processor with Communication processor
- Core: ARMv5 XScale3 core
- PXA955
- Application processor with Communication processor
- Core: ARMv7 compatible Sheeva PJ4 core
Comments:
* This line of SoCs originates from the XScale family developed by
Intel and acquired by Marvell in ~2006. The PXA21x, PXA25x,
PXA26x, PXA27x, PXA3xx and PXA93x were developed by Intel, while
the later PXA95x were developed by Marvell.
* Due to their XScale origin, these SoCs have virtually nothing in
common with the other (Kirkwood, Dove, etc.) families of Marvell
SoCs, except with the MMP/MMP2 family of SoCs.
Linux kernel mach directory:
arch/arm/mach-pxa
Linux kernel plat directory:
arch/arm/plat-pxa
MMP/MMP2/MMP3 family (communication processor)
----------------------------------------------
Flavors:
- PXA168, a.k.a Armada 168
- Homepage : http://www.marvell.com/application-processors/armada-100/armada-168.jsp
- Product brief : http://www.marvell.com/application-processors/armada-100/assets/pxa_168_pb.pdf
- Hardware manual : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_datasheet.pdf
- Software manual : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_software_manual.pdf
- Specification update : http://www.marvell.com/application-processors/armada-100/assets/ARMADA16x_Spec_update.pdf
- Boot ROM manual : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_ref_manual.pdf
- App node package : http://www.marvell.com/application-processors/armada-100/assets/armada_16x_app_note_package.pdf
- Application processor only
- Core: ARMv5 compatible Marvell PJ1 88sv331 (Mohawk)
- PXA910/PXA920
- Homepage : http://www.marvell.com/communication-processors/pxa910/
- Product Brief : http://www.marvell.com/communication-processors/pxa910/assets/Marvell_PXA910_Platform-001_PB_final.pdf
- Application processor with Communication processor
- Core: ARMv5 compatible Marvell PJ1 88sv331 (Mohawk)
- PXA688, a.k.a. MMP2, a.k.a Armada 610
- Product Brief : http://www.marvell.com/application-processors/armada-600/assets/armada610_pb.pdf
- Application processor only
- Core: ARMv7 compatible Sheeva PJ4 88sv581x core
- PXA2128, a.k.a. MMP3 (OLPC XO4, Linux support not upstream)
- Product Brief : http://www.marvell.com/application-processors/armada/pxa2128/assets/Marvell-ARMADA-PXA2128-SoC-PB.pdf
- Application processor only
- Core: Dual-core ARMv7 compatible Sheeva PJ4C core
- PXA960/PXA968/PXA978 (Linux support not upstream)
- Application processor with Communication Processor
- Core: ARMv7 compatible Sheeva PJ4 core
- PXA986/PXA988 (Linux support not upstream)
- Application processor with Communication Processor
- Core: Dual-core ARMv7 compatible Sheeva PJ4B-MP core
- PXA1088/PXA1920 (Linux support not upstream)
- Application processor with Communication Processor
- Core: quad-core ARMv7 Cortex-A7
- PXA1908/PXA1928/PXA1936
- Application processor with Communication Processor
- Core: multi-core ARMv8 Cortex-A53
Comments:
* This line of SoCs originates from the XScale family developed by
Intel and acquired by Marvell in ~2006. All the processors of
this MMP/MMP2 family were developed by Marvell.
* Due to their XScale origin, these SoCs have virtually nothing in
common with the other (Kirkwood, Dove, etc.) families of Marvell
SoCs, except with the PXA family of SoCs listed above.
Linux kernel mach directory:
arch/arm/mach-mmp
Linux kernel plat directory:
arch/arm/plat-pxa
Berlin family (Multimedia Solutions)
-------------------------------------
- Flavors:
- 88DE3010, Armada 1000 (no Linux support)
- Core: Marvell PJ1 (ARMv5TE), Dual-core
- Product Brief: http://www.marvell.com.cn/digital-entertainment/assets/armada_1000_pb.pdf
- 88DE3005, Armada 1500 Mini
- Design name: BG2CD
- Core: ARM Cortex-A9, PL310 L2CC
- 88DE3006, Armada 1500 Mini Plus
- Design name: BG2CDP
- Core: Dual Core ARM Cortex-A7
- 88DE3100, Armada 1500
- Design name: BG2
- Core: Marvell PJ4B-MP (ARMv7), Tauros3 L2CC
- 88DE3114, Armada 1500 Pro
- Design name: BG2Q
- Core: Quad Core ARM Cortex-A9, PL310 L2CC
- 88DE3214, Armada 1500 Pro 4K
- Design name: BG3
- Core: ARM Cortex-A15, CA15 integrated L2CC
- 88DE3218, ARMADA 1500 Ultra
- Core: ARM Cortex-A53
Homepage: https://www.synaptics.com/products/multimedia-solutions
Directory: arch/arm/mach-berlin
Comments:
* This line of SoCs is based on Marvell Sheeva or ARM Cortex CPUs
with Synopsys DesignWare (IRQ, GPIO, Timers, ...) and PXA IP (SDHCI, USB, ETH, ...).
* The Berlin family was acquired by Synaptics from Marvell in 2017.
CPU Cores
---------
The XScale cores were designed by Intel, and shipped by Marvell in the older
PXA processors. Feroceon is a Marvell designed core that developed in-house,
and that evolved into Sheeva. The XScale and Feroceon cores were phased out
over time and replaced with Sheeva cores in later products, which subsequently
got replaced with licensed ARM Cortex-A cores.
XScale 1
CPUID 0x69052xxx
ARMv5, iWMMXt
XScale 2
CPUID 0x69054xxx
ARMv5, iWMMXt
XScale 3
CPUID 0x69056xxx or 0x69056xxx
ARMv5, iWMMXt
Feroceon-1850 88fr331 "Mohawk"
CPUID 0x5615331x or 0x41xx926x
ARMv5TE, single issue
Feroceon-2850 88fr531-vd "Jolteon"
CPUID 0x5605531x or 0x41xx926x
ARMv5TE, VFP, dual-issue
Feroceon 88fr571-vd "Jolteon"
CPUID 0x5615571x
ARMv5TE, VFP, dual-issue
Feroceon 88fr131 "Mohawk-D"
CPUID 0x5625131x
ARMv5TE, single-issue in-order
Sheeva PJ1 88sv331 "Mohawk"
CPUID 0x561584xx
ARMv5, single-issue iWMMXt v2
Sheeva PJ4 88sv581x "Flareon"
CPUID 0x560f581x
ARMv7, idivt, optional iWMMXt v2
Sheeva PJ4B 88sv581x
CPUID 0x561f581x
ARMv7, idivt, optional iWMMXt v2
Sheeva PJ4B-MP / PJ4C
CPUID 0x562f584x
ARMv7, idivt/idiva, LPAE, optional iWMMXt v2 and/or NEON
Long-term plans
---------------
* Unify the mach-dove/, mach-mv78xx0/, mach-orion5x/ into the
mach-mvebu/ to support all SoCs from the Marvell EBU (Engineering
Business Unit) in a single mach-<foo> directory. The plat-orion/
would therefore disappear.
* Unify the mach-mmp/ and mach-pxa/ into the same mach-pxa
directory. The plat-pxa/ would therefore disappear.
Credits
-------
- Maen Suleiman <maen@marvell.com>
- Lior Amsalem <alior@marvell.com>
- Thomas Petazzoni <thomas.petazzoni@free-electrons.com>
- Andrew Lunn <andrew@lunn.ch>
- Nicolas Pitre <nico@fluxnic.net>
- Eric Miao <eric.y.miao@gmail.com>

11
Documentation/arm/mem_alignment → Documentation/arm/mem_alignment.rst
View file

@ -1,3 +1,7 @@
================
Memory alignment
================
Too many problems popped up because of unnoticed misaligned memory access in Too many problems popped up because of unnoticed misaligned memory access in
kernel code lately. Therefore the alignment fixup is now unconditionally kernel code lately. Therefore the alignment fixup is now unconditionally
configured in for SA11x0 based targets. According to Alan Cox, this is a configured in for SA11x0 based targets. According to Alan Cox, this is a
@ -26,9 +30,9 @@ space, and might cause programs to fail unexpectedly.
To change the alignment trap behavior, simply echo a number into To change the alignment trap behavior, simply echo a number into
/proc/cpu/alignment. The number is made up from various bits: /proc/cpu/alignment. The number is made up from various bits:
=== ========================================================
bit behavior when set bit behavior when set
--- ----------------- === ========================================================
0 A user process performing an unaligned memory access 0 A user process performing an unaligned memory access
will cause the kernel to print a message indicating will cause the kernel to print a message indicating
process name, pid, pc, instruction, address, and the process name, pid, pc, instruction, address, and the
@ -41,12 +45,13 @@ bit behavior when set
2 The kernel will send a SIGBUS signal to the user process 2 The kernel will send a SIGBUS signal to the user process
performing the unaligned access. performing the unaligned access.
=== ========================================================
Note that not all combinations are supported - only values 0 through 5. Note that not all combinations are supported - only values 0 through 5.
(6 and 7 don't make sense). (6 and 7 don't make sense).
For example, the following will turn on the warnings, but without For example, the following will turn on the warnings, but without
fixing up or sending SIGBUS signals: fixing up or sending SIGBUS signals::
echo 1 > /proc/cpu/alignment echo 1 > /proc/cpu/alignment

7
Documentation/arm/memory.txt → Documentation/arm/memory.rst
View file

@ -1,6 +1,9 @@
=================================
Kernel Memory Layout on ARM Linux Kernel Memory Layout on ARM Linux
=================================
Russell King <rmk@arm.linux.org.uk> Russell King <rmk@arm.linux.org.uk>
November 17, 2005 (2.6.15) November 17, 2005 (2.6.15)
This document describes the virtual memory layout which the Linux This document describes the virtual memory layout which the Linux
@ -15,8 +18,9 @@ As the ARM architecture matures, it becomes necessary to reserve
certain regions of VM space for use for new facilities; therefore certain regions of VM space for use for new facilities; therefore
this document may reserve more VM space over time. this document may reserve more VM space over time.
=============== =============== ===============================================
Start End Use Start End Use
-------------------------------------------------------------------------- =============== =============== ===============================================
ffff8000 ffffffff copy_user_page / clear_user_page use. ffff8000 ffffffff copy_user_page / clear_user_page use.
For SA11xx and Xscale, this is used to For SA11xx and Xscale, this is used to
setup a minicache mapping. setup a minicache mapping.
@ -77,6 +81,7 @@ MODULES_VADDR MODULES_END-1 Kernel module space
place their vector page here. NULL pointer place their vector page here. NULL pointer
dereferences by both the kernel and user dereferences by both the kernel and user
space are also caught via this mapping. space are also caught via this mapping.
=============== =============== ===============================================
Please note that mappings which collide with the above areas may result Please note that mappings which collide with the above areas may result
in a non-bootable kernel, or may cause the kernel to (eventually) panic in a non-bootable kernel, or may cause the kernel to (eventually) panic

63
Documentation/arm/Microchip/README → Documentation/arm/microchip.rst
View file

@ -1,3 +1,4 @@
=============================
ARM Microchip SoCs (aka AT91) ARM Microchip SoCs (aka AT91)
============================= =============================
@ -22,32 +23,46 @@ the Microchip website: http://www.microchip.com.
Flavors: Flavors:
* ARM 920 based SoC * ARM 920 based SoC
- at91rm9200 - at91rm9200
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-1768-32-bit-ARM920T-Embedded-Microprocessor-AT91RM9200_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-1768-32-bit-ARM920T-Embedded-Microprocessor-AT91RM9200_Datasheet.pdf
* ARM 926 based SoCs * ARM 926 based SoCs
- at91sam9260 - at91sam9260
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6221-32-bit-ARM926EJ-S-Embedded-Microprocessor-SAM9260_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6221-32-bit-ARM926EJ-S-Embedded-Microprocessor-SAM9260_Datasheet.pdf
- at91sam9xe - at91sam9xe
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6254-32-bit-ARM926EJ-S-Embedded-Microprocessor-SAM9XE_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6254-32-bit-ARM926EJ-S-Embedded-Microprocessor-SAM9XE_Datasheet.pdf
- at91sam9261 - at91sam9261
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6062-ARM926EJ-S-Microprocessor-SAM9261_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6062-ARM926EJ-S-Microprocessor-SAM9261_Datasheet.pdf
- at91sam9263 - at91sam9263
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6249-32-bit-ARM926EJ-S-Embedded-Microprocessor-SAM9263_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6249-32-bit-ARM926EJ-S-Embedded-Microprocessor-SAM9263_Datasheet.pdf
- at91sam9rl - at91sam9rl
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/doc6289.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/doc6289.pdf
- at91sam9g20 - at91sam9g20
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/DS60001516A.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/DS60001516A.pdf
- at91sam9g45 family - at91sam9g45 family
@ -55,7 +70,9 @@ the Microchip website: http://www.microchip.com.
- at91sam9g46 - at91sam9g46
- at91sam9m10 - at91sam9m10
- at91sam9m11 (device superset) - at91sam9m11 (device superset)
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6437-32-bit-ARM926-Embedded-Microprocessor-SAM9M11_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-6437-32-bit-ARM926-Embedded-Microprocessor-SAM9M11_Datasheet.pdf
- at91sam9x5 family (aka "The 5 series") - at91sam9x5 family (aka "The 5 series")
@ -64,33 +81,44 @@ the Microchip website: http://www.microchip.com.
- at91sam9g35 - at91sam9g35
- at91sam9x25 - at91sam9x25
- at91sam9x35 - at91sam9x35
+ Datasheet (can be considered as covering the whole family)
* Datasheet (can be considered as covering the whole family)
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-11055-32-bit-ARM926EJ-S-Microcontroller-SAM9X35_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-11055-32-bit-ARM926EJ-S-Microcontroller-SAM9X35_Datasheet.pdf
- at91sam9n12 - at91sam9n12
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/DS60001517A.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/DS60001517A.pdf
* ARM Cortex-A5 based SoCs * ARM Cortex-A5 based SoCs
- sama5d3 family - sama5d3 family
- sama5d31 - sama5d31
- sama5d33 - sama5d33
- sama5d34 - sama5d34
- sama5d35 - sama5d35
- sama5d36 (device superset) - sama5d36 (device superset)
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-11121-32-bit-Cortex-A5-Microcontroller-SAMA5D3_Datasheet.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/Atmel-11121-32-bit-Cortex-A5-Microcontroller-SAMA5D3_Datasheet.pdf
* ARM Cortex-A5 + NEON based SoCs * ARM Cortex-A5 + NEON based SoCs
- sama5d4 family - sama5d4 family
- sama5d41 - sama5d41
- sama5d42 - sama5d42
- sama5d43 - sama5d43
- sama5d44 (device superset) - sama5d44 (device superset)
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/60001525A.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/60001525A.pdf
- sama5d2 family - sama5d2 family
- sama5d21 - sama5d21
- sama5d22 - sama5d22
- sama5d23 - sama5d23
@ -98,11 +126,14 @@ the Microchip website: http://www.microchip.com.
- sama5d26 - sama5d26
- sama5d27 (device superset) - sama5d27 (device superset)
- sama5d28 (device superset + environmental monitors) - sama5d28 (device superset + environmental monitors)
+ Datasheet
* Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/DS60001476B.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/DS60001476B.pdf
* ARM Cortex-M7 MCUs * ARM Cortex-M7 MCUs
- sams70 family - sams70 family
- sams70j19 - sams70j19
- sams70j20 - sams70j20
- sams70j21 - sams70j21
@ -114,6 +145,7 @@ the Microchip website: http://www.microchip.com.
- sams70q21 - sams70q21
- samv70 family - samv70 family
- samv70j19 - samv70j19
- samv70j20 - samv70j20
- samv70n19 - samv70n19
@ -122,6 +154,7 @@ the Microchip website: http://www.microchip.com.
- samv70q20 - samv70q20
- samv71 family - samv71 family
- samv71j19 - samv71j19
- samv71j20 - samv71j20
- samv71j21 - samv71j21
@ -132,7 +165,8 @@ the Microchip website: http://www.microchip.com.
- samv71q20 - samv71q20
- samv71q21 - samv71q21
+ Datasheet * Datasheet
http://ww1.microchip.com/downloads/en/DeviceDoc/60001527A.pdf http://ww1.microchip.com/downloads/en/DeviceDoc/60001527A.pdf
@ -157,6 +191,7 @@ definition of a "Stable" binding/ABI.
This statement will be removed by AT91 MAINTAINERS when appropriate. This statement will be removed by AT91 MAINTAINERS when appropriate.
Naming conventions and best practice: Naming conventions and best practice:
- SoCs Device Tree Source Include files are named after the official name of - SoCs Device Tree Source Include files are named after the official name of
the product (at91sam9g20.dtsi or sama5d33.dtsi for instance). the product (at91sam9g20.dtsi or sama5d33.dtsi for instance).
- Device Tree Source Include files (.dtsi) are used to collect common nodes that can be - Device Tree Source Include files (.dtsi) are used to collect common nodes that can be

85
Documentation/arm/netwinder.rst Normal file
View file

@ -0,0 +1,85 @@
================================
NetWinder specific documentation
================================
The NetWinder is a small low-power computer, primarily designed
to run Linux. It is based around the StrongARM RISC processor,
DC21285 PCI bridge, with PC-type hardware glued around it.
Port usage
==========
======= ====== ===============================
Min Max Description
======= ====== ===============================
0x0000 0x000f DMA1
0x0020 0x0021 PIC1
0x0060 0x006f Keyboard
0x0070 0x007f RTC
0x0080 0x0087 DMA1
0x0088 0x008f DMA2
0x00a0 0x00a3 PIC2
0x00c0 0x00df DMA2
0x0180 0x0187 IRDA
0x01f0 0x01f6 ide0
0x0201 Game port
0x0203 RWA010 configuration read
0x0220 ? SoundBlaster
0x0250 ? WaveArtist
0x0279 RWA010 configuration index
0x02f8 0x02ff Serial ttyS1
0x0300 0x031f Ether10
0x0338 GPIO1
0x033a GPIO2
0x0370 0x0371 W83977F configuration registers
0x0388 ? AdLib
0x03c0 0x03df VGA
0x03f6 ide0
0x03f8 0x03ff Serial ttyS0
0x0400 0x0408 DC21143
0x0480 0x0487 DMA1
0x0488 0x048f DMA2
0x0a79 RWA010 configuration write
0xe800 0xe80f ide0/ide1 BM DMA
======= ====== ===============================
Interrupt usage
===============
======= ======= ========================
IRQ type Description
======= ======= ========================
0 ISA 100Hz timer
1 ISA Keyboard
2 ISA cascade
3 ISA Serial ttyS1
4 ISA Serial ttyS0
5 ISA PS/2 mouse
6 ISA IRDA
7 ISA Printer
8 ISA RTC alarm
9 ISA
10 ISA GP10 (Orange reset button)
11 ISA
12 ISA WaveArtist
13 ISA
14 ISA hda1
15 ISA
======= ======= ========================
DMA usage
=========
======= ======= ===========
DMA type Description
======= ======= ===========
0 ISA IRDA
1 ISA
2 ISA cascade
3 ISA WaveArtist
4 ISA
5 ISA
6 ISA
7 ISA WaveArtist
======= ======= ===========

11
Documentation/arm/nwfpe/index.rst Normal file
View file

@ -0,0 +1,11 @@
===================================
NetWinder's floating point emulator
===================================
.. toctree::
:maxdepth: 1
nwfpe
netwinder-fpe
notes
todo

6
Documentation/arm/nwfpe/README.FPE → Documentation/arm/nwfpe/netwinder-fpe.rst
View file

@ -1,9 +1,15 @@
=============
Current State
=============
The following describes the current state of the NetWinder's floating point The following describes the current state of the NetWinder's floating point
emulator. emulator.
In the following nomenclature is used to describe the floating point In the following nomenclature is used to describe the floating point
instructions. It follows the conventions in the ARM manual. instructions. It follows the conventions in the ARM manual.
::
<S|D|E> = <single|double|extended>, no default <S|D|E> = <single|double|extended>, no default
{P|M|Z} = {round to +infinity,round to -infinity,round to zero}, {P|M|Z} = {round to +infinity,round to -infinity,round to zero},
default = round to nearest default = round to nearest

3
Documentation/arm/nwfpe/NOTES → Documentation/arm/nwfpe/notes.rst
View file

@ -1,3 +1,6 @@
Notes
=====
There seems to be a problem with exp(double) and our emulator. I haven't There seems to be a problem with exp(double) and our emulator. I haven't
been able to track it down yet. This does not occur with the emulator been able to track it down yet. This does not occur with the emulator
supplied by Russell King. supplied by Russell King.

4
Documentation/arm/nwfpe/README → Documentation/arm/nwfpe/nwfpe.rst
View file

@ -1,3 +1,6 @@
Introduction
============
This directory contains the version 0.92 test release of the NetWinder This directory contains the version 0.92 test release of the NetWinder
Floating Point Emulator. Floating Point Emulator.
@ -52,6 +55,7 @@ conditions. Excluded from the above is the SoftFloat code. John Hauser's
legal notice for SoftFloat is included below. legal notice for SoftFloat is included below.
------------------------------------------------------------------------------- -------------------------------------------------------------------------------
SoftFloat Legal Notice SoftFloat Legal Notice
SoftFloat was written by John R. Hauser. This work was made possible in SoftFloat was written by John R. Hauser. This work was made possible in

11
Documentation/arm/nwfpe/TODO → Documentation/arm/nwfpe/todo.rst
View file

@ -1,5 +1,7 @@
TODO LIST TODO LIST
--------- =========
::
POW{cond}<S|D|E>{P,M,Z} Fd, Fn, <Fm,#value> - power POW{cond}<S|D|E>{P,M,Z} Fd, Fn, <Fm,#value> - power
RPW{cond}<S|D|E>{P,M,Z} Fd, Fn, <Fm,#value> - reverse power RPW{cond}<S|D|E>{P,M,Z} Fd, Fn, <Fm,#value> - reverse power
@ -34,6 +36,7 @@ so such a method could be promising, but requires more research to
determine if it is feasible. determine if it is feasible.
Rounding Methods Rounding Methods
----------------
The IEEE standard defines 4 rounding modes. Round to nearest is the The IEEE standard defines 4 rounding modes. Round to nearest is the
default, but rounding to + or - infinity or round to zero are also allowed. default, but rounding to + or - infinity or round to zero are also allowed.
@ -52,7 +55,8 @@ in the FPCR. This requires a kernel call in ArmLinux, as WFC/RFC are
supervisor only instructions. If anyone has any ideas or comments I supervisor only instructions. If anyone has any ideas or comments I
would like to hear them. would like to hear them.
[NOTE: pulled out from some docs on ARM floating point, specifically NOTE:
pulled out from some docs on ARM floating point, specifically
for the Acorn FPE, but not limited to it: for the Acorn FPE, but not limited to it:
The floating point control register (FPCR) may only be present in some The floating point control register (FPCR) may only be present in some
@ -64,4 +68,5 @@ would like to hear them.
Hence, the answer is yes, you could do this, but then you will run a high Hence, the answer is yes, you could do this, but then you will run a high
risk of becoming isolated if and when hardware FP emulation comes out risk of becoming isolated if and when hardware FP emulation comes out
-- Russell].
-- Russell.

26
Documentation/arm/OMAP/DSS → Documentation/arm/omap/dss.rst
View file

@ -1,5 +1,6 @@
=========================
OMAP2/3 Display Subsystem OMAP2/3 Display Subsystem
------------------------- =========================
This is an almost total rewrite of the OMAP FB driver in drivers/video/omap This is an almost total rewrite of the OMAP FB driver in drivers/video/omap
(let's call it DSS1). The main differences between DSS1 and DSS2 are DSI, (let's call it DSS1). The main differences between DSS1 and DSS2 are DSI,
@ -190,6 +191,8 @@ trans_key_value transparency color key (RGB24)
default_color default background color (RGB24) default_color default background color (RGB24)
/sys/devices/platform/omapdss/display? directory: /sys/devices/platform/omapdss/display? directory:
=============== =============================================================
ctrl_name Controller name ctrl_name Controller name
mirror 0=off, 1=on mirror 0=off, 1=on
update_mode 0=off, 1=auto, 2=manual update_mode 0=off, 1=auto, 2=manual
@ -202,6 +205,7 @@ timings Display timings (pixclock,xres/hfp/hbp/hsw,yres/vfp/vbp/vsw)
panel_name panel_name
tear_elim Tearing elimination 0=off, 1=on tear_elim Tearing elimination 0=off, 1=on
output_type Output type (video encoder only): "composite" or "svideo" output_type Output type (video encoder only): "composite" or "svideo"
=============== =============================================================
There are also some debugfs files at <debugfs>/omapdss/ which show information There are also some debugfs files at <debugfs>/omapdss/ which show information
about clocks and registers. about clocks and registers.
@ -209,7 +213,7 @@ about clocks and registers.
Examples Examples
-------- --------
The following definitions have been made for the examples below: The following definitions have been made for the examples below::
ovl0=/sys/devices/platform/omapdss/overlay0 ovl0=/sys/devices/platform/omapdss/overlay0
ovl1=/sys/devices/platform/omapdss/overlay1 ovl1=/sys/devices/platform/omapdss/overlay1
@ -232,14 +236,16 @@ Default setup on OMAP3 SDP
Here's the default setup on OMAP3 SDP board. All planes go to LCD. DVI Here's the default setup on OMAP3 SDP board. All planes go to LCD. DVI
and TV-out are not in use. The columns from left to right are: and TV-out are not in use. The columns from left to right are:
framebuffers, overlays, overlay managers, displays. Framebuffers are framebuffers, overlays, overlay managers, displays. Framebuffers are
handled by omapfb, and the rest by the DSS. handled by omapfb, and the rest by the DSS::
FB0 --- GFX -\ DVI FB0 --- GFX -\ DVI
FB1 --- VID1 --+- LCD ---- LCD FB1 --- VID1 --+- LCD ---- LCD
FB2 --- VID2 -/ TV ----- TV FB2 --- VID2 -/ TV ----- TV
Example: Switch from LCD to DVI Example: Switch from LCD to DVI
---------------------- -------------------------------
::
w=`cat $dvi/timings | cut -d "," -f 2 | cut -d "/" -f 1` w=`cat $dvi/timings | cut -d "," -f 2 | cut -d "/" -f 1`
h=`cat $dvi/timings | cut -d "," -f 3 | cut -d "/" -f 1` h=`cat $dvi/timings | cut -d "," -f 3 | cut -d "/" -f 1`
@ -251,14 +257,16 @@ fbset -fb /dev/fb0 -xres $w -yres $h -vxres $w -vyres $h
echo "dvi" > $mgr0/display echo "dvi" > $mgr0/display
echo "1" > $dvi/enabled echo "1" > $dvi/enabled
After this the configuration looks like: After this the configuration looks like:::
FB0 --- GFX -\ -- DVI FB0 --- GFX -\ -- DVI
FB1 --- VID1 --+- LCD -/ LCD FB1 --- VID1 --+- LCD -/ LCD
FB2 --- VID2 -/ TV ----- TV FB2 --- VID2 -/ TV ----- TV
Example: Clone GFX overlay to LCD and TV Example: Clone GFX overlay to LCD and TV
------------------------------- ----------------------------------------
::
w=`cat $tv/timings | cut -d "," -f 2 | cut -d "/" -f 1` w=`cat $tv/timings | cut -d "," -f 2 | cut -d "/" -f 1`
h=`cat $tv/timings | cut -d "," -f 3 | cut -d "/" -f 1` h=`cat $tv/timings | cut -d "," -f 3 | cut -d "/" -f 1`
@ -277,7 +285,7 @@ echo "1" > $ovl1/enabled
echo "1" > $tv/enabled echo "1" > $tv/enabled
After this the configuration looks like (only relevant parts shown): After this the configuration looks like (only relevant parts shown)::
FB0 +-- GFX ---- LCD ---- LCD FB0 +-- GFX ---- LCD ---- LCD
\- VID1 ---- TV ---- TV \- VID1 ---- TV ---- TV
@ -351,12 +359,14 @@ TODO
DSS locking DSS locking
Error checking Error checking
- Lots of checks are missing or implemented just as BUG() - Lots of checks are missing or implemented just as BUG()
System DMA update for DSI System DMA update for DSI
- Can be used for RGB16 and RGB24P modes. Probably not for RGB24U (how - Can be used for RGB16 and RGB24P modes. Probably not for RGB24U (how
to skip the empty byte?) to skip the empty byte?)
OMAP1 support OMAP1 support
- Not sure if needed
- Not sure if needed

10
Documentation/arm/omap/index.rst Normal file
View file

@ -0,0 +1,10 @@
=======
TI OMAP
=======
.. toctree::
:maxdepth: 1
omap
omap_pm
dss

7
Documentation/arm/OMAP/README → Documentation/arm/omap/omap.rst
View file

@ -1,7 +1,13 @@
============
OMAP history
============
This file contains documentation for running mainline This file contains documentation for running mainline
kernel on omaps. kernel on omaps.
====== ======================================================
KERNEL NEW DEPENDENCIES KERNEL NEW DEPENDENCIES
====== ======================================================
v4.3+ Update is needed for custom .config files to make sure v4.3+ Update is needed for custom .config files to make sure
CONFIG_REGULATOR_PBIAS is enabled for MMC1 to work CONFIG_REGULATOR_PBIAS is enabled for MMC1 to work
properly. properly.
@ -9,3 +15,4 @@ v4.3+ Update is needed for custom .config files to make sure
v4.18+ Update is needed for custom .config files to make sure v4.18+ Update is needed for custom .config files to make sure
CONFIG_MMC_SDHCI_OMAP is enabled for all MMC instances CONFIG_MMC_SDHCI_OMAP is enabled for all MMC instances
to work in DRA7 and K2G based boards. to work in DRA7 and K2G based boards.
====== ======================================================

47
Documentation/arm/OMAP/omap_pm → Documentation/arm/omap/omap_pm.rst
View file

@ -1,4 +1,4 @@
=====================
The OMAP PM interface The OMAP PM interface
===================== =====================
@ -31,19 +31,24 @@ Drivers need to express PM parameters which:
This document proposes the OMAP PM interface, including the following This document proposes the OMAP PM interface, including the following
five power management functions for driver code: five power management functions for driver code:
1. Set the maximum MPU wakeup latency: 1. Set the maximum MPU wakeup latency::
(*pdata->set_max_mpu_wakeup_lat)(struct device *dev, unsigned long t) (*pdata->set_max_mpu_wakeup_lat)(struct device *dev, unsigned long t)
2. Set the maximum device wakeup latency: 2. Set the maximum device wakeup latency::
(*pdata->set_max_dev_wakeup_lat)(struct device *dev, unsigned long t) (*pdata->set_max_dev_wakeup_lat)(struct device *dev, unsigned long t)
3. Set the maximum system DMA transfer start latency (CORE pwrdm): 3. Set the maximum system DMA transfer start latency (CORE pwrdm)::
(*pdata->set_max_sdma_lat)(struct device *dev, long t) (*pdata->set_max_sdma_lat)(struct device *dev, long t)
4. Set the minimum bus throughput needed by a device: 4. Set the minimum bus throughput needed by a device::
(*pdata->set_min_bus_tput)(struct device *dev, u8 agent_id, unsigned long r) (*pdata->set_min_bus_tput)(struct device *dev, u8 agent_id, unsigned long r)
5. Return the number of times the device has lost context 5. Return the number of times the device has lost context::
(*pdata->get_dev_context_loss_count)(struct device *dev) (*pdata->get_dev_context_loss_count)(struct device *dev)
@ -65,12 +70,13 @@ Driver usage of the OMAP PM functions
As the 'pdata' in the above examples indicates, these functions are As the 'pdata' in the above examples indicates, these functions are
exposed to drivers through function pointers in driver .platform_data exposed to drivers through function pointers in driver .platform_data
structures. The function pointers are initialized by the board-*.c structures. The function pointers are initialized by the `board-*.c`
files to point to the corresponding OMAP PM functions: files to point to the corresponding OMAP PM functions:
.set_max_dev_wakeup_lat will point to
- set_max_dev_wakeup_lat will point to
omap_pm_set_max_dev_wakeup_lat(), etc. Other architectures which do omap_pm_set_max_dev_wakeup_lat(), etc. Other architectures which do
not support these functions should leave these function pointers set not support these functions should leave these function pointers set
to NULL. Drivers should use the following idiom: to NULL. Drivers should use the following idiom::
if (pdata->set_max_dev_wakeup_lat) if (pdata->set_max_dev_wakeup_lat)
(*pdata->set_max_dev_wakeup_lat)(dev, t); (*pdata->set_max_dev_wakeup_lat)(dev, t);
@ -81,7 +87,7 @@ becomes accessible. To accomplish this, driver writers should use the
set_max_mpu_wakeup_lat() function to constrain the MPU wakeup set_max_mpu_wakeup_lat() function to constrain the MPU wakeup
latency, and the set_max_dev_wakeup_lat() function to constrain the latency, and the set_max_dev_wakeup_lat() function to constrain the
device wakeup latency (from clk_enable() to accessibility). For device wakeup latency (from clk_enable() to accessibility). For
example, example::
/* Limit MPU wakeup latency */ /* Limit MPU wakeup latency */
if (pdata->set_max_mpu_wakeup_lat) if (pdata->set_max_mpu_wakeup_lat)
@ -116,17 +122,17 @@ specialized cases to convert that input information (OPPs/MPU
frequency) into the form that the underlying power management frequency) into the form that the underlying power management
implementation needs: implementation needs:
6. (*pdata->dsp_get_opp_table)(void) 6. `(*pdata->dsp_get_opp_table)(void)`
7. (*pdata->dsp_set_min_opp)(u8 opp_id) 7. `(*pdata->dsp_set_min_opp)(u8 opp_id)`
8. (*pdata->dsp_get_opp)(void) 8. `(*pdata->dsp_get_opp)(void)`
9. (*pdata->cpu_get_freq_table)(void) 9. `(*pdata->cpu_get_freq_table)(void)`
10. (*pdata->cpu_set_freq)(unsigned long f) 10. `(*pdata->cpu_set_freq)(unsigned long f)`
11. (*pdata->cpu_get_freq)(void) 11. `(*pdata->cpu_get_freq)(void)`
Customizing OPP for platform Customizing OPP for platform
============================ ============================
@ -134,12 +140,15 @@ Defining CONFIG_PM should enable OPP layer for the silicon
and the registration of OPP table should take place automatically. and the registration of OPP table should take place automatically.
However, in special cases, the default OPP table may need to be However, in special cases, the default OPP table may need to be
tweaked, for e.g.: tweaked, for e.g.:
* enable default OPPs which are disabled by default, but which * enable default OPPs which are disabled by default, but which
could be enabled on a platform could be enabled on a platform
* Disable an unsupported OPP on the platform * Disable an unsupported OPP on the platform
* Define and add a custom opp table entry * Define and add a custom opp table entry
in these cases, the board file needs to do additional steps as follows: in these cases, the board file needs to do additional steps as follows:
arch/arm/mach-omapx/board-xyz.c
arch/arm/mach-omapx/board-xyz.c::
#include "pm.h" #include "pm.h"
.... ....
static void __init omap_xyz_init_irq(void) static void __init omap_xyz_init_irq(void)
@ -150,5 +159,7 @@ arch/arm/mach-omapx/board-xyz.c
/* Do customization to the defaults */ /* Do customization to the defaults */
.... ....
} }
NOTE: omapx_opp_init will be omap3_opp_init or as required
NOTE:
omapx_opp_init will be omap3_opp_init or as required
based on the omap family. based on the omap family.

14
Documentation/arm/Porting → Documentation/arm/porting.rst
View file

@ -1,3 +1,7 @@
=======
Porting
=======
Taken from list archive at http://lists.arm.linux.org.uk/pipermail/linux-arm-kernel/2001-July/004064.html Taken from list archive at http://lists.arm.linux.org.uk/pipermail/linux-arm-kernel/2001-July/004064.html
Initial definitions Initial definitions
@ -89,8 +93,7 @@ DATAADDR
Virtual address for the kernel data segment. Must not be defined Virtual address for the kernel data segment. Must not be defined
when using the decompressor. when using the decompressor.
VMALLOC_START VMALLOC_START / VMALLOC_END
VMALLOC_END
Virtual addresses bounding the vmalloc() area. There must not be Virtual addresses bounding the vmalloc() area. There must not be
any static mappings in this area; vmalloc will overwrite them. any static mappings in this area; vmalloc will overwrite them.
The addresses must also be in the kernel segment (see above). The addresses must also be in the kernel segment (see above).
@ -107,13 +110,13 @@ Architecture Specific Macros
---------------------------- ----------------------------
BOOT_MEM(pram,pio,vio) BOOT_MEM(pram,pio,vio)
`pram' specifies the physical start address of RAM. Must always `pram` specifies the physical start address of RAM. Must always
be present, and should be the same as PHYS_OFFSET. be present, and should be the same as PHYS_OFFSET.
`pio' is the physical address of an 8MB region containing IO for `pio` is the physical address of an 8MB region containing IO for
use with the debugging macros in arch/arm/kernel/debug-armv.S. use with the debugging macros in arch/arm/kernel/debug-armv.S.
`vio' is the virtual address of the 8MB debugging region. `vio` is the virtual address of the 8MB debugging region.
It is expected that the debugging region will be re-initialised It is expected that the debugging region will be re-initialised
by the architecture specific code later in the code (via the by the architecture specific code later in the code (via the
@ -132,4 +135,3 @@ MAPIO(func)
INITIRQ(func) INITIRQ(func)
Machine specific function to initialise interrupts. Machine specific function to initialise interrupts.

20
Documentation/arm/pxa/mfp.txt → Documentation/arm/pxa/mfp.rst
View file

@ -1,4 +1,6 @@
==============================================
MFP Configuration for PXA2xx/PXA3xx Processors MFP Configuration for PXA2xx/PXA3xx Processors
==============================================
Eric Miao <eric.miao@marvell.com> Eric Miao <eric.miao@marvell.com>
@ -7,14 +9,14 @@ later PXA series processors. This document describes the existing MFP API,
and how board/platform driver authors could make use of it. and how board/platform driver authors could make use of it.
Basic Concept Basic Concept
=============== =============
Unlike the GPIO alternate function settings on PXA25x and PXA27x, a new MFP Unlike the GPIO alternate function settings on PXA25x and PXA27x, a new MFP
mechanism is introduced from PXA3xx to completely move the pin-mux functions mechanism is introduced from PXA3xx to completely move the pin-mux functions
out of the GPIO controller. In addition to pin-mux configurations, the MFP out of the GPIO controller. In addition to pin-mux configurations, the MFP
also controls the low power state, driving strength, pull-up/down and event also controls the low power state, driving strength, pull-up/down and event
detection of each pin. Below is a diagram of internal connections between detection of each pin. Below is a diagram of internal connections between
the MFP logic and the remaining SoC peripherals: the MFP logic and the remaining SoC peripherals::
+--------+ +--------+
| |--(GPIO19)--+ | |--(GPIO19)--+
@ -70,7 +72,7 @@ mean it is a GPIO signal, and by MFP<xxx> or pin xxx, we mean a physical
pad (or ball). pad (or ball).
MFP API Usage MFP API Usage
=============== =============
For board code writers, here are some guidelines: For board code writers, here are some guidelines:
@ -94,7 +96,7 @@ For board code writers, here are some guidelines:
PXA310 supporting some additional ones), thus the difference is actually PXA310 supporting some additional ones), thus the difference is actually
covered in a single mfp-pxa300.h. covered in a single mfp-pxa300.h.
2. prepare an array for the initial pin configurations, e.g.: 2. prepare an array for the initial pin configurations, e.g.::
static unsigned long mainstone_pin_config[] __initdata = { static unsigned long mainstone_pin_config[] __initdata = {
/* Chip Select */ /* Chip Select */
@ -148,12 +150,12 @@ For board code writers, here are some guidelines:
MFP on PXA3xx MFP on PXA3xx
=============== =============
Every external I/O pad on PXA3xx (excluding those for special purpose) has Every external I/O pad on PXA3xx (excluding those for special purpose) has
one MFP logic associated, and is controlled by one MFP register (MFPR). one MFP logic associated, and is controlled by one MFP register (MFPR).
The MFPR has the following bit definitions (for PXA300/PXA310/PXA320): The MFPR has the following bit definitions (for PXA300/PXA310/PXA320)::
31 16 15 14 13 12 11 10 9 8 7 6 5 4 3 2 1 0 31 16 15 14 13 12 11 10 9 8 7 6 5 4 3 2 1 0
+-------------------------+--+--+--+--+--+--+--+--+--+--+--+--+--+--+--+--+ +-------------------------+--+--+--+--+--+--+--+--+--+--+--+--+--+--+--+--+
@ -184,7 +186,7 @@ The MFPR has the following bit definitions (for PXA300/PXA310/PXA320):
0b007 - fast 10mA 0b007 - fast 10mA
MFP Design for PXA2xx/PXA3xx MFP Design for PXA2xx/PXA3xx
============================== ============================
Due to the difference of pin-mux handling between PXA2xx and PXA3xx, a unified Due to the difference of pin-mux handling between PXA2xx and PXA3xx, a unified
MFP API is introduced to cover both series of processors. MFP API is introduced to cover both series of processors.
@ -230,7 +232,7 @@ make them effective there-after.
----------------- -----------------
The following comments are copied from mfp.h (see the actual source code The following comments are copied from mfp.h (see the actual source code
for most updated info) for most updated info)::
/* /*
* a possible MFP configuration is represented by a 32-bit integer * a possible MFP configuration is represented by a 32-bit integer
@ -259,7 +261,7 @@ make them effective there-after.
* pin drive strength and low power mode * pin drive strength and low power mode
*/ */
Examples of pin configurations are: Examples of pin configurations are::
#define GPIO94_SSP3_RXD MFP_CFG_X(GPIO94, AF1, DS08X, FLOAT) #define GPIO94_SSP3_RXD MFP_CFG_X(GPIO94, AF1, DS08X, FLOAT)

14
Documentation/arm/SA1100/ADSBitsy → Documentation/arm/sa1100/adsbitsy.rst
View file

@ -1,4 +1,7 @@
===============================
ADS Bitsy Single Board Computer ADS Bitsy Single Board Computer
===============================
(It is different from Bitsy(iPAQ) of Compaq) (It is different from Bitsy(iPAQ) of Compaq)
For more details, contact Applied Data Systems or see For more details, contact Applied Data Systems or see
@ -15,7 +18,9 @@ The kernel zImage is linked to be loaded and executed at 0xc0400000.
Linux can be used with the ADS BootLoader that ships with the Linux can be used with the ADS BootLoader that ships with the
newer rev boards. See their documentation on how to load Linux. newer rev boards. See their documentation on how to load Linux.
Supported peripherals: Supported peripherals
=====================
- SA1100 LCD frame buffer (8/16bpp...sort of) - SA1100 LCD frame buffer (8/16bpp...sort of)
- SA1111 USB Master - SA1111 USB Master
- SA1100 serial port - SA1100 serial port
@ -25,10 +30,13 @@ Supported peripherals:
- serial ports (ttyS[0-2]) - serial ports (ttyS[0-2])
- ttyS0 is default for serial console - ttyS0 is default for serial console
To do: To do
=====
- everything else! :-) - everything else! :-)
Notes: Notes
=====
- The flash on board is divided into 3 partitions. - The flash on board is divided into 3 partitions.
You should be careful to use flash on board. You should be careful to use flash on board.

115
Documentation/arm/SA1100/Assabet → Documentation/arm/sa1100/assabet.rst
View file

@ -1,3 +1,4 @@
============================================
The Intel Assabet (SA-1110 evaluation) board The Intel Assabet (SA-1110 evaluation) board
============================================ ============================================
@ -11,7 +12,7 @@ http://www.cs.cmu.edu/~wearable/software/assabet.html
Building the kernel Building the kernel
------------------- -------------------
To build the kernel with current defaults: To build the kernel with current defaults::
make assabet_config make assabet_config
make oldconfig make oldconfig
@ -51,9 +52,9 @@ Brief examples on how to boot Linux with RedBoot are shown below. But first
you need to have RedBoot installed in your flash memory. A known to work you need to have RedBoot installed in your flash memory. A known to work
precompiled RedBoot binary is available from the following location: precompiled RedBoot binary is available from the following location:
ftp://ftp.netwinder.org/users/n/nico/ - ftp://ftp.netwinder.org/users/n/nico/
ftp://ftp.arm.linux.org.uk/pub/linux/arm/people/nico/ - ftp://ftp.arm.linux.org.uk/pub/linux/arm/people/nico/
ftp://ftp.handhelds.org/pub/linux/arm/sa-1100-patches/ - ftp://ftp.handhelds.org/pub/linux/arm/sa-1100-patches/
Look for redboot-assabet*.tgz. Some installation infos are provided in Look for redboot-assabet*.tgz. Some installation infos are provided in
redboot-assabet*.txt. redboot-assabet*.txt.
@ -71,12 +72,12 @@ Socket Communications Inc.), you should strongly consider using it for TFTP
file transfers. You must insert it before RedBoot runs since it can't detect file transfers. You must insert it before RedBoot runs since it can't detect
it dynamically. it dynamically.
To initialize the flash directory: To initialize the flash directory::
fis init -f fis init -f
To initialize the non-volatile settings, like whether you want to use BOOTP or To initialize the non-volatile settings, like whether you want to use BOOTP or
a static IP address, etc, use this command: a static IP address, etc, use this command::
fconfig -i fconfig -i
@ -85,15 +86,15 @@ Writing a kernel image into flash
--------------------------------- ---------------------------------
First, the kernel image must be loaded into RAM. If you have the zImage file First, the kernel image must be loaded into RAM. If you have the zImage file
available on a TFTP server: available on a TFTP server::
load zImage -r -b 0x100000 load zImage -r -b 0x100000
If you rather want to use Y-Modem upload over the serial port: If you rather want to use Y-Modem upload over the serial port::
load -m ymodem -r -b 0x100000 load -m ymodem -r -b 0x100000
To write it to flash: To write it to flash::
fis create "Linux kernel" -b 0x100000 -l 0xc0000 fis create "Linux kernel" -b 0x100000 -l 0xc0000
@ -102,18 +103,18 @@ Booting the kernel
------------------ ------------------
The kernel still requires a filesystem to boot. A ramdisk image can be loaded The kernel still requires a filesystem to boot. A ramdisk image can be loaded
as follows: as follows::
load ramdisk_image.gz -r -b 0x800000 load ramdisk_image.gz -r -b 0x800000
Again, Y-Modem upload can be used instead of TFTP by replacing the file name Again, Y-Modem upload can be used instead of TFTP by replacing the file name
by '-y ymodem'. by '-y ymodem'.
Now the kernel can be retrieved from flash like this: Now the kernel can be retrieved from flash like this::
fis load "Linux kernel" fis load "Linux kernel"
or loaded as described previously. To boot the kernel: or loaded as described previously. To boot the kernel::
exec -b 0x100000 -l 0xc0000 exec -b 0x100000 -l 0xc0000
@ -134,20 +135,20 @@ creating JFFS/JFFS2 images is available from the same site.
For instance, a sample JFFS2 image can be retrieved from the same FTP sites For instance, a sample JFFS2 image can be retrieved from the same FTP sites
mentioned below for the precompiled RedBoot image. mentioned below for the precompiled RedBoot image.
To load this file: To load this file::
load sample_img.jffs2 -r -b 0x100000 load sample_img.jffs2 -r -b 0x100000
The result should look like: The result should look like::
RedBoot> load sample_img.jffs2 -r -b 0x100000 RedBoot> load sample_img.jffs2 -r -b 0x100000
Raw file loaded 0x00100000-0x00377424 Raw file loaded 0x00100000-0x00377424
Now we must know the size of the unallocated flash: Now we must know the size of the unallocated flash::
fis free fis free
Result: Result::
RedBoot> fis free RedBoot> fis free
0x500E0000 .. 0x503C0000 0x500E0000 .. 0x503C0000
@ -156,13 +157,13 @@ The values above may be different depending on the size of the filesystem and
the type of flash. See their usage below as an example and take care of the type of flash. See their usage below as an example and take care of
substituting yours appropriately. substituting yours appropriately.
We must determine some values: We must determine some values::
size of unallocated flash: 0x503c0000 - 0x500e0000 = 0x2e0000 size of unallocated flash: 0x503c0000 - 0x500e0000 = 0x2e0000
size of the filesystem image: 0x00377424 - 0x00100000 = 0x277424 size of the filesystem image: 0x00377424 - 0x00100000 = 0x277424
We want to fit the filesystem image of course, but we also want to give it all We want to fit the filesystem image of course, but we also want to give it all
the remaining flash space as well. To write it: the remaining flash space as well. To write it::
fis unlock -f 0x500E0000 -l 0x2e0000 fis unlock -f 0x500E0000 -l 0x2e0000
fis erase -f 0x500E0000 -l 0x2e0000 fis erase -f 0x500E0000 -l 0x2e0000
@ -171,7 +172,7 @@ the remaining flash space as well. To write it:
Now the filesystem is associated to a MTD "partition" once Linux has discovered Now the filesystem is associated to a MTD "partition" once Linux has discovered
what they are in the boot process. From Redboot, the 'fis list' command what they are in the boot process. From Redboot, the 'fis list' command
displays them: displays them::
RedBoot> fis list RedBoot> fis list
Name FLASH addr Mem addr Length Entry point Name FLASH addr Mem addr Length Entry point
@ -181,7 +182,7 @@ FIS directory 0x503E0000 0x503E0000 0x00020000 0x00000000
Linux kernel 0x50020000 0x00100000 0x000C0000 0x00000000 Linux kernel 0x50020000 0x00100000 0x000C0000 0x00000000
JFFS2 0x500E0000 0x500E0000 0x002E0000 0x00000000 JFFS2 0x500E0000 0x500E0000 0x002E0000 0x00000000
However Linux should display something like: However Linux should display something like::
SA1100 flash: probing 32-bit flash bus SA1100 flash: probing 32-bit flash bus
SA1100 flash: Found 2 x16 devices at 0x0 in 32-bit mode SA1100 flash: Found 2 x16 devices at 0x0 in 32-bit mode
@ -196,7 +197,7 @@ Creating 5 MTD partitions on "SA1100 flash":
What's important here is the position of the partition we are interested in, What's important here is the position of the partition we are interested in,
which is the third one. Within Linux, this correspond to /dev/mtdblock2. which is the third one. Within Linux, this correspond to /dev/mtdblock2.
Therefore to boot Linux with the kernel and its root filesystem in flash, we Therefore to boot Linux with the kernel and its root filesystem in flash, we
need this RedBoot command: need this RedBoot command::
fis load "Linux kernel" fis load "Linux kernel"
exec -b 0x100000 -l 0xc0000 -c "root=/dev/mtdblock2" exec -b 0x100000 -l 0xc0000 -c "root=/dev/mtdblock2"
@ -218,7 +219,7 @@ time the Assabet is rebooted. Therefore it's possible to automate the boot
process using RedBoot's scripting capability. process using RedBoot's scripting capability.
For example, I use this to boot Linux with both the kernel and the ramdisk For example, I use this to boot Linux with both the kernel and the ramdisk
images retrieved from a TFTP server on the network: images retrieved from a TFTP server on the network::
RedBoot> fconfig RedBoot> fconfig
Run script at boot: false true Run script at boot: false true
@ -240,6 +241,7 @@ Then, rebooting the Assabet is just a matter of waiting for the login prompt.
Nicolas Pitre Nicolas Pitre
nico@fluxnic.net nico@fluxnic.net
June 12, 2001 June 12, 2001
@ -249,52 +251,51 @@ Status of peripherals in -rmk tree (updated 14/10/2001)
Assabet: Assabet:
Serial ports: Serial ports:
Radio: TX, RX, CTS, DSR, DCD, RI Radio: TX, RX, CTS, DSR, DCD, RI
PM: Not tested. - PM: Not tested.
COM: TX, RX, CTS, DSR, DCD, RTS, DTR, PM - COM: TX, RX, CTS, DSR, DCD, RTS, DTR, PM
PM: Not tested. - PM: Not tested.
I2C: Implemented, not fully tested. - I2C: Implemented, not fully tested.
L3: Fully tested, pass. - L3: Fully tested, pass.
PM: Not tested. - PM: Not tested.
Video: Video:
LCD: Fully tested. PM - LCD: Fully tested. PM
(LCD doesn't like being blanked with
neponset connected) (LCD doesn't like being blanked with neponset connected)
Video out: Not fully
- Video out: Not fully
Audio: Audio:
UDA1341: UDA1341:
Playback: Fully tested, pass. - Playback: Fully tested, pass.
Record: Implemented, not tested. - Record: Implemented, not tested.
PM: Not tested. - PM: Not tested.
UCB1200: UCB1200:
Audio play: Implemented, not heavily tested. - Audio play: Implemented, not heavily tested.
Audio rec: Implemented, not heavily tested. - Audio rec: Implemented, not heavily tested.
Telco audio play: Implemented, not heavily tested. - Telco audio play: Implemented, not heavily tested.
Telco audio rec: Implemented, not heavily tested. - Telco audio rec: Implemented, not heavily tested.
POTS control: No - POTS control: No
Touchscreen: Yes - Touchscreen: Yes
PM: Not tested. - PM: Not tested.
Other: Other:
PCMCIA: - PCMCIA:
LPE: Fully tested, pass. - LPE: Fully tested, pass.
USB: No - USB: No
IRDA: - IRDA:
SIR: Fully tested, pass. - SIR: Fully tested, pass.
FIR: Fully tested, pass. - FIR: Fully tested, pass.
PM: Not tested. - PM: Not tested.
Neponset: Neponset:
Serial ports: Serial ports:
COM1,2: TX, RX, CTS, DSR, DCD, RTS, DTR - COM1,2: TX, RX, CTS, DSR, DCD, RTS, DTR
PM: Not tested. - PM: Not tested.
USB: Implemented, not heavily tested. - USB: Implemented, not heavily tested.
PCMCIA: Implemented, not heavily tested. - PCMCIA: Implemented, not heavily tested.
PM: Not tested. - CF: Implemented, not heavily tested.
CF: Implemented, not heavily tested. - PM: Not tested.
PM: Not tested.
More stuff can be found in the -np (Nicolas Pitre's) tree. More stuff can be found in the -np (Nicolas Pitre's) tree.

17
Documentation/arm/SA1100/Brutus → Documentation/arm/sa1100/brutus.rst
View file

@ -1,9 +1,13 @@
======
Brutus
======
Brutus is an evaluation platform for the SA1100 manufactured by Intel. Brutus is an evaluation platform for the SA1100 manufactured by Intel.
For more details, see: For more details, see:
http://developer.intel.com http://developer.intel.com
To compile for Brutus, you must issue the following commands: To compile for Brutus, you must issue the following commands::
make brutus_config make brutus_config
make config make config
@ -20,9 +24,8 @@ memory. Use memory address 0xd8000000 for this. Note that the file
containing the (compressed) ramdisk image must not exceed 4 MB. containing the (compressed) ramdisk image must not exceed 4 MB.
Typically, you'll need angelboot to load the kernel. Typically, you'll need angelboot to load the kernel.
The following angelboot.opt file should be used: The following angelboot.opt file should be used::
----- begin angelboot.opt -----
base 0xc0008000 base 0xc0008000
entry 0xc0008000 entry 0xc0008000
r0 0x00000000 r0 0x00000000
@ -32,9 +35,8 @@ options "9600 8N1"
baud 115200 baud 115200
otherfile ramdisk_img.gz otherfile ramdisk_img.gz
otherbase 0xd8000000 otherbase 0xd8000000
----- end angelboot.opt -----
Then load the kernel and ramdisk with: Then load the kernel and ramdisk with::
angelboot -f angelboot.opt zImage angelboot -f angelboot.opt zImage
@ -44,7 +46,9 @@ console is provided through the second Brutus serial port. To access it,
you may use minicom configured with /dev/ttyS1, 9600 baud, 8N1, no flow you may use minicom configured with /dev/ttyS1, 9600 baud, 8N1, no flow
control. control.
Currently supported: Currently supported
===================
- RS232 serial ports - RS232 serial ports
- audio output - audio output
- LCD screen - LCD screen
@ -63,4 +67,3 @@ Any contribution is welcome.
Please send patches to nico@fluxnic.net Please send patches to nico@fluxnic.net
Have Fun ! Have Fun !

10
Documentation/arm/SA1100/CERF → Documentation/arm/sa1100/cerf.rst
View file

@ -1,3 +1,7 @@
==============
CerfBoard/Cube
==============
*** The StrongARM version of the CerfBoard/Cube has been discontinued *** *** The StrongARM version of the CerfBoard/Cube has been discontinued ***
The Intrinsyc CerfBoard is a StrongARM 1110-based computer on a board The Intrinsyc CerfBoard is a StrongARM 1110-based computer on a board
@ -9,7 +13,9 @@ Intrinsyc website, http://www.intrinsyc.com.
This document describes the support in the Linux kernel for the This document describes the support in the Linux kernel for the
Intrinsyc CerfBoard. Intrinsyc CerfBoard.
Supported in this version: Supported in this version
=========================
- CompactFlash+ slot (select PCMCIA in General Setup and any options - CompactFlash+ slot (select PCMCIA in General Setup and any options
that may be required) that may be required)
- Onboard Crystal CS8900 Ethernet controller (Cerf CS8900A support in - Onboard Crystal CS8900 Ethernet controller (Cerf CS8900A support in
@ -19,7 +25,7 @@ Supported in this version:
In order to get this kernel onto your Cerf, you need a server that runs In order to get this kernel onto your Cerf, you need a server that runs
both BOOTP and TFTP. Detailed instructions should have come with your both BOOTP and TFTP. Detailed instructions should have come with your
evaluation kit on how to use the bootloader. This series of commands evaluation kit on how to use the bootloader. This series of commands
will suffice: will suffice::
make ARCH=arm CROSS_COMPILE=arm-linux- cerfcube_defconfig make ARCH=arm CROSS_COMPILE=arm-linux- cerfcube_defconfig
make ARCH=arm CROSS_COMPILE=arm-linux- zImage make ARCH=arm CROSS_COMPILE=arm-linux- zImage

25
Documentation/arm/sa1100/freebird.rst Normal file
View file

@ -0,0 +1,25 @@
========
Freebird
========
Freebird-1.1 is produced by Legend(C), Inc.
`http://web.archive.org/web/*/http://www.legend.com.cn`
and software/linux maintained by Coventive(C), Inc.
(http://www.coventive.com)
Based on the Nicolas's strongarm kernel tree.
Maintainer:
Chester Kuo
- <chester@coventive.com>
- <chester@linux.org.tw>
Author:
- Tim wu <timwu@coventive.com>
- CIH <cih@coventive.com>
- Eric Peng <ericpeng@coventive.com>
- Jeff Lee <jeff_lee@coventive.com>
- Allen Cheng
- Tony Liu <tonyliu@coventive.com>

22
Documentation/arm/SA1100/GraphicsClient → Documentation/arm/sa1100/graphicsclient.rst
View file

@ -1,4 +1,6 @@
=============================================
ADS GraphicsClient Plus Single Board Computer ADS GraphicsClient Plus Single Board Computer
=============================================
For more details, contact Applied Data Systems or see For more details, contact Applied Data Systems or see
http://www.applieddata.net/products.html http://www.applieddata.net/products.html
@ -15,7 +17,7 @@ Use 'make graphicsclient_config' before any 'make config'. This will set up
defaults for GraphicsClient Plus support. defaults for GraphicsClient Plus support.
The kernel zImage is linked to be loaded and executed at 0xc0200000. The kernel zImage is linked to be loaded and executed at 0xc0200000.
Also the following registers should have the specified values upon entry: Also the following registers should have the specified values upon entry::
r0 = 0 r0 = 0
r1 = 29 (this is the GraphicsClient architecture number) r1 = 29 (this is the GraphicsClient architecture number)
@ -31,9 +33,8 @@ as outlined below. In any case, if you're planning on deploying
something en masse, you should probably get the newer board. something en masse, you should probably get the newer board.
If using Angel on the older boards, here is a typical angel.opt option file If using Angel on the older boards, here is a typical angel.opt option file
if the kernel is loaded through the Angel Debug Monitor: if the kernel is loaded through the Angel Debug Monitor::
----- begin angelboot.opt -----
base 0xc0200000 base 0xc0200000
entry 0xc0200000 entry 0xc0200000
r0 0x00000000 r0 0x00000000
@ -44,10 +45,9 @@ baud 115200
#otherfile ramdisk.gz #otherfile ramdisk.gz
#otherbase 0xc0800000 #otherbase 0xc0800000
exec minicom exec minicom
----- end angelboot.opt -----
Then the kernel (and ramdisk if otherfile/otherbase lines above are Then the kernel (and ramdisk if otherfile/otherbase lines above are
uncommented) would be loaded with: uncommented) would be loaded with::
angelboot -f angelboot.opt zImage angelboot -f angelboot.opt zImage
@ -59,7 +59,9 @@ If any other bootloader is used, ensure it accomplish the same, especially
for r0/r1 register values before jumping into the kernel. for r0/r1 register values before jumping into the kernel.
Supported peripherals: Supported peripherals
=====================
- SA1100 LCD frame buffer (8/16bpp...sort of) - SA1100 LCD frame buffer (8/16bpp...sort of)
- on-board SMC 92C96 ethernet NIC - on-board SMC 92C96 ethernet NIC
- SA1100 serial port - SA1100 serial port
@ -74,11 +76,14 @@ Supported peripherals:
See http://www.eurotech-inc.com/linux-sbc.asp for IOCTL documentation See http://www.eurotech-inc.com/linux-sbc.asp for IOCTL documentation
and example user space code. ps/2 keybd is multiplexed through this driver and example user space code. ps/2 keybd is multiplexed through this driver
To do: To do
=====
- UCB1200 audio with new ucb_generic layer - UCB1200 audio with new ucb_generic layer
- everything else! :-) - everything else! :-)
Notes: Notes
=====
- The flash on board is divided into 3 partitions. mtd0 is where - The flash on board is divided into 3 partitions. mtd0 is where
the ADS boot ROM and zImage is stored. It's been marked as the ADS boot ROM and zImage is stored. It's been marked as
@ -95,4 +100,3 @@ Notes:
fixed soon. fixed soon.
Any contribution can be sent to nico@fluxnic.net and will be greatly welcome! Any contribution can be sent to nico@fluxnic.net and will be greatly welcome!

13
Documentation/arm/SA1100/GraphicsMaster → Documentation/arm/sa1100/graphicsmaster.rst
View file

@ -1,4 +1,6 @@
========================================
ADS GraphicsMaster Single Board Computer ADS GraphicsMaster Single Board Computer
========================================
For more details, contact Applied Data Systems or see For more details, contact Applied Data Systems or see
http://www.applieddata.net/products.html http://www.applieddata.net/products.html
@ -15,7 +17,9 @@ The kernel zImage is linked to be loaded and executed at 0xc0400000.
Linux can be used with the ADS BootLoader that ships with the Linux can be used with the ADS BootLoader that ships with the
newer rev boards. See their documentation on how to load Linux. newer rev boards. See their documentation on how to load Linux.
Supported peripherals: Supported peripherals
=====================
- SA1100 LCD frame buffer (8/16bpp...sort of) - SA1100 LCD frame buffer (8/16bpp...sort of)
- SA1111 USB Master - SA1111 USB Master
- on-board SMC 92C96 ethernet NIC - on-board SMC 92C96 ethernet NIC
@ -31,10 +35,13 @@ Supported peripherals:
See http://www.eurotech-inc.com/linux-sbc.asp for IOCTL documentation See http://www.eurotech-inc.com/linux-sbc.asp for IOCTL documentation
and example user space code. ps/2 keybd is multiplexed through this driver and example user space code. ps/2 keybd is multiplexed through this driver
To do: To do
=====
- everything else! :-) - everything else! :-)
Notes: Notes
=====
- The flash on board is divided into 3 partitions. mtd0 is where - The flash on board is divided into 3 partitions. mtd0 is where
the zImage is stored. It's been marked as read-only to keep you the zImage is stored. It's been marked as read-only to keep you

8
Documentation/arm/SA1100/HUW_WEBPANEL → Documentation/arm/sa1100/huw_webpanel.rst
View file

@ -1,9 +1,14 @@
=======================
Hoeft & Wessel Webpanel
=======================
The HUW_WEBPANEL is a product of the german company Hoeft & Wessel AG The HUW_WEBPANEL is a product of the german company Hoeft & Wessel AG
If you want more information, please visit If you want more information, please visit
http://www.hoeft-wessel.de http://www.hoeft-wessel.de
To build the kernel: To build the kernel::
make huw_webpanel_config make huw_webpanel_config
make oldconfig make oldconfig
[accept all defaults] [accept all defaults]
@ -14,4 +19,3 @@ Roman Jordan jor@hoeft-wessel.de
Christoph Schulz schu@hoeft-wessel.de Christoph Schulz schu@hoeft-wessel.de
2000/12/18/ 2000/12/18/

23
Documentation/arm/sa1100/index.rst Normal file
View file

@ -0,0 +1,23 @@
====================
Intel StrongARM 1100
====================
.. toctree::
:maxdepth: 1
adsbitsy
assabet
brutus
cerf
freebird
graphicsclient
graphicsmaster
huw_webpanel
itsy
lart
nanoengine
pangolin
pleb
serial_uart
tifon
yopy

10
Documentation/arm/SA1100/Itsy → Documentation/arm/sa1100/itsy.rst
View file

@ -1,3 +1,7 @@
====
Itsy
====
Itsy is a research project done by the Western Research Lab, and Systems Itsy is a research project done by the Western Research Lab, and Systems
Research Center in Palo Alto, CA. The Itsy project is one of several Research Center in Palo Alto, CA. The Itsy project is one of several
research projects at Compaq that are related to pocket computing. research projects at Compaq that are related to pocket computing.
@ -7,6 +11,7 @@ For more information, see:
http://www.hpl.hp.com/downloads/crl/itsy/ http://www.hpl.hp.com/downloads/crl/itsy/
Notes on initial 2.4 Itsy support (8/27/2000) : Notes on initial 2.4 Itsy support (8/27/2000) :
The port was done on an Itsy version 1.5 machine with a daughtercard with The port was done on an Itsy version 1.5 machine with a daughtercard with
64 Meg of DRAM and 32 Meg of Flash. The initial work includes support for 64 Meg of DRAM and 32 Meg of Flash. The initial work includes support for
serial console (to see what you're doing). No other devices have been serial console (to see what you're doing). No other devices have been
@ -18,8 +23,10 @@ Finally, you will need to cd to arch/arm/boot/tools and execute a make there
to build the params-itsy program used to boot the kernel. to build the params-itsy program used to boot the kernel.
In order to install the port of 2.4 to the itsy, You will need to set the In order to install the port of 2.4 to the itsy, You will need to set the
configuration parameters in the monitor as follows: configuration parameters in the monitor as follows::
Arg 1:0x08340000, Arg2: 0xC0000000, Arg3:18 (0x12), Arg4:0 Arg 1:0x08340000, Arg2: 0xC0000000, Arg3:18 (0x12), Arg4:0
Make sure the start-routine address is set to 0x00060000. Make sure the start-routine address is set to 0x00060000.
Next, flash the params-itsy program to 0x00060000 ("p 1 0x00060000" in the Next, flash the params-itsy program to 0x00060000 ("p 1 0x00060000" in the
@ -29,6 +36,7 @@ flash menu) Flash the kernel in arch/arm/boot/zImage into 0x08340000
handhelds.org. handhelds.org.
The serial connection we established was at: The serial connection we established was at:
8-bit data, no parity, 1 stop bit(s), 115200.00 b/s. in the monitor, in the 8-bit data, no parity, 1 stop bit(s), 115200.00 b/s. in the monitor, in the
params-itsy program, and in the kernel itself. This can be changed, but params-itsy program, and in the kernel itself. This can be changed, but
not easily. The monitor parameters are easily changed, the params program not easily. The monitor parameters are easily changed, the params program

3
Documentation/arm/SA1100/LART → Documentation/arm/sa1100/lart.rst
View file

@ -1,5 +1,6 @@
====================================
Linux Advanced Radio Terminal (LART) Linux Advanced Radio Terminal (LART)
------------------------------------ ====================================
The LART is a small (7.5 x 10cm) SA-1100 board, designed for embedded The LART is a small (7.5 x 10cm) SA-1100 board, designed for embedded
applications. It has 32 MB DRAM, 4MB Flash ROM, double RS232 and all applications. It has 32 MB DRAM, 4MB Flash ROM, double RS232 and all

4
Documentation/arm/SA1100/nanoEngine → Documentation/arm/sa1100/nanoengine.rst
View file

@ -1,5 +1,6 @@
==========
nanoEngine nanoEngine
---------- ==========
"nanoEngine" is a SA1110 based single board computer from "nanoEngine" is a SA1110 based single board computer from
Bright Star Engineering Inc. See www.brightstareng.com/arm Bright Star Engineering Inc. See www.brightstareng.com/arm
@ -8,4 +9,3 @@ for more info.
Also visit Larry Doolittle's "Linux for the nanoEngine" site: Also visit Larry Doolittle's "Linux for the nanoEngine" site:
http://www.brightstareng.com/arm/nanoeng.htm http://www.brightstareng.com/arm/nanoeng.htm

10
Documentation/arm/SA1100/Pangolin → Documentation/arm/sa1100/pangolin.rst
View file

@ -1,16 +1,22 @@
========
Pangolin
========
Pangolin is a StrongARM 1110-based evaluation platform produced Pangolin is a StrongARM 1110-based evaluation platform produced
by Dialogue Technology (http://www.dialogue.com.tw/). by Dialogue Technology (http://www.dialogue.com.tw/).
It has EISA slots for ease of configuration with SDRAM/Flash It has EISA slots for ease of configuration with SDRAM/Flash
memory card, USB/Serial/Audio card, Compact Flash card, memory card, USB/Serial/Audio card, Compact Flash card,
PCMCIA/IDE card and TFT-LCD card. PCMCIA/IDE card and TFT-LCD card.
To compile for Pangolin, you must issue the following commands: To compile for Pangolin, you must issue the following commands::
make pangolin_config make pangolin_config
make oldconfig make oldconfig
make zImage make zImage
Supported peripherals: Supported peripherals
=====================
- SA1110 serial port (UART1/UART2/UART3) - SA1110 serial port (UART1/UART2/UART3)
- flash memory access - flash memory access
- compact flash driver - compact flash driver

6
Documentation/arm/SA1100/PLEB → Documentation/arm/sa1100/pleb.rst
View file

@ -1,3 +1,7 @@
====
PLEB
====
The PLEB project was started as a student initiative at the School of The PLEB project was started as a student initiative at the School of
Computer Science and Engineering, University of New South Wales to make a Computer Science and Engineering, University of New South Wales to make a
pocket computer capable of running the Linux Kernel. pocket computer capable of running the Linux Kernel.
@ -7,5 +11,3 @@ PLEB support has yet to be fully integrated.
For more information, see: For more information, see:
http://www.cse.unsw.edu.au http://www.cse.unsw.edu.au

51
Documentation/arm/sa1100/serial_uart.rst Normal file
View file

@ -0,0 +1,51 @@
==================
SA1100 serial port
==================
The SA1100 serial port had its major/minor numbers officially assigned::
> Date: Sun, 24 Sep 2000 21:40:27 -0700
> From: H. Peter Anvin <hpa@transmeta.com>
> To: Nicolas Pitre <nico@CAM.ORG>
> Cc: Device List Maintainer <device@lanana.org>
> Subject: Re: device
>
> Okay. Note that device numbers 204 and 205 are used for "low density
> serial devices", so you will have a range of minors on those majors (the
> tty device layer handles this just fine, so you don't have to worry about
> doing anything special.)
>
> So your assignments are:
>
> 204 char Low-density serial ports
> 5 = /dev/ttySA0 SA1100 builtin serial port 0
> 6 = /dev/ttySA1 SA1100 builtin serial port 1
> 7 = /dev/ttySA2 SA1100 builtin serial port 2
>
> 205 char Low-density serial ports (alternate device)
> 5 = /dev/cusa0 Callout device for ttySA0
> 6 = /dev/cusa1 Callout device for ttySA1
> 7 = /dev/cusa2 Callout device for ttySA2
>
You must create those inodes in /dev on the root filesystem used
by your SA1100-based device::
mknod ttySA0 c 204 5
mknod ttySA1 c 204 6
mknod ttySA2 c 204 7
mknod cusa0 c 205 5
mknod cusa1 c 205 6
mknod cusa2 c 205 7
In addition to the creation of the appropriate device nodes above, you
must ensure your user space applications make use of the correct device
name. The classic example is the content of the /etc/inittab file where
you might have a getty process started on ttyS0.
In this case:
- replace occurrences of ttyS0 with ttySA0, ttyS1 with ttySA1, etc.
- don't forget to add 'ttySA0', 'console', or the appropriate tty name
in /etc/securetty for root to be allowed to login as well.

4
Documentation/arm/SA1100/Tifon → Documentation/arm/sa1100/tifon.rst
View file

@ -1,7 +1,7 @@
=====
Tifon Tifon
----- =====
More info has to come... More info has to come...
Contact: Peter Danielsson <peter.danielsson@era-t.ericsson.se> Contact: Peter Danielsson <peter.danielsson@era-t.ericsson.se>

5
Documentation/arm/SA1100/Yopy → Documentation/arm/sa1100/yopy.rst
View file

@ -1,2 +1,5 @@
See http://www.yopydeveloper.org for more. ====
Yopy
====
See http://www.yopydeveloper.org for more.

1
Documentation/arm/Samsung-S3C24XX/CPUfreq.txt → Documentation/arm/samsung-s3c24xx/cpufreq.rst
View file

@ -1,3 +1,4 @@
=======================
S3C24XX CPUfreq support S3C24XX CPUfreq support
======================= =======================

1
Documentation/arm/Samsung-S3C24XX/EB2410ITX.txt → Documentation/arm/samsung-s3c24xx/eb2410itx.rst
View file

@ -1,3 +1,4 @@
===================================
Simtec Electronics EB2410ITX (BAST) Simtec Electronics EB2410ITX (BAST)
=================================== ===================================

19
Documentation/arm/Samsung-S3C24XX/GPIO.txt → Documentation/arm/samsung-s3c24xx/gpio.rst
View file

@ -1,3 +1,4 @@
====================
S3C24XX GPIO Control S3C24XX GPIO Control
==================== ====================
@ -12,7 +13,7 @@ Introduction
of the s3c2410 GPIO system, please read the Samsung provided of the s3c2410 GPIO system, please read the Samsung provided
data-sheet/users manual to find out the complete list. data-sheet/users manual to find out the complete list.
See Documentation/arm/Samsung/GPIO.txt for the core implementation. See Documentation/arm/samsung/gpio.rst for the core implementation.
GPIOLIB GPIOLIB
@ -26,16 +27,16 @@ GPIOLIB
listed below will be removed (they may be marked as __deprecated listed below will be removed (they may be marked as __deprecated
in the near future). in the near future).
The following functions now either have a s3c_ specific variant The following functions now either have a `s3c_` specific variant
or are merged into gpiolib. See the definitions in or are merged into gpiolib. See the definitions in
arch/arm/plat-samsung/include/plat/gpio-cfg.h: arch/arm/plat-samsung/include/plat/gpio-cfg.h:
s3c2410_gpio_setpin() gpio_set_value() or gpio_direction_output() - s3c2410_gpio_setpin() gpio_set_value() or gpio_direction_output()
s3c2410_gpio_getpin() gpio_get_value() or gpio_direction_input() - s3c2410_gpio_getpin() gpio_get_value() or gpio_direction_input()
s3c2410_gpio_getirq() gpio_to_irq() - s3c2410_gpio_getirq() gpio_to_irq()
s3c2410_gpio_cfgpin() s3c_gpio_cfgpin() - s3c2410_gpio_cfgpin() s3c_gpio_cfgpin()
s3c2410_gpio_getcfg() s3c_gpio_getcfg() - s3c2410_gpio_getcfg() s3c_gpio_getcfg()
s3c2410_gpio_pullup() s3c_gpio_setpull() - s3c2410_gpio_pullup() s3c_gpio_setpull()
GPIOLIB conversion GPIOLIB conversion
@ -77,7 +78,7 @@ out s3c2410 API, then here are some notes on the process.
6) s3c2410_gpio_getirq() should be directly replaceable with the 6) s3c2410_gpio_getirq() should be directly replaceable with the
gpio_to_irq() call. gpio_to_irq() call.
The s3c2410_gpio and gpio_ calls have always operated on the same gpio The s3c2410_gpio and `gpio_` calls have always operated on the same gpio
numberspace, so there is no problem with converting the gpio numbering numberspace, so there is no problem with converting the gpio numbering
between the calls. between the calls.

1
Documentation/arm/Samsung-S3C24XX/H1940.txt → Documentation/arm/samsung-s3c24xx/h1940.rst
View file

@ -1,3 +1,4 @@
=============
HP IPAQ H1940 HP IPAQ H1940
============= =============

18
Documentation/arm/samsung-s3c24xx/index.rst Normal file
View file

@ -0,0 +1,18 @@
==========================
Samsung S3C24XX SoC Family
==========================
.. toctree::
:maxdepth: 1
h1940
gpio
cpufreq
suspend
usb-host
s3c2412
eb2410itx
nand
smdk2440
s3c2413
overview

2
Documentation/arm/Samsung-S3C24XX/NAND.txt → Documentation/arm/samsung-s3c24xx/nand.rst
View file

@ -1,3 +1,4 @@
====================
S3C24XX NAND Support S3C24XX NAND Support
==================== ====================
@ -27,4 +28,3 @@ Document Author
--------------- ---------------
Ben Dooks, Copyright 2007 Simtec Electronics Ben Dooks, Copyright 2007 Simtec Electronics

9
Documentation/arm/Samsung-S3C24XX/Overview.txt → Documentation/arm/samsung-s3c24xx/overview.rst
View file

@ -1,3 +1,4 @@
==========================
S3C24XX ARM Linux Overview S3C24XX ARM Linux Overview
========================== ==========================
@ -182,7 +183,7 @@ NAND
controller. If there are any problems the latest linux-mtd controller. If there are any problems the latest linux-mtd
code can be found from http://www.linux-mtd.infradead.org/ code can be found from http://www.linux-mtd.infradead.org/
For more information see Documentation/arm/Samsung-S3C24XX/NAND.txt For more information see Documentation/arm/samsung-s3c24xx/nand.rst
SD/MMC SD/MMC
@ -221,8 +222,8 @@ GPIO
As of v2.6.34, the move towards using gpiolib support is almost As of v2.6.34, the move towards using gpiolib support is almost
complete, and very little of the old calls are left. complete, and very little of the old calls are left.
See Documentation/arm/Samsung-S3C24XX/GPIO.txt for the S3C24XX specific See Documentation/arm/samsung-s3c24xx/gpio.rst for the S3C24XX specific
support and Documentation/arm/Samsung/GPIO.txt for the core Samsung support and Documentation/arm/samsung/gpio.rst for the core Samsung
implementation. implementation.
@ -276,7 +277,7 @@ Platform Data
kmalloc()s an area of memory, and copies the __initdata kmalloc()s an area of memory, and copies the __initdata
and then sets the relevant device's platform data. Making and then sets the relevant device's platform data. Making
the function `__init` takes care of ensuring it is discarded the function `__init` takes care of ensuring it is discarded
with the rest of the initialisation code with the rest of the initialisation code::
static __init void s3c24xx_xxx_set_platdata(struct xxx_data *pd) static __init void s3c24xx_xxx_set_platdata(struct xxx_data *pd)
{ {

1
Documentation/arm/Samsung-S3C24XX/S3C2412.txt → Documentation/arm/samsung-s3c24xx/s3c2412.rst
View file

@ -1,3 +1,4 @@
==========================
S3C2412 ARM Linux Overview S3C2412 ARM Linux Overview
========================== ==========================

3
Documentation/arm/Samsung-S3C24XX/S3C2413.txt → Documentation/arm/samsung-s3c24xx/s3c2413.rst
View file

@ -1,3 +1,4 @@
==========================
S3C2413 ARM Linux Overview S3C2413 ARM Linux Overview
========================== ==========================
@ -10,7 +11,7 @@ Introduction
Camera Interface Camera Interface
--------------- ----------------
This block is currently not supported. This block is currently not supported.

1
Documentation/arm/Samsung-S3C24XX/SMDK2440.txt → Documentation/arm/samsung-s3c24xx/smdk2440.rst
View file

@ -1,3 +1,4 @@
=========================
Samsung/Meritech SMDK2440 Samsung/Meritech SMDK2440
========================= =========================

4
Documentation/arm/Samsung-S3C24XX/Suspend.txt → Documentation/arm/samsung-s3c24xx/suspend.rst
View file

@ -1,3 +1,4 @@
=======================
S3C24XX Suspend Support S3C24XX Suspend Support
======================= =======================
@ -57,7 +58,7 @@ Machine Support
and will end up initialising all compiled machines' pm init! and will end up initialising all compiled machines' pm init!
The following is an example of code used for testing wakeup from The following is an example of code used for testing wakeup from
an falling edge on IRQ_EINT0: an falling edge on IRQ_EINT0::
static irqreturn_t button_irq(int irq, void *pw) static irqreturn_t button_irq(int irq, void *pw)
@ -134,4 +135,3 @@ Document Author
--------------- ---------------
Ben Dooks, Copyright 2004 Simtec Electronics Ben Dooks, Copyright 2004 Simtec Electronics

12
Documentation/arm/Samsung-S3C24XX/USB-Host.txt → Documentation/arm/samsung-s3c24xx/usb-host.rst
View file

@ -1,3 +1,4 @@
========================
S3C24XX USB Host support S3C24XX USB Host support
======================== ========================
@ -13,7 +14,7 @@ Configuration
Enable at least the following kernel options: Enable at least the following kernel options:
menuconfig: menuconfig::
Device Drivers ---> Device Drivers --->
USB support ---> USB support --->
@ -22,8 +23,9 @@ Configuration
.config: .config:
CONFIG_USB
CONFIG_USB_OHCI_HCD - CONFIG_USB
- CONFIG_USB_OHCI_HCD
Once these options are configured, the standard set of USB device Once these options are configured, the standard set of USB device
@ -60,17 +62,14 @@ Platform Data
The ports are numbered 0 and 1. The ports are numbered 0 and 1.
power_control: power_control:
Called to enable or disable the power on the port. Called to enable or disable the power on the port.
enable_oc: enable_oc:
Called to enable or disable the over-current monitoring. Called to enable or disable the over-current monitoring.
This should claim or release the resources being used to This should claim or release the resources being used to
check the power condition on the port, such as an IRQ. check the power condition on the port, such as an IRQ.
report_oc: report_oc:
The OHCI driver fills this field in for the over-current code The OHCI driver fills this field in for the over-current code
to call when there is a change to the over-current state on to call when there is a change to the over-current state on
an port. The ports argument is a bitmask of 1 bit per port, an port. The ports argument is a bitmask of 1 bit per port,
@ -80,7 +79,6 @@ Platform Data
ensure this is called correctly. ensure this is called correctly.
port[x]: port[x]:
This is struct describes each port, 0 or 1. The platform driver This is struct describes each port, 0 or 1. The platform driver
should set the flags field of each port to S3C_HCDFLG_USED if should set the flags field of each port to S3C_HCDFLG_USED if
the port is enabled. the port is enabled.

23
Documentation/arm/Samsung/Bootloader-interface.txt → Documentation/arm/samsung/bootloader-interface.rst
View file

@ -1,7 +1,9 @@
==========================================================
Interface between kernel and boot loaders on Exynos boards Interface between kernel and boot loaders on Exynos boards
========================================================== ==========================================================
Author: Krzysztof Kozlowski Author: Krzysztof Kozlowski
Date : 6 June 2015 Date : 6 June 2015
The document tries to describe currently used interface between Linux kernel The document tries to describe currently used interface between Linux kernel
@ -17,8 +19,10 @@ executing kernel.
1. Non-Secure mode 1. Non-Secure mode
Address: sysram_ns_base_addr Address: sysram_ns_base_addr
============= ============================================ ==================
Offset Value Purpose Offset Value Purpose
============================================================================= ============= ============================================ ==================
0x08 exynos_cpu_resume_ns, mcpm_entry_point System suspend 0x08 exynos_cpu_resume_ns, mcpm_entry_point System suspend
0x0c 0x00000bad (Magic cookie) System suspend 0x0c 0x00000bad (Magic cookie) System suspend
0x1c exynos4_secondary_startup Secondary CPU boot 0x1c exynos4_secondary_startup Secondary CPU boot
@ -27,22 +31,28 @@ Offset Value Purpose
0x24 exynos_cpu_resume_ns AFTR 0x24 exynos_cpu_resume_ns AFTR
0x28 + 4*cpu 0x8 (Magic cookie, Exynos3250) AFTR 0x28 + 4*cpu 0x8 (Magic cookie, Exynos3250) AFTR
0x28 0x0 or last value during resume (Exynos542x) System suspend 0x28 0x0 or last value during resume (Exynos542x) System suspend
============= ============================================ ==================
2. Secure mode 2. Secure mode
Address: sysram_base_addr Address: sysram_base_addr
============= ============================================ ==================
Offset Value Purpose Offset Value Purpose
============================================================================= ============= ============================================ ==================
0x00 exynos4_secondary_startup Secondary CPU boot 0x00 exynos4_secondary_startup Secondary CPU boot
0x04 exynos4_secondary_startup (Exynos542x) Secondary CPU boot 0x04 exynos4_secondary_startup (Exynos542x) Secondary CPU boot
4*cpu exynos4_secondary_startup (Exynos4412) Secondary CPU boot 4*cpu exynos4_secondary_startup (Exynos4412) Secondary CPU boot
0x20 exynos_cpu_resume (Exynos4210 r1.0) AFTR 0x20 exynos_cpu_resume (Exynos4210 r1.0) AFTR
0x24 0xfcba0d10 (Magic cookie, Exynos4210 r1.0) AFTR 0x24 0xfcba0d10 (Magic cookie, Exynos4210 r1.0) AFTR
============= ============================================ ==================
Address: pmu_base_addr Address: pmu_base_addr
============= ============================================ ==================
Offset Value Purpose Offset Value Purpose
============================================================================= ============= ============================================ ==================
0x0800 exynos_cpu_resume AFTR, suspend 0x0800 exynos_cpu_resume AFTR, suspend
0x0800 mcpm_entry_point (Exynos542x with MCPM) AFTR, suspend 0x0800 mcpm_entry_point (Exynos542x with MCPM) AFTR, suspend
0x0804 0xfcba0d10 (Magic cookie) AFTR 0x0804 0xfcba0d10 (Magic cookie) AFTR
@ -50,15 +60,18 @@ Offset Value Purpose
0x0814 exynos4_secondary_startup (Exynos4210 r1.1) Secondary CPU boot 0x0814 exynos4_secondary_startup (Exynos4210 r1.1) Secondary CPU boot
0x0818 0xfcba0d10 (Magic cookie, Exynos4210 r1.1) AFTR 0x0818 0xfcba0d10 (Magic cookie, Exynos4210 r1.1) AFTR
0x081C exynos_cpu_resume (Exynos4210 r1.1) AFTR 0x081C exynos_cpu_resume (Exynos4210 r1.1) AFTR
============= ============================================ ==================
3. Other (regardless of secure/non-secure mode) 3. Other (regardless of secure/non-secure mode)
Address: pmu_base_addr Address: pmu_base_addr
============= =============================== ===============================
Offset Value Purpose Offset Value Purpose
============================================================================= ============= =============================== ===============================
0x0908 Non-zero Secondary CPU boot up indicator 0x0908 Non-zero Secondary CPU boot up indicator
on Exynos3250 and Exynos542x on Exynos3250 and Exynos542x
============= =============================== ===============================
4. Glossary 4. Glossary

0
Documentation/arm/Samsung/clksrc-change-registers.awk → Documentation/arm/samsung/clksrc-change-registers.awk
View file

3
Documentation/arm/Samsung/GPIO.txt → Documentation/arm/samsung/gpio.rst
View file

@ -1,3 +1,4 @@
===========================
Samsung GPIO implementation Samsung GPIO implementation
=========================== ===========================
@ -11,7 +12,7 @@ specific calls provided alongside the drivers/gpio core.
S3C24XX (Legacy) S3C24XX (Legacy)
---------------- ----------------
See Documentation/arm/Samsung-S3C24XX/GPIO.txt for more information See Documentation/arm/samsung-s3c24xx/gpio.rst for more information
about these devices. Their implementation has been brought into line about these devices. Their implementation has been brought into line
with the core samsung implementation described in this document. with the core samsung implementation described in this document.

10
Documentation/arm/samsung/index.rst Normal file
View file

@ -0,0 +1,10 @@
===========
Samsung SoC
===========
.. toctree::
:maxdepth: 1
gpio
bootloader-interface
overview

11
Documentation/arm/Samsung/Overview.txt → Documentation/arm/samsung/overview.rst
View file

@ -1,3 +1,4 @@
==========================
Samsung ARM Linux Overview Samsung ARM Linux Overview
========================== ==========================
@ -11,7 +12,7 @@ Introduction
The currently supported SoCs are: The currently supported SoCs are:
- S3C24XX: See Documentation/arm/Samsung-S3C24XX/Overview.txt for full list - S3C24XX: See Documentation/arm/samsung-s3c24xx/overview.rst for full list
- S3C64XX: S3C6400 and S3C6410 - S3C64XX: S3C6400 and S3C6410
- S5PC110 / S5PV210 - S5PC110 / S5PV210
@ -22,7 +23,7 @@ S3C24XX Systems
There is still documentation in Documnetation/arm/Samsung-S3C24XX/ which There is still documentation in Documnetation/arm/Samsung-S3C24XX/ which
deals with the architecture and drivers specific to these devices. deals with the architecture and drivers specific to these devices.
See Documentation/arm/Samsung-S3C24XX/Overview.txt for more information See Documentation/arm/samsung-s3c24xx/overview.rst for more information
on the implementation details and specific support. on the implementation details and specific support.
@ -32,8 +33,10 @@ Configuration
A number of configurations are supplied, as there is no current way of A number of configurations are supplied, as there is no current way of
unifying all the SoCs into one kernel. unifying all the SoCs into one kernel.
s5pc110_defconfig - S5PC110 specific default configuration s5pc110_defconfig
s5pv210_defconfig - S5PV210 specific default configuration - S5PC110 specific default configuration
s5pv210_defconfig
- S5PV210 specific default configuration
Layout Layout

49
Documentation/arm/Setup → Documentation/arm/setup.rst
View file

@ -1,5 +1,6 @@
=============================================
Kernel initialisation parameters on ARM Linux Kernel initialisation parameters on ARM Linux
--------------------------------------------- =============================================
The following document describes the kernel initialisation parameter The following document describes the kernel initialisation parameter
structure, otherwise known as 'struct param_struct' which is used structure, otherwise known as 'struct param_struct' which is used
@ -14,12 +15,10 @@ There are a lot of parameters listed in there, and they are described
below: below:
page_size page_size
This parameter must be set to the page size of the machine, and This parameter must be set to the page size of the machine, and
will be checked by the kernel. will be checked by the kernel.
nr_pages nr_pages
This is the total number of pages of memory in the system. If This is the total number of pages of memory in the system. If
the memory is banked, then this should contain the total number the memory is banked, then this should contain the total number
of pages in the system. of pages in the system.
@ -28,24 +27,22 @@ below:
include this information. include this information.
ramdisk_size ramdisk_size
This is now obsolete, and should not be used. This is now obsolete, and should not be used.
flags flags
Various kernel flags, including: Various kernel flags, including:
bit 0 - 1 = mount root read only
bit 1 - unused ===== ========================
bit 2 - 0 = load ramdisk bit 0 1 = mount root read only
bit 3 - 0 = prompt for ramdisk bit 1 unused
bit 2 0 = load ramdisk
bit 3 0 = prompt for ramdisk
===== ========================
rootdev rootdev
major/minor number pair of device to mount as the root filesystem. major/minor number pair of device to mount as the root filesystem.
video_num_cols video_num_cols / video_num_rows
video_num_rows
These two together describe the character size of the dummy console, These two together describe the character size of the dummy console,
or VGA console character size. They should not be used for any other or VGA console character size. They should not be used for any other
purpose. purpose.
@ -54,66 +51,50 @@ below:
the equivalent character size of your fbcon display. This then allows the equivalent character size of your fbcon display. This then allows
all the bootup messages to be displayed correctly. all the bootup messages to be displayed correctly.
video_x video_x / video_y
video_y
This describes the character position of cursor on VGA console, and This describes the character position of cursor on VGA console, and
is otherwise unused. (should not be used for other console types, and is otherwise unused. (should not be used for other console types, and
should not be used for other purposes). should not be used for other purposes).
memc_control_reg memc_control_reg
MEMC chip control register for Acorn Archimedes and Acorn A5000 MEMC chip control register for Acorn Archimedes and Acorn A5000
based machines. May be used differently by different architectures. based machines. May be used differently by different architectures.
sounddefault sounddefault
Default sound setting on Acorn machines. May be used differently by Default sound setting on Acorn machines. May be used differently by
different architectures. different architectures.
adfsdrives adfsdrives
Number of ADFS/MFM disks. May be used differently by different Number of ADFS/MFM disks. May be used differently by different
architectures. architectures.
bytes_per_char_h bytes_per_char_h / bytes_per_char_v
bytes_per_char_v
These are now obsolete, and should not be used. These are now obsolete, and should not be used.
pages_in_bank[4] pages_in_bank[4]
Number of pages in each bank of the systems memory (used for RiscPC). Number of pages in each bank of the systems memory (used for RiscPC).
This is intended to be used on systems where the physical memory This is intended to be used on systems where the physical memory
is non-contiguous from the processors point of view. is non-contiguous from the processors point of view.
pages_in_vram pages_in_vram
Number of pages in VRAM (used on Acorn RiscPC). This value may also Number of pages in VRAM (used on Acorn RiscPC). This value may also
be used by loaders if the size of the video RAM can't be obtained be used by loaders if the size of the video RAM can't be obtained
from the hardware. from the hardware.
initrd_start initrd_start / initrd_size
initrd_size
This describes the kernel virtual start address and size of the This describes the kernel virtual start address and size of the
initial ramdisk. initial ramdisk.
rd_start rd_start
Start address in sectors of the ramdisk image on a floppy disk. Start address in sectors of the ramdisk image on a floppy disk.
system_rev system_rev
system revision number. system revision number.
system_serial_low system_serial_low / system_serial_high
system_serial_high
system 64-bit serial number system 64-bit serial number
mem_fclk_21285 mem_fclk_21285
The speed of the external oscillator to the 21285 (footbridge), The speed of the external oscillator to the 21285 (footbridge),
which control's the speed of the memory bus, timer & serial port. which control's the speed of the memory bus, timer & serial port.
Depending upon the speed of the cpu its value can be between Depending upon the speed of the cpu its value can be between
@ -121,9 +102,7 @@ below:
then a value of 50 Mhz is the default on 21285 architectures. then a value of 50 Mhz is the default on 21285 architectures.
paths[8][128] paths[8][128]
These are now obsolete, and should not be used. These are now obsolete, and should not be used.
commandline commandline
Kernel command line parameters. Details can be found elsewhere. Kernel command line parameters. Details can be found elsewhere.

0
Documentation/arm/SH-Mobile/.gitignore → Documentation/arm/sh-mobile/.gitignore vendored
View file

6
Documentation/arm/SPEAr/overview.txt → Documentation/arm/spear/overview.rst
View file

@ -1,5 +1,6 @@
========================
SPEAr ARM Linux Overview SPEAr ARM Linux Overview
========================== ========================
Introduction Introduction
------------ ------------
@ -34,7 +35,8 @@ Introduction
------------- -------------
A generic configuration is provided for each machine, and can be used as the A generic configuration is provided for each machine, and can be used as the
default by default by::
make spear13xx_defconfig make spear13xx_defconfig
make spear3xx_defconfig make spear3xx_defconfig
make spear6xx_defconfig make spear6xx_defconfig

7
Documentation/arm/sti/overview.txt → Documentation/arm/sti/overview.rst
View file

@ -1,5 +1,6 @@
======================
STi ARM Linux Overview STi ARM Linux Overview
========================== ======================
Introduction Introduction
------------ ------------
@ -14,11 +15,13 @@ Introduction
------------- -------------
A generic configuration is provided for both STiH415/416, and can be used as the A generic configuration is provided for both STiH415/416, and can be used as the
default by default by::
make stih41x_defconfig make stih41x_defconfig
Layout Layout
------ ------
All the files for multiple machine families (STiH415, STiH416, and STiG125) All the files for multiple machine families (STiH415, STiH416, and STiG125)
are located in the platform code contained in arch/arm/mach-sti are located in the platform code contained in arch/arm/mach-sti

1
Documentation/arm/sti/stih407-overview.txt → Documentation/arm/sti/stih407-overview.rst
View file

@ -1,3 +1,4 @@
================
STiH407 Overview STiH407 Overview
================ ================

4
Documentation/arm/sti/stih415-overview.txt → Documentation/arm/sti/stih415-overview.rst
View file

@ -1,3 +1,4 @@
================
STiH415 Overview STiH415 Overview
================ ================
@ -7,6 +8,7 @@ Introduction
The STiH415 is the next generation of HD, AVC set-top box processors The STiH415 is the next generation of HD, AVC set-top box processors
for satellite, cable, terrestrial and IP-STB markets. for satellite, cable, terrestrial and IP-STB markets.
Features Features:
- ARM Cortex-A9 1.0 GHz, dual-core CPU - ARM Cortex-A9 1.0 GHz, dual-core CPU
- SATA2x2,USB 2.0x3, PCIe, Gbit Ethernet MACx2 - SATA2x2,USB 2.0x3, PCIe, Gbit Ethernet MACx2

1
Documentation/arm/sti/stih416-overview.txt → Documentation/arm/sti/stih416-overview.rst
View file

@ -1,3 +1,4 @@
================
STiH416 Overview STiH416 Overview
================ ================

1
Documentation/arm/sti/stih418-overview.txt → Documentation/arm/sti/stih418-overview.rst
View file

@ -1,3 +1,4 @@
================
STiH418 Overview STiH418 Overview
================ ================

2
Documentation/arm/stm32/overview.rst
View file

@ -1,5 +1,3 @@
:orphan:
======================== ========================
STM32 ARM Linux Overview STM32 ARM Linux Overview
======================== ========================

7
Documentation/arm/stm32/stm32f429-overview.rst
View file

@ -1,5 +1,4 @@
:orphan: ==================
STM32F429 Overview STM32F429 Overview
================== ==================
@ -23,6 +22,4 @@ Datasheet and reference manual are publicly available on ST website (STM32F429_)
.. _STM32F429: http://www.st.com/web/en/catalog/mmc/FM141/SC1169/SS1577/LN1806?ecmp=stm32f429-439_pron_pr-ces2014_nov2013 .. _STM32F429: http://www.st.com/web/en/catalog/mmc/FM141/SC1169/SS1577/LN1806?ecmp=stm32f429-439_pron_pr-ces2014_nov2013
:Authors: :Authors: Maxime Coquelin <mcoquelin.stm32@gmail.com>
Maxime Coquelin <mcoquelin.stm32@gmail.com>

7
Documentation/arm/stm32/stm32f746-overview.rst
View file

@ -1,5 +1,4 @@
:orphan: ==================
STM32F746 Overview STM32F746 Overview
================== ==================
@ -30,6 +29,4 @@ Datasheet and reference manual are publicly available on ST website (STM32F746_)
.. _STM32F746: http://www.st.com/content/st_com/en/products/microcontrollers/stm32-32-bit-arm-cortex-mcus/stm32f7-series/stm32f7x6/stm32f746ng.html .. _STM32F746: http://www.st.com/content/st_com/en/products/microcontrollers/stm32-32-bit-arm-cortex-mcus/stm32f7-series/stm32f7x6/stm32f746ng.html
:Authors: :Authors: Alexandre Torgue <alexandre.torgue@st.com>
Alexandre Torgue <alexandre.torgue@st.com>

7
Documentation/arm/stm32/stm32f769-overview.rst
View file

@ -1,5 +1,4 @@
:orphan: ==================
STM32F769 Overview STM32F769 Overview
================== ==================
@ -32,6 +31,4 @@ Datasheet and reference manual are publicly available on ST website (STM32F769_)
.. _STM32F769: http://www.st.com/content/st_com/en/products/microcontrollers/stm32-32-bit-arm-cortex-mcus/stm32-high-performance-mcus/stm32f7-series/stm32f7x9/stm32f769ni.html .. _STM32F769: http://www.st.com/content/st_com/en/products/microcontrollers/stm32-32-bit-arm-cortex-mcus/stm32-high-performance-mcus/stm32f7-series/stm32f7x9/stm32f769ni.html
:Authors: :Authors: Alexandre Torgue <alexandre.torgue@st.com>
Alexandre Torgue <alexandre.torgue@st.com>

7
Documentation/arm/stm32/stm32h743-overview.rst
View file

@ -1,5 +1,4 @@
:orphan: ==================
STM32H743 Overview STM32H743 Overview
================== ==================
@ -31,6 +30,4 @@ Datasheet and reference manual are publicly available on ST website (STM32H743_)
.. _STM32H743: http://www.st.com/en/microcontrollers/stm32h7x3.html?querycriteria=productId=LN2033 .. _STM32H743: http://www.st.com/en/microcontrollers/stm32h7x3.html?querycriteria=productId=LN2033
:Authors: :Authors: Alexandre Torgue <alexandre.torgue@st.com>
Alexandre Torgue <alexandre.torgue@st.com>

3
Documentation/arm/stm32/stm32mp157-overview.rst
View file

@ -1,5 +1,4 @@
:orphan: ===================
STM32MP157 Overview STM32MP157 Overview
=================== ===================

98
Documentation/arm/sunxi/README → Documentation/arm/sunxi.rst
View file

@ -1,3 +1,4 @@
==================
ARM Allwinner SoCs ARM Allwinner SoCs
================== ==================
@ -10,93 +11,140 @@ SunXi family
Linux kernel mach directory: arch/arm/mach-sunxi Linux kernel mach directory: arch/arm/mach-sunxi
Flavors: Flavors:
* ARM926 based SoCs * ARM926 based SoCs
- Allwinner F20 (sun3i) - Allwinner F20 (sun3i)
+ Not Supported
* Not Supported
* ARM Cortex-A8 based SoCs * ARM Cortex-A8 based SoCs
- Allwinner A10 (sun4i) - Allwinner A10 (sun4i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A10/A10%20Datasheet%20-%20v1.21%20%282012-04-06%29.pdf http://dl.linux-sunxi.org/A10/A10%20Datasheet%20-%20v1.21%20%282012-04-06%29.pdf
+ User Manual * User Manual
http://dl.linux-sunxi.org/A10/A10%20User%20Manual%20-%20v1.20%20%282012-04-09%2c%20DECRYPTED%29.pdf http://dl.linux-sunxi.org/A10/A10%20User%20Manual%20-%20v1.20%20%282012-04-09%2c%20DECRYPTED%29.pdf
- Allwinner A10s (sun5i) - Allwinner A10s (sun5i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A10s/A10s%20Datasheet%20-%20v1.20%20%282012-03-27%29.pdf http://dl.linux-sunxi.org/A10s/A10s%20Datasheet%20-%20v1.20%20%282012-03-27%29.pdf
- Allwinner A13 / R8 (sun5i) - Allwinner A13 / R8 (sun5i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A13/A13%20Datasheet%20-%20v1.12%20%282012-03-29%29.pdf http://dl.linux-sunxi.org/A13/A13%20Datasheet%20-%20v1.12%20%282012-03-29%29.pdf
+ User Manual * User Manual
http://dl.linux-sunxi.org/A13/A13%20User%20Manual%20-%20v1.2%20%282013-01-08%29.pdf http://dl.linux-sunxi.org/A13/A13%20User%20Manual%20-%20v1.2%20%282013-01-08%29.pdf
- Next Thing Co GR8 (sun5i) - Next Thing Co GR8 (sun5i)
* Single ARM Cortex-A7 based SoCs * Single ARM Cortex-A7 based SoCs
- Allwinner V3s (sun8i) - Allwinner V3s (sun8i)
+ Datasheet
* Datasheet
http://linux-sunxi.org/File:Allwinner_V3s_Datasheet_V1.0.pdf http://linux-sunxi.org/File:Allwinner_V3s_Datasheet_V1.0.pdf
* Dual ARM Cortex-A7 based SoCs * Dual ARM Cortex-A7 based SoCs
- Allwinner A20 (sun7i) - Allwinner A20 (sun7i)
+ User Manual
* User Manual
http://dl.linux-sunxi.org/A20/A20%20User%20Manual%202013-03-22.pdf http://dl.linux-sunxi.org/A20/A20%20User%20Manual%202013-03-22.pdf
- Allwinner A23 (sun8i) - Allwinner A23 (sun8i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A23/A23%20Datasheet%20V1.0%2020130830.pdf http://dl.linux-sunxi.org/A23/A23%20Datasheet%20V1.0%2020130830.pdf
+ User Manual
* User Manual
http://dl.linux-sunxi.org/A23/A23%20User%20Manual%20V1.0%2020130830.pdf http://dl.linux-sunxi.org/A23/A23%20User%20Manual%20V1.0%2020130830.pdf
* Quad ARM Cortex-A7 based SoCs * Quad ARM Cortex-A7 based SoCs
- Allwinner A31 (sun6i) - Allwinner A31 (sun6i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A31/A3x_release_document/A31/IC/A31%20datasheet%20V1.3%2020131106.pdf http://dl.linux-sunxi.org/A31/A3x_release_document/A31/IC/A31%20datasheet%20V1.3%2020131106.pdf
+ User Manual
* User Manual
http://dl.linux-sunxi.org/A31/A3x_release_document/A31/IC/A31%20user%20manual%20V1.1%2020130630.pdf http://dl.linux-sunxi.org/A31/A3x_release_document/A31/IC/A31%20user%20manual%20V1.1%2020130630.pdf
- Allwinner A31s (sun6i) - Allwinner A31s (sun6i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A31/A3x_release_document/A31s/IC/A31s%20datasheet%20V1.3%2020131106.pdf http://dl.linux-sunxi.org/A31/A3x_release_document/A31s/IC/A31s%20datasheet%20V1.3%2020131106.pdf
+ User Manual
* User Manual
http://dl.linux-sunxi.org/A31/A3x_release_document/A31s/IC/A31s%20User%20Manual%20%20V1.0%2020130322.pdf http://dl.linux-sunxi.org/A31/A3x_release_document/A31s/IC/A31s%20User%20Manual%20%20V1.0%2020130322.pdf
- Allwinner A33 (sun8i) - Allwinner A33 (sun8i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A33/A33%20Datasheet%20release%201.1.pdf http://dl.linux-sunxi.org/A33/A33%20Datasheet%20release%201.1.pdf
+ User Manual
* User Manual
http://dl.linux-sunxi.org/A33/A33%20user%20manual%20release%201.1.pdf http://dl.linux-sunxi.org/A33/A33%20user%20manual%20release%201.1.pdf
- Allwinner H2+ (sun8i) - Allwinner H2+ (sun8i)
+ No document available now, but is known to be working properly with
* No document available now, but is known to be working properly with
H3 drivers and memory map. H3 drivers and memory map.
- Allwinner H3 (sun8i) - Allwinner H3 (sun8i)
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/H3/Allwinner_H3_Datasheet_V1.0.pdf http://dl.linux-sunxi.org/H3/Allwinner_H3_Datasheet_V1.0.pdf
- Allwinner R40 (sun8i) - Allwinner R40 (sun8i)
+ Datasheet
* Datasheet
https://github.com/tinalinux/docs/raw/r40-v1.y/R40_Datasheet_V1.0.pdf https://github.com/tinalinux/docs/raw/r40-v1.y/R40_Datasheet_V1.0.pdf
+ User Manual
* User Manual
https://github.com/tinalinux/docs/raw/r40-v1.y/Allwinner_R40_User_Manual_V1.0.pdf https://github.com/tinalinux/docs/raw/r40-v1.y/Allwinner_R40_User_Manual_V1.0.pdf
* Quad ARM Cortex-A15, Quad ARM Cortex-A7 based SoCs * Quad ARM Cortex-A15, Quad ARM Cortex-A7 based SoCs
- Allwinner A80 - Allwinner A80
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A80/A80_Datasheet_Revision_1.0_0404.pdf http://dl.linux-sunxi.org/A80/A80_Datasheet_Revision_1.0_0404.pdf
* Octa ARM Cortex-A7 based SoCs * Octa ARM Cortex-A7 based SoCs
- Allwinner A83T - Allwinner A83T
+ Datasheet
* Datasheet
https://github.com/allwinner-zh/documents/raw/master/A83T/A83T_Datasheet_v1.3_20150510.pdf https://github.com/allwinner-zh/documents/raw/master/A83T/A83T_Datasheet_v1.3_20150510.pdf
+ User Manual
* User Manual
https://github.com/allwinner-zh/documents/raw/master/A83T/A83T_User_Manual_v1.5.1_20150513.pdf https://github.com/allwinner-zh/documents/raw/master/A83T/A83T_User_Manual_v1.5.1_20150513.pdf
* Quad ARM Cortex-A53 based SoCs * Quad ARM Cortex-A53 based SoCs
- Allwinner A64 - Allwinner A64
+ Datasheet
* Datasheet
http://dl.linux-sunxi.org/A64/A64_Datasheet_V1.1.pdf http://dl.linux-sunxi.org/A64/A64_Datasheet_V1.1.pdf
+ User Manual
* User Manual
http://dl.linux-sunxi.org/A64/Allwinner%20A64%20User%20Manual%20v1.0.pdf http://dl.linux-sunxi.org/A64/Allwinner%20A64%20User%20Manual%20v1.0.pdf

7
Documentation/arm/sunxi/clocks.txt → Documentation/arm/sunxi/clocks.rst
View file

@ -1,3 +1,4 @@
=======================================================
Frequently asked questions about the sunxi clock system Frequently asked questions about the sunxi clock system
======================================================= =======================================================
@ -12,7 +13,7 @@ A: The 24MHz oscillator allows gating to save power. Indeed, if gated
steps, one can gate it and keep the system running. Consider this steps, one can gate it and keep the system running. Consider this
simplified suspend example: simplified suspend example:
While the system is operational, you would see something like While the system is operational, you would see something like::
24MHz 32kHz 24MHz 32kHz
| |
@ -23,7 +24,7 @@ A: The 24MHz oscillator allows gating to save power. Indeed, if gated
[CPU] [CPU]
When you are about to suspend, you switch the CPU Mux to the 32kHz When you are about to suspend, you switch the CPU Mux to the 32kHz
oscillator: oscillator::
24Mhz 32kHz 24Mhz 32kHz
| | | |
@ -33,7 +34,7 @@ A: The 24MHz oscillator allows gating to save power. Indeed, if gated
| |
[CPU] [CPU]
Finally you can gate the main oscillator Finally you can gate the main oscillator::
32kHz 32kHz
| |

10
Documentation/arm/swp_emulation → Documentation/arm/swp_emulation.rst
View file

@ -11,17 +11,17 @@ sequence. If a memory access fault (an abort) occurs, a segmentation fault is
signalled to the triggering process. signalled to the triggering process.
/proc/cpu/swp_emulation holds some statistics/information, including the PID of /proc/cpu/swp_emulation holds some statistics/information, including the PID of
the last process to trigger the emulation to be invocated. For example: the last process to trigger the emulation to be invocated. For example::
---
Emulated SWP: 12 Emulated SWP: 12
Emulated SWPB: 0 Emulated SWPB: 0
Aborted SWP{B}: 1 Aborted SWP{B}: 1
Last process: 314 Last process: 314
---
NOTE: when accessing uncached shared regions, LDREX/STREX rely on an external
NOTE:
when accessing uncached shared regions, LDREX/STREX rely on an external
transaction monitoring block called a global monitor to maintain update transaction monitoring block called a global monitor to maintain update
atomicity. If your system does not implement a global monitor, this option can atomicity. If your system does not implement a global monitor, this option can
cause programs that perform SWP operations to uncached memory to deadlock, as cause programs that perform SWP operations to uncached memory to deadlock, as
the STREX operation will always fail. the STREX operation will always fail.

16
Documentation/arm/tcm.txt → Documentation/arm/tcm.rst
View file

@ -1,5 +1,7 @@
==================================================
ARM TCM (Tightly-Coupled Memory) handling in Linux ARM TCM (Tightly-Coupled Memory) handling in Linux
---- ==================================================
Written by Linus Walleij <linus.walleij@stericsson.com> Written by Linus Walleij <linus.walleij@stericsson.com>
Some ARM SoC:s have a so-called TCM (Tightly-Coupled Memory). Some ARM SoC:s have a so-called TCM (Tightly-Coupled Memory).
@ -85,17 +87,21 @@ to have functions called locally inside the TCM without
wasting space, there is also the __tcmlocalfunc prefix that wasting space, there is also the __tcmlocalfunc prefix that
will make the call relative. will make the call relative.
Variables to go into dtcm can be tagged like this: Variables to go into dtcm can be tagged like this::
int __tcmdata foo; int __tcmdata foo;
Constants can be tagged like this: Constants can be tagged like this::
int __tcmconst foo; int __tcmconst foo;
To put assembler into TCM just use To put assembler into TCM just use::
.section ".tcm.text" or .section ".tcm.data" .section ".tcm.text" or .section ".tcm.data"
respectively. respectively.
Example code: Example code::
#include <asm/tcm.h> #include <asm/tcm.h>

39
Documentation/arm/uefi.txt → Documentation/arm/uefi.rst
View file

@ -1,3 +1,7 @@
================================================
The Unified Extensible Firmware Interface (UEFI)
================================================
UEFI, the Unified Extensible Firmware Interface, is a specification UEFI, the Unified Extensible Firmware Interface, is a specification
governing the behaviours of compatible firmware interfaces. It is governing the behaviours of compatible firmware interfaces. It is
maintained by the UEFI Forum - http://www.uefi.org/. maintained by the UEFI Forum - http://www.uefi.org/.
@ -11,11 +15,13 @@ UEFI support in Linux
===================== =====================
Booting on a platform with firmware compliant with the UEFI specification Booting on a platform with firmware compliant with the UEFI specification
makes it possible for the kernel to support additional features: makes it possible for the kernel to support additional features:
- UEFI Runtime Services - UEFI Runtime Services
- Retrieving various configuration information through the standardised - Retrieving various configuration information through the standardised
interface of UEFI configuration tables. (ACPI, SMBIOS, ...) interface of UEFI configuration tables. (ACPI, SMBIOS, ...)
For actually enabling [U]EFI support, enable: For actually enabling [U]EFI support, enable:
- CONFIG_EFI=y - CONFIG_EFI=y
- CONFIG_EFI_VARS=y or m - CONFIG_EFI_VARS=y or m
@ -42,19 +48,20 @@ Instead, the kernel reads the UEFI memory map.
The stub populates the FDT /chosen node with (and the kernel scans for) the The stub populates the FDT /chosen node with (and the kernel scans for) the
following parameters: following parameters:
________________________________________________________________________________
Name | Size | Description ========================== ====== ===========================================
================================================================================ Name Size Description
linux,uefi-system-table | 64-bit | Physical address of the UEFI System Table. ========================== ====== ===========================================
-------------------------------------------------------------------------------- linux,uefi-system-table 64-bit Physical address of the UEFI System Table.
linux,uefi-mmap-start | 64-bit | Physical address of the UEFI memory map,
| | populated by the UEFI GetMemoryMap() call. linux,uefi-mmap-start 64-bit Physical address of the UEFI memory map,
-------------------------------------------------------------------------------- populated by the UEFI GetMemoryMap() call.
linux,uefi-mmap-size | 32-bit | Size in bytes of the UEFI memory map
| | pointed to in previous entry. linux,uefi-mmap-size 32-bit Size in bytes of the UEFI memory map
-------------------------------------------------------------------------------- pointed to in previous entry.
linux,uefi-mmap-desc-size | 32-bit | Size in bytes of each entry in the UEFI
| | memory map. linux,uefi-mmap-desc-size 32-bit Size in bytes of each entry in the UEFI
-------------------------------------------------------------------------------- memory map.
linux,uefi-mmap-desc-ver | 32-bit | Version of the mmap descriptor format.
-------------------------------------------------------------------------------- linux,uefi-mmap-desc-ver 32-bit Version of the mmap descriptor format.
========================== ====== ===========================================

4
Documentation/arm/VFP/release-notes.txt → Documentation/arm/vfp/release-notes.rst
View file

@ -1,7 +1,9 @@
===============================================
Release notes for Linux Kernel VFP support code Release notes for Linux Kernel VFP support code
----------------------------------------------- ===============================================
Date: 20 May 2004 Date: 20 May 2004
Author: Russell King Author: Russell King
This is the first release of the Linux Kernel VFP support code. It This is the first release of the Linux Kernel VFP support code. It

9
Documentation/arm/vlocks.txt → Documentation/arm/vlocks.rst
View file

@ -1,3 +1,4 @@
======================================
vlocks for Bare-Metal Mutual Exclusion vlocks for Bare-Metal Mutual Exclusion
====================================== ======================================
@ -26,7 +27,7 @@ started yet.
Algorithm Algorithm
--------- ---------
The easiest way to explain the vlocks algorithm is with some pseudo-code: The easiest way to explain the vlocks algorithm is with some pseudo-code::
int currently_voting[NR_CPUS] = { 0, }; int currently_voting[NR_CPUS] = { 0, };
@ -93,7 +94,7 @@ Features and limitations
number of CPUs. number of CPUs.
vlocks can be cascaded in a voting hierarchy to permit better scaling vlocks can be cascaded in a voting hierarchy to permit better scaling
if necessary, as in the following hypothetical example for 4096 CPUs: if necessary, as in the following hypothetical example for 4096 CPUs::
/* first level: local election */ /* first level: local election */
my_town = towns[(this_cpu >> 4) & 0xf]; my_town = towns[(this_cpu >> 4) & 0xf];
@ -127,12 +128,12 @@ the basic algorithm:
reduces the number of round-trips required to external memory. reduces the number of round-trips required to external memory.
In the ARM implementation, this means that we can use a single load In the ARM implementation, this means that we can use a single load
and comparison: and comparison::
LDR Rt, [Rn] LDR Rt, [Rn]
CMP Rt, #0 CMP Rt, #0
...in place of code equivalent to: ...in place of code equivalent to::
LDRB Rt, [Rn] LDRB Rt, [Rn]
CMP Rt, #0 CMP Rt, #0

2
Documentation/devicetree/bindings/arm/xen.txt
View file

@ -54,7 +54,7 @@ hypervisor {
}; };
The format and meaning of the "xen,uefi-*" parameters are similar to those in The format and meaning of the "xen,uefi-*" parameters are similar to those in
Documentation/arm/uefi.txt, which are provided by the regular UEFI stub. However Documentation/arm/uefi.rst, which are provided by the regular UEFI stub. However
they differ because they are provided by the Xen hypervisor, together with a set they differ because they are provided by the Xen hypervisor, together with a set
of UEFI runtime services implemented via hypercalls, see of UEFI runtime services implemented via hypercalls, see
http://xenbits.xen.org/docs/unstable/hypercall/x86_64/include,public,platform.h.html. http://xenbits.xen.org/docs/unstable/hypercall/x86_64/include,public,platform.h.html.

4
Documentation/devicetree/booting-without-of.txt
View file

@ -160,7 +160,7 @@ it with special cases.
of the kernel image. That entry point supports two calling of the kernel image. That entry point supports two calling
conventions. A summary of the interface is described here. A full conventions. A summary of the interface is described here. A full
description of the boot requirements is documented in description of the boot requirements is documented in
Documentation/arm/Booting Documentation/arm/booting.rst
a) ATAGS interface. Minimal information is passed from firmware a) ATAGS interface. Minimal information is passed from firmware
to the kernel with a tagged list of predefined parameters. to the kernel with a tagged list of predefined parameters.
@ -174,7 +174,7 @@ it with special cases.
b) Entry with a flattened device-tree block. Firmware loads the b) Entry with a flattened device-tree block. Firmware loads the
physical address of the flattened device tree block (dtb) into r2, physical address of the flattened device tree block (dtb) into r2,
r1 is not used, but it is considered good practice to use a valid r1 is not used, but it is considered good practice to use a valid
machine number as described in Documentation/arm/Booting. machine number as described in Documentation/arm/booting.rst.
r0 : 0 r0 : 0

1
Documentation/index.rst
View file

@ -1,3 +1,4 @@
.. The Linux Kernel documentation master file, created by .. The Linux Kernel documentation master file, created by
sphinx-quickstart on Fri Feb 12 13:51:46 2016. sphinx-quickstart on Fri Feb 12 13:51:46 2016.
You can adapt this file completely to your liking, but it should at least You can adapt this file completely to your liking, but it should at least

4
Documentation/translations/zh_CN/arm/Booting
View file

@ -1,4 +1,4 @@
Chinese translated version of Documentation/arm/Booting Chinese translated version of Documentation/arm/booting.rst
If you have any comment or update to the content, please contact the If you have any comment or update to the content, please contact the
original document maintainer directly. However, if you have a problem original document maintainer directly. However, if you have a problem
@ -9,7 +9,7 @@ or if there is a problem with the translation.
Maintainer: Russell King <linux@arm.linux.org.uk> Maintainer: Russell King <linux@arm.linux.org.uk>
Chinese maintainer: Fu Wei <tekkamanninja@gmail.com> Chinese maintainer: Fu Wei <tekkamanninja@gmail.com>
--------------------------------------------------------------------- ---------------------------------------------------------------------
Documentation/arm/Booting 的中文翻译 Documentation/arm/booting.rst 的中文翻译
如果想评论或更新本文的内容，请直接联系原文档的维护者。如果你使用英文 如果想评论或更新本文的内容，请直接联系原文档的维护者。如果你使用英文
交流有困难的话，也可以向中文版维护者求助。如果本翻译更新不及时或者翻 交流有困难的话，也可以向中文版维护者求助。如果本翻译更新不及时或者翻

4
Documentation/translations/zh_CN/arm/kernel_user_helpers.txt
View file

@ -1,4 +1,4 @@
Chinese translated version of Documentation/arm/kernel_user_helpers.txt Chinese translated version of Documentation/arm/kernel_user_helpers.rst
If you have any comment or update to the content, please contact the If you have any comment or update to the content, please contact the
original document maintainer directly. However, if you have a problem original document maintainer directly. However, if you have a problem
@ -10,7 +10,7 @@ Maintainer: Nicolas Pitre <nicolas.pitre@linaro.org>
Dave Martin <dave.martin@linaro.org> Dave Martin <dave.martin@linaro.org>
Chinese maintainer: Fu Wei <tekkamanninja@gmail.com> Chinese maintainer: Fu Wei <tekkamanninja@gmail.com>
--------------------------------------------------------------------- ---------------------------------------------------------------------
Documentation/arm/kernel_user_helpers.txt 的中文翻译 Documentation/arm/kernel_user_helpers.rst 的中文翻译
如果想评论或更新本文的内容，请直接联系原文档的维护者。如果你使用英文 如果想评论或更新本文的内容，请直接联系原文档的维护者。如果你使用英文
交流有困难的话，也可以向中文版维护者求助。如果本翻译更新不及时或者翻 交流有困难的话，也可以向中文版维护者求助。如果本翻译更新不及时或者翻

4
MAINTAINERS
View file

@ -2218,7 +2218,7 @@ F: drivers/*/*s3c64xx*
F: drivers/*/*s5pv210* F: drivers/*/*s5pv210*
F: drivers/memory/samsung/* F: drivers/memory/samsung/*
F: drivers/soc/samsung/* F: drivers/soc/samsung/*
F: Documentation/arm/Samsung/ F: Documentation/arm/samsung/
F: Documentation/devicetree/bindings/arm/samsung/ F: Documentation/devicetree/bindings/arm/samsung/
F: Documentation/devicetree/bindings/sram/samsung-sram.txt F: Documentation/devicetree/bindings/sram/samsung-sram.txt
F: Documentation/devicetree/bindings/power/pd-samsung.txt F: Documentation/devicetree/bindings/power/pd-samsung.txt
@ -11571,7 +11571,7 @@ L: linux-omap@vger.kernel.org
L: linux-fbdev@vger.kernel.org L: linux-fbdev@vger.kernel.org
S: Orphan S: Orphan
F: drivers/video/fbdev/omap2/ F: drivers/video/fbdev/omap2/
F: Documentation/arm/OMAP/DSS F: Documentation/arm/omap/dss.rst
OMAP FRAMEBUFFER SUPPORT OMAP FRAMEBUFFER SUPPORT
L: linux-fbdev@vger.kernel.org L: linux-fbdev@vger.kernel.org

2
arch/arm/Kconfig
View file

@ -2142,7 +2142,7 @@ config VFP
Say Y to include VFP support code in the kernel. This is needed Say Y to include VFP support code in the kernel. This is needed
if your hardware includes a VFP unit. if your hardware includes a VFP unit.
Please see <file:Documentation/arm/VFP/release-notes.txt> for Please see <file:Documentation/arm/vfp/release-notes.rst> for
release notes and additional status information. release notes and additional status information.
Say N if your target does not have VFP hardware. Say N if your target does not have VFP hardware.

2
arch/arm/common/mcpm_entry.c
View file

@ -21,7 +21,7 @@
/* /*
* The public API for this code is documented in arch/arm/include/asm/mcpm.h. * The public API for this code is documented in arch/arm/include/asm/mcpm.h.
* For a comprehensive description of the main algorithm used here, please * For a comprehensive description of the main algorithm used here, please
* see Documentation/arm/cluster-pm-race-avoidance.txt. * see Documentation/arm/cluster-pm-race-avoidance.rst.
*/ */
struct sync_struct mcpm_sync; struct sync_struct mcpm_sync;

2
arch/arm/common/mcpm_head.S
View file

@ -5,7 +5,7 @@
* Created by: Nicolas Pitre, March 2012 * Created by: Nicolas Pitre, March 2012
* Copyright: (C) 2012-2013 Linaro Limited * Copyright: (C) 2012-2013 Linaro Limited
* *
* Refer to Documentation/arm/cluster-pm-race-avoidance.txt * Refer to Documentation/arm/cluster-pm-race-avoidance.rst
* for details of the synchronisation algorithms used here. * for details of the synchronisation algorithms used here.
*/ */

2
arch/arm/common/vlock.S
View file

@ -6,7 +6,7 @@
* Copyright: (C) 2012-2013 Linaro Limited * Copyright: (C) 2012-2013 Linaro Limited
* *
* This algorithm is described in more detail in * This algorithm is described in more detail in
* Documentation/arm/vlocks.txt. * Documentation/arm/vlocks.rst.
*/ */
#include <linux/linkage.h> #include <linux/linkage.h>

2
arch/arm/include/asm/setup.h
View file

@ -5,7 +5,7 @@
* Copyright (C) 1997-1999 Russell King * Copyright (C) 1997-1999 Russell King
* *
* Structure passed to kernel to tell it about the * Structure passed to kernel to tell it about the
* hardware it's running on. See Documentation/arm/Setup * hardware it's running on. See Documentation/arm/setup.rst
* for more info. * for more info.
*/ */
#ifndef __ASMARM_SETUP_H #ifndef __ASMARM_SETUP_H

2
arch/arm/include/uapi/asm/setup.h
View file

@ -9,7 +9,7 @@
* published by the Free Software Foundation. * published by the Free Software Foundation.
* *
* Structure passed to kernel to tell it about the * Structure passed to kernel to tell it about the
* hardware it's running on. See Documentation/arm/Setup * hardware it's running on. See Documentation/arm/setup.rst
* for more info. * for more info.
*/ */
#ifndef _UAPI__ASMARM_SETUP_H #ifndef _UAPI__ASMARM_SETUP_H

2
arch/arm/kernel/entry-armv.S
View file

@ -826,7 +826,7 @@ ENDPROC(__switch_to)
* existing ones. This mechanism should be used only for things that are * existing ones. This mechanism should be used only for things that are
* really small and justified, and not be abused freely. * really small and justified, and not be abused freely.
* *
* See Documentation/arm/kernel_user_helpers.txt for formal definitions. * See Documentation/arm/kernel_user_helpers.rst for formal definitions.
*/ */
THUMB( .arm ) THUMB( .arm )

Some files were not shown because too many files have changed in this diff Show more