CUDA Academy · 강의

memcheck로 누수 찾기

범위를 벗어난 접근과 잘못된 장치 포인터를 찾습니다

레슨 2/413개 단계

memcheck로 누수 찾기은(는) CoddyKit의 무료 CUDA Academy 강의입니다. 이것은 4개 중 2번째 강의입니다. 아래에서 전체 강의를 무료로 읽을 수 있으며, 내장 코드 에디터와 24/7 AI 튜터와 함께 브라우저에서 직접 실습할 수 있습니다. 이 강의는 CUDA Academy 학습 경로의 일부이며, 진행 상황이 웹과 CoddyKit 앱에 동기화됩니다. CUDA Academy 강의에는 총 4개의 강의가 포함되어 있습니다.

memcheck가 필요한 이유

GPU 메모리 버그는 큰 오류 없이 발생하는 경우가 많습니다. 따라서 compute-sanitizer의 memcheck 도구가 모든 접근을 감시하고 문제를 알려 줍니다. 🛡️

범위를 벗어난 읽기

memcheck가 찾아내는 대표적인 버그는 범위를 벗어난 접근입니다. 이는 스레드가 장치 배열의 끝을 넘어 읽거나 쓰는 경우입니다.

누락된 범위 확인

보호 조건을 빼먹으면 여분의 스레드가 제멋대로 실행되므로, 이 인덱스가 n을 넘어가 잘못된 전역 메모리 쓰기를 일으킬 수 있습니다.

int i = blockIdx.x * blockDim.x + threadIdx.x;
out[i] = a[i] + b[i];

보고서 읽기

memcheck는 오류 종류, 문제가 발생한 주소, 그리고 오류를 일으킨 스레드를 출력하여 잘못된 접근을 바로 찾을 수 있게 해 줍니다.

줄 번호 가져오기

-lineinfo와 함께 컴파일하면 memcheck가 각 오류를 원시 주소가 아닌 정확한 소스 줄에 대응시킬 수 있습니다.

nvcc -lineinfo vecadd.cu -o vecadd

누수 감지하기

--leak-check 옵션을 켜면 memcheck가 프로그램 종료 전에 할당했지만 해제하지 않은 장치 메모리를 모두 알려 줍니다.

compute-sanitizer --leak-check full ./vecadd

전형적인 메모리 누수

해당하는 해제가 없이 할당하면 버퍼가 누수됩니다. 이런 작업이 여러 번 반복되면 장치 메모리가 서서히 고갈됩니다.

cudaMalloc(&d_a, bytes);
// ...used, but cudaFree(d_a) is missing

잘못된 장치 포인터

memcheck는 커널이 장치 포인터를 예상하는 곳에 호스트 포인터를 전달하는 경우도 표시합니다. 이는 결과를 조용히 손상시키는 실수입니다.

정렬되지 않은 접근

일부 로드는 정렬된 주소를 필요로 하므로, memcheck는 그렇지 않으면 잘못된 값이나 오류를 일으킬 수 있는 정렬되지 않은 접근을 경고합니다.

수정하고 다시 실행하기

수정할 때마다 memcheck를 다시 실행하여 오류가 0개로 보고될 때까지 반복하십시오. 오류 없는 실행은 메모리 버그가 사라졌다는 신호입니다.

빠른 확인

memcheck 도구는 주로 어떤 종류의 버그를 찾도록 설계되었습니까?

인터랙티브 레슨에서 답해보세요

복습

memcheck를 실행하고, 소스 줄 정보를 위해 -lineinfo를 추가했으며, 누수 검사를 활성화하고, 자주 발생하는 오류 종류를 배웠습니다. 오류 없는 실행은 안전한 메모리를 의미합니다. ✅

무료로 시작

AI 튜터와 함께 C++을(를) 배우세요 — 무료

브라우저에서 실제 코드를 작성하고 실행하며, 24/7 AI 튜터로부터 즉각적인 도움을 받고, 웹이나 앱에서 중단한 부분부터 계속 학습하세요.

코스: 30
레슨: 120

무료로 학습 시작 전체 코스 보기

자주 묻는 질문