NVIDIA CUDA编程指南.pdf

NVIDIA CUDA 编程指南

NVIDIA

GPU

NVIDIA CUDA

Chapter1

1.1

………………………….............................................11

1.2 CUDA

GPU

..............................................................................................12

Chapter2

............................................................................................................................... 15

2.1

.....................................................................................................................15

2.2

2.2.1

..........................................................................................................................................16

2.2.2

3.5

Chapter4

...................................................................................................21

4.1

C

..............................................................................................................................21

4.2

4.2.1

......................................................................................................................... 22

4.2.1.1 __device__..................................................................................................................22

4.2.1.2 __global__..........................................................................................................22

4.2.1.3 __host__............................................................................................................22

4.2.1.4

....................................................................................................................22

4.2.2

4.2.4.2 blockIdx...........................................................................................................................26

4.2.4.3 blockDim............................................................................................................................26

4.2.4.4 threadIdx......................................................................................................................... 26

4.2.4.5

4.2.5 NVCC

4.2.5.1 __noinline__ ...................................................................................................................27

4.2.5.2 #pragmaunroll .................................................................................................................27

4.3

Runtime

........................................................................................................................... 28

4.3.1

............................................................................................................................. 28

4.3.1.1

4.3.3

4.3.4

4.3.4.1 Texture Reference

.......................................................................................................29

4.3.4.2 RuntimeTexture Reference

.........................................................................................30

4.3.4.3

CUDA

.......................................................................................31

4.4

Runtime

........................................................................................................................... 31

4.4.1

4.4.2

4.4.3

............................................................................................................................. 32

4.4.4 TypeCasting

........................................................................................................................32

4.4.5

4.5.1.2

4.5.1.3 OpenGL Interoperability ...................................................................................................... 36

4.5.1.4 Direct3D Interoperability ..................................................................................................... 36

4.5.1.5

4.5.2 RuntimeAPI.................................................................................................................................... 38

4.5.2.1

..................................................................................................................................... 38

4.5.2.2

.................................................................................................................................. 38

4.5.2.3

.................................................................................................................................. 39

4.5.2.4

..................................................................................................................................... 40

4.5.2.5

.................................................................................................................................. 41

4.5.2.6 Texture Reference

...........................................................................................................42

4.5.2.7 OpenGL Interoperability .......................................................................................................... 44

4.5.2.8 Direct3D Interoperability ......................................................................................................... 44

4.5.3.4

................................................................................................................................. 48

4.5.3.5

................................................................................................................................. 49

4.5.3.6

................................................................................................................................. 49

4.5.3.7

..................................................................................................................................... 51

4.5.3.8

................................................................................................................................. 51

4.5.3.9 Texture Reference

..........................................................................................................52

Chapter5

................................................................................................................................ 54

5.1

5.1.1

5.1.2.2

............................................................................................................................. 62

5.1.2.3

............................................................................................................................. 63

5.1.2.4

............................................................................................................................. 63

5.1.2.5

5.2

5.3

....................................................................................................................71

5.4 Texture Fetch

5.5

Chapter6

6.1

............................................................................................................................................... 74

6.2

6.3

B.1

runtime

............................................................................................................................. 83

B.2

runtime

........................................................................................................................... 86

C

C.1

....................................................................................................................................... 88

C.1.1 atomicAdd() ................................................................................................................... 88

C.1.2 atomicSub() ................................................................................................................... 88

C.1.3 atomicExch() ................................................................................................................. 88

C.1.4 atomicMin() ................................................................................................................... 88

C.2.3 atomicXor() ................................................................................................................... 90

D.1

........................................................................................................................................ 91

D.1.1 cudaGetDeviceCount().......................................................................................................91

D.1.2 cudaSetDevice()..................................................................................................................91

D.1.3 cudaGetDevice()..................................................................................................................91

D.1.4 cudaGetDeviceProperties() .............................................................................91

D.1.5 cudaChooseDevice() .......................................................................................................93