Seminar LinuxBootSMM Portierung & Board-Integration: SoC-Hooks, ACPI, Register, Bring-up

Inhaltsverzeichnis

• Abstract
• Zielgruppe
• Voraussetzungen
• Lernziele
• Inhalte und Agenda
• Praxis-Workshops
• Ergebnisse und Transfer

Abstract

Dieses Seminar überführt LinuxBootSMM von der QEMU-Referenz in reale Plattformbedingungen. Schwerpunkt ist die Integration in SoC-spezifische coreboot-SMI-Handler-Pfade, inklusive “Hooking” des payload-eigenen Handlers in die coreboot-Logik für höherstufige Features (u. a. ACPI enable/disable). Zusätzlich werden Anforderungen an SoC-Registerdefinitionen, deren Verifikation sowie Debugging-Strategien behandelt. Kernpunkt ist das Verständnis, dass der payload-seitige Handler ohne echte Plattformkenntnis auf korrekte Datenstrukturen angewiesen ist und daher Validierung und Testdesign auf Firmware-Seite essenziell sind.

Zielgruppe

• Platform Enablement, Board Support Package (BSP) Teams
• Firmware-Entwicklung mit SoC-Nähe (Intel/AMD)
• Validation/QA für Firmwarefeatures

Voraussetzungen

• LinuxBootSMM Architektur: SMM Ownership Transition, SMM-Payload vs. MM-Payload und LinuxBootSMM PoC Hands-on (QEMU Q35): Build, Boot, Logs, Debug empfohlen (Architektur + PoC)
• Gute Kenntnisse coreboot-Konfiguration und Bootlogs

Lernziele

• Anforderungen an “Hooking” in SoC-spezifische coreboot-Handlerpfade ableiten und implementierbar beschreiben
• Datenstrukturen für payload-seitige Handler korrekt bereitstellen (Register/Offsets) und verifizieren
• Bring-up-Plan für neue Boards erstellen (Iterationsschleifen, Debug-Signale, Abbruchkriterien)

Inhalte und Agenda

Tag 1

• Portierungsmodell: Was ist “plattformunabhängig”, was bleibt SoC-abhängig
• Hooking in coreboot SMI Handler: Redirection höherer Features an payload Handler

Tag 2

• SoC-spezifische Definitionen: Strukturinhalt, Base/Offset-Logik, Plausibilitätsprüfungen
• Debugging: Verifikation der Definitionskorrektheit (Write-Formate, Registerzugriffe)

Tag 3

• Bring-up und Rollout: Minimal-Feature-Set, Erweiterungen, Risiken
• Ausblick auf “nächste Features” (z. B. Variable Store als Ersatz für SMMSTORE)

Praxis-Workshops

• Hooking-Plan erstellen
  • SMI-Dispatch-Punkte im SoC-Handler lokalisieren
  • Feature-Liste definieren, die über payload abgewickelt werden soll (z. B. ACPI toggles)
  • Redirection-Logik entwerfen: “payload first, fallback to coreboot”
• Definitionen verifizieren
  • Erwartete Registerbasis und Offsets dokumentieren
  • Testfall definieren: Write-Pattern prüfen (Wertänderung, Statusbits)
  • Logs/Instrumentierung festlegen, die die Korrektheit beweisen

Ergebnisse und Transfer

• Portierungs-Checkliste pro Plattform
• Risiko-/Testmatrix für Register- und Handler-Integrationen