LIME YAO
0 followers · 759 views
on the atlas — 24
- A Parallel Computing Primer1 savers
- The 2026 AI Index Report | Stanford HAI1 savers
- CodeCarbon.io2 savers
- Worklog: Optimising GEMM on NVIDIA H100 for cuBLAS-like Performance (WIP) | Hamza's Blog1 savers
- How to Optimize a CUDA Matmul Kernel for cuBLAS-like Performance: a Worklog24 savers
- Katakana Writing Practice | Characters | Japanese-Lesson.com1 savers
- Hiragana Writing Practice | Characters | Japanese-Lesson.com1 savers
- The Smol Training Playbook: The Secrets to Building World-Class LLMs - a Hugging Face Space by HuggingFaceTB13 savers
- A Deep Dive into LLM Inference Latencies1 savers
- KV cache strategies1 savers
- API Reference — TensorRT LLM1 savers
- Efficient GEMM in CUDA — NVIDIA CUTLASS Documentation1 savers
- Inside NVIDIA GPUs: Anatomy of high performance matmul kernels - Aleksa Gordić9 savers
- NVIDIA Tensor Core Evolution: From Volta To Blackwell1 savers
- CVPR2023_eff_tutorial_molchanov.pdf1 savers
- How to Think About GPUs | How To Scale Your Model5 savers
- How to Think About TPUs | How To Scale Your Model5 savers
- All About Rooflines | How To Scale Your Model10 savers
- Formula for Human Genius and Creativity1 savers
- Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysis1 savers
- BIST for Analog Weenies | Analog Devices1 savers
- Python API reference — nvMatmulHeuristics1 savers
- GPU Performance Background User's Guide - NVIDIA Docs2 savers
- H100 vs GB200 NVL72 Training Benchmarks – Power, TCO, and Reliability Analysis, Software Improvement Over Time – SemiAnalysis1 savers
highlights — 37
30 TFLOPs that the GPU can provide
How to Optimize a CUDA Matmul Kernel for cuBLAS-like Performance: a WorklogHigh occupancy is useful because it allows us to hide the high latency of our operations, by having a bigger pool of issue-able instructions available
How to Optimize a CUDA Matmul Kernel for cuBLAS-like Performance: a Worklogonfiguration for the build cache. cache_root
API Reference — TensorRT LLM-llama/Llama-2-7b-chat-hf")
KV cache strategiesHowever, for small requests, TMA loads have higher latency than regular async data copies because of the address generation overhead. Thus, NVIDIA recommends programmers to use TMAs for large data copies to amortize the overhead. For example, in LLM inference, TMA is not suitable for workloads that load KV cache in small chunks, but works well when each chunk is a multiple of 16 bytes
NVIDIA Tensor Core Evolution: From Volta To Blackwellup to 64 “resident warps” per S
How to Think About GPUs | How To Scale Your ModelTPUs have a lot more fast cache memory. TPUs also have a lot more VMEM than GPUs have SMEM (+TMEM), and this memory can be used for storing weights and activations in a way that lets them be loaded and used extremely fast. This can make them faster for LLM inference if you can consistently store or prefetch model weights into VMEM.
How to Think About GPUs | How To Scale Your ModelA GPU programmer can just launch dozens of different kernels, each running on a totally independent SM. On the other hand, those kernels might get horrible performance because they are thrashing the L2 cache or failing to coalesce memory loads; because the hardware controls so much of the runtime, it becomes hard to reason about what’s going on behind the scenes. As a result, TPUs can often get closer to peak roofline performance with less work.
How to Think About GPUs | How To Scale Your ModelSMEM is used for storing activations and inputs to TC matmuls.
How to Think About GPUs | How To Scale Your Modelthe critical threshhold now depends on and not
All About Rooflines | How To Scale Your Modelwe need to keep on learning and we need to pay special attention to how we represent things in our memory to ensure we understand the implications of the things we learn.
Formula for Human Genius and CreativityIntuition is an inability to explicitly express knowledge that is already wired in the neural network of the brain.
Formula for Human Genius and Creativitywhat new powers our brains can acquire with relatively little effort if the new knowledge is selected in the right way
Formula for Human Genius and CreativityThis person is really intelligent! Look at his record! To use a computer metaphor, the scientist is endowed with the best hardware and software money can buy. He or she is optimally equipped for problem solving
Formula for Human Genius and CreativityThis kid is really intelligent! The sky is the limit for him. The kid is equipped with high quality extensible hardware infrastructure
Formula for Human Genius and CreativityThis guy is really intelligent! See how fast his brain reacts! The student has a fast processor installed and his RAM has a lightning access time
Formula for Human Genius and Creativityone key disadvantage of the Vera Rubin NVL144 CPX is that it has a fixed number and ratio of Rubin and Rubin CPX chips, which makes it less flexible should one wish to change the PD ratio
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisPP will tend to deliver higher token throughput per GPU than Expert Parallelism (EP), but the tradeoff is that PP suffers from a higher time to first token (TTFT) than EP
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisRubin CPX’s off-chip I/O is limited to 16 lanes of PCIe Gen6 which is approximately 1Tbit/s of unidirectional bandwidth vs 14.4Tbit/s of NVLink for R200. This is enough I/O for performing prefill even for modern MoE frontier LLMs.
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisThis complete disaggregation only seems to provide excellent results under certain input/output sequence length ratios and for long decode lengths, with other scenarios seeing underwhelming benefits
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisSince prefill is inherently going to underutilize memory bandwidth resources one approach to reduce wastage is to reduce the quantity and cost of the memory
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysiswhen sequence length exceeds 32k, the FLOPS utilization reaches 100% while the memory bandwidth utilization drops
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisOnce specialized inference hardware becomes ubiquitous, using uniform hardware will feel like buying a jackhammer to squash a bug
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisgains are likely from reducing higher precision compute units to have more FP4 ALUs
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisDense PFLOPs for the Rubin CPX follow the same 3:2 sparse to dense ratio as the R200 because it inherits a similar tensor core architecture as Rubin R200
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisgeneration of KVCache is much less bandwidth intensive due to the parallel nature of prefill, therefore the HBM is underutilized during this step
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisunning prefill on a chip with lots of expensive HBM featuring very high memory bandwidth is a waste
Another Giant Leap: The Rubin CPX Specialized Accelerator & Rack – SemiAnalysisHowever, the way the device is stimulated can provide some information about the type of fault. For example, different test patterns could isolate the fault to a specific input pin
BIST for Analog Weenies | Analog DevicesThe process of compressing the response introduces the possibility of enabling a faulty CUT to produce a correct signature, but the probability of a fault going undetected becomes vanishingly small as the pattern length increases.
BIST for Analog Weenies | Analog DevicesSince an SM can execute multiple thread blocks concurrently, typically one wants the number of thread blocks to be several times higher than the number of SMs
GPU Performance Background User's Guide - NVIDIA Docsterm wave to refer to a set of thread blocks that run concurrently
GPU Performance Background User's Guide - NVIDIA DocsTo train to convergence using 15T tokens, Meta would require an amount of energy equal to the annual consumption of an entire neighborhood of 3,400 US households.
H100 vs GB200 NVL72 Training Benchmarks – Power, TCO, and Reliability Analysis, Software Improvement Over Time – SemiAnalysisAmdahl’s Law, which describes the speedup that can be achieved by parallelizing computing steps, can be used to quantify the speedup of strong scaling
H100 vs GB200 NVL72 Training Benchmarks – Power, TCO, and Reliability Analysis, Software Improvement Over Time – SemiAnalysisExtending this calculation further, training 300B tokens on GPT3 175B would require 19 annual US households’ worth of energy consumption for FP8 and 28 households’ worth of annual energy consumption for BF16.
H100 vs GB200 NVL72 Training Benchmarks – Power, TCO, and Reliability Analysis, Software Improvement Over Time – SemiAnalysisThe average annual US household in 2022 consumed 10,791kWh of energy or approximately 38,847,600,000 Joules. Dividing this 10,791 kWh by 8,760 hours per year gives us 1,232 W of power on average over the year – a little more than the 1,200W used by a single GB200 GPU!
H100 vs GB200 NVL72 Training Benchmarks – Power, TCO, and Reliability Analysis, Software Improvement Over Time – SemiAnalysisThis improvement results from NVIDIA CuDNN/CuBLAS engineers writing more optimized fused wgmma kernels, NCCL engineers writing more optimized collectives that use fewer SMs for communication among other improvements. At the end of the day, it is the full software stack optimization that matters.
H100 vs GB200 NVL72 Training Benchmarks – Power, TCO, and Reliability Analysis, Software Improvement Over Time – SemiAnalysisGB200 chip consumes 1200W per chip vs 700W for the H100
H100 vs GB200 NVL72 Training Benchmarks – Power, TCO, and Reliability Analysis, Software Improvement Over Time – SemiAnalysis