Закреплённая память с помощью cudaMallocHost
Используйте буферы с блокировкой страниц для быстрой передачи DMA.
«Закреплённая память с помощью cudaMallocHost» — бесплатный урок CUDA Academy на CoddyKit. Это урок 2 из 4. Ты можешь прочитать весь урок бесплатно ниже — а потом практиковать его прямо в браузере с встроенным редактором кода и ИИ-репетитором 24/7. Это часть пути обучения CUDA Academy, и твой прогресс синхронизируется между веб-версией и приложением CoddyKit. Курс CUDA Academy содержит 4 уроков всего.
Части этого урока еще не переведены и отображаются на английском.
Meet Pinned Memory
Pinned memory is host memory the operating system promises never to move or swap out. Because its physical address is fixed, the GPU can read it directly.
Also Called Page-Locked
You will see the term page-locked used as a synonym for pinned. Both mean the same thing: pages locked in place so no swapping can ever happen.
Allocate It Right
Ask CUDA for pinned memory with cudaMallocHost. It hands back an ordinary host pointer you can read and write just like any C++ array.
float* h_data;
cudaMallocHost(&h_data, N * sizeof(float));Use It Like Normal
The returned pointer behaves like any host buffer, so your CPU code stays unchanged. You just fill it and read it exactly as before.
for (int i = 0; i < N; ++i) h_data[i] = i * 1.0f;No More Staging
Since the pages cannot move, the driver skips its hidden staging copy. The GPU pulls straight from your buffer, so the doubled copy disappears.
Faster Transfers
The payoff is real bandwidth. Pinned transfers often run near the link's peak speed, sometimes roughly twice as fast as the pageable version.
Free It Correctly
Pinned memory needs its own matching release. Use cudaFreeHost, never the plain free, or you risk a crash and a leak.
cudaFreeHost(h_data);It Is Not Free Real Estate
Pinned pages cannot be swapped, so they hold real RAM hostage. Pin too much and you starve the rest of the system of usable memory.
Allocation Is Slower
Locking pages takes work, so cudaMallocHost is slower to allocate than malloc. Reuse one pinned buffer across many transfers instead of reallocating.
The Real Superpower
Beyond speed, pinned memory is the key that unlocks truly asynchronous copies. Without it, cudaMemcpyAsync cannot overlap with anything.
When to Reach for It
Pin buffers that you transfer often or that feed streams. For a one-off copy of a tiny array, plain malloc is perfectly fine. 🙂
Quick Check
You allocated a buffer with cudaMallocHost. How should you release it?
Recap
cudaMallocHost pins host pages so the GPU reads them directly, giving faster copies and enabling async overlap. Always release with cudaFreeHost. 🔒
Часто задаваемые вопросы
Урок «Закреплённая память с помощью cudaMallocHost» бесплатный?
Да — полный текст урока «Закреплённая память с помощью cudaMallocHost» бесплатно доступен здесь в веб-версии. Чтобы практиковать его интерактивно (встроенный редактор кода и ИИ-репетитор 24/7) и разблокировать остальной курс CUDA Academy, подпишись на CoddyKit PRO. Курс CUDA Academy содержит 4 уроков всего.
Чему я научусь в уроке «Закреплённая память с помощью cudaMallocHost»?
Используйте буферы с блокировкой страниц для быстрой передачи DMA. Ты практикуешь CUDA Academy с помощью реального кода, который запускаешь прямо в браузере, и ИИ-репетитор 24/7 отвечает на твои вопросы во время урока.
Нужен ли мне опыт, чтобы начать CUDA Academy?
Предыдущий опыт не требуется. CUDA Academy на CoddyKit структурирован для всех уровней — от новичков до продвинутых, поэтому ты можешь начать отсюда или с самого начала и учиться в своем темпе. Это урок 2 из 4.
Сколько времени занимает урок «Закреплённая память с помощью cudaMallocHost»?
Большинство уроков CoddyKit занимают около 5–10 минут. Каждый из них компактный и интерактивный, поэтому ты постоянно делаешь прогресс и продолжаешь с того же места в веб-версии и приложении.
Можно ли писать и запускать код в этом уроке CUDA Academy?
Да. Каждый урок CUDA Academy включает встроенный редактор кода, поэтому ты пишешь и запускаешь реальный код прямо в браузере и получаешь моментальную обратную связь от AI — локальная установка не требуется.
Все уроки этого курса
- Почему страничная память медленная
- Закреплённая память с помощью cudaMallocHost
- cudaMemcpyAsync в потоке выполнения
- Конвейер с двойной буферизацией