CS计算机代考程序代写 scheme compiler cache arm assembly Chapter …

Chapter …

Chapter 4
The Processor

Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Introduction
CPU performance factors
Instruction count
Determined by ISA and compiler
CPI and Cycle time
Determined by CPU hardware
We will examine two LEGv8 implementations
A simplified version
A more realistic pipelined version
Simple subset, shows most aspects
Memory reference: LDUR, STUR
Arithmetic/logical: add, sub, and, or, slt
Control transfer: beq, j

§4.1 Introduction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Instruction Execution
PC  instruction memory, fetch instruction
Register numbers  register file, read registers
Depending on instruction class
Use ALU to calculate
Arithmetic result
Memory address for load/store
Branch target address
Access data memory for load/store
PC  target address or PC + 4

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
CPU Overview

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *

Multiplexers

Can’t just join wires together
Use multiplexers

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Control

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Logic Design Basics
§4.2 Logic Design Conventions
Information encoded in binary
Low voltage = 0, High voltage = 1
One wire per bit
Multi-bit data encoded on multi-wire buses
Combinational element
Operate on data
Output is a function of input
State (sequential) elements
Store information

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Combinational Elements
AND-gate
Y = A & B

Multiplexer
Y = S ? I1 : I0

Adder
Y = A + B

Arithmetic/Logic Unit
Y = F(A, B)

A
B
Y

I0
I1
Y

M
u
x

S

A
B
Y

+

A
B
Y

ALU

F

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Sequential Elements
Register: stores data in a circuit
Uses a clock signal to determine when to update the stored value
Edge-triggered: update when Clk changes from 0 to 1

D
Clk
Q

Clk
D
Q

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Sequential Elements
Register with write control
Only updates on clock edge when write control input is 1
Used when stored value is required later

D
Clk
Q

Write

Write
D
Q

Clk

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Clocking Methodology
Combinational logic transforms data during clock cycles
Between clock edges
Input from state elements, output to state element
Longest delay determines clock period

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Building a Datapath
Datapath
Elements that process data and addresses
in the CPU
Registers, ALUs, mux’s, memories, …
We will build a LEGv8 datapath incrementally
Refining the overview design

§4.3 Building a Datapath

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Instruction Fetch
32-bit register
Increment by 4 for next instruction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
R-Format Instructions
Read two register operands
Perform arithmetic/logical operation
Write register result

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Load/Store Instructions
Read register operands
Calculate address using 16-bit offset
Use ALU, but sign-extend offset
Load: Read memory and update register
Store: Write register value to memory

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Branch Instructions
Read register operands
Compare operands
Use ALU, subtract and check Zero output
Calculate target address
Sign-extend displacement
Shift left 2 places (word displacement)
Add to PC + 4
Already calculated by instruction fetch

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Branch Instructions
Just
re-routes wires
Sign-bit wire replicated

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Composing the Elements
First-cut data path does an instruction in one clock cycle
Each datapath element can only do one function at a time
Hence, we need separate instruction and data memories
Use multiplexers where alternate data sources are used for different instructions

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
R-Type/Load/Store Datapath

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Full Datapath

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
ALU Control
ALU used for
Load/Store: F = add
Branch: F = subtract
R-type: F depends on opcode

§4.4 A Simple Implementation Scheme
ALU control Function
0000 AND
0001 OR
0010 add
0110 subtract
0111 pass input b
1100 NOR

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
ALU Control
Assume 2-bit ALUOp derived from opcode
Combinational logic derives ALU control

opcode ALUOp Operation Opcode field ALU function ALU control
LDUR 00 load register XXXXXXXXXXX add 0010
STUR 00 store register XXXXXXXXXXX add 0010
CBZ 01 compare and branch on zero XXXXXXXXXXX pass input b 0111
R-type 10 add 100000 add 0010
subtract 100010 subtract 0110
AND 100100 AND 0000
ORR 100101 OR 0001

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
The Main Control Unit
Control signals derived from instruction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Datapath With Control

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
R-Type Instruction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Load Instruction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
CBZ Instruction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Implementing Uncnd’l Branch
Jump uses word address
Update PC with concatenation of
Top 4 bits of old PC
26-bit jump address
00
Need an extra control signal decoded from opcode

Jump
2
address
31:26
25:0

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Datapath With B Added

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Performance Issues
Longest delay determines clock period
Critical path: load instruction
Instruction memory  register file  ALU  data memory  register file
Not feasible to vary period for different instructions
Violates design principle
Making the common case fast
We will improve performance by pipelining

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipelining Analogy
Pipelined laundry: overlapping execution
Parallelism improves performance

§4.5 An Overview of Pipelining
Four loads:
Speedup
= 8/3.5 = 2.3
Non-stop:
Speedup
= 2n/0.5n + 1.5 ≈ 4
= number of stages

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
LEGv8 Pipeline
Five stages, one step per stage

IF: Instruction fetch from memory
ID: Instruction decode & register read
EX: Execute operation or calculate address
MEM: Access memory operand
WB: Write result back to register

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipeline Performance
Assume time for stages is
100ps for register read or write
200ps for other stages
Compare pipelined datapath with single-cycle datapath

Instr Instr fetch Register read ALU op Memory access Register write Total time
LDUR 200ps 100 ps 200ps 200ps 100 ps 800ps
STUR 200ps 100 ps 200ps 200ps 700ps
R-format 200ps 100 ps 200ps 100 ps 600ps
CBZ 200ps 100 ps 200ps 500ps

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipeline Performance
Single-cycle (Tc= 800ps)
Pipelined (Tc= 200ps)

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipeline Speedup
If all stages are balanced
i.e., all take the same time
Time between instructionspipelined
= Time between instructionsnonpipelined
Number of stages
If not balanced, speedup is less
Speedup due to increased throughput
Latency (time for each instruction) does not decrease

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipelining and ISA Design
LEGv8 ISA designed for pipelining
All instructions are 32-bits
Easier to fetch and decode in one cycle
c.f. x86: 1- to 17-byte instructions
Few and regular instruction formats
Can decode and read registers in one step
Load/store addressing
Can calculate address in 3rd stage, access memory in 4th stage
Alignment of memory operands
Memory access takes only one cycle

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Hazards
Situations that prevent starting the next instruction in the next cycle
Structure hazards
A required resource is busy
Data hazard
Need to wait for previous instruction to complete its data read/write
Control hazard
Deciding on control action depends on previous instruction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Structure Hazards
Conflict for use of a resource
In LEGv8 pipeline with a single memory
Load/store requires data access
Instruction fetch would have to stall for that cycle
Would cause a pipeline “bubble”
Hence, pipelined datapaths require separate instruction/data memories
Or separate instruction/data caches

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Data Hazards
An instruction depends on completion of data access by a previous instruction
ADD X19, X0, X1
SUB X2, X19, X3

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Forwarding (aka Bypassing)
Use result when it is computed
Don’t wait for it to be stored in a register
Requires extra connections in the datapath

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Load-Use Data Hazard
Can’t always avoid stalls by forwarding
If value not computed when needed
Can’t forward backward in time!

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Code Scheduling to Avoid Stalls
Reorder code to avoid use of load result in the next instruction
C code for A = B + E; C = B + F;

LDUR X1, [X0,#0]
LDUR X2, [X0,#8]
ADD X3, X1, X2
STUR X3, [X0,#24]
LDUR X4, [X0,#16]
ADD X5, X1, X4
STUR X5, [X0,#32]
stall
stall
LDUR X1, [X0,#0]
LDUR X2, [X0,#8]
LDUR X4, [X0,#16]
ADD X3, X1, X2
STUR X3, [X0,#24]
ADD X5, X1, X4
STUR X5, [X0,#32]

11 cycles
13 cycles

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Control Hazards
Branch determines flow of control
Fetching next instruction depends on branch outcome
Pipeline can’t always fetch correct instruction
Still working on ID stage of branch

In LEGv8 pipeline
Need to compare registers and compute target early in the pipeline
Add hardware to do it in ID stage

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Stall on Branch
Wait until branch outcome determined before fetching next instruction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Branch Prediction
Longer pipelines can’t readily determine branch outcome early
Stall penalty becomes unacceptable
Predict outcome of branch
Only stall if prediction is wrong
In LEGv8 pipeline
Can predict branches not taken
Fetch instruction after branch, with no delay

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
More-Realistic Branch Prediction
Static branch prediction
Based on typical branch behavior
Example: loop and if-statement branches
Predict backward branches taken
Predict forward branches not taken
Dynamic branch prediction
Hardware measures actual branch behavior
e.g., record recent history of each branch
Assume future behavior will continue the trend
When wrong, stall while re-fetching, and update history

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipeline Summary
Pipelining improves performance by increasing instruction throughput
Executes multiple instructions in parallel
Each instruction has the same latency
Subject to hazards
Structure, data, control
Instruction set design affects complexity of pipeline implementation

The BIG Picture

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
LEGv8 Pipelined Datapath
§4.6 Pipelined Datapath and Control
WB
MEM
Right-to-left flow leads to hazards

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipeline registers
Need registers between stages
To hold information produced in previous cycle

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipeline Operation
Cycle-by-cycle flow of instructions through the pipelined datapath
“Single-clock-cycle” pipeline diagram
Shows pipeline usage in a single cycle
Highlight resources used
c.f. “multi-clock-cycle” diagram
Graph of operation over time
We’ll look at “single-clock-cycle” diagrams for load & store

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
IF for Load, Store, …

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
ID for Load, Store, …

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
EX for Load

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
MEM for Load

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
WB for Load

Wrong
register
number

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Corrected Datapath for Load

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
EX for Store

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
MEM for Store

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
WB for Store

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Multi-Cycle Pipeline Diagram
Form showing resource usage

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Multi-Cycle Pipeline Diagram
Traditional form

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Single-Cycle Pipeline Diagram
State of pipeline in a given cycle

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipelined Control (Simplified)

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipelined Control
Control signals derived from instruction
As in single-cycle implementation

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipelined Control

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Data Hazards in ALU Instructions
Consider this sequence:

SUB X2, X1,X3
AND X12,X2,X5
OR X13,X6,X2
ADD X14,X2,X2
STUR X15,[X2,#100]

We can resolve hazards with forwarding
How do we detect when to forward?

§4.7 Data Hazards: Forwarding vs. Stalling

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Dependencies & Forwarding

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Detecting the Need to Forward
Pass register numbers along pipeline
e.g., ID/EX.RegisterRs = register number for Rs sitting in ID/EX pipeline register
ALU operand register numbers in EX stage are given by
ID/EX.RegisterRn1, ID/EX.RegisterRm2
Data hazards when

1a. EX/MEM.RegisterRd = ID/EX.RegisterRn1
1b. EX/MEM.RegisterRd = ID/EX.RegisterRm2
2a. MEM/WB.RegisterRd = ID/EX.RegisterRn1
2b. MEM/WB.RegisterRd = ID/EX.RegisterRm2
Fwd from
EX/MEM
pipeline reg

Fwd from
MEM/WB
pipeline reg

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Detecting the Need to Forward
But only if forwarding instruction will write to a register!
EX/MEM.RegWrite, MEM/WB.RegWrite

And only if Rd for that instruction is not XZR
EX/MEM.RegisterRd ≠ 31,
MEM/WB.RegisterRd ≠ 31

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Forwarding Paths

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Forwarding Conditions
Mux control Source Explanation
ForwardA = 00 ID/EX The first ALU operand comes from the register file.
ForwardA = 10 EX/MEM The first ALU operand is forwarded from the prior ALU result.
ForwardA = 01 MEM/WB The first ALU operand is forwarded from data memory or an earlier
ALU result.
ForwardB = 00 ID/EX The second ALU operand comes from the register file.
ForwardB = 10 EX/MEM The second ALU operand is forwarded from the prior ALU result.
ForwardB = 01 MEM/WB The second ALU operand is forwarded from data memory or an
earlier ALU result.

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Double Data Hazard
Consider the sequence:

add X1,X1,X2
add X1,X1,X3
add X1,X1,X4
Both hazards occur
Want to use the most recent
Revise MEM hazard condition
Only fwd if EX hazard condition isn’t true

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Revised Forwarding Condition
MEM hazard
if (MEM/WB.RegWrite

and (MEM/WB.RegisterRd ≠ 31)
and not(EX/MEM.RegWrite and (EX/MEM.RegisterRd ≠ 31)
and (EX/MEM.RegisterRd ≠ ID/EX.RegisterRn1))
and (MEM/WB.RegisterRd = ID/EX.RegisterRn1)) ForwardA = 01
if (MEM/WB.RegWrite

and (MEM/WB.RegisterRd ≠ 31)
and not(EX/MEM.RegWrite and (EX/MEM.RegisterRd ≠ 31)
and (EX/MEM.RegisterRd ≠ ID/EX.RegisterRm2))
and (MEM/WB.RegisterRd = ID/EX.RegisterRm2)) ForwardB = 01

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *

Datapath with Forwarding

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Load-Use Hazard Detection
Check when using instruction is decoded in ID stage
ALU operand register numbers in ID stage are given by
IF/ID.RegisterRn1, IF/ID.RegisterRm2
Load-use hazard when
ID/EX.MemRead and
((ID/EX.RegisterRd = IF/ID.RegisterRn1) or
(ID/EX.RegisterRd = IF/ID.RegisterRm1))
If detected, stall and insert bubble

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
How to Stall the Pipeline
Force control values in ID/EX register
to 0
EX, MEM and WB do nop (no-operation)
Prevent update of PC and IF/ID register
Using instruction is decoded again
Following instruction is fetched again
1-cycle stall allows MEM to read data for LDUI
Can subsequently forward to EX stage

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Load-Use Data Hazard
Stall inserted here

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Datapath with Hazard Detection

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Stalls and Performance
Stalls reduce performance
But are required to get correct results
Compiler can arrange code to avoid hazards and stalls
Requires knowledge of the pipeline structure

The BIG Picture

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Branch Hazards
If branch outcome determined in MEM

§4.8 Control Hazards
PC
Flush these
instructions
(Set control
values to 0)

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Reducing Branch Delay
Move hardware to determine outcome to ID stage
Target address adder
Register comparator
Example: branch taken

36: SUB X10, X4, X8
40: CBZ X1, X3, 8
44: AND X12, X2, X5
48: ORR X13, X2, X6
52: ADD X14, X4, X2
56: SUB X15, X6, X7

72: LDUR X4, [X7,#50]

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Example: Branch Taken

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Example: Branch Taken

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Dynamic Branch Prediction
In deeper and superscalar pipelines, branch penalty is more significant
Use dynamic prediction
Branch prediction buffer (aka branch history table)
Indexed by recent branch instruction addresses
Stores outcome (taken/not taken)
To execute a branch
Check table, expect the same outcome
Start fetching from fall-through or target
If wrong, flush pipeline and flip prediction

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *

1-Bit Predictor: Shortcoming
Inner loop branches mispredicted twice!

outer: …

inner: …

CBZ …, …, inner

CBZ …, …, outer
Mispredict as taken on last iteration of inner loop
Then mispredict as not taken on first iteration of inner loop next time around

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
2-Bit Predictor
Only change prediction on two successive mispredictions

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Calculating the Branch Target
Even with predictor, still need to calculate the target address
1-cycle penalty for a taken branch
Branch target buffer
Cache of target addresses
Indexed by PC when instruction fetched
If hit and instruction is branch predicted taken, can fetch target immediately

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Exceptions and Interrupts
“Unexpected” events requiring change
in flow of control
Different ISAs use the terms differently
Exception
Arises within the CPU
e.g., undefined opcode, overflow, syscall, …
Interrupt
From an external I/O controller
Dealing with them without sacrificing performance is hard

§4.9 Exceptions

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Handling Exceptions
Save PC of offending (or interrupted) instruction
In LEGv8: Exception Link Register (ELR)

Save indication of the problem
In LEGv8: Exception Syndrome Rregister (ESR)
We’ll assume 1-bit
0 for undefined opcode, 1 for overflow

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
An Alternate Mechanism
Vectored Interrupts
Handler address determined by the cause
Exception vector address to be added to a vector table base register:
Unknown Reason: 00 0000two
Overflow: 10 1100two
…: 11 1111two
Instructions either
Deal with the interrupt, or
Jump to real handler

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Handler Actions
Read cause, and transfer to relevant handler
Determine action required
If restartable
Take corrective action
use EPC to return to program
Otherwise
Terminate program
Report error using EPC, cause, …

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Exceptions in a Pipeline
Another form of control hazard
Consider overflow on add in EX stage

ADD X1, X2, X1
Prevent X1 from being clobbered
Complete previous instructions
Flush add and subsequent instructions
Set ESR and ELR register values
Transfer control to handler
Similar to mispredicted branch
Use much of the same hardware

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pipeline with Exceptions

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Exception Properties
Restartable exceptions
Pipeline can flush the instruction
Handler executes, then returns to the instruction
Refetched and executed from scratch
PC saved in ELR register
Identifies causing instruction
Actually PC + 4 is saved
Handler must adjust

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Exception Example
Exception on ADD in

40 SUB X11, X2, X4
44 AND X12, X2, X5
48 ORR X13, X2, X6
4C ADD X1, X2, X1
50 SUB X15, X6, X7
54 LDUR X16, [X7,#100]

Handler

80000180 STUR X26, [X0,#1000]
80000184 STUR X27, [X0,#1008]

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Exception Example

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Exception Example

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Multiple Exceptions
Pipelining overlaps multiple instructions
Could have multiple exceptions at once
Simple approach: deal with exception from earliest instruction
Flush subsequent instructions
“Precise” exceptions
In complex pipelines
Multiple instructions issued per cycle
Out-of-order completion
Maintaining precise exceptions is difficult!

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Imprecise Exceptions
Just stop pipeline and save state
Including exception cause(s)
Let the handler work out
Which instruction(s) had exceptions
Which to complete or flush
May require “manual” completion
Simplifies hardware, but more complex handler software
Not feasible for complex multiple-issue
out-of-order pipelines

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Instruction-Level Parallelism (ILP)
Pipelining: executing multiple instructions in parallel
To increase ILP
Deeper pipeline
Less work per stage  shorter clock cycle
Multiple issue
Replicate pipeline stages  multiple pipelines
Start multiple instructions per clock cycle
CPI < 1, so use Instructions Per Cycle (IPC) E.g., 4GHz 4-way multiple-issue 16 BIPS, peak CPI = 0.25, peak IPC = 4 But dependencies reduce this in practice §4.10 Parallelism via Instructions Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Multiple Issue Static multiple issue Compiler groups instructions to be issued together Packages them into “issue slots” Compiler detects and avoids hazards Dynamic multiple issue CPU examines instruction stream and chooses instructions to issue each cycle Compiler can help by reordering instructions CPU resolves hazards using advanced techniques at runtime Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Speculation “Guess” what to do with an instruction Start operation as soon as possible Check whether guess was right If so, complete the operation If not, roll-back and do the right thing Common to static and dynamic multiple issue Examples Speculate on branch outcome Roll back if path taken is different Speculate on load Roll back if location is updated Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Compiler/Hardware Speculation Compiler can reorder instructions e.g., move load before branch Can include “fix-up” instructions to recover from incorrect guess Hardware can look ahead for instructions to execute Buffer results until it determines they are actually needed Flush buffers on incorrect speculation Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Speculation and Exceptions What if exception occurs on a speculatively executed instruction? e.g., speculative load before null-pointer check Static speculation Can add ISA support for deferring exceptions Dynamic speculation Can buffer exceptions until instruction completion (which may not occur) Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Static Multiple Issue Compiler groups instructions into “issue packets” Group of instructions that can be issued on a single cycle Determined by pipeline resources required Think of an issue packet as a very long instruction Specifies multiple concurrent operations  Very Long Instruction Word (VLIW) Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Scheduling Static Multiple Issue Compiler must remove some/all hazards Reorder instructions into issue packets No dependencies with a packet Possibly some dependencies between packets Varies between ISAs; compiler must know! Pad with nop if necessary Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * LEGv8 with Static Dual Issue Two-issue packets One ALU/branch instruction One load/store instruction 64-bit aligned ALU/branch, then load/store Pad an unused instruction with nop Address Instruction type Pipeline Stages n ALU/branch IF ID EX MEM WB n + 4 Load/store IF ID EX MEM WB n + 8 ALU/branch IF ID EX MEM WB n + 12 Load/store IF ID EX MEM WB n + 16 ALU/branch IF ID EX MEM WB n + 20 Load/store IF ID EX MEM WB Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * LEGv8 with Static Dual Issue Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Hazards in the Dual-Issue LEGv8 More instructions executing in parallel EX data hazard Forwarding avoided stalls with single-issue Now can’t use ALU result in load/store in same packet ADD X0, X0, X1 LDUR X2, [X0,#0] Split into two packets, effectively a stall Load-use hazard Still one cycle use latency, but now two instructions More aggressive scheduling required Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Scheduling Example Schedule this for dual-issue LEGv8 Loop: LDUR X0, [X20,#0] // X0=array element ADD X0, X0,X21 // add scalar in X21 STUR X0, [X20,#0] // store result SUBI X20, X20,#4 // decrement pointer CMP X20, X22 // branch $s1!=0 BGT Loop IPC = 7/6 = 1.17 (c.f. peak IPC = 2) ALU/branch Load/store cycle Loop: nop LDUR X0, [X20,#0] 1 SUBI X20, X20,#4 nop 2 ADD X0, X0,X21 nop 3 CMP X20, X22 sw $t0, 4($s1) 4 BGT Loop STUR X0, [X20,#0] 5 Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Loop Unrolling Replicate loop body to expose more parallelism Reduces loop-control overhead Use different registers per replication Called “register renaming” Avoid loop-carried “anti-dependencies” Store followed by a load of the same register Aka “name dependence” Reuse of a register name Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Loop Unrolling Example IPC = 15/8 = 1.875 Closer to 2, but at cost of registers and code size ALU/branch Load/store cycle Loop: SUBI X20, X20,#32 LDUR X0, [X20,#0] 1 nop LDUR X1, [X20,#24] 2 ADD X0, X0, X21 LDUR X2, [X20,#16] 3 ADD X1, X1, X21 LDUR X3, [X20,#8] 4 ADD X2, X2, X21 STUR X0, [X20,#32] 5 ADD X3, X3, X21 sw X1, [X20,#24] 6 CMP X20,X22 sw X2, [X20,#16] 7 BGT Loop sw X3, [X20,#8] 8 Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Dynamic Multiple Issue “Superscalar” processors CPU decides whether to issue 0, 1, 2, … each cycle Avoiding structural and data hazards Avoids the need for compiler scheduling Though it may still help Code semantics ensured by the CPU Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Dynamic Pipeline Scheduling Allow the CPU to execute instructions out of order to avoid stalls But commit result to registers in order Example LDUR X0, [X21,#20] ADD X1, X0, X2 SUB X23,X23,X3 ANDI X5, X23,#20 Can start sub while ADD is waiting for LDUI Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Dynamically Scheduled CPU Results also sent to any waiting reservation stations Reorders buffer for register writes Can supply operands for issued instructions Preserves dependencies Hold pending operands Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Register Renaming Reservation stations and reorder buffer effectively provide register renaming On instruction issue to reservation station If operand is available in register file or reorder buffer Copied to reservation station No longer required in the register; can be overwritten If operand is not yet available It will be provided to the reservation station by a function unit Register update may not be required Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Speculation Predict branch and continue issuing Don’t commit until branch outcome determined Load speculation Avoid load and cache miss delay Predict the effective address Predict loaded value Load before completing outstanding stores Bypass stored values to load unit Don’t commit load until speculation cleared Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Why Do Dynamic Scheduling? Why not just let the compiler schedule code? Not all stalls are predicable e.g., cache misses Can’t always schedule around branches Branch outcome is dynamically determined Different implementations of an ISA have different latencies and hazards Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Does Multiple Issue Work? Yes, but not as much as we’d like Programs have real dependencies that limit ILP Some dependencies are hard to eliminate e.g., pointer aliasing Some parallelism is hard to expose Limited window size during instruction issue Memory delays and limited bandwidth Hard to keep pipelines full Speculation can help if done well The BIG Picture Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Chapter 4 — The Processor — * Power Efficiency Complexity of dynamic scheduling and speculations requires power Multiple simpler cores may be better Microprocessor Year Clock Rate Pipeline Stages Issue width Out-of-order/ Speculation Cores Power i486 1989 25MHz 5 1 No 1 5W Pentium 1993 66MHz 5 2 No 1 10W Pentium Pro 1997 200MHz 10 3 Yes 1 29W P4 Willamette 2001 2000MHz 22 3 Yes 1 75W P4 Prescott 2004 3600MHz 31 3 Yes 1 103W Core 2006 2930MHz 14 4 Yes 2 75W UltraSparc III 2003 1950MHz 14 4 No 1 90W UltraSparc T1 2005 1200MHz 6 1 No 8 70W Chapter 4 — The Processor — * Morgan Kaufmann Publishers Morgan Kaufmann Publishers * Chapter 4 — The Processor * Chapter 4 — The Processor Cortex A53 and Intel i7 Chapter 4 — The Processor — * §4.11 Real Stuff: The ARM Cortex-A8 and Intel Core i7 Pipelines Processor ARM A53 Intel Core i7 920 Market Personal Mobile Device Server, cloud Thermal design power 100 milliWatts (1 core @ 1 GHz) 130 Watts Clock rate 1.5 GHz 2.66 GHz Cores/Chip 4 (configurable) 4 Floating point? Yes Yes Multiple issue? Dynamic Dynamic Peak instructions/clock cycle 2 4 Pipeline stages 8 14 Pipeline schedule Static in-order Dynamic out-of-order with speculation Branch prediction Hybrid 2-level 1st level caches/core 16-64 KiB I, 16-64 KiB D 32 KiB I, 32 KiB D 2nd level caches/core 128-2048 KiB 256 KiB (per core) 3rd level caches (shared) (platform dependent) 2-8 MB Chapter 4 — The Processor — * ARM Cortex-A53 Pipeline Chapter 4 — The Processor — * Chapter 4 — The Processor — * ARM Cortex-A53 Performance Chapter 4 — The Processor — * Chapter 4 — The Processor — * Core i7 Pipeline Chapter 4 — The Processor — * Chapter 4 — The Processor — * Core i7 Performance Chapter 4 — The Processor — * Chapter 4 — The Processor — * Matrix Multiply Unrolled C code 1 #include
2 #define UNROLL (4)
3
4 void dgemm (int n, double* A, double* B, double* C)
5 {
6 for ( int i = 0; i < n; i+=UNROLL*4 ) 7 for ( int j = 0; j < n; j++ ) { 8 __m256d c[4]; 9 for ( int x = 0; x < UNROLL; x++ ) 10 c[x] = _mm256_load_pd(C+i+x*4+j*n); 11 12 for( int k = 0; k < n; k++ ) 13 { 14 __m256d b = _mm256_broadcast_sd(B+k+j*n); 15 for (int x = 0; x < UNROLL; x++) 16 c[x] = _mm256_add_pd(c[x], 17 _mm256_mul_pd(_mm256_load_pd(A+n*k+x*4+i), b)); 18 } 19 20 for ( int x = 0; x < UNROLL; x++ ) 21 _mm256_store_pd(C+i+x*4+j*n, c[x]); 22 } 23 } Chapter 4 — The Processor — * §4.12 Instruction-Level Parallelism and Matrix Multiply Chapter 4 — The Processor — * Matrix Multiply Assembly code: 1 vmovapd (%r11),%ymm4 # Load 4 elements of C into %ymm4 2 mov %rbx,%rax # register %rax = %rbx 3 xor %ecx,%ecx # register %ecx = 0 4 vmovapd 0x20(%r11),%ymm3 # Load 4 elements of C into %ymm3 5 vmovapd 0x40(%r11),%ymm2 # Load 4 elements of C into %ymm2 6 vmovapd 0x60(%r11),%ymm1 # Load 4 elements of C into %ymm1 7 vbroadcastsd (%rcx,%r9,1),%ymm0 # Make 4 copies of B element 8 add $0x8,%rcx # register %rcx = %rcx + 8 9 vmulpd (%rax),%ymm0,%ymm5 # Parallel mul %ymm1,4 A elements 10 vaddpd %ymm5,%ymm4,%ymm4 # Parallel add %ymm5, %ymm4 11 vmulpd 0x20(%rax),%ymm0,%ymm5 # Parallel mul %ymm1,4 A elements 12 vaddpd %ymm5,%ymm3,%ymm3 # Parallel add %ymm5, %ymm3 13 vmulpd 0x40(%rax),%ymm0,%ymm5 # Parallel mul %ymm1,4 A elements 14 vmulpd 0x60(%rax),%ymm0,%ymm0 # Parallel mul %ymm1,4 A elements 15 add %r8,%rax # register %rax = %rax + %r8 16 cmp %r10,%rcx # compare %r8 to %rax 17 vaddpd %ymm5,%ymm2,%ymm2 # Parallel add %ymm5, %ymm2 18 vaddpd %ymm0,%ymm1,%ymm1 # Parallel add %ymm0, %ymm1 19 jne 68 # jump if not %r8 != %rax
20 add $0x1,%esi # register % esi = % esi + 1
21 vmovapd %ymm4,(%r11) # Store %ymm4 into 4 C elements
22 vmovapd %ymm3,0x20(%r11) # Store %ymm3 into 4 C elements
23 vmovapd %ymm2,0x40(%r11) # Store %ymm2 into 4 C elements
24 vmovapd %ymm1,0x60(%r11) # Store %ymm1 into 4 C elements
Chapter 4 — The Processor — *
§4.12 Instruction-Level Parallelism and Matrix Multiply

Chapter 4 — The Processor — *

Performance Impact
Chapter 4 — The Processor — *

Chapter 4 — The Processor — *

Chapter 4 — The Processor — *
Fallacies
Pipelining is easy (!)
The basic idea is easy
The devil is in the details
e.g., detecting data hazards
Pipelining is independent of technology
So why haven’t we always done pipelining?
More transistors make more advanced techniques feasible
Pipeline-related ISA design needs to take account of technology trends
e.g., predicated instructions

§4.14 Fallacies and Pitfalls

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Pitfalls
Poor ISA design can make pipelining harder
e.g., complex instruction sets (VAX, IA-32)
Significant overhead to make pipelining work
IA-32 micro-op approach
e.g., complex addressing modes
Register update side effects, memory indirection
e.g., delayed branches
Advanced pipelines have long delay slots

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor

Chapter 4 — The Processor — *
Concluding Remarks
ISA influences design of datapath and control
Datapath and control influence design of ISA
Pipelining improves instruction throughput
using parallelism
More instructions completed per second
Latency for each instruction not reduced
Hazards: structural, data, control
Multiple issue and dynamic scheduling (ILP)
Dependencies limit achievable parallelism
Complexity leads to the power wall

§4.14 Concluding Remarks

Chapter 4 — The Processor — *
Morgan Kaufmann Publishers
Morgan Kaufmann Publishers
*
Chapter 4 — The Processor
*

Chapter 4 — The Processor