<!DOCTYPE html
PUBLIC "-//W3C//DTD XHTML 1.0 Transitional//EN" "http://www.w3.org/TR/xhtml1/DTD/xhtml1-transitional.dtd">
<html xmlns="http://www.w3.org/1999/xhtml" lang="en-us" xml:lang="en-us">
<head>
<meta http-equiv="Content-Type" content="text/html; charset=utf-8"></meta>
<meta http-equiv="X-UA-Compatible" content="IE=edge"></meta>
<meta name="copyright" content="(C) Copyright 2005"></meta>
<meta name="DC.rights.owner" content="(C) Copyright 2005"></meta>
<meta name="DC.Type" content="cppModule"></meta>
<meta name="DC.Title" content="Data types used by CUDA Runtime"></meta>
<meta name="abstract" content=""></meta>
<meta name="description" content=""></meta>
<meta name="DC.Format" content="XHTML"></meta>
<meta name="DC.Identifier" content="group__CUDART__TYPES"></meta>
<link rel="stylesheet" type="text/css" href="../common/formatting/commonltr.css"></link>
<link rel="stylesheet" type="text/css" href="../common/formatting/site.css"></link>
<title>CUDA Runtime API :: CUDA Toolkit Documentation</title>
<!--[if lt IE 9]>
<script src="../common/formatting/html5shiv-printshiv.min.js"></script>
<![endif]-->
<script type="text/javascript" charset="utf-8" src="//assets.adobedtm.com/b92787824f2e0e9b68dc2e993f9bd995339fe417/satelliteLib-7ba51e58dc61bcb0e9311aadd02a0108ab24cc6c.js"></script>
<script type="text/javascript" charset="utf-8" src="../common/formatting/jquery.min.js"></script>
<script type="text/javascript" charset="utf-8" src="../common/formatting/jquery.ba-hashchange.min.js"></script>
<script type="text/javascript" charset="utf-8" src="../common/formatting/jquery.scrollintoview.min.js"></script>
<script type="text/javascript" src="../search/htmlFileList.js"></script>
<script type="text/javascript" src="../search/htmlFileInfoList.js"></script>
<script type="text/javascript" src="../search/nwSearchFnt.min.js"></script>
<script type="text/javascript" src="../search/stemmers/en_stemmer.min.js"></script>
<script type="text/javascript" src="../search/index-1.js"></script>
<script type="text/javascript" src="../search/index-2.js"></script>
<script type="text/javascript" src="../search/index-3.js"></script>
<link rel="canonical" href="http://docs.nvidia.com/cuda/cuda-runtime-api/index.html"></link>
<link rel="stylesheet" type="text/css" href="../common/formatting/qwcode.highlight.css"></link>
</head>
<body>
<header id="header"><span id="company">NVIDIA</span><span id="site-title">CUDA Toolkit Documentation</span><form id="search" method="get" action="search">
<input type="text" name="search-text"></input><fieldset id="search-location">
<legend>Search In:</legend>
<label><input type="radio" name="search-type" value="site"></input>Entire Site</label>
<label><input type="radio" name="search-type" value="document"></input>Just This Document</label></fieldset>
<button type="reset">clear search</button>
<button id="submit" type="submit">search</button></form>
</header>
<div id="site-content">
<nav id="site-nav">
<div class="category closed"><a href="../index.html" title="The root of the site.">CUDA Toolkit
v10.1.168</a></div>
<div class="category"><a href="index.html" title="CUDA Runtime API">CUDA Runtime API</a></div>
<ul>
<li>
<div class="section-link"><a href="driver-vs-runtime-api.html#driver-vs-runtime-api">1. Difference between the driver and runtime APIs </a></div>
</li>
<li>
<div class="section-link"><a href="api-sync-behavior.html#api-sync-behavior">2. API synchronization behavior </a></div>
</li>
<li>
<div class="section-link"><a href="stream-sync-behavior.html#stream-sync-behavior">3. Stream synchronization behavior</a></div>
</li>
<li>
<div class="section-link"><a href="graphs-thread-safety.html#graphs-thread-safety">4. Graph object thread safety</a></div>
</li>
<li>
<div class="section-link"><a href="modules.html#modules">5. Modules</a></div>
<ul>
<li>
<div class="section-link"><a href="group__CUDART__DEVICE.html#group__CUDART__DEVICE">5.1. Device Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED">5.2. Thread Management [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__ERROR.html#group__CUDART__ERROR">5.3. Error Handling</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__STREAM.html#group__CUDART__STREAM">5.4. Stream Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__EVENT.html#group__CUDART__EVENT">5.5. Event Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__EXTRES__INTEROP.html#group__CUDART__EXTRES__INTEROP">5.6. External Resource Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION">5.7. Execution Control</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__OCCUPANCY.html#group__CUDART__OCCUPANCY">5.8. Occupancy</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__MEMORY.html#group__CUDART__MEMORY">5.9. Memory Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__MEMORY__DEPRECATED.html#group__CUDART__MEMORY__DEPRECATED">5.10. Memory Management [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__UNIFIED.html#group__CUDART__UNIFIED">5.11. Unified Addressing</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__PEER.html#group__CUDART__PEER">5.12. Peer Device Memory Access</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__OPENGL.html#group__CUDART__OPENGL">5.13. OpenGL Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__OPENGL__DEPRECATED.html#group__CUDART__OPENGL__DEPRECATED">5.14. OpenGL Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D9.html#group__CUDART__D3D9">5.15. Direct3D 9 Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D9__DEPRECATED.html#group__CUDART__D3D9__DEPRECATED">5.16. Direct3D 9 Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D10.html#group__CUDART__D3D10">5.17. Direct3D 10 Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D10__DEPRECATED.html#group__CUDART__D3D10__DEPRECATED">5.18. Direct3D 10 Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D11.html#group__CUDART__D3D11">5.19. Direct3D 11 Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__D3D11__DEPRECATED.html#group__CUDART__D3D11__DEPRECATED">5.20. Direct3D 11 Interoperability [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__VDPAU.html#group__CUDART__VDPAU">5.21. VDPAU Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__EGL.html#group__CUDART__EGL">5.22. EGL Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__INTEROP.html#group__CUDART__INTEROP">5.23. Graphics Interoperability</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE">5.24. Texture Reference Management [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__SURFACE.html#group__CUDART__SURFACE">5.25. Surface Reference Management [DEPRECATED]</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__TEXTURE__OBJECT.html#group__CUDART__TEXTURE__OBJECT">5.26. Texture Object Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__SURFACE__OBJECT.html#group__CUDART__SURFACE__OBJECT">5.27. Surface Object Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART____VERSION.html#group__CUDART____VERSION">5.28. Version Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__GRAPH.html#group__CUDART__GRAPH">5.29. Graph Management</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL">5.30. C++ API Routines</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__DRIVER.html#group__CUDART__DRIVER">5.31. Interactions with the CUDA Driver API</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__PROFILER.html#group__CUDART__PROFILER">5.32. Profiler Control</a></div>
</li>
<li>
<div class="section-link"><a href="group__CUDART__TYPES.html#group__CUDART__TYPES">5.33. Data types used by CUDA Runtime</a></div>
</li>
</ul>
</li>
<li>
<div class="section-link"><a href="annotated.html#annotated">6. Data Structures</a></div>
<ul>
<li>
<div class="section-link"><a href="class____cudaOccupancyB2DHelper.html#class____cudaOccupancyB2DHelper">6.1. __cudaOccupancyB2DHelper</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc">6.2. cudaChannelFormatDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaDeviceProp.html#structcudaDeviceProp">6.3. cudaDeviceProp</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaEglFrame.html#structcudaEglFrame">6.4. cudaEglFrame</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaEglPlaneDesc.html#structcudaEglPlaneDesc">6.5. cudaEglPlaneDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExtent.html#structcudaExtent">6.6. cudaExtent</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExternalMemoryBufferDesc.html#structcudaExternalMemoryBufferDesc">6.7. cudaExternalMemoryBufferDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExternalMemoryHandleDesc.html#structcudaExternalMemoryHandleDesc">6.8. cudaExternalMemoryHandleDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExternalMemoryMipmappedArrayDesc.html#structcudaExternalMemoryMipmappedArrayDesc">6.9. cudaExternalMemoryMipmappedArrayDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExternalSemaphoreHandleDesc.html#structcudaExternalSemaphoreHandleDesc">6.10. cudaExternalSemaphoreHandleDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExternalSemaphoreSignalParams.html#structcudaExternalSemaphoreSignalParams">6.11. cudaExternalSemaphoreSignalParams</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaExternalSemaphoreWaitParams.html#structcudaExternalSemaphoreWaitParams">6.12. cudaExternalSemaphoreWaitParams</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaFuncAttributes.html#structcudaFuncAttributes">6.13. cudaFuncAttributes</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaHostNodeParams.html#structcudaHostNodeParams">6.14. cudaHostNodeParams</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t">6.15. cudaIpcEventHandle_t</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t">6.16. cudaIpcMemHandle_t</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaKernelNodeParams.html#structcudaKernelNodeParams">6.17. cudaKernelNodeParams</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaLaunchParams.html#structcudaLaunchParams">6.18. cudaLaunchParams</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms">6.19. cudaMemcpy3DParms</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms">6.20. cudaMemcpy3DPeerParms</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaMemsetParams.html#structcudaMemsetParams">6.21. cudaMemsetParams</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaPitchedPtr.html#structcudaPitchedPtr">6.22. cudaPitchedPtr</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaPointerAttributes.html#structcudaPointerAttributes">6.23. cudaPointerAttributes</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaPos.html#structcudaPos">6.24. cudaPos</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaResourceDesc.html#structcudaResourceDesc">6.25. cudaResourceDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaResourceViewDesc.html#structcudaResourceViewDesc">6.26. cudaResourceViewDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structcudaTextureDesc.html#structcudaTextureDesc">6.27. cudaTextureDesc</a></div>
</li>
<li>
<div class="section-link"><a href="structCUuuid__st.html#structCUuuid__st">6.28. CUuuid_st</a></div>
</li>
<li>
<div class="section-link"><a href="structsurfaceReference.html#structsurfaceReference">6.29. surfaceReference</a></div>
</li>
<li>
<div class="section-link"><a href="structtextureReference.html#structtextureReference">6.30. textureReference</a></div>
</li>
</ul>
</li>
<li>
<div class="section-link"><a href="functions.html#functions">7. Data Fields</a></div>
</li>
<li>
<div class="section-link"><a href="deprecated.html#deprecated">8. Deprecated List</a></div>
</li>
<li>
<div class="section-link"><a href="notices-header.html#notices-header">Notices</a></div>
<ul></ul>
</li>
</ul>
</nav>
<div id="resize-nav"></div>
<nav id="search-results">
<h2>Search Results</h2>
<ol></ol>
</nav>
<div id="contents-container">
<div id="breadcrumbs-container">
<div id="breadcrumbs"><a href="group__CUDART__PROFILER.html" shape="rect">< Previous</a> | <a href="annotated.html" shape="rect">Next ></a></div>
<div id="release-info">CUDA Runtime API
(<a href="../../pdf/CUDA_Runtime_API.pdf">PDF</a>)
-
v10.1.168
(<a href="https://developer.nvidia.com/cuda-toolkit-archive">older</a>)
-
Last updated April 24, 2019
-
<a href="mailto:CUDAIssues@nvidia.com?subject=CUDA Toolkit Documentation Feedback: CUDA Runtime API">Send Feedback</a></div>
</div>
<article id="contents">
<div class="topic reference apiRef apiPackage cppModule" id="group__CUDART__TYPES"><a name="group__CUDART__TYPES" shape="rect">
<!-- --></a><h2 class="topictitle2 cppModule">5.33. Data types used by CUDA Runtime</h2>
<div class="section">
<p></p>
</div>
<h3 class="fake_sectiontitle member_header">Classes</h3>
<dl class="members">
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structCUuuid__st.html#structCUuuid__st" shape="rect">CUuuid_st</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structCUuuid__st.html#structCUuuid__st" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" shape="rect">cudaChannelFormatDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaDeviceProp.html#structcudaDeviceProp" shape="rect">cudaDeviceProp</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaDeviceProp.html#structcudaDeviceProp" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaEglFrame.html#structcudaEglFrame" shape="rect">cudaEglFrame</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaEglFrame.html#structcudaEglFrame" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaEglPlaneDesc.html#structcudaEglPlaneDesc" shape="rect">cudaEglPlaneDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaEglPlaneDesc.html#structcudaEglPlaneDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExtent.html#structcudaExtent" shape="rect">cudaExtent</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExtent.html#structcudaExtent" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExternalMemoryBufferDesc.html#structcudaExternalMemoryBufferDesc" shape="rect">cudaExternalMemoryBufferDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExternalMemoryBufferDesc.html#structcudaExternalMemoryBufferDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExternalMemoryHandleDesc.html#structcudaExternalMemoryHandleDesc" shape="rect">cudaExternalMemoryHandleDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExternalMemoryHandleDesc.html#structcudaExternalMemoryHandleDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExternalMemoryMipmappedArrayDesc.html#structcudaExternalMemoryMipmappedArrayDesc" shape="rect">cudaExternalMemoryMipmappedArrayDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExternalMemoryMipmappedArrayDesc.html#structcudaExternalMemoryMipmappedArrayDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExternalSemaphoreHandleDesc.html#structcudaExternalSemaphoreHandleDesc" shape="rect">cudaExternalSemaphoreHandleDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExternalSemaphoreHandleDesc.html#structcudaExternalSemaphoreHandleDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExternalSemaphoreSignalParams.html#structcudaExternalSemaphoreSignalParams" shape="rect">cudaExternalSemaphoreSignalParams</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExternalSemaphoreSignalParams.html#structcudaExternalSemaphoreSignalParams" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaExternalSemaphoreWaitParams.html#structcudaExternalSemaphoreWaitParams" shape="rect">cudaExternalSemaphoreWaitParams</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaExternalSemaphoreWaitParams.html#structcudaExternalSemaphoreWaitParams" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaFuncAttributes.html#structcudaFuncAttributes" shape="rect">cudaFuncAttributes</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaFuncAttributes.html#structcudaFuncAttributes" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaHostNodeParams.html#structcudaHostNodeParams" shape="rect">cudaHostNodeParams</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaHostNodeParams.html#structcudaHostNodeParams" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t" shape="rect">cudaIpcEventHandle_t</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t" shape="rect">cudaIpcMemHandle_t</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaKernelNodeParams.html#structcudaKernelNodeParams" shape="rect">cudaKernelNodeParams</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaKernelNodeParams.html#structcudaKernelNodeParams" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaLaunchParams.html#structcudaLaunchParams" shape="rect">cudaLaunchParams</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaLaunchParams.html#structcudaLaunchParams" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms" shape="rect">cudaMemcpy3DParms</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms" shape="rect">cudaMemcpy3DPeerParms</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaMemsetParams.html#structcudaMemsetParams" shape="rect">cudaMemsetParams</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaMemsetParams.html#structcudaMemsetParams" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaPitchedPtr.html#structcudaPitchedPtr" shape="rect">cudaPitchedPtr</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaPitchedPtr.html#structcudaPitchedPtr" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaPointerAttributes.html#structcudaPointerAttributes" shape="rect">cudaPointerAttributes</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaPointerAttributes.html#structcudaPointerAttributes" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaPos.html#structcudaPos" shape="rect">cudaPos</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaPos.html#structcudaPos" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaResourceDesc.html#structcudaResourceDesc" shape="rect">cudaResourceDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaResourceDesc.html#structcudaResourceDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaResourceViewDesc.html#structcudaResourceViewDesc" shape="rect">cudaResourceViewDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaResourceViewDesc.html#structcudaResourceViewDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structcudaTextureDesc.html#structcudaTextureDesc" shape="rect">cudaTextureDesc</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structcudaTextureDesc.html#structcudaTextureDesc" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structsurfaceReference.html#structsurfaceReference" shape="rect">surfaceReference</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structsurfaceReference.html#structsurfaceReference" class="link" title="" shape="rect"></a></dd>
<dt><span class="member_type">struct </span><span class="member_name">
<div><a class="link" href="structtextureReference.html#structtextureReference" shape="rect">textureReference</a></div></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span><a href="structtextureReference.html#structtextureReference" class="link" title="" shape="rect"></a></dd>
</dl>
<h3 class="fake_sectiontitle member_header">Defines</h3>
<dl class="members">
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g804d292b8842ce5fb4e77d71b979615f" shape="rect">CUDA_EGL_MAX_PLANES</a> 3</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g38818d647e61a5d15fb8012fe54c2d24" shape="rect">CUDA_IPC_HANDLE_SIZE</a> 64</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gfec2b519ab85854efaa40e12f4e34ad3" shape="rect">cudaArrayColorAttachment</a> 0x20</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g802843d69ca8be35ee050ff66782179e" shape="rect">cudaArrayCubemap</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6c47e87081bfd4f6030937f99ef12412" shape="rect">cudaArrayDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6d9a27dfb1207df13de0e822f75f4ab8" shape="rect">cudaArrayLayered</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g8cb5bdac32ad53c423992a125b3f9a66" shape="rect">cudaArraySurfaceLoadStore</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g142b19a14d56a03b1e410430aa5202d1" shape="rect">cudaArrayTextureGather</a> 0x08</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4b4ed6dd17d7c0950e5127138279f86a" shape="rect">cudaCooperativeLaunchMultiDeviceNoPostSync</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g310f49178bf4b06b546f83124fa191f2" shape="rect">cudaCooperativeLaunchMultiDeviceNoPreSync</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gb3de5e703b559507c39a6a02127e2967" shape="rect">cudaCpuDeviceId</a> ((int)-1)</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g130ddae663f1873258fee5a6e0808b71" shape="rect">cudaDeviceBlockingSync</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gda5f97298bf704dd3b04cbac4819e6e3" shape="rect">cudaDeviceLmemResizeToMax</a> 0x10</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3762be9cccdd809a4ca128354fd134b0" shape="rect">cudaDeviceMapHost</a> 0x08</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gc50dd5d226be88b768de22e849c9bf7a" shape="rect">cudaDeviceMask</a> 0x1f</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g1f938b9d13391758b22f0d0d2faa3e47" shape="rect">cudaDevicePropDontCare</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3ade1dbaf4b222b22733cdfdcc026075" shape="rect">cudaDeviceScheduleAuto</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" shape="rect">cudaDeviceScheduleBlockingSync</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g008de63abd7ba8da0f5f13ef7317fd29" shape="rect">cudaDeviceScheduleMask</a> 0x07</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gf01347c3dafebf07e1a0b4321a030a63" shape="rect">cudaDeviceScheduleSpin</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gbc13c52d342c67ebf0f1f7af937735a8" shape="rect">cudaDeviceScheduleYield</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" shape="rect">cudaEventBlockingSync</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6f8811acffcc133b5e4a50de6646d18e" shape="rect">cudaEventDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1ga5d3eff7c3623e2be533968d9cc1ee7e" shape="rect">cudaEventDisableTiming</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g49ec9cd742f8a3f6fde4ee72a66326f6" shape="rect">cudaEventInterprocess</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gea2031488a28bcdb7695e9bbaf25e149" shape="rect">cudaExternalMemoryDedicated</a> 0x1</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g1e00f7734325eb38d75f3ffeae6acac8" shape="rect">cudaHostAllocDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" shape="rect">cudaHostAllocMapped</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" shape="rect">cudaHostAllocPortable</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3a7db37d02ce0b2350067ab639ef321c" shape="rect">cudaHostAllocWriteCombined</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g91ca01bef4ecb16ca98b8e129ff6427f" shape="rect">cudaHostRegisterDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g27d1406f2a35d23fd8f70cb25c408d8a" shape="rect">cudaHostRegisterIoMemory</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g838b73458521c60f502efd19db0e365d" shape="rect">cudaHostRegisterMapped</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g36977255e5c778f7e4362d32d6b1cecd" shape="rect">cudaHostRegisterPortable</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g5ca8f199bd18a2fadd964e3582dcd937" shape="rect">cudaInvalidDeviceId</a> ((int)-2)</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g60f28a5142ee7ae0336dfa83fd54e006" shape="rect">cudaIpcMemLazyEnablePeerAccess</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">cudaMemAttachGlobal</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">cudaMemAttachHost</a> 0x02</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">cudaMemAttachSingle</a> 0x04</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g11570371f508845a9df47b17f85d90ac" shape="rect">cudaOccupancyDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g0a30e61b561f0678f1bf39eb051033bf" shape="rect">cudaOccupancyDisableCachingOverride</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g666bfab4a42e799d74bc07269f9bcd9b" shape="rect">cudaPeerAccessDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1ged347a89ec289c787faa116b851708fc" shape="rect">cudaStreamDefault</a> 0x00</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4e62d09dde16ba457b0a97f3a5262246" shape="rect">cudaStreamLegacy</a> ((cudaStream_t)0x1)</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g5dbd11a1723d9f5938a133cedbc525e3" shape="rect">cudaStreamNonBlocking</a> 0x01</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">#define </span><span class="member_name"><a href="#group__CUDART__TYPES_1g7b7129befd6f52708309acafd1c46197" shape="rect">cudaStreamPerThread</a> ((cudaStream_t)0x2)</span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
</dl>
<h3 class="fake_sectiontitle member_header">Typedefs</h3>
<dl class="members">
<dt><span class="member_type">typedef cudaArray * </span><span class="member_name"><a href="#group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" shape="rect">cudaArray_const_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef cudaArray * </span><span class="member_name"><a href="#group__CUDART__TYPES_1gaf8b3ba752727d996074a71ee997ce68" shape="rect">cudaArray_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef CUeglStreamConnection_st * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g8d98c18806b2361aeb23e07a3bda96da" shape="rect">cudaEglStreamConnection</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" title="" shape="rect">enumcudaError</a> </span><span class="member_name"><a href="#group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" shape="rect">cudaError_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUevent_st * </span><span class="member_name"><a href="#group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" shape="rect">cudaEvent_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef CUexternalMemory_st * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g79a2bf6a3a2aa9011a96dc17d476faf7" shape="rect">cudaExternalMemory_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef CUexternalSemaphore_st * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1gf8bc7ab93d638c5835e5289ac7d683c4" shape="rect">cudaExternalSemaphore_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUgraphExec_st * </span><span class="member_name"><a href="#group__CUDART__TYPES_1g2fee13c408fb7da16401e25c1ae6bdb9" shape="rect">cudaGraphExec_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUgraphNode_st * </span><span class="member_name"><a href="#group__CUDART__TYPES_1g7eed9297e04a8e4b5100200d5e69c124" shape="rect">cudaGraphNode_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUgraph_st * </span><span class="member_name"><a href="#group__CUDART__TYPES_1g5707132c494c91db57db5a6da0beba4c" shape="rect">cudaGraph_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef cudaGraphicsResource * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1gf58dd8d3c7a65714ff7f5459adbf7e6f" shape="rect">cudaGraphicsResource_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef
void(CUDART_CB*
</span><span class="member_name"><a href="#group__CUDART__TYPES_1g30104c99d85403b72b7c7ad72a4782fc" shape="rect">cudaHostFn_t</a> )( void*
<span> </span><span class="keyword keyword apiItemName">userData</span> ) </span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef cudaMipmappedArray * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" shape="rect">cudaMipmappedArray_const_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef cudaMipmappedArray * </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g1b03ad14fc0ab86f8b033837f5562d8a" shape="rect">cudaMipmappedArray_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" title="" shape="rect">enumcudaOutputMode</a> </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1ge1e4fa3423d204e9f927703561c36c8f" shape="rect">cudaOutputMode_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">typedef CUstream_st * </span><span class="member_name"><a href="#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" shape="rect">cudaStream_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef unsigned long long </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1gbe57cf2ccbe7f9d696f18808dd634c0a" shape="rect">cudaSurfaceObject_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_long_type">typedef unsigned long long </span><span class="member_name_long_type"><a href="#group__CUDART__TYPES_1g83eb271ebc4cb2817e66d7c752f0c29b" shape="rect">cudaTextureObject_t</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
</dl>
<h3 class="fake_sectiontitle member_header">Enumerations</h3>
<dl class="members">
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gd343aef6d93073cfc0d0851fc2b47471" shape="rect">cudaCGScope</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">cudaChannelFormatKind</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" shape="rect">cudaComputeMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g49e2f8c2c0bd6fe264f2fc970912e5cd" shape="rect">cudaDeviceAttr</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g2f597e2acceab33f60bd61c41fea0c1b" shape="rect">cudaDeviceP2PAttr</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gb6ba961c95f712b86ed7a52e73970a69" shape="rect">cudaEglColorFormat</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gbe68551b4eb6dfd6964e674c89d210b1" shape="rect">cudaEglFrameType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g1b8600d3bc8514e841e093921c10ebe4" shape="rect">cudaEglResourceLocationFlags</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" shape="rect">cudaError</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g62ab2fcc2eb066702c3694148383749e" shape="rect">cudaExternalMemoryHandleType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gb35390be1e170db8671b0abfb57ad3d9" shape="rect">cudaExternalSemaphoreHandleType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gc6c537b33d22c871a103f0fda8ac8bbe" shape="rect">cudaFuncAttribute</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" shape="rect">cudaFuncCache</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g649fb64bad79fc6f2f531860c0eb777c" shape="rect">cudaGraphNodeType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gbf3ce16a621826a09263b8a58902fee8" shape="rect">cudaGraphicsCubeFace</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g2c3c3a69caaf333d29d0b38b75de5ffd" shape="rect">cudaGraphicsMapFlags</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gd17cc29b28205bbe32ac575eba16c277" shape="rect">cudaGraphicsRegisterFlags</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">cudaLimit</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gdfcc848da2b9f49661333f861ad1a379" shape="rect">cudaMemRangeAttribute</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" shape="rect">cudaMemcpyKind</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gc314a8b14091f7e02a7ad15dcb36c857" shape="rect">cudaMemoryAdvise</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g13de56a8fe75569530ecc3a3106e9b6d" shape="rect">cudaMemoryType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" shape="rect">cudaOutputMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g067b774c0e639817a00a972c8e2c203c" shape="rect">cudaResourceType</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6b3a50368a0aa592f65e928adca9b929" shape="rect">cudaResourceViewFormat</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gb0a2adc3971b31a19b6ce2729bb5ce9f" shape="rect">cudaSharedCarveout</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g6e62d15f3c224625e8c9aa946f1709a6" shape="rect">cudaSharedMemConfig</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g24ae5ae00cc50614957ff8eba43e560e" shape="rect">cudaStreamCaptureMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g0ec4aacc66fe76c145252d12b189e233" shape="rect">cudaStreamCaptureStatus</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gdc002e3c2a4fd592efa944e2c73a10fb" shape="rect">cudaSurfaceBoundaryMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g427be57cb8aa90479139bba92267150f" shape="rect">cudaSurfaceFormatMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1g03e1bbd2c491d809279c7a47e2cd0351" shape="rect">cudaTextureAddressMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gee4adb3d1b062cf05374de09325a82d5" shape="rect">cudaTextureFilterMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
<dt><span class="member_type">enum </span><span class="member_name"><a href="#group__CUDART__TYPES_1gd9266d02be93809558036ec4f3d5f43d" shape="rect">cudaTextureReadMode</a></span></dt>
<dd class="shortdesc"><span></span><span class="desc"></span></dd>
</dl>
<div class="description">
<h3 class="sectiontitle">Defines</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__TYPES_1g804d292b8842ce5fb4e77d71b979615f" id="group__CUDART__TYPES_1g804d292b8842ce5fb4e77d71b979615f" shape="rect">
<!-- --></a><span>#define CUDA_EGL_MAX_PLANES 3</span></dt>
<dd class="description">
<div class="section">
<p>Maximum number of planes per frame </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g38818d647e61a5d15fb8012fe54c2d24" id="group__CUDART__TYPES_1g38818d647e61a5d15fb8012fe54c2d24" shape="rect">
<!-- --></a><span>#define CUDA_IPC_HANDLE_SIZE 64</span></dt>
<dd class="description">
<div class="section">
<p>CUDA IPC Handle Size </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gfec2b519ab85854efaa40e12f4e34ad3" id="group__CUDART__TYPES_1gfec2b519ab85854efaa40e12f4e34ad3" shape="rect">
<!-- --></a><span>#define cudaArrayColorAttachment 0x20</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaExternalMemoryGetMappedMipmappedArray if the mipmapped array is used as a color target in a graphics API
</p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g802843d69ca8be35ee050ff66782179e" id="group__CUDART__TYPES_1g802843d69ca8be35ee050ff66782179e" shape="rect">
<!-- --></a><span>#define cudaArrayCubemap 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMalloc3DArray to create a cubemap CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6c47e87081bfd4f6030937f99ef12412" id="group__CUDART__TYPES_1g6c47e87081bfd4f6030937f99ef12412" shape="rect">
<!-- --></a><span>#define cudaArrayDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default CUDA array allocation flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6d9a27dfb1207df13de0e822f75f4ab8" id="group__CUDART__TYPES_1g6d9a27dfb1207df13de0e822f75f4ab8" shape="rect">
<!-- --></a><span>#define cudaArrayLayered 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMalloc3DArray to create a layered CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g8cb5bdac32ad53c423992a125b3f9a66" id="group__CUDART__TYPES_1g8cb5bdac32ad53c423992a125b3f9a66" shape="rect">
<!-- --></a><span>#define cudaArraySurfaceLoadStore 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMallocArray or cudaMalloc3DArray in order to bind surfaces to the CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g142b19a14d56a03b1e410430aa5202d1" id="group__CUDART__TYPES_1g142b19a14d56a03b1e410430aa5202d1" shape="rect">
<!-- --></a><span>#define cudaArrayTextureGather 0x08</span></dt>
<dd class="description">
<div class="section">
<p>Must be set in cudaMallocArray or cudaMalloc3DArray in order to perform texture gather operations on the CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4b4ed6dd17d7c0950e5127138279f86a" id="group__CUDART__TYPES_1g4b4ed6dd17d7c0950e5127138279f86a" shape="rect">
<!-- --></a><span>#define cudaCooperativeLaunchMultiDeviceNoPostSync 0x02</span></dt>
<dd class="description">
<div class="section">
<p>If set, any subsequent work pushed in a stream that participated in a call to <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g20f8d75d8786c54cc168c47fde66ee52" title="Launches device functions on multiple devices where thread blocks can cooperate and synchronize as they execute." shape="rect">cudaLaunchCooperativeKernelMultiDevice</a> will only wait for the kernel launched on the GPU corresponding to that stream to complete before it begins execution.
</p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g310f49178bf4b06b546f83124fa191f2" id="group__CUDART__TYPES_1g310f49178bf4b06b546f83124fa191f2" shape="rect">
<!-- --></a><span>#define cudaCooperativeLaunchMultiDeviceNoPreSync 0x01</span></dt>
<dd class="description">
<div class="section">
<p>If set, each kernel launched as part of <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g20f8d75d8786c54cc168c47fde66ee52" title="Launches device functions on multiple devices where thread blocks can cooperate and synchronize as they execute." shape="rect">cudaLaunchCooperativeKernelMultiDevice</a> only waits for prior work in the stream corresponding to that GPU to complete before the kernel begins execution.
</p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gb3de5e703b559507c39a6a02127e2967" id="group__CUDART__TYPES_1gb3de5e703b559507c39a6a02127e2967" shape="rect">
<!-- --></a><span>#define cudaCpuDeviceId ((int)-1)</span></dt>
<dd class="description">
<div class="section">
<p>Device id that represents the CPU </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g130ddae663f1873258fee5a6e0808b71" id="group__CUDART__TYPES_1g130ddae663f1873258fee5a6e0808b71" shape="rect">
<!-- --></a><span>#define cudaDeviceBlockingSync 0x04</span></dt>
<dd class="description">
<div class="section">
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000055" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This flag was deprecated as of CUDA 4.0 and replaced with <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" shape="rect">cudaDeviceScheduleBlockingSync</a>. </span></p>
<p>Device flag - Use blocking synchronization </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gda5f97298bf704dd3b04cbac4819e6e3" id="group__CUDART__TYPES_1gda5f97298bf704dd3b04cbac4819e6e3" shape="rect">
<!-- --></a><span>#define cudaDeviceLmemResizeToMax 0x10</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Keep local memory allocation after launch </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3762be9cccdd809a4ca128354fd134b0" id="group__CUDART__TYPES_1g3762be9cccdd809a4ca128354fd134b0" shape="rect">
<!-- --></a><span>#define cudaDeviceMapHost 0x08</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Support mapped pinned allocations </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gc50dd5d226be88b768de22e849c9bf7a" id="group__CUDART__TYPES_1gc50dd5d226be88b768de22e849c9bf7a" shape="rect">
<!-- --></a><span>#define cudaDeviceMask 0x1f</span></dt>
<dd class="description">
<div class="section">
<p>Device flags mask </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g1f938b9d13391758b22f0d0d2faa3e47" id="group__CUDART__TYPES_1g1f938b9d13391758b22f0d0d2faa3e47" shape="rect">
<!-- --></a><span>#define cudaDevicePropDontCare </span></dt>
<dd class="description">
<div class="section">
<p>Empty device properties </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3ade1dbaf4b222b22733cdfdcc026075" id="group__CUDART__TYPES_1g3ade1dbaf4b222b22733cdfdcc026075" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleAuto 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Automatic scheduling </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" id="group__CUDART__TYPES_1g057e6912c52708b6aa86e79dd83d007c" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleBlockingSync 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Use blocking synchronization </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g008de63abd7ba8da0f5f13ef7317fd29" id="group__CUDART__TYPES_1g008de63abd7ba8da0f5f13ef7317fd29" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleMask 0x07</span></dt>
<dd class="description">
<div class="section">
<p>Device schedule flags mask </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gf01347c3dafebf07e1a0b4321a030a63" id="group__CUDART__TYPES_1gf01347c3dafebf07e1a0b4321a030a63" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleSpin 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Spin default scheduling </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbc13c52d342c67ebf0f1f7af937735a8" id="group__CUDART__TYPES_1gbc13c52d342c67ebf0f1f7af937735a8" shape="rect">
<!-- --></a><span>#define cudaDeviceScheduleYield 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Device flag - Yield default scheduling </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" id="group__CUDART__TYPES_1g26509a522be9d449aa7c8c279612452d" shape="rect">
<!-- --></a><span>#define cudaEventBlockingSync 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Event uses blocking synchronization </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6f8811acffcc133b5e4a50de6646d18e" id="group__CUDART__TYPES_1g6f8811acffcc133b5e4a50de6646d18e" shape="rect">
<!-- --></a><span>#define cudaEventDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default event flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ga5d3eff7c3623e2be533968d9cc1ee7e" id="group__CUDART__TYPES_1ga5d3eff7c3623e2be533968d9cc1ee7e" shape="rect">
<!-- --></a><span>#define cudaEventDisableTiming 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Event will not record timing data </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g49ec9cd742f8a3f6fde4ee72a66326f6" id="group__CUDART__TYPES_1g49ec9cd742f8a3f6fde4ee72a66326f6" shape="rect">
<!-- --></a><span>#define cudaEventInterprocess 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Event is suitable for interprocess use. cudaEventDisableTiming must be set </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gea2031488a28bcdb7695e9bbaf25e149" id="group__CUDART__TYPES_1gea2031488a28bcdb7695e9bbaf25e149" shape="rect">
<!-- --></a><span>#define cudaExternalMemoryDedicated 0x1</span></dt>
<dd class="description">
<div class="section">
<p>Indicates that the external memory object is a dedicated resource </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g1e00f7734325eb38d75f3ffeae6acac8" id="group__CUDART__TYPES_1g1e00f7734325eb38d75f3ffeae6acac8" shape="rect">
<!-- --></a><span>#define cudaHostAllocDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default page-locked allocation flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" id="group__CUDART__TYPES_1g01e600c738b962c8f973dda7708f7a70" shape="rect">
<!-- --></a><span>#define cudaHostAllocMapped 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Map allocation into device space </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" id="group__CUDART__TYPES_1gc46ce76be41cf79774331cc8cfceb52b" shape="rect">
<!-- --></a><span>#define cudaHostAllocPortable 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Pinned memory accessible by all CUDA contexts </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3a7db37d02ce0b2350067ab639ef321c" id="group__CUDART__TYPES_1g3a7db37d02ce0b2350067ab639ef321c" shape="rect">
<!-- --></a><span>#define cudaHostAllocWriteCombined 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Write-combined memory </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g91ca01bef4ecb16ca98b8e129ff6427f" id="group__CUDART__TYPES_1g91ca01bef4ecb16ca98b8e129ff6427f" shape="rect">
<!-- --></a><span>#define cudaHostRegisterDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default host memory registration flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g27d1406f2a35d23fd8f70cb25c408d8a" id="group__CUDART__TYPES_1g27d1406f2a35d23fd8f70cb25c408d8a" shape="rect">
<!-- --></a><span>#define cudaHostRegisterIoMemory 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Memory-mapped I/O space </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g838b73458521c60f502efd19db0e365d" id="group__CUDART__TYPES_1g838b73458521c60f502efd19db0e365d" shape="rect">
<!-- --></a><span>#define cudaHostRegisterMapped 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Map registered memory into device space </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g36977255e5c778f7e4362d32d6b1cecd" id="group__CUDART__TYPES_1g36977255e5c778f7e4362d32d6b1cecd" shape="rect">
<!-- --></a><span>#define cudaHostRegisterPortable 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Pinned memory accessible by all CUDA contexts </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g5ca8f199bd18a2fadd964e3582dcd937" id="group__CUDART__TYPES_1g5ca8f199bd18a2fadd964e3582dcd937" shape="rect">
<!-- --></a><span>#define cudaInvalidDeviceId ((int)-2)</span></dt>
<dd class="description">
<div class="section">
<p>Device id that represents an invalid device </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g60f28a5142ee7ae0336dfa83fd54e006" id="group__CUDART__TYPES_1g60f28a5142ee7ae0336dfa83fd54e006" shape="rect">
<!-- --></a><span>#define cudaIpcMemLazyEnablePeerAccess 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Automatically enable peer access between remote devices as needed </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" id="group__CUDART__TYPES_1g4808e47eba73eb94622ec70a9f9b91ff" shape="rect">
<!-- --></a><span>#define cudaMemAttachGlobal 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Memory can be accessed by any stream on any device </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" id="group__CUDART__TYPES_1g4f9a428d18fdd89a99441d0dd27131c0" shape="rect">
<!-- --></a><span>#define cudaMemAttachHost 0x02</span></dt>
<dd class="description">
<div class="section">
<p>Memory cannot be accessed by any stream on any device </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" id="group__CUDART__TYPES_1gdc191442d08fc3a9de4cf055edfd2dbe" shape="rect">
<!-- --></a><span>#define cudaMemAttachSingle 0x04</span></dt>
<dd class="description">
<div class="section">
<p>Memory can only be accessed by a single stream on the associated device </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g11570371f508845a9df47b17f85d90ac" id="group__CUDART__TYPES_1g11570371f508845a9df47b17f85d90ac" shape="rect">
<!-- --></a><span>#define cudaOccupancyDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default behavior </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g0a30e61b561f0678f1bf39eb051033bf" id="group__CUDART__TYPES_1g0a30e61b561f0678f1bf39eb051033bf" shape="rect">
<!-- --></a><span>#define cudaOccupancyDisableCachingOverride 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Assume global caching is enabled and cannot be automatically turned off </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g666bfab4a42e799d74bc07269f9bcd9b" id="group__CUDART__TYPES_1g666bfab4a42e799d74bc07269f9bcd9b" shape="rect">
<!-- --></a><span>#define cudaPeerAccessDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default peer addressing enable flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ged347a89ec289c787faa116b851708fc" id="group__CUDART__TYPES_1ged347a89ec289c787faa116b851708fc" shape="rect">
<!-- --></a><span>#define cudaStreamDefault 0x00</span></dt>
<dd class="description">
<div class="section">
<p>Default stream flag </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4e62d09dde16ba457b0a97f3a5262246" id="group__CUDART__TYPES_1g4e62d09dde16ba457b0a97f3a5262246" shape="rect">
<!-- --></a><span>#define cudaStreamLegacy ((cudaStream_t)0x1)</span></dt>
<dd class="description">
<div class="section">
<p>Legacy stream handle</p>
<p class="p">Stream handle that can be passed as a cudaStream_t to use an implicit stream with legacy synchronization behavior.</p>
<p class="p">See details of the <a class="xref xmlonly" href="stream-sync-behavior.html#stream-sync-behavior" shape="rect">synchronization behavior</a>.
</p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g5dbd11a1723d9f5938a133cedbc525e3" id="group__CUDART__TYPES_1g5dbd11a1723d9f5938a133cedbc525e3" shape="rect">
<!-- --></a><span>#define cudaStreamNonBlocking 0x01</span></dt>
<dd class="description">
<div class="section">
<p>Stream does not synchronize with stream 0 (the NULL stream) </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g7b7129befd6f52708309acafd1c46197" id="group__CUDART__TYPES_1g7b7129befd6f52708309acafd1c46197" shape="rect">
<!-- --></a><span>#define cudaStreamPerThread ((cudaStream_t)0x2)</span></dt>
<dd class="description">
<div class="section">
<p>Per-thread stream handle</p>
<p class="p">Stream handle that can be passed as a cudaStream_t to use an implicit stream with per-thread synchronization behavior.</p>
<p class="p">See details of the <a class="xref xmlonly" href="stream-sync-behavior.html#stream-sync-behavior" shape="rect">synchronization behavior</a>.
</p>
</div>
</dd>
</dl>
</div>
<div class="description">
<h3 class="sectiontitle">Typedefs</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" id="group__CUDART__TYPES_1g1259f0b7bcff80ba46267c9117f9bb21" shape="rect">
<!-- --></a><span>typedef cudaArray * cudaArray_const_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA array (as source copy argument) </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gaf8b3ba752727d996074a71ee997ce68" id="group__CUDART__TYPES_1gaf8b3ba752727d996074a71ee997ce68" shape="rect">
<!-- --></a><span>typedef cudaArray * cudaArray_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g8d98c18806b2361aeb23e07a3bda96da" id="group__CUDART__TYPES_1g8d98c18806b2361aeb23e07a3bda96da" shape="rect">
<!-- --></a><span>typedef CUeglStreamConnection_st * cudaEglStreamConnection</span></dt>
<dd class="description">
<div class="section">
<p> CUDA EGLSream Connection </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" id="group__CUDART__TYPES_1gf599e5b8b829ce7db0f5216928f6ecb6" shape="rect">
<!-- --></a><span>typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" title="" shape="rect">enumcudaError</a> cudaError_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA Error types </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" id="group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" shape="rect">
<!-- --></a><span>typedef CUevent_st * cudaEvent_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA event types </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g79a2bf6a3a2aa9011a96dc17d476faf7" id="group__CUDART__TYPES_1g79a2bf6a3a2aa9011a96dc17d476faf7" shape="rect">
<!-- --></a><span>typedef CUexternalMemory_st * cudaExternalMemory_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA external memory </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gf8bc7ab93d638c5835e5289ac7d683c4" id="group__CUDART__TYPES_1gf8bc7ab93d638c5835e5289ac7d683c4" shape="rect">
<!-- --></a><span>typedef CUexternalSemaphore_st * cudaExternalSemaphore_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA external semaphore </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g2fee13c408fb7da16401e25c1ae6bdb9" id="group__CUDART__TYPES_1g2fee13c408fb7da16401e25c1ae6bdb9" shape="rect">
<!-- --></a><span>typedef CUgraphExec_st * cudaGraphExec_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA executable (launchable) graph </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g7eed9297e04a8e4b5100200d5e69c124" id="group__CUDART__TYPES_1g7eed9297e04a8e4b5100200d5e69c124" shape="rect">
<!-- --></a><span>typedef CUgraphNode_st * cudaGraphNode_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA graph node. </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g5707132c494c91db57db5a6da0beba4c" id="group__CUDART__TYPES_1g5707132c494c91db57db5a6da0beba4c" shape="rect">
<!-- --></a><span>typedef CUgraph_st * cudaGraph_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA graph </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gf58dd8d3c7a65714ff7f5459adbf7e6f" id="group__CUDART__TYPES_1gf58dd8d3c7a65714ff7f5459adbf7e6f" shape="rect">
<!-- --></a><span>typedef cudaGraphicsResource * cudaGraphicsResource_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA graphics resource types </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g30104c99d85403b72b7c7ad72a4782fc" id="group__CUDART__TYPES_1g30104c99d85403b72b7c7ad72a4782fc" shape="rect">
<!-- --></a><span>
void(CUDART_CB*
cudaHostFn_t )( void*
<span> </span><span class="keyword keyword apiItemName">userData</span> ) </span></dt>
<dd class="description">
<div class="section">
<p> CUDA host function
</p>
</div>
</dd>
<div class="section">
<h6 class="parameter_header">
Parameters
</h6>
<dl class="table-display-params">
<dt><tt class="code"><span class="keyword keyword apiItemName">userData</span></tt></dt>
<dd>Argument value passed to the function </dd>
</dl>
</div>
<dt class="description"><a name="group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" id="group__CUDART__TYPES_1g99f602628e1c5159da2dc2cefb5bdc04" shape="rect">
<!-- --></a><span>typedef cudaMipmappedArray * cudaMipmappedArray_const_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA mipmapped array (as source argument) </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g1b03ad14fc0ab86f8b033837f5562d8a" id="group__CUDART__TYPES_1g1b03ad14fc0ab86f8b033837f5562d8a" shape="rect">
<!-- --></a><span>typedef cudaMipmappedArray * cudaMipmappedArray_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA mipmapped array </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ge1e4fa3423d204e9f927703561c36c8f" id="group__CUDART__TYPES_1ge1e4fa3423d204e9f927703561c36c8f" shape="rect">
<!-- --></a><span>typedef <a href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" title="" shape="rect">enumcudaOutputMode</a> cudaOutputMode_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA output file modes </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" id="group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" shape="rect">
<!-- --></a><span>typedef CUstream_st * cudaStream_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA stream </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbe57cf2ccbe7f9d696f18808dd634c0a" id="group__CUDART__TYPES_1gbe57cf2ccbe7f9d696f18808dd634c0a" shape="rect">
<!-- --></a><span>typedef unsigned long long cudaSurfaceObject_t</span></dt>
<dd class="description">
<div class="section">
<p> An opaque value that represents a CUDA Surface object </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g83eb271ebc4cb2817e66d7c752f0c29b" id="group__CUDART__TYPES_1g83eb271ebc4cb2817e66d7c752f0c29b" shape="rect">
<!-- --></a><span>typedef unsigned long long cudaTextureObject_t</span></dt>
<dd class="description">
<div class="section">
<p> An opaque value that represents a CUDA texture object </p>
</div>
</dd>
</dl>
</div>
<div class="description">
<h3 class="sectiontitle">Enumerations</h3>
<dl class="description">
<dt class="description"><a name="group__CUDART__TYPES_1gd343aef6d93073cfc0d0851fc2b47471" id="group__CUDART__TYPES_1gd343aef6d93073cfc0d0851fc2b47471" shape="rect">
<!-- --></a><span>enum cudaCGScope</span></dt>
<dd class="description">
<div class="section">
<p>CUDA cooperative group scope </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaCGScopeInvalid = <span class="ph ph apiData">0</span></span></dt>
<dd>Invalid cooperative group scope </dd>
<dt><span class="enum-member-name-def">cudaCGScopeGrid = <span class="ph ph apiData">1</span></span></dt>
<dd>Scope represented by a grid_group </dd>
<dt><span class="enum-member-name-def">cudaCGScopeMultiGrid = <span class="ph ph apiData">2</span></span></dt>
<dd>Scope represented by a multi_grid_group </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" id="group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">
<!-- --></a><span>enum cudaChannelFormatKind</span></dt>
<dd class="description">
<div class="section">
<p>Channel format kind </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaChannelFormatKindSigned = <span class="ph ph apiData">0</span></span></dt>
<dd>Signed channel format </dd>
<dt><span class="enum-member-name-def">cudaChannelFormatKindUnsigned = <span class="ph ph apiData">1</span></span></dt>
<dd>Unsigned channel format </dd>
<dt><span class="enum-member-name-def">cudaChannelFormatKindFloat = <span class="ph ph apiData">2</span></span></dt>
<dd>Float channel format </dd>
<dt><span class="enum-member-name-def">cudaChannelFormatKindNone = <span class="ph ph apiData">3</span></span></dt>
<dd>No channel format </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" id="group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" shape="rect">
<!-- --></a><span>enum cudaComputeMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA device compute modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaComputeModeDefault = <span class="ph ph apiData">0</span></span></dt>
<dd>Default compute mode (Multiple threads can use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g159587909ffa0791bbe4b40187a4c6bb" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
<dt><span class="enum-member-name-def">cudaComputeModeExclusive = <span class="ph ph apiData">1</span></span></dt>
<dd>Compute-exclusive-thread mode (Only one thread in one process will be able to use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g159587909ffa0791bbe4b40187a4c6bb" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
<dt><span class="enum-member-name-def">cudaComputeModeProhibited = <span class="ph ph apiData">2</span></span></dt>
<dd>Compute-prohibited mode (No threads can use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g159587909ffa0791bbe4b40187a4c6bb" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
<dt><span class="enum-member-name-def">cudaComputeModeExclusiveProcess = <span class="ph ph apiData">3</span></span></dt>
<dd>Compute-exclusive-process mode (Many threads in one process will be able to use <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g159587909ffa0791bbe4b40187a4c6bb" title="Set device to be used for GPU executions." shape="rect">cudaSetDevice()</a> with this device)
</dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g49e2f8c2c0bd6fe264f2fc970912e5cd" id="group__CUDART__TYPES_1g49e2f8c2c0bd6fe264f2fc970912e5cd" shape="rect">
<!-- --></a><span>enum cudaDeviceAttr</span></dt>
<dd class="description">
<div class="section">
<p>CUDA device attributes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaDevAttrMaxThreadsPerBlock = <span class="ph ph apiData">1</span></span></dt>
<dd>Maximum number of threads per block </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxBlockDimX = <span class="ph ph apiData">2</span></span></dt>
<dd>Maximum block dimension X </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxBlockDimY = <span class="ph ph apiData">3</span></span></dt>
<dd>Maximum block dimension Y </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxBlockDimZ = <span class="ph ph apiData">4</span></span></dt>
<dd>Maximum block dimension Z </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxGridDimX = <span class="ph ph apiData">5</span></span></dt>
<dd>Maximum grid dimension X </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxGridDimY = <span class="ph ph apiData">6</span></span></dt>
<dd>Maximum grid dimension Y </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxGridDimZ = <span class="ph ph apiData">7</span></span></dt>
<dd>Maximum grid dimension Z </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSharedMemoryPerBlock = <span class="ph ph apiData">8</span></span></dt>
<dd>Maximum shared memory available per block in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTotalConstantMemory = <span class="ph ph apiData">9</span></span></dt>
<dd>Memory available on device for __constant__ variables in a CUDA C kernel in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrWarpSize = <span class="ph ph apiData">10</span></span></dt>
<dd>Warp size in threads </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxPitch = <span class="ph ph apiData">11</span></span></dt>
<dd>Maximum pitch in bytes allowed by memory copies </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxRegistersPerBlock = <span class="ph ph apiData">12</span></span></dt>
<dd>Maximum number of 32-bit registers available per block </dd>
<dt><span class="enum-member-name-def">cudaDevAttrClockRate = <span class="ph ph apiData">13</span></span></dt>
<dd>Peak clock frequency in kilohertz </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTextureAlignment = <span class="ph ph apiData">14</span></span></dt>
<dd>Alignment requirement for textures </dd>
<dt><span class="enum-member-name-def">cudaDevAttrGpuOverlap = <span class="ph ph apiData">15</span></span></dt>
<dd>Device can possibly copy memory and execute a kernel concurrently </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMultiProcessorCount = <span class="ph ph apiData">16</span></span></dt>
<dd>Number of multiprocessors on device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrKernelExecTimeout = <span class="ph ph apiData">17</span></span></dt>
<dd>Specifies whether there is a run time limit on kernels </dd>
<dt><span class="enum-member-name-def">cudaDevAttrIntegrated = <span class="ph ph apiData">18</span></span></dt>
<dd>Device is integrated with host memory </dd>
<dt><span class="enum-member-name-def">cudaDevAttrCanMapHostMemory = <span class="ph ph apiData">19</span></span></dt>
<dd>Device can map host memory into CUDA address space </dd>
<dt><span class="enum-member-name-def">cudaDevAttrComputeMode = <span class="ph ph apiData">20</span></span></dt>
<dd>Compute mode (See <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g7eb25f5413a962faad0956d92bae10d0" shape="rect">cudaComputeMode</a> for details)
</dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DWidth = <span class="ph ph apiData">21</span></span></dt>
<dd>Maximum 1D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DWidth = <span class="ph ph apiData">22</span></span></dt>
<dd>Maximum 2D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DHeight = <span class="ph ph apiData">23</span></span></dt>
<dd>Maximum 2D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DWidth = <span class="ph ph apiData">24</span></span></dt>
<dd>Maximum 3D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DHeight = <span class="ph ph apiData">25</span></span></dt>
<dd>Maximum 3D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DDepth = <span class="ph ph apiData">26</span></span></dt>
<dd>Maximum 3D texture depth </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLayeredWidth = <span class="ph ph apiData">27</span></span></dt>
<dd>Maximum 2D layered texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLayeredHeight = <span class="ph ph apiData">28</span></span></dt>
<dd>Maximum 2D layered texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLayeredLayers = <span class="ph ph apiData">29</span></span></dt>
<dd>Maximum layers in a 2D layered texture </dd>
<dt><span class="enum-member-name-def">cudaDevAttrSurfaceAlignment = <span class="ph ph apiData">30</span></span></dt>
<dd>Alignment requirement for surfaces </dd>
<dt><span class="enum-member-name-def">cudaDevAttrConcurrentKernels = <span class="ph ph apiData">31</span></span></dt>
<dd>Device can possibly execute multiple kernels concurrently </dd>
<dt><span class="enum-member-name-def">cudaDevAttrEccEnabled = <span class="ph ph apiData">32</span></span></dt>
<dd>Device has ECC support enabled </dd>
<dt><span class="enum-member-name-def">cudaDevAttrPciBusId = <span class="ph ph apiData">33</span></span></dt>
<dd>PCI bus ID of the device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrPciDeviceId = <span class="ph ph apiData">34</span></span></dt>
<dd>PCI device ID of the device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTccDriver = <span class="ph ph apiData">35</span></span></dt>
<dd>Device is using TCC driver model </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMemoryClockRate = <span class="ph ph apiData">36</span></span></dt>
<dd>Peak memory clock frequency in kilohertz </dd>
<dt><span class="enum-member-name-def">cudaDevAttrGlobalMemoryBusWidth = <span class="ph ph apiData">37</span></span></dt>
<dd>Global memory bus width in bits </dd>
<dt><span class="enum-member-name-def">cudaDevAttrL2CacheSize = <span class="ph ph apiData">38</span></span></dt>
<dd>Size of L2 cache in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxThreadsPerMultiProcessor = <span class="ph ph apiData">39</span></span></dt>
<dd>Maximum resident threads per multiprocessor </dd>
<dt><span class="enum-member-name-def">cudaDevAttrAsyncEngineCount = <span class="ph ph apiData">40</span></span></dt>
<dd>Number of asynchronous engines </dd>
<dt><span class="enum-member-name-def">cudaDevAttrUnifiedAddressing = <span class="ph ph apiData">41</span></span></dt>
<dd>Device shares a unified address space with the host </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DLayeredWidth = <span class="ph ph apiData">42</span></span></dt>
<dd>Maximum 1D layered texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DLayeredLayers = <span class="ph ph apiData">43</span></span></dt>
<dd>Maximum layers in a 1D layered texture </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DGatherWidth = <span class="ph ph apiData">45</span></span></dt>
<dd>Maximum 2D texture width if cudaArrayTextureGather is set </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DGatherHeight = <span class="ph ph apiData">46</span></span></dt>
<dd>Maximum 2D texture height if cudaArrayTextureGather is set </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DWidthAlt = <span class="ph ph apiData">47</span></span></dt>
<dd>Alternate maximum 3D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DHeightAlt = <span class="ph ph apiData">48</span></span></dt>
<dd>Alternate maximum 3D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture3DDepthAlt = <span class="ph ph apiData">49</span></span></dt>
<dd>Alternate maximum 3D texture depth </dd>
<dt><span class="enum-member-name-def">cudaDevAttrPciDomainId = <span class="ph ph apiData">50</span></span></dt>
<dd>PCI domain ID of the device </dd>
<dt><span class="enum-member-name-def">cudaDevAttrTexturePitchAlignment = <span class="ph ph apiData">51</span></span></dt>
<dd>Pitch alignment requirement for textures </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTextureCubemapWidth = <span class="ph ph apiData">52</span></span></dt>
<dd>Maximum cubemap texture width/height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTextureCubemapLayeredWidth = <span class="ph ph apiData">53</span></span></dt>
<dd>Maximum cubemap layered texture width/height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTextureCubemapLayeredLayers = <span class="ph ph apiData">54</span></span></dt>
<dd>Maximum layers in a cubemap layered texture </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface1DWidth = <span class="ph ph apiData">55</span></span></dt>
<dd>Maximum 1D surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DWidth = <span class="ph ph apiData">56</span></span></dt>
<dd>Maximum 2D surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DHeight = <span class="ph ph apiData">57</span></span></dt>
<dd>Maximum 2D surface height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface3DWidth = <span class="ph ph apiData">58</span></span></dt>
<dd>Maximum 3D surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface3DHeight = <span class="ph ph apiData">59</span></span></dt>
<dd>Maximum 3D surface height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface3DDepth = <span class="ph ph apiData">60</span></span></dt>
<dd>Maximum 3D surface depth </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface1DLayeredWidth = <span class="ph ph apiData">61</span></span></dt>
<dd>Maximum 1D layered surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface1DLayeredLayers = <span class="ph ph apiData">62</span></span></dt>
<dd>Maximum layers in a 1D layered surface </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DLayeredWidth = <span class="ph ph apiData">63</span></span></dt>
<dd>Maximum 2D layered surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DLayeredHeight = <span class="ph ph apiData">64</span></span></dt>
<dd>Maximum 2D layered surface height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurface2DLayeredLayers = <span class="ph ph apiData">65</span></span></dt>
<dd>Maximum layers in a 2D layered surface </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurfaceCubemapWidth = <span class="ph ph apiData">66</span></span></dt>
<dd>Maximum cubemap surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurfaceCubemapLayeredWidth = <span class="ph ph apiData">67</span></span></dt>
<dd>Maximum cubemap layered surface width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSurfaceCubemapLayeredLayers = <span class="ph ph apiData">68</span></span></dt>
<dd>Maximum layers in a cubemap layered surface </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DLinearWidth = <span class="ph ph apiData">69</span></span></dt>
<dd>Maximum 1D linear texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLinearWidth = <span class="ph ph apiData">70</span></span></dt>
<dd>Maximum 2D linear texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLinearHeight = <span class="ph ph apiData">71</span></span></dt>
<dd>Maximum 2D linear texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DLinearPitch = <span class="ph ph apiData">72</span></span></dt>
<dd>Maximum 2D linear texture pitch in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DMipmappedWidth = <span class="ph ph apiData">73</span></span></dt>
<dd>Maximum mipmapped 2D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture2DMipmappedHeight = <span class="ph ph apiData">74</span></span></dt>
<dd>Maximum mipmapped 2D texture height </dd>
<dt><span class="enum-member-name-def">cudaDevAttrComputeCapabilityMajor = <span class="ph ph apiData">75</span></span></dt>
<dd>Major compute capability version number </dd>
<dt><span class="enum-member-name-def">cudaDevAttrComputeCapabilityMinor = <span class="ph ph apiData">76</span></span></dt>
<dd>Minor compute capability version number </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxTexture1DMipmappedWidth = <span class="ph ph apiData">77</span></span></dt>
<dd>Maximum mipmapped 1D texture width </dd>
<dt><span class="enum-member-name-def">cudaDevAttrStreamPrioritiesSupported = <span class="ph ph apiData">78</span></span></dt>
<dd>Device supports stream priorities </dd>
<dt><span class="enum-member-name-def">cudaDevAttrGlobalL1CacheSupported = <span class="ph ph apiData">79</span></span></dt>
<dd>Device supports caching globals in L1 </dd>
<dt><span class="enum-member-name-def">cudaDevAttrLocalL1CacheSupported = <span class="ph ph apiData">80</span></span></dt>
<dd>Device supports caching locals in L1 </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSharedMemoryPerMultiprocessor = <span class="ph ph apiData">81</span></span></dt>
<dd>Maximum shared memory available per multiprocessor in bytes </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxRegistersPerMultiprocessor = <span class="ph ph apiData">82</span></span></dt>
<dd>Maximum number of 32-bit registers available per multiprocessor </dd>
<dt><span class="enum-member-name-def">cudaDevAttrManagedMemory = <span class="ph ph apiData">83</span></span></dt>
<dd>Device can allocate managed memory on this system </dd>
<dt><span class="enum-member-name-def">cudaDevAttrIsMultiGpuBoard = <span class="ph ph apiData">84</span></span></dt>
<dd>Device is on a multi-GPU board </dd>
<dt><span class="enum-member-name-def">cudaDevAttrMultiGpuBoardGroupID = <span class="ph ph apiData">85</span></span></dt>
<dd>Unique identifier for a group of devices on the same multi-GPU board </dd>
<dt><span class="enum-member-name-def">cudaDevAttrHostNativeAtomicSupported = <span class="ph ph apiData">86</span></span></dt>
<dd>Link between the device and the host supports native atomic operations </dd>
<dt><span class="enum-member-name-def">cudaDevAttrSingleToDoublePrecisionPerfRatio = <span class="ph ph apiData">87</span></span></dt>
<dd>Ratio of single precision performance (in floating-point operations per second) to double precision performance </dd>
<dt><span class="enum-member-name-def">cudaDevAttrPageableMemoryAccess = <span class="ph ph apiData">88</span></span></dt>
<dd>Device supports coherently accessing pageable memory without calling cudaHostRegister on it </dd>
<dt><span class="enum-member-name-def">cudaDevAttrConcurrentManagedAccess = <span class="ph ph apiData">89</span></span></dt>
<dd>Device can coherently access managed memory concurrently with the CPU </dd>
<dt><span class="enum-member-name-def">cudaDevAttrComputePreemptionSupported = <span class="ph ph apiData">90</span></span></dt>
<dd>Device supports Compute Preemption </dd>
<dt><span class="enum-member-name-def">cudaDevAttrCanUseHostPointerForRegisteredMem = <span class="ph ph apiData">91</span></span></dt>
<dd>Device can access host registered memory at the same virtual address as the CPU </dd>
<dt><span class="enum-member-name-def">cudaDevAttrReserved92 = <span class="ph ph apiData">92</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaDevAttrReserved93 = <span class="ph ph apiData">93</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaDevAttrReserved94 = <span class="ph ph apiData">94</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaDevAttrCooperativeLaunch = <span class="ph ph apiData">95</span></span></dt>
<dd>Device supports launching cooperative kernels via <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gc0210b928f9bf4e212af07d35ac11d67" title="Launches a device function." shape="rect">cudaLaunchCooperativeKernel</a></dd>
<dt><span class="enum-member-name-def">cudaDevAttrCooperativeMultiDeviceLaunch = <span class="ph ph apiData">96</span></span></dt>
<dd>Device can participate in cooperative kernels launched via <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g20f8d75d8786c54cc168c47fde66ee52" title="Launches device functions on multiple devices where thread blocks can cooperate and synchronize as they execute." shape="rect">cudaLaunchCooperativeKernelMultiDevice</a></dd>
<dt><span class="enum-member-name-def">cudaDevAttrMaxSharedMemoryPerBlockOptin = <span class="ph ph apiData">97</span></span></dt>
<dd>The maximum optin shared memory per block. This value may vary by chip. See <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g422642bfa0c035a590e4c43ff7c11f8d" title="[C++ API] Set attributes for a given function" shape="rect">cudaFuncSetAttribute</a></dd>
<dt><span class="enum-member-name-def">cudaDevAttrCanFlushRemoteWrites = <span class="ph ph apiData">98</span></span></dt>
<dd>Device supports flushing of outstanding remote writes. </dd>
<dt><span class="enum-member-name-def">cudaDevAttrHostRegisterSupported = <span class="ph ph apiData">99</span></span></dt>
<dd>Device supports host memory registration via <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1ge8d5c17670f16ac4fc8fcb4181cb490c" title="Registers an existing host memory range for use by CUDA." shape="rect">cudaHostRegister</a>.
</dd>
<dt><span class="enum-member-name-def">cudaDevAttrPageableMemoryAccessUsesHostPageTables = <span class="ph ph apiData">100</span></span></dt>
<dd>Device accesses pageable memory via the host's page tables. </dd>
<dt><span class="enum-member-name-def">cudaDevAttrDirectManagedMemAccessFromHost = <span class="ph ph apiData">101</span></span></dt>
<dd>Host can directly access managed memory on the device without migration. </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g2f597e2acceab33f60bd61c41fea0c1b" id="group__CUDART__TYPES_1g2f597e2acceab33f60bd61c41fea0c1b" shape="rect">
<!-- --></a><span>enum cudaDeviceP2PAttr</span></dt>
<dd class="description">
<div class="section">
<p>CUDA device P2P attributes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaDevP2PAttrPerformanceRank = <span class="ph ph apiData">1</span></span></dt>
<dd>A relative value indicating the performance of the link between two devices </dd>
<dt><span class="enum-member-name-def">cudaDevP2PAttrAccessSupported = <span class="ph ph apiData">2</span></span></dt>
<dd>Peer access is enabled </dd>
<dt><span class="enum-member-name-def">cudaDevP2PAttrNativeAtomicSupported = <span class="ph ph apiData">3</span></span></dt>
<dd>Native atomic operation over the link supported </dd>
<dt><span class="enum-member-name-def">cudaDevP2PAttrCudaArrayAccessSupported = <span class="ph ph apiData">4</span></span></dt>
<dd>Accessing CUDA arrays over the link supported </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gb6ba961c95f712b86ed7a52e73970a69" id="group__CUDART__TYPES_1gb6ba961c95f712b86ed7a52e73970a69" shape="rect">
<!-- --></a><span>enum cudaEglColorFormat</span></dt>
<dd class="description">
<div class="section">
<p>CUDA EGL Color Format - The different planar and multiplanar formats currently supported for CUDA_EGL interops. </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV420Planar = <span class="ph ph apiData">0</span></span></dt>
<dd>Y, U, V in three surfaces, each in a separate surface, U/V width = 1/2 Y width, U/V height = 1/2 Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV420SemiPlanar = <span class="ph ph apiData">1</span></span></dt>
<dd>Y, UV in two surfaces (UV as one surface) with VU byte ordering, width, height ratio same as YUV420Planar. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV422Planar = <span class="ph ph apiData">2</span></span></dt>
<dd>Y, U, V each in a separate surface, U/V width = 1/2 Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV422SemiPlanar = <span class="ph ph apiData">3</span></span></dt>
<dd>Y, UV in two surfaces with VU byte ordering, width, height ratio same as YUV422Planar. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatRGB = <span class="ph ph apiData">4</span></span></dt>
<dd>R/G/B three channels in one surface with BGR byte ordering. Only pitch linear format supported. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBGR = <span class="ph ph apiData">5</span></span></dt>
<dd>R/G/B three channels in one surface with RGB byte ordering. Only pitch linear format supported. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatARGB = <span class="ph ph apiData">6</span></span></dt>
<dd>R/G/B/A four channels in one surface with BGRA byte ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatRGBA = <span class="ph ph apiData">7</span></span></dt>
<dd>R/G/B/A four channels in one surface with ABGR byte ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatL = <span class="ph ph apiData">8</span></span></dt>
<dd>single luminance channel in one surface. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatR = <span class="ph ph apiData">9</span></span></dt>
<dd>single color channel in one surface. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV444Planar = <span class="ph ph apiData">10</span></span></dt>
<dd>Y, U, V in three surfaces, each in a separate surface, U/V width = Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV444SemiPlanar = <span class="ph ph apiData">11</span></span></dt>
<dd>Y, UV in two surfaces (UV as one surface) with VU byte ordering, width, height ratio same as YUV444Planar. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUYV422 = <span class="ph ph apiData">12</span></span></dt>
<dd>Y, U, V in one surface, interleaved as UYVY. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatUYVY422 = <span class="ph ph apiData">13</span></span></dt>
<dd>Y, U, V in one surface, interleaved as YUYV. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatABGR = <span class="ph ph apiData">14</span></span></dt>
<dd>R/G/B/A four channels in one surface with RGBA byte ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBGRA = <span class="ph ph apiData">15</span></span></dt>
<dd>R/G/B/A four channels in one surface with ARGB byte ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatA = <span class="ph ph apiData">16</span></span></dt>
<dd>Alpha color format - one channel in one surface. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatRG = <span class="ph ph apiData">17</span></span></dt>
<dd>R/G color format - two channels in one surface with GR byte ordering </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatAYUV = <span class="ph ph apiData">18</span></span></dt>
<dd>Y, U, V, A four channels in one surface, interleaved as VUYA. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU444SemiPlanar = <span class="ph ph apiData">19</span></span></dt>
<dd>Y, VU in two surfaces (VU as one surface) with UV byte ordering, U/V width = Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU422SemiPlanar = <span class="ph ph apiData">20</span></span></dt>
<dd>Y, VU in two surfaces (VU as one surface) with UV byte ordering, U/V width = 1/2 Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU420SemiPlanar = <span class="ph ph apiData">21</span></span></dt>
<dd>Y, VU in two surfaces (VU as one surface) with UV byte ordering, U/V width = 1/2 Y width, U/V height = 1/2 Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatY10V10U10_444SemiPlanar = <span class="ph ph apiData">22</span></span></dt>
<dd>Y10, V10U10 in two surfaces (VU as one surface) with UV byte ordering, U/V width = Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatY10V10U10_420SemiPlanar = <span class="ph ph apiData">23</span></span></dt>
<dd>Y10, V10U10 in two surfaces (VU as one surface) with UV byte ordering, U/V width = 1/2 Y width, U/V height = 1/2 Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatY12V12U12_444SemiPlanar = <span class="ph ph apiData">24</span></span></dt>
<dd>Y12, V12U12 in two surfaces (VU as one surface) with UV byte ordering, U/V width = Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatY12V12U12_420SemiPlanar = <span class="ph ph apiData">25</span></span></dt>
<dd>Y12, V12U12 in two surfaces (VU as one surface) with UV byte ordering, U/V width = 1/2 Y width, U/V height = 1/2 Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatVYUY_ER = <span class="ph ph apiData">26</span></span></dt>
<dd>Extended Range Y, U, V in one surface, interleaved as YVYU. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatUYVY_ER = <span class="ph ph apiData">27</span></span></dt>
<dd>Extended Range Y, U, V in one surface, interleaved as YUYV. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUYV_ER = <span class="ph ph apiData">28</span></span></dt>
<dd>Extended Range Y, U, V in one surface, interleaved as UYVY. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVYU_ER = <span class="ph ph apiData">29</span></span></dt>
<dd>Extended Range Y, U, V in one surface, interleaved as VYUY. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV_ER = <span class="ph ph apiData">30</span></span></dt>
<dd>Extended Range Y, U, V three channels in one surface, interleaved as VUY. Only pitch linear format supported. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUVA_ER = <span class="ph ph apiData">31</span></span></dt>
<dd>Extended Range Y, U, V, A four channels in one surface, interleaved as AVUY. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatAYUV_ER = <span class="ph ph apiData">32</span></span></dt>
<dd>Extended Range Y, U, V, A four channels in one surface, interleaved as VUYA. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV444Planar_ER = <span class="ph ph apiData">33</span></span></dt>
<dd>Extended Range Y, U, V in three surfaces, U/V width = Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV422Planar_ER = <span class="ph ph apiData">34</span></span></dt>
<dd>Extended Range Y, U, V in three surfaces, U/V width = 1/2 Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV420Planar_ER = <span class="ph ph apiData">35</span></span></dt>
<dd>Extended Range Y, U, V in three surfaces, U/V width = 1/2 Y width, U/V height = 1/2 Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV444SemiPlanar_ER = <span class="ph ph apiData">36</span></span></dt>
<dd>Extended Range Y, UV in two surfaces (UV as one surface) with VU byte ordering, U/V width = Y width, U/V height = Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV422SemiPlanar_ER = <span class="ph ph apiData">37</span></span></dt>
<dd>Extended Range Y, UV in two surfaces (UV as one surface) with VU byte ordering, U/V width = 1/2 Y width, U/V height = Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYUV420SemiPlanar_ER = <span class="ph ph apiData">38</span></span></dt>
<dd>Extended Range Y, UV in two surfaces (UV as one surface) with VU byte ordering, U/V width = 1/2 Y width, U/V height = 1/2
Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU444Planar_ER = <span class="ph ph apiData">39</span></span></dt>
<dd>Extended Range Y, V, U in three surfaces, U/V width = Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU422Planar_ER = <span class="ph ph apiData">40</span></span></dt>
<dd>Extended Range Y, V, U in three surfaces, U/V width = 1/2 Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU420Planar_ER = <span class="ph ph apiData">41</span></span></dt>
<dd>Extended Range Y, V, U in three surfaces, U/V width = 1/2 Y width, U/V height = 1/2 Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU444SemiPlanar_ER = <span class="ph ph apiData">42</span></span></dt>
<dd>Extended Range Y, VU in two surfaces (VU as one surface) with UV byte ordering, U/V width = Y width, U/V height = Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU422SemiPlanar_ER = <span class="ph ph apiData">43</span></span></dt>
<dd>Extended Range Y, VU in two surfaces (VU as one surface) with UV byte ordering, U/V width = 1/2 Y width, U/V height = Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU420SemiPlanar_ER = <span class="ph ph apiData">44</span></span></dt>
<dd>Extended Range Y, VU in two surfaces (VU as one surface) with UV byte ordering, U/V width = 1/2 Y width, U/V height = 1/2
Y height.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerRGGB = <span class="ph ph apiData">45</span></span></dt>
<dd>Bayer format - one channel in one surface with interleaved RGGB ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerBGGR = <span class="ph ph apiData">46</span></span></dt>
<dd>Bayer format - one channel in one surface with interleaved BGGR ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerGRBG = <span class="ph ph apiData">47</span></span></dt>
<dd>Bayer format - one channel in one surface with interleaved GRBG ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerGBRG = <span class="ph ph apiData">48</span></span></dt>
<dd>Bayer format - one channel in one surface with interleaved GBRG ordering. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer10RGGB = <span class="ph ph apiData">49</span></span></dt>
<dd>Bayer10 format - one channel in one surface with interleaved RGGB ordering. Out of 16 bits, 10 bits used 6 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer10BGGR = <span class="ph ph apiData">50</span></span></dt>
<dd>Bayer10 format - one channel in one surface with interleaved BGGR ordering. Out of 16 bits, 10 bits used 6 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer10GRBG = <span class="ph ph apiData">51</span></span></dt>
<dd>Bayer10 format - one channel in one surface with interleaved GRBG ordering. Out of 16 bits, 10 bits used 6 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer10GBRG = <span class="ph ph apiData">52</span></span></dt>
<dd>Bayer10 format - one channel in one surface with interleaved GBRG ordering. Out of 16 bits, 10 bits used 6 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer12RGGB = <span class="ph ph apiData">53</span></span></dt>
<dd>Bayer12 format - one channel in one surface with interleaved RGGB ordering. Out of 16 bits, 12 bits used 4 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer12BGGR = <span class="ph ph apiData">54</span></span></dt>
<dd>Bayer12 format - one channel in one surface with interleaved BGGR ordering. Out of 16 bits, 12 bits used 4 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer12GRBG = <span class="ph ph apiData">55</span></span></dt>
<dd>Bayer12 format - one channel in one surface with interleaved GRBG ordering. Out of 16 bits, 12 bits used 4 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer12GBRG = <span class="ph ph apiData">56</span></span></dt>
<dd>Bayer12 format - one channel in one surface with interleaved GBRG ordering. Out of 16 bits, 12 bits used 4 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer14RGGB = <span class="ph ph apiData">57</span></span></dt>
<dd>Bayer14 format - one channel in one surface with interleaved RGGB ordering. Out of 16 bits, 14 bits used 2 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer14BGGR = <span class="ph ph apiData">58</span></span></dt>
<dd>Bayer14 format - one channel in one surface with interleaved BGGR ordering. Out of 16 bits, 14 bits used 2 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer14GRBG = <span class="ph ph apiData">59</span></span></dt>
<dd>Bayer14 format - one channel in one surface with interleaved GRBG ordering. Out of 16 bits, 14 bits used 2 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer14GBRG = <span class="ph ph apiData">60</span></span></dt>
<dd>Bayer14 format - one channel in one surface with interleaved GBRG ordering. Out of 16 bits, 14 bits used 2 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer20RGGB = <span class="ph ph apiData">61</span></span></dt>
<dd>Bayer20 format - one channel in one surface with interleaved RGGB ordering. Out of 32 bits, 20 bits used 12 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer20BGGR = <span class="ph ph apiData">62</span></span></dt>
<dd>Bayer20 format - one channel in one surface with interleaved BGGR ordering. Out of 32 bits, 20 bits used 12 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer20GRBG = <span class="ph ph apiData">63</span></span></dt>
<dd>Bayer20 format - one channel in one surface with interleaved GRBG ordering. Out of 32 bits, 20 bits used 12 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayer20GBRG = <span class="ph ph apiData">64</span></span></dt>
<dd>Bayer20 format - one channel in one surface with interleaved GBRG ordering. Out of 32 bits, 20 bits used 12 bits No-op. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU444Planar = <span class="ph ph apiData">65</span></span></dt>
<dd>Y, V, U in three surfaces, each in a separate surface, U/V width = Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU422Planar = <span class="ph ph apiData">66</span></span></dt>
<dd>Y, V, U in three surfaces, each in a separate surface, U/V width = 1/2 Y width, U/V height = Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatYVU420Planar = <span class="ph ph apiData">67</span></span></dt>
<dd>Y, V, U in three surfaces, each in a separate surface, U/V width = 1/2 Y width, U/V height = 1/2 Y height. </dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerIspRGGB = <span class="ph ph apiData">68</span></span></dt>
<dd>Nvidia proprietary Bayer ISP format - one channel in one surface with interleaved RGGB ordering and mapped to opaque integer
datatype.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerIspBGGR = <span class="ph ph apiData">69</span></span></dt>
<dd>Nvidia proprietary Bayer ISP format - one channel in one surface with interleaved BGGR ordering and mapped to opaque integer
datatype.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerIspGRBG = <span class="ph ph apiData">70</span></span></dt>
<dd>Nvidia proprietary Bayer ISP format - one channel in one surface with interleaved GRBG ordering and mapped to opaque integer
datatype.
</dd>
<dt><span class="enum-member-name-def">cudaEglColorFormatBayerIspGBRG = <span class="ph ph apiData">71</span></span></dt>
<dd>Nvidia proprietary Bayer ISP format - one channel in one surface with interleaved GBRG ordering and mapped to opaque integer
datatype.
</dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbe68551b4eb6dfd6964e674c89d210b1" id="group__CUDART__TYPES_1gbe68551b4eb6dfd6964e674c89d210b1" shape="rect">
<!-- --></a><span>enum cudaEglFrameType</span></dt>
<dd class="description">
<div class="section">
<p>CUDA EglFrame type - array or pointer </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaEglFrameTypeArray = <span class="ph ph apiData">0</span></span></dt>
<dd>Frame type CUDA array </dd>
<dt><span class="enum-member-name-def">cudaEglFrameTypePitch = <span class="ph ph apiData">1</span></span></dt>
<dd>Frame type CUDA pointer </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g1b8600d3bc8514e841e093921c10ebe4" id="group__CUDART__TYPES_1g1b8600d3bc8514e841e093921c10ebe4" shape="rect">
<!-- --></a><span>enum cudaEglResourceLocationFlags</span></dt>
<dd class="description">
<div class="section">
<p>Resource location flags- sysmem or vidmem</p>
<p class="p">For CUDA context on iGPU, since video and system memory are equivalent - these flags will not have an effect on the execution.</p>
<p class="p">For CUDA context on dGPU, applications can use the flag <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g1b8600d3bc8514e841e093921c10ebe4" shape="rect">cudaEglResourceLocationFlags</a> to give a hint about the desired location.
</p>
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg1b8600d3bc8514e841e093921c10ebe4502da824e4d8837a90e09aec82727f9e" shape="rect">cudaEglResourceLocationSysmem</a> - the frame data is made resident on the system memory to be accessed by CUDA.
</p>
<p class="p"><a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg1b8600d3bc8514e841e093921c10ebe4f3361b86e6f88245861cac54cb58f58e" shape="rect">cudaEglResourceLocationVidmem</a> - the frame data is made resident on the dedicated video memory to be accessed by CUDA.
</p>
<p class="p">There may be an additional latency due to new allocation and data migration, if the frame is produced on a different memory.
</p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaEglResourceLocationSysmem = <span class="ph ph apiData">0x00</span></span></dt>
<dd>Resource location sysmem </dd>
<dt><span class="enum-member-name-def">cudaEglResourceLocationVidmem = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Resource location vidmem </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" id="group__CUDART__TYPES_1g3f51e3575c2178246db0a94a430e0038" shape="rect">
<!-- --></a><span>enum cudaError</span></dt>
<dd class="description">
<div class="section">
<p>CUDA error types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaSuccess = <span class="ph ph apiData">0</span></span></dt>
<dd>The API call returned with no errors. In the case of query calls, this also means that the operation being queried is complete
(see <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1g2bf738909b4a059023537eaa29d8a5b7" title="Queries an event's status." shape="rect">cudaEventQuery()</a> and <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g2021adeb17905c7ec2a3c1bf125c5435" title="Queries an asynchronous stream for completion status." shape="rect">cudaStreamQuery()</a>).
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidValue = <span class="ph ph apiData">1</span></span></dt>
<dd>This indicates that one or more of the parameters passed to the API call is not within an acceptable range of values. </dd>
<dt><span class="enum-member-name-def">cudaErrorMemoryAllocation = <span class="ph ph apiData">2</span></span></dt>
<dd>The API call failed because it was unable to allocate enough memory to perform the requested operation. </dd>
<dt><span class="enum-member-name-def">cudaErrorInitializationError = <span class="ph ph apiData">3</span></span></dt>
<dd>The API call failed because the CUDA driver and runtime could not be initialized. </dd>
<dt><span class="enum-member-name-def">cudaErrorCudartUnloading = <span class="ph ph apiData">4</span></span></dt>
<dd>This indicates that a CUDA Runtime API call cannot be executed because it is being called during process shut down, at a point
in time after CUDA driver has been unloaded.
</dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerDisabled = <span class="ph ph apiData">5</span></span></dt>
<dd>This indicates profiler is not initialized for this run. This can happen when the application is running with external profiling
tools like visual profiler.
</dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerNotInitialized = <span class="ph ph apiData">6</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000056" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 5.0. It is no longer an error to attempt to enable/disable the profiling via <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1gf536d75bb382356e10e3b4e89f4a5374" title="Enable profiling." shape="rect">cudaProfilerStart</a> or <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1g826922d9d1d0090d4a9a6b8b249cebb5" title="Disable profiling." shape="rect">cudaProfilerStop</a> without initialization. </span></p>
<p></p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerAlreadyStarted = <span class="ph ph apiData">7</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000057" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 5.0. It is no longer an error to call <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1gf536d75bb382356e10e3b4e89f4a5374" title="Enable profiling." shape="rect">cudaProfilerStart()</a> when profiling is already enabled. </span></p>
<p></p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorProfilerAlreadyStopped = <span class="ph ph apiData">8</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000058" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 5.0. It is no longer an error to call <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1g826922d9d1d0090d4a9a6b8b249cebb5" title="Disable profiling." shape="rect">cudaProfilerStop()</a> when profiling is already disabled. </span></p>
<p></p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidConfiguration = <span class="ph ph apiData">9</span></span></dt>
<dd>This indicates that a kernel launch is requesting resources that can never be satisfied by the current device. Requesting
more shared memory per block than the device supports will trigger this error, as will requesting too many threads or blocks.
See <a class="xref" href="structcudaDeviceProp.html#structcudaDeviceProp" shape="rect">cudaDeviceProp</a> for more device limitations.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidPitchValue = <span class="ph ph apiData">12</span></span></dt>
<dd>This indicates that one or more of the pitch-related parameters passed to the API call is not within the acceptable range
for pitch.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidSymbol = <span class="ph ph apiData">13</span></span></dt>
<dd>This indicates that the symbol name/identifier passed to the API call is not a valid name or identifier. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidHostPointer = <span class="ph ph apiData">16</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000059" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 10.1. </span></p>
<p>This indicates that at least one host pointer passed to the API call is not a valid host pointer.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidDevicePointer = <span class="ph ph apiData">17</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000060" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 10.1. </span></p>
<p>This indicates that at least one device pointer passed to the API call is not a valid device pointer.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidTexture = <span class="ph ph apiData">18</span></span></dt>
<dd>This indicates that the texture passed to the API call is not a valid texture. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidTextureBinding = <span class="ph ph apiData">19</span></span></dt>
<dd>This indicates that the texture binding is not valid. This occurs if you call <a class="xref" href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE_1ga1134e3ee365dca1e3df9b29f161e13e" title="Get the alignment offset of a texture." shape="rect">cudaGetTextureAlignmentOffset()</a> with an unbound texture.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidChannelDescriptor = <span class="ph ph apiData">20</span></span></dt>
<dd>This indicates that the channel descriptor passed to the API call is not valid. This occurs if the format is not one of the
formats specified by <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g8085eac5cb54b4228f3619a60f235119" shape="rect">cudaChannelFormatKind</a>, or if one of the dimensions is invalid.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidMemcpyDirection = <span class="ph ph apiData">21</span></span></dt>
<dd>This indicates that the direction of the memcpy passed to the API call is not one of the types specified by <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" shape="rect">cudaMemcpyKind</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorAddressOfConstant = <span class="ph ph apiData">22</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000061" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Variables in constant memory may now have their address taken by the runtime
via <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g4f513be54d3794667c2017146b3d6a2b" title="Finds the address associated with a CUDA symbol." shape="rect">cudaGetSymbolAddress()</a>. </span></p>
<p>This indicated that the user has taken the address of a constant variable, which was forbidden up until the CUDA 3.1 release.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorTextureFetchFailed = <span class="ph ph apiData">23</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000062" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a texture fetch was not able to be performed. This was previously used for device emulation of texture
operations.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorTextureNotBound = <span class="ph ph apiData">24</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000063" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a texture was not bound for access. This was previously used for device emulation of texture operations.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorSynchronizationError = <span class="ph ph apiData">25</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000064" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a synchronization operation had failed. This was previously used for some device emulation functions.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidFilterSetting = <span class="ph ph apiData">26</span></span></dt>
<dd>This indicates that a non-float texture was being accessed with linear filtering. This is not supported by CUDA. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidNormSetting = <span class="ph ph apiData">27</span></span></dt>
<dd>This indicates that an attempt was made to read a non-float texture as a normalized float. This is not supported by CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorMixedDeviceExecution = <span class="ph ph apiData">28</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000065" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>Mixing of device and device emulation code was not allowed.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorNotYetImplemented = <span class="ph ph apiData">31</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000066" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 4.1. </span></p>
<p>This indicates that the API call is not yet implemented. Production releases of CUDA will never return this error.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorMemoryValueTooLarge = <span class="ph ph apiData">32</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000067" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that an emulated device pointer exceeded the 32-bit address range.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorInsufficientDriver = <span class="ph ph apiData">35</span></span></dt>
<dd>This indicates that the installed NVIDIA CUDA driver is older than the CUDA runtime library. This is not a supported configuration.
Users should install an updated NVIDIA display driver to allow the application to run.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidSurface = <span class="ph ph apiData">37</span></span></dt>
<dd>This indicates that the surface passed to the API call is not a valid surface. </dd>
<dt><span class="enum-member-name-def">cudaErrorDuplicateVariableName = <span class="ph ph apiData">43</span></span></dt>
<dd>This indicates that multiple global or constant variables (across separate CUDA source files in the application) share the
same string name.
</dd>
<dt><span class="enum-member-name-def">cudaErrorDuplicateTextureName = <span class="ph ph apiData">44</span></span></dt>
<dd>This indicates that multiple textures (across separate CUDA source files in the application) share the same string name. </dd>
<dt><span class="enum-member-name-def">cudaErrorDuplicateSurfaceName = <span class="ph ph apiData">45</span></span></dt>
<dd>This indicates that multiple surfaces (across separate CUDA source files in the application) share the same string name. </dd>
<dt><span class="enum-member-name-def">cudaErrorDevicesUnavailable = <span class="ph ph apiData">46</span></span></dt>
<dd>This indicates that all CUDA devices are busy or unavailable at the current time. Devices are often busy/unavailable due to
use of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg7eb25f5413a962faad0956d92bae10d06965403d087b7f1153726c999bbc879c" shape="rect">cudaComputeModeExclusive</a>, <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg7eb25f5413a962faad0956d92bae10d0fc71b88518e4501544d6e65b5f3671b6" shape="rect">cudaComputeModeProhibited</a> or when long running CUDA kernels have filled up the GPU and are blocking new work from starting. They can also be unavailable
due to memory constraints on a device that already has active CUDA work being performed.
</dd>
<dt><span class="enum-member-name-def">cudaErrorIncompatibleDriverContext = <span class="ph ph apiData">49</span></span></dt>
<dd>This indicates that the current context is not compatible with this the CUDA Runtime. This can only occur if you are using
CUDA Runtime/Driver interoperability and have created an existing Driver context using the driver API. The Driver context
may be incompatible either because the Driver context was created using an older version of the API, because the Runtime API
call expects a primary driver context and the Driver context is not primary, or because the Driver context has been destroyed.
Please see <a class="xref" href="group__CUDART__DRIVER.html#group__CUDART__DRIVER" shape="rect">Interactions</a> with the CUDA Driver API" for more information.
</dd>
<dt><span class="enum-member-name-def">cudaErrorMissingConfiguration = <span class="ph ph apiData">52</span></span></dt>
<dd>The device function being invoked (usually via <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g5064cdf5d8e6741ace56fd8be951783c" title="Launches a device function." shape="rect">cudaLaunchKernel()</a>) was not previously configured via the cudaConfigureCall() function.
</dd>
<dt><span class="enum-member-name-def">cudaErrorPriorLaunchFailure = <span class="ph ph apiData">53</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000068" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 3.1. Device emulation mode was removed with the CUDA 3.1 release. </span></p>
<p>This indicated that a previous kernel launch failed. This was previously used for device emulation of kernel launches.
</p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchMaxDepthExceeded = <span class="ph ph apiData">65</span></span></dt>
<dd>This error indicates that a device runtime grid launch did not occur because the depth of the child grid would exceed the
maximum supported number of nested grid launches.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchFileScopedTex = <span class="ph ph apiData">66</span></span></dt>
<dd>This error indicates that a grid launch did not occur because the kernel uses file-scoped textures which are unsupported by
the device runtime. Kernels launched via the device runtime only support textures created with the Texture Object API's.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchFileScopedSurf = <span class="ph ph apiData">67</span></span></dt>
<dd>This error indicates that a grid launch did not occur because the kernel uses file-scoped surfaces which are unsupported by
the device runtime. Kernels launched via the device runtime only support surfaces created with the Surface Object API's.
</dd>
<dt><span class="enum-member-name-def">cudaErrorSyncDepthExceeded = <span class="ph ph apiData">68</span></span></dt>
<dd>This error indicates that a call to <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g10e20b05a95f638a4071a655503df25d" title="Wait for compute device to finish." shape="rect">cudaDeviceSynchronize</a> made from the device runtime failed because the call was made at grid depth greater than than either the default (2 levels
of grids) or user specified device limit <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365123c4900be4af436cb769e4c72d07be11" shape="rect">cudaLimitDevRuntimeSyncDepth</a>. To be able to synchronize on launched grids at a greater depth successfully, the maximum nested depth at which <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g10e20b05a95f638a4071a655503df25d" title="Wait for compute device to finish." shape="rect">cudaDeviceSynchronize</a> will be called must be specified with the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365123c4900be4af436cb769e4c72d07be11" shape="rect">cudaLimitDevRuntimeSyncDepth</a> limit to the <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g05956f16eaa47ef3a4efee84563ccb7d" title="Set resource limits." shape="rect">cudaDeviceSetLimit</a> api before the host-side launch of a kernel using the device runtime. Keep in mind that additional levels of sync depth require
the runtime to reserve large amounts of device memory that cannot be used for user allocations.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchPendingCountExceeded = <span class="ph ph apiData">69</span></span></dt>
<dd>This error indicates that a device runtime grid launch failed because the launch would exceed the limit <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365118712cb05d2c3efaeea73afba823d916" shape="rect">cudaLimitDevRuntimePendingLaunchCount</a>. For this launch to proceed successfully, <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g05956f16eaa47ef3a4efee84563ccb7d" title="Set resource limits." shape="rect">cudaDeviceSetLimit</a> must be called to set the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg4c4b34c054d383b0e9a63ab0ffc9365118712cb05d2c3efaeea73afba823d916" shape="rect">cudaLimitDevRuntimePendingLaunchCount</a> to be higher than the upper bound of outstanding launches that can be issued to the device runtime. Keep in mind that raising
the limit of pending device runtime launches will require the runtime to reserve device memory that cannot be used for user
allocations.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidDeviceFunction = <span class="ph ph apiData">98</span></span></dt>
<dd>The requested device function does not exist or is not compiled for the proper device architecture. </dd>
<dt><span class="enum-member-name-def">cudaErrorNoDevice = <span class="ph ph apiData">100</span></span></dt>
<dd>This indicates that no CUDA-capable devices were detected by the installed CUDA driver. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidDevice = <span class="ph ph apiData">101</span></span></dt>
<dd>This indicates that the device ordinal supplied by the user does not correspond to a valid CUDA device. </dd>
<dt><span class="enum-member-name-def">cudaErrorStartupFailure = <span class="ph ph apiData">127</span></span></dt>
<dd>This indicates an internal startup failure in the CUDA runtime. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidKernelImage = <span class="ph ph apiData">200</span></span></dt>
<dd>This indicates that the device kernel image is invalid. </dd>
<dt><span class="enum-member-name-def">cudaErrorDeviceUninitilialized = <span class="ph ph apiData">201</span></span></dt>
<dd>This most frequently indicates that there is no context bound to the current thread. This can also be returned if the context
passed to an API call is not a valid handle (such as a context that has had <a class="xref" href="../cuda-driver-api/group__CUDA__CTX.html#group__CUDA__CTX_1g27a365aebb0eb548166309f58a1e8b8e" target="_blank" shape="rect">cuCtxDestroy()</a> invoked on it). This can also be returned if a user mixes different API versions (i.e. 3010 context with 3020 API calls).
See <a class="xref" href="../cuda-driver-api/group__CUDA__CTX.html#group__CUDA__CTX_1g088a90490dafca5893ef6fbebc8de8fb" target="_blank" shape="rect">cuCtxGetApiVersion()</a> for more details.
</dd>
<dt><span class="enum-member-name-def">cudaErrorMapBufferObjectFailed = <span class="ph ph apiData">205</span></span></dt>
<dd>This indicates that the buffer object could not be mapped. </dd>
<dt><span class="enum-member-name-def">cudaErrorUnmapBufferObjectFailed = <span class="ph ph apiData">206</span></span></dt>
<dd>This indicates that the buffer object could not be unmapped. </dd>
<dt><span class="enum-member-name-def">cudaErrorArrayIsMapped = <span class="ph ph apiData">207</span></span></dt>
<dd>This indicates that the specified array is currently mapped and thus cannot be destroyed. </dd>
<dt><span class="enum-member-name-def">cudaErrorAlreadyMapped = <span class="ph ph apiData">208</span></span></dt>
<dd>This indicates that the resource is already mapped. </dd>
<dt><span class="enum-member-name-def">cudaErrorNoKernelImageForDevice = <span class="ph ph apiData">209</span></span></dt>
<dd>This indicates that there is no kernel image available that is suitable for the device. This can occur when a user specifies
code generation options for a particular CUDA source file that do not include the corresponding device configuration.
</dd>
<dt><span class="enum-member-name-def">cudaErrorAlreadyAcquired = <span class="ph ph apiData">210</span></span></dt>
<dd>This indicates that a resource has already been acquired. </dd>
<dt><span class="enum-member-name-def">cudaErrorNotMapped = <span class="ph ph apiData">211</span></span></dt>
<dd>This indicates that a resource is not mapped. </dd>
<dt><span class="enum-member-name-def">cudaErrorNotMappedAsArray = <span class="ph ph apiData">212</span></span></dt>
<dd>This indicates that a mapped resource is not available for access as an array. </dd>
<dt><span class="enum-member-name-def">cudaErrorNotMappedAsPointer = <span class="ph ph apiData">213</span></span></dt>
<dd>This indicates that a mapped resource is not available for access as a pointer. </dd>
<dt><span class="enum-member-name-def">cudaErrorECCUncorrectable = <span class="ph ph apiData">214</span></span></dt>
<dd>This indicates that an uncorrectable ECC error was detected during execution. </dd>
<dt><span class="enum-member-name-def">cudaErrorUnsupportedLimit = <span class="ph ph apiData">215</span></span></dt>
<dd>This indicates that the <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">cudaLimit</a> passed to the API call is not supported by the active device.
</dd>
<dt><span class="enum-member-name-def">cudaErrorDeviceAlreadyInUse = <span class="ph ph apiData">216</span></span></dt>
<dd>This indicates that a call tried to access an exclusive-thread device that is already in use by a different thread. </dd>
<dt><span class="enum-member-name-def">cudaErrorPeerAccessUnsupported = <span class="ph ph apiData">217</span></span></dt>
<dd>This error indicates that P2P access is not supported across the given devices. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidPtx = <span class="ph ph apiData">218</span></span></dt>
<dd>A PTX compilation failed. The runtime may fall back to compiling PTX if an application does not contain a suitable binary
for the current device.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidGraphicsContext = <span class="ph ph apiData">219</span></span></dt>
<dd>This indicates an error with the OpenGL or DirectX context. </dd>
<dt><span class="enum-member-name-def">cudaErrorNvlinkUncorrectable = <span class="ph ph apiData">220</span></span></dt>
<dd>This indicates that an uncorrectable NVLink error was detected during the execution. </dd>
<dt><span class="enum-member-name-def">cudaErrorJitCompilerNotFound = <span class="ph ph apiData">221</span></span></dt>
<dd>This indicates that the PTX JIT compiler library was not found. The JIT Compiler library is used for PTX compilation. The
runtime may fall back to compiling PTX if an application does not contain a suitable binary for the current device.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidSource = <span class="ph ph apiData">300</span></span></dt>
<dd>This indicates that the device kernel source is invalid. </dd>
<dt><span class="enum-member-name-def">cudaErrorFileNotFound = <span class="ph ph apiData">301</span></span></dt>
<dd>This indicates that the file specified was not found. </dd>
<dt><span class="enum-member-name-def">cudaErrorSharedObjectSymbolNotFound = <span class="ph ph apiData">302</span></span></dt>
<dd>This indicates that a link to a shared object failed to resolve. </dd>
<dt><span class="enum-member-name-def">cudaErrorSharedObjectInitFailed = <span class="ph ph apiData">303</span></span></dt>
<dd>This indicates that initialization of a shared object failed. </dd>
<dt><span class="enum-member-name-def">cudaErrorOperatingSystem = <span class="ph ph apiData">304</span></span></dt>
<dd>This error indicates that an OS call failed. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidResourceHandle = <span class="ph ph apiData">400</span></span></dt>
<dd>This indicates that a resource handle passed to the API call was not valid. Resource handles are opaque types like <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ge15d9c8b7a240312b533d6122558085a" shape="rect">cudaStream_t</a> and <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gea2f543a9fc0e52fe4ae712920fd1247" shape="rect">cudaEvent_t</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorIllegalState = <span class="ph ph apiData">401</span></span></dt>
<dd>This indicates that a resource required by the API call is not in a valid state to perform the requested operation. </dd>
<dt><span class="enum-member-name-def">cudaErrorSymbolNotFound = <span class="ph ph apiData">500</span></span></dt>
<dd>This indicates that a named symbol was not found. Examples of symbols are global/constant variable names, texture names, and
surface names.
</dd>
<dt><span class="enum-member-name-def">cudaErrorNotReady = <span class="ph ph apiData">600</span></span></dt>
<dd>This indicates that asynchronous operations issued previously have not completed yet. This result is not actually an error,
but must be indicated differently than <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038e355f04607d824883b4a50662830d591" shape="rect">cudaSuccess</a> (which indicates completion). Calls that may return this value include <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1g2bf738909b4a059023537eaa29d8a5b7" title="Queries an event's status." shape="rect">cudaEventQuery()</a> and <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g2021adeb17905c7ec2a3c1bf125c5435" title="Queries an asynchronous stream for completion status." shape="rect">cudaStreamQuery()</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorIllegalAddress = <span class="ph ph apiData">700</span></span></dt>
<dd>The device encountered a load or store instruction on an invalid memory address. This leaves the process in an inconsistent
state and any further CUDA work will return the same error. To continue using CUDA, the process must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchOutOfResources = <span class="ph ph apiData">701</span></span></dt>
<dd>This indicates that a launch did not occur because it did not have appropriate resources. Although this error is similar to
<a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg3f51e3575c2178246db0a94a430e0038d3934977826b2e1488dfeb7e0614e776" shape="rect">cudaErrorInvalidConfiguration</a>, this error usually indicates that the user has attempted to pass too many arguments to the device kernel, or the kernel
launch specifies too many threads for the kernel's register count.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchTimeout = <span class="ph ph apiData">702</span></span></dt>
<dd>This indicates that the device kernel took too long to execute. This can only occur if timeouts are enabled - see the device
property <a class="xref" href="structcudaDeviceProp.html#structcudaDeviceProp_19a63114766c4d2309f00403c1bf056c8" shape="rect">kernelExecTimeoutEnabled</a> for more information. This leaves the process in an inconsistent state and any further CUDA work will return the same error.
To continue using CUDA, the process must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchIncompatibleTexturing = <span class="ph ph apiData">703</span></span></dt>
<dd>This error indicates a kernel launch that uses an incompatible texturing mode. </dd>
<dt><span class="enum-member-name-def">cudaErrorPeerAccessAlreadyEnabled = <span class="ph ph apiData">704</span></span></dt>
<dd>This error indicates that a call to <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1g2b0adabf90db37e5cfddc92cbb2589f3" title="Enables direct access to memory allocations on a peer device." shape="rect">cudaDeviceEnablePeerAccess()</a> is trying to re-enable peer addressing on from a context which has already had peer addressing enabled.
</dd>
<dt><span class="enum-member-name-def">cudaErrorPeerAccessNotEnabled = <span class="ph ph apiData">705</span></span></dt>
<dd>This error indicates that <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1g9663734ad02653207ad6836053bf572e" title="Disables direct access to memory allocations on a peer device." shape="rect">cudaDeviceDisablePeerAccess()</a> is trying to disable peer addressing which has not been enabled yet via <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1g2b0adabf90db37e5cfddc92cbb2589f3" title="Enables direct access to memory allocations on a peer device." shape="rect">cudaDeviceEnablePeerAccess()</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorSetOnActiveProcess = <span class="ph ph apiData">708</span></span></dt>
<dd>This indicates that the user has called <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g1b9336c70f2299405f67a4f8496d7cfe" title="Set a list of devices that can be used for CUDA." shape="rect">cudaSetValidDevices()</a>, <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g69e73c7dda3fc05306ae7c811a690fac" title="Sets flags to be used for device executions." shape="rect">cudaSetDeviceFlags()</a>, <a class="xref" href="group__CUDART__D3D9.html#group__CUDART__D3D9_1g0733a6f0bdc8aca6c6812da66c6d814a" title="Sets the Direct3D 9 device to use for interoperability with a CUDA device." shape="rect">cudaD3D9SetDirect3DDevice()</a>, <a class="xref" href="group__CUDART__D3D10__DEPRECATED.html#group__CUDART__D3D10__DEPRECATED_1g7c942225222284fbfc3794a4ed6edf98" title="Sets the Direct3D 10 device to use for interoperability with a CUDA device." shape="rect">cudaD3D10SetDirect3DDevice</a>, <a class="xref" href="group__CUDART__D3D11__DEPRECATED.html#group__CUDART__D3D11__DEPRECATED_1g533524c773e7ca4ef57c0698b157d670" title="Sets the Direct3D 11 device to use for interoperability with a CUDA device." shape="rect">cudaD3D11SetDirect3DDevice()</a>, or <a class="xref" href="group__CUDART__VDPAU.html#group__CUDART__VDPAU_1g2a9ccfe8e6c87fe694bafd8cfcc67586" title="Sets a CUDA device to use VDPAU interoperability." shape="rect">cudaVDPAUSetVDPAUDevice()</a> after initializing the CUDA runtime by calling non-device management operations (allocating memory and launching kernels
are examples of non-device management operations). This error can also be returned if using runtime/driver interoperability
and there is an existing <a class="xref" href="../cuda-driver-api/group__CUDA__TYPES.html#group__CUDA__TYPES_1gf9f5bd81658f866613785b3a0bb7d7d9" target="_blank" shape="rect">CUcontext</a> active on the host thread.
</dd>
<dt><span class="enum-member-name-def">cudaErrorContextIsDestroyed = <span class="ph ph apiData">709</span></span></dt>
<dd>This error indicates that the context current to the calling thread has been destroyed using <a class="xref" href="../cuda-driver-api/group__CUDA__CTX.html#group__CUDA__CTX_1g27a365aebb0eb548166309f58a1e8b8e" target="_blank" shape="rect">cuCtxDestroy</a>, or is a primary context which has not yet been initialized.
</dd>
<dt><span class="enum-member-name-def">cudaErrorAssert = <span class="ph ph apiData">710</span></span></dt>
<dd>An assert triggered in device code during kernel execution. The device cannot be used again. All existing allocations are
invalid. To continue using CUDA, the process must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorTooManyPeers = <span class="ph ph apiData">711</span></span></dt>
<dd>This error indicates that the hardware resources required to enable peer access have been exhausted for one or more of the
devices passed to cudaEnablePeerAccess().
</dd>
<dt><span class="enum-member-name-def">cudaErrorHostMemoryAlreadyRegistered = <span class="ph ph apiData">712</span></span></dt>
<dd>This error indicates that the memory range passed to <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1ge8d5c17670f16ac4fc8fcb4181cb490c" title="Registers an existing host memory range for use by CUDA." shape="rect">cudaHostRegister()</a> has already been registered.
</dd>
<dt><span class="enum-member-name-def">cudaErrorHostMemoryNotRegistered = <span class="ph ph apiData">713</span></span></dt>
<dd>This error indicates that the pointer passed to <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g81fd4101862bbefdb42a62d60e515eea" title="Unregisters a memory range that was registered with cudaHostRegister." shape="rect">cudaHostUnregister()</a> does not correspond to any currently registered memory region.
</dd>
<dt><span class="enum-member-name-def">cudaErrorHardwareStackError = <span class="ph ph apiData">714</span></span></dt>
<dd>Device encountered an error in the call stack during kernel execution, possibly due to stack corruption or exceeding the stack
size limit. This leaves the process in an inconsistent state and any further CUDA work will return the same error. To continue
using CUDA, the process must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorIllegalInstruction = <span class="ph ph apiData">715</span></span></dt>
<dd>The device encountered an illegal instruction during kernel execution This leaves the process in an inconsistent state and
any further CUDA work will return the same error. To continue using CUDA, the process must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorMisalignedAddress = <span class="ph ph apiData">716</span></span></dt>
<dd>The device encountered a load or store instruction on a memory address which is not aligned. This leaves the process in an
inconsistent state and any further CUDA work will return the same error. To continue using CUDA, the process must be terminated
and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidAddressSpace = <span class="ph ph apiData">717</span></span></dt>
<dd>While executing a kernel, the device encountered an instruction which can only operate on memory locations in certain address
spaces (global, shared, or local), but was supplied a memory address not belonging to an allowed address space. This leaves
the process in an inconsistent state and any further CUDA work will return the same error. To continue using CUDA, the process
must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidPc = <span class="ph ph apiData">718</span></span></dt>
<dd>The device encountered an invalid program counter. This leaves the process in an inconsistent state and any further CUDA work
will return the same error. To continue using CUDA, the process must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchFailure = <span class="ph ph apiData">719</span></span></dt>
<dd>An exception occurred on the device while executing a kernel. Common causes include dereferencing an invalid device pointer
and accessing out of bounds shared memory. Less common cases can be system specific - more information about these cases can
be found in the system specific user guide. This leaves the process in an inconsistent state and any further CUDA work will
return the same error. To continue using CUDA, the process must be terminated and relaunched.
</dd>
<dt><span class="enum-member-name-def">cudaErrorCooperativeLaunchTooLarge = <span class="ph ph apiData">720</span></span></dt>
<dd>This error indicates that the number of blocks launched per grid for a kernel that was launched via either <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1gc0210b928f9bf4e212af07d35ac11d67" title="Launches a device function." shape="rect">cudaLaunchCooperativeKernel</a> or <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g20f8d75d8786c54cc168c47fde66ee52" title="Launches device functions on multiple devices where thread blocks can cooperate and synchronize as they execute." shape="rect">cudaLaunchCooperativeKernelMultiDevice</a> exceeds the maximum number of blocks as allowed by <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g5a5d67a3c907371559ba692195e8a38c" title="Returns occupancy for a device function." shape="rect">cudaOccupancyMaxActiveBlocksPerMultiprocessor</a> or <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g603b86b20b37823253ff89fe8688ba83" title="Returns occupancy for a device function with the specified flags." shape="rect">cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags</a> times the number of multiprocessors as specified by the device attribute <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1gg49e2f8c2c0bd6fe264f2fc970912e5cd74de9ed281f917c8e4ef272da09f338a" shape="rect">cudaDevAttrMultiProcessorCount</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorNotPermitted = <span class="ph ph apiData">800</span></span></dt>
<dd>This error indicates the attempted operation is not permitted. </dd>
<dt><span class="enum-member-name-def">cudaErrorNotSupported = <span class="ph ph apiData">801</span></span></dt>
<dd>This error indicates the attempted operation is not supported on the current system or device. </dd>
<dt><span class="enum-member-name-def">cudaErrorSystemNotReady = <span class="ph ph apiData">802</span></span></dt>
<dd>This error indicates that the system is not yet ready to start any CUDA work. To continue using CUDA, verify the system configuration
is in a valid state and all required driver daemons are actively running. More information about this error can be found in
the system specific user guide.
</dd>
<dt><span class="enum-member-name-def">cudaErrorSystemDriverMismatch = <span class="ph ph apiData">803</span></span></dt>
<dd>This error indicates that there is a mismatch between the versions of the display driver and the CUDA driver. Refer to the
compatibility documentation for supported versions.
</dd>
<dt><span class="enum-member-name-def">cudaErrorCompatNotSupportedOnDevice = <span class="ph ph apiData">804</span></span></dt>
<dd>This error indicates that the system was upgraded to run with forward compatibility but the visible hardware detected by CUDA
does not support this configuration. Refer to the compatibility documentation for the supported hardware matrix or ensure
that only supported hardware is visible during initialization via the CUDA_VISIBLE_DEVICES environment variable.
</dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureUnsupported = <span class="ph ph apiData">900</span></span></dt>
<dd>The operation is not permitted when the stream is capturing. </dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureInvalidated = <span class="ph ph apiData">901</span></span></dt>
<dd>The current capture sequence on the stream has been invalidated due to a previous error. </dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureMerge = <span class="ph ph apiData">902</span></span></dt>
<dd>The operation would have resulted in a merge of two independent capture sequences. </dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureUnmatched = <span class="ph ph apiData">903</span></span></dt>
<dd>The capture was not initiated in this stream. </dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureUnjoined = <span class="ph ph apiData">904</span></span></dt>
<dd>The capture sequence contains a fork that was not joined to the primary stream. </dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureIsolation = <span class="ph ph apiData">905</span></span></dt>
<dd>A dependency would have been created which crosses the capture sequence boundary. Only implicit in-stream ordering dependencies
are allowed to cross the boundary.
</dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureImplicit = <span class="ph ph apiData">906</span></span></dt>
<dd>The operation would have resulted in a disallowed implicit dependency on a current capture sequence from cudaStreamLegacy.
</dd>
<dt><span class="enum-member-name-def">cudaErrorCapturedEvent = <span class="ph ph apiData">907</span></span></dt>
<dd>The operation is not permitted on an event which was last recorded in a capturing stream. </dd>
<dt><span class="enum-member-name-def">cudaErrorStreamCaptureWrongThread = <span class="ph ph apiData">908</span></span></dt>
<dd>A stream capture sequence not initiated with the cudaStreamCaptureModeRelaxed argument to <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g793d7d4e474388ddfda531603dc34aa3" title="Begins graph capture on a stream." shape="rect">cudaStreamBeginCapture</a> was passed to <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1gf5a0efebc818054ceecd1e3e5e76d93e" title="Ends capture on a stream, returning the captured graph." shape="rect">cudaStreamEndCapture</a> in a different thread.
</dd>
<dt><span class="enum-member-name-def">cudaErrorUnknown = <span class="ph ph apiData">999</span></span></dt>
<dd>This indicates that an unknown internal error has occurred. </dd>
<dt><span class="enum-member-name-def">cudaErrorApiFailureBase = <span class="ph ph apiData">10000</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000069" shape="rect">Deprecated</a></h6>
<p><span class="ph xrefsect-description">This error return is deprecated as of CUDA 4.1. </span></p>
<p>Any unhandled CUDA driver error is added to this value and returned via the runtime. Production releases of CUDA should not
return such errors.
</p>
</dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g62ab2fcc2eb066702c3694148383749e" id="group__CUDART__TYPES_1g62ab2fcc2eb066702c3694148383749e" shape="rect">
<!-- --></a><span>enum cudaExternalMemoryHandleType</span></dt>
<dd class="description">
<div class="section">
<p>External memory handle types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaExternalMemoryHandleTypeOpaqueFd = <span class="ph ph apiData">1</span></span></dt>
<dd>Handle is an opaque file descriptor </dd>
<dt><span class="enum-member-name-def">cudaExternalMemoryHandleTypeOpaqueWin32 = <span class="ph ph apiData">2</span></span></dt>
<dd>Handle is an opaque shared NT handle </dd>
<dt><span class="enum-member-name-def">cudaExternalMemoryHandleTypeOpaqueWin32Kmt = <span class="ph ph apiData">3</span></span></dt>
<dd>Handle is an opaque, globally shared handle </dd>
<dt><span class="enum-member-name-def">cudaExternalMemoryHandleTypeD3D12Heap = <span class="ph ph apiData">4</span></span></dt>
<dd>Handle is a D3D12 heap object </dd>
<dt><span class="enum-member-name-def">cudaExternalMemoryHandleTypeD3D12Resource = <span class="ph ph apiData">5</span></span></dt>
<dd>Handle is a D3D12 committed resource </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gb35390be1e170db8671b0abfb57ad3d9" id="group__CUDART__TYPES_1gb35390be1e170db8671b0abfb57ad3d9" shape="rect">
<!-- --></a><span>enum cudaExternalSemaphoreHandleType</span></dt>
<dd class="description">
<div class="section">
<p>External semaphore handle types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaExternalSemaphoreHandleTypeOpaqueFd = <span class="ph ph apiData">1</span></span></dt>
<dd>Handle is an opaque file descriptor </dd>
<dt><span class="enum-member-name-def">cudaExternalSemaphoreHandleTypeOpaqueWin32 = <span class="ph ph apiData">2</span></span></dt>
<dd>Handle is an opaque shared NT handle </dd>
<dt><span class="enum-member-name-def">cudaExternalSemaphoreHandleTypeOpaqueWin32Kmt = <span class="ph ph apiData">3</span></span></dt>
<dd>Handle is an opaque, globally shared handle </dd>
<dt><span class="enum-member-name-def">cudaExternalSemaphoreHandleTypeD3D12Fence = <span class="ph ph apiData">4</span></span></dt>
<dd>Handle is a shared NT handle referencing a D3D12 fence object </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gc6c537b33d22c871a103f0fda8ac8bbe" id="group__CUDART__TYPES_1gc6c537b33d22c871a103f0fda8ac8bbe" shape="rect">
<!-- --></a><span>enum cudaFuncAttribute</span></dt>
<dd class="description">
<div class="section">
<p>CUDA function attributes that can be set using <a class="xref" href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL_1g422642bfa0c035a590e4c43ff7c11f8d" title="[C++ API] Set attributes for a given function" shape="rect">cudaFuncSetAttribute</a></p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaFuncAttributeMaxDynamicSharedMemorySize = <span class="ph ph apiData">8</span></span></dt>
<dd>Maximum dynamic shared memory size </dd>
<dt><span class="enum-member-name-def">cudaFuncAttributePreferredSharedMemoryCarveout = <span class="ph ph apiData">9</span></span></dt>
<dd>Preferred shared memory-L1 cache split </dd>
<dt><span class="enum-member-name-def">cudaFuncAttributeMax</span></dt>
<dd></dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" id="group__CUDART__TYPES_1gb980f35ed69ee7991704de29a13de49b" shape="rect">
<!-- --></a><span>enum cudaFuncCache</span></dt>
<dd class="description">
<div class="section">
<p>CUDA function cache configurations </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaFuncCachePreferNone = <span class="ph ph apiData">0</span></span></dt>
<dd>Default function cache configuration, no preference </dd>
<dt><span class="enum-member-name-def">cudaFuncCachePreferShared = <span class="ph ph apiData">1</span></span></dt>
<dd>Prefer larger shared memory and smaller L1 cache </dd>
<dt><span class="enum-member-name-def">cudaFuncCachePreferL1 = <span class="ph ph apiData">2</span></span></dt>
<dd>Prefer larger L1 cache and smaller shared memory </dd>
<dt><span class="enum-member-name-def">cudaFuncCachePreferEqual = <span class="ph ph apiData">3</span></span></dt>
<dd>Prefer equal size L1 cache and shared memory </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g649fb64bad79fc6f2f531860c0eb777c" id="group__CUDART__TYPES_1g649fb64bad79fc6f2f531860c0eb777c" shape="rect">
<!-- --></a><span>enum cudaGraphNodeType</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Graph node types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaGraphNodeTypeKernel = <span class="ph ph apiData">0x00</span></span></dt>
<dd>GPU kernel node </dd>
<dt><span class="enum-member-name-def">cudaGraphNodeTypeMemcpy = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Memcpy node </dd>
<dt><span class="enum-member-name-def">cudaGraphNodeTypeMemset = <span class="ph ph apiData">0x02</span></span></dt>
<dd>Memset node </dd>
<dt><span class="enum-member-name-def">cudaGraphNodeTypeHost = <span class="ph ph apiData">0x03</span></span></dt>
<dd>Host (executable) node </dd>
<dt><span class="enum-member-name-def">cudaGraphNodeTypeGraph = <span class="ph ph apiData">0x04</span></span></dt>
<dd>Node which executes an embedded graph </dd>
<dt><span class="enum-member-name-def">cudaGraphNodeTypeEmpty = <span class="ph ph apiData">0x05</span></span></dt>
<dd>Empty (no-op) node </dd>
<dt><span class="enum-member-name-def">cudaGraphNodeTypeCount</span></dt>
<dd></dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbf3ce16a621826a09263b8a58902fee8" id="group__CUDART__TYPES_1gbf3ce16a621826a09263b8a58902fee8" shape="rect">
<!-- --></a><span>enum cudaGraphicsCubeFace</span></dt>
<dd class="description">
<div class="section">
<p>CUDA graphics interop array indices for cube maps </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaGraphicsCubeFacePositiveX = <span class="ph ph apiData">0x00</span></span></dt>
<dd>Positive X face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFaceNegativeX = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Negative X face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFacePositiveY = <span class="ph ph apiData">0x02</span></span></dt>
<dd>Positive Y face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFaceNegativeY = <span class="ph ph apiData">0x03</span></span></dt>
<dd>Negative Y face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFacePositiveZ = <span class="ph ph apiData">0x04</span></span></dt>
<dd>Positive Z face of cubemap </dd>
<dt><span class="enum-member-name-def">cudaGraphicsCubeFaceNegativeZ = <span class="ph ph apiData">0x05</span></span></dt>
<dd>Negative Z face of cubemap </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g2c3c3a69caaf333d29d0b38b75de5ffd" id="group__CUDART__TYPES_1g2c3c3a69caaf333d29d0b38b75de5ffd" shape="rect">
<!-- --></a><span>enum cudaGraphicsMapFlags</span></dt>
<dd class="description">
<div class="section">
<p>CUDA graphics interop map flags </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaGraphicsMapFlagsNone = <span class="ph ph apiData">0</span></span></dt>
<dd>Default; Assume resource can be read/written </dd>
<dt><span class="enum-member-name-def">cudaGraphicsMapFlagsReadOnly = <span class="ph ph apiData">1</span></span></dt>
<dd>CUDA will not write to this resource </dd>
<dt><span class="enum-member-name-def">cudaGraphicsMapFlagsWriteDiscard = <span class="ph ph apiData">2</span></span></dt>
<dd>CUDA will only write to and will not read from this resource </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gd17cc29b28205bbe32ac575eba16c277" id="group__CUDART__TYPES_1gd17cc29b28205bbe32ac575eba16c277" shape="rect">
<!-- --></a><span>enum cudaGraphicsRegisterFlags</span></dt>
<dd class="description">
<div class="section">
<p>CUDA graphics interop register flags </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsNone = <span class="ph ph apiData">0</span></span></dt>
<dd>Default </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsReadOnly = <span class="ph ph apiData">1</span></span></dt>
<dd>CUDA will not write to this resource </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsWriteDiscard = <span class="ph ph apiData">2</span></span></dt>
<dd>CUDA will only write to and will not read from this resource </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsSurfaceLoadStore = <span class="ph ph apiData">4</span></span></dt>
<dd>CUDA will bind this resource to a surface reference </dd>
<dt><span class="enum-member-name-def">cudaGraphicsRegisterFlagsTextureGather = <span class="ph ph apiData">8</span></span></dt>
<dd>CUDA will perform texture gather operations on this resource </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" id="group__CUDART__TYPES_1g4c4b34c054d383b0e9a63ab0ffc93651" shape="rect">
<!-- --></a><span>enum cudaLimit</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Limits </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaLimitStackSize = <span class="ph ph apiData">0x00</span></span></dt>
<dd>GPU thread stack size </dd>
<dt><span class="enum-member-name-def">cudaLimitPrintfFifoSize = <span class="ph ph apiData">0x01</span></span></dt>
<dd>GPU printf FIFO size </dd>
<dt><span class="enum-member-name-def">cudaLimitMallocHeapSize = <span class="ph ph apiData">0x02</span></span></dt>
<dd>GPU malloc heap size </dd>
<dt><span class="enum-member-name-def">cudaLimitDevRuntimeSyncDepth = <span class="ph ph apiData">0x03</span></span></dt>
<dd>GPU device runtime synchronize depth </dd>
<dt><span class="enum-member-name-def">cudaLimitDevRuntimePendingLaunchCount = <span class="ph ph apiData">0x04</span></span></dt>
<dd>GPU device runtime pending launch count </dd>
<dt><span class="enum-member-name-def">cudaLimitMaxL2FetchGranularity = <span class="ph ph apiData">0x05</span></span></dt>
<dd>A value between 0 and 128 that indicates the maximum fetch granularity of L2 (in Bytes). This is a hint </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gdfcc848da2b9f49661333f861ad1a379" id="group__CUDART__TYPES_1gdfcc848da2b9f49661333f861ad1a379" shape="rect">
<!-- --></a><span>enum cudaMemRangeAttribute</span></dt>
<dd class="description">
<div class="section">
<p>CUDA range attributes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaMemRangeAttributeReadMostly = <span class="ph ph apiData">1</span></span></dt>
<dd>Whether the range will mostly be read and only occassionally be written to </dd>
<dt><span class="enum-member-name-def">cudaMemRangeAttributePreferredLocation = <span class="ph ph apiData">2</span></span></dt>
<dd>The preferred location of the range </dd>
<dt><span class="enum-member-name-def">cudaMemRangeAttributeAccessedBy = <span class="ph ph apiData">3</span></span></dt>
<dd>Memory range has <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggc314a8b14091f7e02a7ad15dcb36c85750a22279bce0dc29956ad4f257084623" shape="rect">cudaMemAdviseSetAccessedBy</a> set for specified device
</dd>
<dt><span class="enum-member-name-def">cudaMemRangeAttributeLastPrefetchLocation = <span class="ph ph apiData">4</span></span></dt>
<dd>The last location to which the range was prefetched </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" id="group__CUDART__TYPES_1g18fa99055ee694244a270e4d5101e95b" shape="rect">
<!-- --></a><span>enum cudaMemcpyKind</span></dt>
<dd class="description">
<div class="section">
<p>CUDA memory copy types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaMemcpyHostToHost = <span class="ph ph apiData">0</span></span></dt>
<dd>Host -> Host </dd>
<dt><span class="enum-member-name-def">cudaMemcpyHostToDevice = <span class="ph ph apiData">1</span></span></dt>
<dd>Host -> Device </dd>
<dt><span class="enum-member-name-def">cudaMemcpyDeviceToHost = <span class="ph ph apiData">2</span></span></dt>
<dd>Device -> Host </dd>
<dt><span class="enum-member-name-def">cudaMemcpyDeviceToDevice = <span class="ph ph apiData">3</span></span></dt>
<dd>Device -> Device </dd>
<dt><span class="enum-member-name-def">cudaMemcpyDefault = <span class="ph ph apiData">4</span></span></dt>
<dd>Direction of the transfer is inferred from the pointer values. Requires unified virtual addressing </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gc314a8b14091f7e02a7ad15dcb36c857" id="group__CUDART__TYPES_1gc314a8b14091f7e02a7ad15dcb36c857" shape="rect">
<!-- --></a><span>enum cudaMemoryAdvise</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Memory Advise values </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaMemAdviseSetReadMostly = <span class="ph ph apiData">1</span></span></dt>
<dd>Data will mostly be read and only occassionally be written to </dd>
<dt><span class="enum-member-name-def">cudaMemAdviseUnsetReadMostly = <span class="ph ph apiData">2</span></span></dt>
<dd>Undo the effect of <a class="xref" href="group__CUDART__TYPES.html#group__CUDART__TYPES_1ggc314a8b14091f7e02a7ad15dcb36c857441d911811beda174627f403142d5ff0" shape="rect">cudaMemAdviseSetReadMostly</a></dd>
<dt><span class="enum-member-name-def">cudaMemAdviseSetPreferredLocation = <span class="ph ph apiData">3</span></span></dt>
<dd>Set the preferred location for the data as the specified device </dd>
<dt><span class="enum-member-name-def">cudaMemAdviseUnsetPreferredLocation = <span class="ph ph apiData">4</span></span></dt>
<dd>Clear the preferred location for the data </dd>
<dt><span class="enum-member-name-def">cudaMemAdviseSetAccessedBy = <span class="ph ph apiData">5</span></span></dt>
<dd>Data will be accessed by the specified device, so prevent page faults as much as possible </dd>
<dt><span class="enum-member-name-def">cudaMemAdviseUnsetAccessedBy = <span class="ph ph apiData">6</span></span></dt>
<dd>Let the Unified Memory subsystem decide on the page faulting policy for the specified device </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g13de56a8fe75569530ecc3a3106e9b6d" id="group__CUDART__TYPES_1g13de56a8fe75569530ecc3a3106e9b6d" shape="rect">
<!-- --></a><span>enum cudaMemoryType</span></dt>
<dd class="description">
<div class="section">
<p>CUDA memory types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaMemoryTypeUnregistered = <span class="ph ph apiData">0</span></span></dt>
<dd>Unregistered memory </dd>
<dt><span class="enum-member-name-def">cudaMemoryTypeHost = <span class="ph ph apiData">1</span></span></dt>
<dd>Host memory </dd>
<dt><span class="enum-member-name-def">cudaMemoryTypeDevice = <span class="ph ph apiData">2</span></span></dt>
<dd>Device memory </dd>
<dt><span class="enum-member-name-def">cudaMemoryTypeManaged = <span class="ph ph apiData">3</span></span></dt>
<dd>Managed memory </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" id="group__CUDART__TYPES_1g4d08d35d3a07b79e125df157c65dd9e9" shape="rect">
<!-- --></a><span>enum cudaOutputMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Profiler Output modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaKeyValuePair = <span class="ph ph apiData">0x00</span></span></dt>
<dd>Output mode Key-Value pair format. </dd>
<dt><span class="enum-member-name-def">cudaCSV = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Output mode Comma separated values format. </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g067b774c0e639817a00a972c8e2c203c" id="group__CUDART__TYPES_1g067b774c0e639817a00a972c8e2c203c" shape="rect">
<!-- --></a><span>enum cudaResourceType</span></dt>
<dd class="description">
<div class="section">
<p>CUDA resource types </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaResourceTypeArray = <span class="ph ph apiData">0x00</span></span></dt>
<dd>Array resource </dd>
<dt><span class="enum-member-name-def">cudaResourceTypeMipmappedArray = <span class="ph ph apiData">0x01</span></span></dt>
<dd>Mipmapped array resource </dd>
<dt><span class="enum-member-name-def">cudaResourceTypeLinear = <span class="ph ph apiData">0x02</span></span></dt>
<dd>Linear resource </dd>
<dt><span class="enum-member-name-def">cudaResourceTypePitch2D = <span class="ph ph apiData">0x03</span></span></dt>
<dd>Pitch 2D resource </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6b3a50368a0aa592f65e928adca9b929" id="group__CUDART__TYPES_1g6b3a50368a0aa592f65e928adca9b929" shape="rect">
<!-- --></a><span>enum cudaResourceViewFormat</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture resource view formats </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaResViewFormatNone = <span class="ph ph apiData">0x00</span></span></dt>
<dd>No resource view format (use underlying resource format) </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedChar1 = <span class="ph ph apiData">0x01</span></span></dt>
<dd>1 channel unsigned 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedChar2 = <span class="ph ph apiData">0x02</span></span></dt>
<dd>2 channel unsigned 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedChar4 = <span class="ph ph apiData">0x03</span></span></dt>
<dd>4 channel unsigned 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedChar1 = <span class="ph ph apiData">0x04</span></span></dt>
<dd>1 channel signed 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedChar2 = <span class="ph ph apiData">0x05</span></span></dt>
<dd>2 channel signed 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedChar4 = <span class="ph ph apiData">0x06</span></span></dt>
<dd>4 channel signed 8-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedShort1 = <span class="ph ph apiData">0x07</span></span></dt>
<dd>1 channel unsigned 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedShort2 = <span class="ph ph apiData">0x08</span></span></dt>
<dd>2 channel unsigned 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedShort4 = <span class="ph ph apiData">0x09</span></span></dt>
<dd>4 channel unsigned 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedShort1 = <span class="ph ph apiData">0x0a</span></span></dt>
<dd>1 channel signed 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedShort2 = <span class="ph ph apiData">0x0b</span></span></dt>
<dd>2 channel signed 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedShort4 = <span class="ph ph apiData">0x0c</span></span></dt>
<dd>4 channel signed 16-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedInt1 = <span class="ph ph apiData">0x0d</span></span></dt>
<dd>1 channel unsigned 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedInt2 = <span class="ph ph apiData">0x0e</span></span></dt>
<dd>2 channel unsigned 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedInt4 = <span class="ph ph apiData">0x0f</span></span></dt>
<dd>4 channel unsigned 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedInt1 = <span class="ph ph apiData">0x10</span></span></dt>
<dd>1 channel signed 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedInt2 = <span class="ph ph apiData">0x11</span></span></dt>
<dd>2 channel signed 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedInt4 = <span class="ph ph apiData">0x12</span></span></dt>
<dd>4 channel signed 32-bit integers </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatHalf1 = <span class="ph ph apiData">0x13</span></span></dt>
<dd>1 channel 16-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatHalf2 = <span class="ph ph apiData">0x14</span></span></dt>
<dd>2 channel 16-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatHalf4 = <span class="ph ph apiData">0x15</span></span></dt>
<dd>4 channel 16-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatFloat1 = <span class="ph ph apiData">0x16</span></span></dt>
<dd>1 channel 32-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatFloat2 = <span class="ph ph apiData">0x17</span></span></dt>
<dd>2 channel 32-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatFloat4 = <span class="ph ph apiData">0x18</span></span></dt>
<dd>4 channel 32-bit floating point </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed1 = <span class="ph ph apiData">0x19</span></span></dt>
<dd>Block compressed 1 </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed2 = <span class="ph ph apiData">0x1a</span></span></dt>
<dd>Block compressed 2 </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed3 = <span class="ph ph apiData">0x1b</span></span></dt>
<dd>Block compressed 3 </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed4 = <span class="ph ph apiData">0x1c</span></span></dt>
<dd>Block compressed 4 unsigned </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedBlockCompressed4 = <span class="ph ph apiData">0x1d</span></span></dt>
<dd>Block compressed 4 signed </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed5 = <span class="ph ph apiData">0x1e</span></span></dt>
<dd>Block compressed 5 unsigned </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedBlockCompressed5 = <span class="ph ph apiData">0x1f</span></span></dt>
<dd>Block compressed 5 signed </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed6H = <span class="ph ph apiData">0x20</span></span></dt>
<dd>Block compressed 6 unsigned half-float </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatSignedBlockCompressed6H = <span class="ph ph apiData">0x21</span></span></dt>
<dd>Block compressed 6 signed half-float </dd>
<dt><span class="enum-member-name-def">cudaResViewFormatUnsignedBlockCompressed7 = <span class="ph ph apiData">0x22</span></span></dt>
<dd>Block compressed 7 </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gb0a2adc3971b31a19b6ce2729bb5ce9f" id="group__CUDART__TYPES_1gb0a2adc3971b31a19b6ce2729bb5ce9f" shape="rect">
<!-- --></a><span>enum cudaSharedCarveout</span></dt>
<dd class="description">
<div class="section">
<p>Shared memory carveout configurations. These may be passed to cudaFuncSetAttribute </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaSharedmemCarveoutDefault = <span class="ph ph apiData">-1</span></span></dt>
<dd>No preference for shared memory or L1 (default) </dd>
<dt><span class="enum-member-name-def">cudaSharedmemCarveoutMaxShared = <span class="ph ph apiData">100</span></span></dt>
<dd>Prefer maximum available shared memory, minimum L1 cache </dd>
<dt><span class="enum-member-name-def">cudaSharedmemCarveoutMaxL1 = <span class="ph ph apiData">0</span></span></dt>
<dd>Prefer maximum available L1 cache, minimum shared memory </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g6e62d15f3c224625e8c9aa946f1709a6" id="group__CUDART__TYPES_1g6e62d15f3c224625e8c9aa946f1709a6" shape="rect">
<!-- --></a><span>enum cudaSharedMemConfig</span></dt>
<dd class="description">
<div class="section">
<p>CUDA shared memory configuration </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaSharedMemBankSizeDefault = <span class="ph ph apiData">0</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaSharedMemBankSizeFourByte = <span class="ph ph apiData">1</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaSharedMemBankSizeEightByte = <span class="ph ph apiData">2</span></span></dt>
<dd></dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g24ae5ae00cc50614957ff8eba43e560e" id="group__CUDART__TYPES_1g24ae5ae00cc50614957ff8eba43e560e" shape="rect">
<!-- --></a><span>enum cudaStreamCaptureMode</span></dt>
<dd class="description">
<div class="section">
<p>Possible modes for stream capture thread interactions. For more details see <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g793d7d4e474388ddfda531603dc34aa3" title="Begins graph capture on a stream." shape="rect">cudaStreamBeginCapture</a> and <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1g9d0535d93a214cbf126835257b16ba85" title="Swaps the stream capture interaction mode for a thread." shape="rect">cudaThreadExchangeStreamCaptureMode</a></p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaStreamCaptureModeGlobal = <span class="ph ph apiData">0</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaStreamCaptureModeThreadLocal = <span class="ph ph apiData">1</span></span></dt>
<dd></dd>
<dt><span class="enum-member-name-def">cudaStreamCaptureModeRelaxed = <span class="ph ph apiData">2</span></span></dt>
<dd></dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g0ec4aacc66fe76c145252d12b189e233" id="group__CUDART__TYPES_1g0ec4aacc66fe76c145252d12b189e233" shape="rect">
<!-- --></a><span>enum cudaStreamCaptureStatus</span></dt>
<dd class="description">
<div class="section">
<p>Possible stream capture statuses returned by <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1ge564e8434c67d716367931c4bc7db1cc" title="Returns a stream's capture status." shape="rect">cudaStreamIsCapturing</a></p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaStreamCaptureStatusNone = <span class="ph ph apiData">0</span></span></dt>
<dd>Stream is not capturing </dd>
<dt><span class="enum-member-name-def">cudaStreamCaptureStatusActive = <span class="ph ph apiData">1</span></span></dt>
<dd>Stream is actively capturing </dd>
<dt><span class="enum-member-name-def">cudaStreamCaptureStatusInvalidated = <span class="ph ph apiData">2</span></span></dt>
<dd>Stream is part of a capture sequence that has been invalidated, but not terminated </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gdc002e3c2a4fd592efa944e2c73a10fb" id="group__CUDART__TYPES_1gdc002e3c2a4fd592efa944e2c73a10fb" shape="rect">
<!-- --></a><span>enum cudaSurfaceBoundaryMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Surface boundary modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaBoundaryModeZero = <span class="ph ph apiData">0</span></span></dt>
<dd>Zero boundary mode </dd>
<dt><span class="enum-member-name-def">cudaBoundaryModeClamp = <span class="ph ph apiData">1</span></span></dt>
<dd>Clamp boundary mode </dd>
<dt><span class="enum-member-name-def">cudaBoundaryModeTrap = <span class="ph ph apiData">2</span></span></dt>
<dd>Trap boundary mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g427be57cb8aa90479139bba92267150f" id="group__CUDART__TYPES_1g427be57cb8aa90479139bba92267150f" shape="rect">
<!-- --></a><span>enum cudaSurfaceFormatMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA Surface format modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaFormatModeForced = <span class="ph ph apiData">0</span></span></dt>
<dd>Forced format mode </dd>
<dt><span class="enum-member-name-def">cudaFormatModeAuto = <span class="ph ph apiData">1</span></span></dt>
<dd>Auto format mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1g03e1bbd2c491d809279c7a47e2cd0351" id="group__CUDART__TYPES_1g03e1bbd2c491d809279c7a47e2cd0351" shape="rect">
<!-- --></a><span>enum cudaTextureAddressMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture address modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaAddressModeWrap = <span class="ph ph apiData">0</span></span></dt>
<dd>Wrapping address mode </dd>
<dt><span class="enum-member-name-def">cudaAddressModeClamp = <span class="ph ph apiData">1</span></span></dt>
<dd>Clamp to edge address mode </dd>
<dt><span class="enum-member-name-def">cudaAddressModeMirror = <span class="ph ph apiData">2</span></span></dt>
<dd>Mirror address mode </dd>
<dt><span class="enum-member-name-def">cudaAddressModeBorder = <span class="ph ph apiData">3</span></span></dt>
<dd>Border address mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gee4adb3d1b062cf05374de09325a82d5" id="group__CUDART__TYPES_1gee4adb3d1b062cf05374de09325a82d5" shape="rect">
<!-- --></a><span>enum cudaTextureFilterMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture filter modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaFilterModePoint = <span class="ph ph apiData">0</span></span></dt>
<dd>Point filter mode </dd>
<dt><span class="enum-member-name-def">cudaFilterModeLinear = <span class="ph ph apiData">1</span></span></dt>
<dd>Linear filter mode </dd>
</dl>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gd9266d02be93809558036ec4f3d5f43d" id="group__CUDART__TYPES_1gd9266d02be93809558036ec4f3d5f43d" shape="rect">
<!-- --></a><span>enum cudaTextureReadMode</span></dt>
<dd class="description">
<div class="section">
<p>CUDA texture read modes </p>
</div>
<div class="enum-members">
<h6 class="enumerator_header">
Values
</h6>
<dl class="enumerator">
<dt><span class="enum-member-name-def">cudaReadModeElementType = <span class="ph ph apiData">0</span></span></dt>
<dd>Read texture as specified element type </dd>
<dt><span class="enum-member-name-def">cudaReadModeNormalizedFloat = <span class="ph ph apiData">1</span></span></dt>
<dd>Read texture as normalized float </dd>
</dl>
</div>
</dd>
</dl>
</div>
</div>
<hr id="contents-end"></hr>
</article>
</div>
</div>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/formatting/common.min.js"></script>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/scripts/google-analytics/google-analytics-write.js"></script>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/scripts/google-analytics/google-analytics-tracker.js"></script>
<script type="text/javascript">var switchTo5x=true;</script><script type="text/javascript" src="http://w.sharethis.com/button/buttons.js"></script><script type="text/javascript">stLight.options({publisher: "998dc202-a267-4d8e-bce9-14debadb8d92", doNotHash: false, doNotCopy: false, hashAddressBar: false});</script><script type="text/javascript">_satellite.pageBottom();</script></body>
</html>
distrib
>
Mageia
>
7
>
x86_64
>
media
>
nonfree-updates
>
by-pkgid
>
b86a85131cc739c1c53d0b55840a4328
>
files
>
1522
