<!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="../common/formatting/jquery.min.js"></script>
<script type="text/javascript" charset="utf-8" src="../common/formatting/jquery.ba-hashchange.min.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>
<article id="contents">
<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>)
-
CUDA Toolkit v5.5
(<a href="https://developer.nvidia.com/cuda-toolkit-archive">older</a>)
-
Last updated
July 19, 2013
-
<a href="mailto:cudatools@nvidia.com?subject=CUDA Tools Documentation Feedback: cuda-runtime-api">Send Feedback</a></div>
<div class="topic reference apiRef apiPackage cppModule" id="group__CUDART__TYPES"><a name="group__CUDART__TYPES" shape="rect">
<!-- --></a><h2 class="topictitle2 cppModule">2.28. 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="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="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="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="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="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="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_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_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_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_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_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_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_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_1g5dbd11a1723d9f5938a133cedbc525e3" shape="rect">cudaStreamNonBlocking</a> 0x01</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_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 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_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>
<dt><span class="member_type">typedef CUuuid_st </span><span class="member_name"><a href="#group__CUDART__TYPES_1gbc782b3ec2c70c11b945629e1e0542b9" shape="rect">cudaUUID_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_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_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_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_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_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_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_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_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_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_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_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_deprecated000039" 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_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_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_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_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_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>
</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_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_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_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> 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> CUDA texture object </p>
</div>
</dd>
<dt class="description"><a name="group__CUDART__TYPES_1gbc782b3ec2c70c11b945629e1e0542b9" id="group__CUDART__TYPES_1gbc782b3ec2c70c11b945629e1e0542b9" shape="rect">
<!-- --></a><span>typedef CUuuid_st cudaUUID_t</span></dt>
<dd class="description">
<div class="section">
<p> CUDA UUID types </p>
</div>
</dd>
</dl>
</div>
<div class="description">
<h3 class="sectiontitle">Enumerations</h3>
<dl class="description">
<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_1g418c299b069c4803bfb7cab4943da383" 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_1g418c299b069c4803bfb7cab4943da383" 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_1g418c299b069c4803bfb7cab4943da383" 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_1g418c299b069c4803bfb7cab4943da383" 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>
</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 can also mean that the operation being queried is complete
(see <a class="xref" href="group__CUDART__EVENT.html#group__CUDART__EVENT_1gf8e4ddb569b1da032c060f0c54da698f" title="Queries an event's status." shape="rect">cudaEventQuery()</a> and <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1ge78feba9080b59fe0fff536a42c13e6d" title="Queries an asynchronous stream for completion status." shape="rect">cudaStreamQuery()</a>).
</dd>
<dt><span class="enum-member-name-def">cudaErrorMissingConfiguration = <span class="ph ph apiData">1</span></span></dt>
<dd>The device function being invoked (usually via <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1gf4f3215d06b6d90849a3d977f9440002" title="Launches a device function." shape="rect">cudaLaunch()</a>) was not previously configured via the <a class="xref" href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION_1g19a7dd5a102b499c39f6a7648bec757a" title="Configure a device-launch." shape="rect">cudaConfigureCall()</a> function.
</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">cudaErrorLaunchFailure = <span class="ph ph apiData">4</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. The device cannot be used until <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" title="Exit and clean up from CUDA launches." shape="rect">cudaThreadExit()</a> is called. All existing device memory allocations are invalid and must be reconstructed if the program is to continue using
CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorPriorLaunchFailure = <span class="ph ph apiData">5</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000040" 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">cudaErrorLaunchTimeout = <span class="ph ph apiData">6</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. The device cannot be used until <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" title="Exit and clean up from CUDA launches." shape="rect">cudaThreadExit()</a> is called. All existing device memory allocations are invalid and must be reconstructed if the program is to continue using
CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorLaunchOutOfResources = <span class="ph ph apiData">7</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">cudaErrorInvalidDeviceFunction = <span class="ph ph apiData">8</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">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">cudaErrorInvalidDevice = <span class="ph ph apiData">10</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">cudaErrorInvalidValue = <span class="ph ph apiData">11</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">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">cudaErrorMapBufferObjectFailed = <span class="ph ph apiData">14</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">15</span></span></dt>
<dd>This indicates that the buffer object could not be unmapped. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidHostPointer = <span class="ph ph apiData">16</span></span></dt>
<dd>This indicates that at least one host pointer passed to the API call is not a valid host pointer. </dd>
<dt><span class="enum-member-name-def">cudaErrorInvalidDevicePointer = <span class="ph ph apiData">17</span></span></dt>
<dd>This indicates that at least one device pointer passed to the API call is not a valid device pointer. </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_1g6076c6bf0b1f2e52a36cd51af9d78fb4" 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_deprecated000041" 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_1g1b2a5ca2b220e77deb6a777bf3f75a65" 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_deprecated000042" 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_deprecated000043" 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_deprecated000044" 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_deprecated000045" 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">cudaErrorCudartUnloading = <span class="ph ph apiData">29</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">cudaErrorUnknown = <span class="ph ph apiData">30</span></span></dt>
<dd>This indicates that an unknown internal error has occurred. </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_deprecated000046" 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_deprecated000047" 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">cudaErrorInvalidResourceHandle = <span class="ph ph apiData">33</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">cudaErrorNotReady = <span class="ph ph apiData">34</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_1gf8e4ddb569b1da032c060f0c54da698f" title="Queries an event's status." shape="rect">cudaEventQuery()</a> and <a class="xref" href="group__CUDART__STREAM.html#group__CUDART__STREAM_1ge78feba9080b59fe0fff536a42c13e6d" title="Queries an asynchronous stream for completion status." shape="rect">cudaStreamQuery()</a>.
</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">cudaErrorSetOnActiveProcess = <span class="ph ph apiData">36</span></span></dt>
<dd>This indicates that the user has called <a class="xref" href="group__CUDART__DEVICE.html#group__CUDART__DEVICE_1g5754b9d4e409b6cc0e252ba240d7468b" 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_1g18074e885b4d89f5a0fe1beab589e0c8" title="Sets flags to be used for device executions." shape="rect">cudaSetDeviceFlags()</a>, <a class="xref" href="group__CUDART__D3D9.html#group__CUDART__D3D9_1g3b7a9c5a5f249fa1f8fb5743304474b5" 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_1geec2934147774dd7a611df971a548675" 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_1g447d066794c8070432514185d1326446" 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_1g93a9727b90c526a3493918bceafcb3f7" 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 CUcontext active on the host thread.
</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">cudaErrorNoDevice = <span class="ph ph apiData">38</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">cudaErrorECCUncorrectable = <span class="ph ph apiData">39</span></span></dt>
<dd>This indicates that an uncorrectable ECC error was detected during execution. </dd>
<dt><span class="enum-member-name-def">cudaErrorSharedObjectSymbolNotFound = <span class="ph ph apiData">40</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">41</span></span></dt>
<dd>This indicates that initialization of a shared object failed. </dd>
<dt><span class="enum-member-name-def">cudaErrorUnsupportedLimit = <span class="ph ph apiData">42</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">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">cudaErrorInvalidKernelImage = <span class="ph ph apiData">47</span></span></dt>
<dd>This indicates that the device kernel image is invalid. </dd>
<dt><span class="enum-member-name-def">cudaErrorNoKernelImageForDevice = <span class="ph ph apiData">48</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">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">cudaErrorPeerAccessAlreadyEnabled = <span class="ph ph apiData">50</span></span></dt>
<dd>This error indicates that a call to <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1g9e5ea65a18938c2b8715a5602105c306" 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">51</span></span></dt>
<dd>This error indicates that <a class="xref" href="group__CUDART__PEER.html#group__CUDART__PEER_1gae24fc50bd0f1ce7f69032f91bde87ac" 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_1g9e5ea65a18938c2b8715a5602105c306" title="Enables direct access to memory allocations on a peer device." shape="rect">cudaDeviceEnablePeerAccess()</a>.
</dd>
<dt><span class="enum-member-name-def">cudaErrorDeviceAlreadyInUse = <span class="ph ph apiData">54</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">cudaErrorProfilerDisabled = <span class="ph ph apiData">55</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">56</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000048" 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_1gde61d4a32c92d43d5d3f28847d89fe68" title="Enable profiling." shape="rect">cudaProfilerStart</a> or <a class="xref" href="group__CUDART__PROFILER.html#group__CUDART__PROFILER_1gfbae1163a2c1086eac72e1908c2597f1" 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">57</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000049" 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_1gde61d4a32c92d43d5d3f28847d89fe68" 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">58</span></span></dt>
<dd>
<h6 class="deprecated_header"><a class="xref xrefsect-title" href="deprecated.html#deprecated__deprecated_1_deprecated000050" 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_1gfbae1163a2c1086eac72e1908c2597f1" title="Disable profiling." shape="rect">cudaProfilerStop()</a> when profiling is already disabled. </span></p>
<p></p>
</dd>
<dt><span class="enum-member-name-def">cudaErrorAssert = <span class="ph ph apiData">59</span></span></dt>
<dd>An assert triggered in device code during kernel execution. The device cannot be used again until <a class="xref" href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED_1gf423ba04af587d42b52799455a7c094d" title="Exit and clean up from CUDA launches." shape="rect">cudaThreadExit()</a> is called. All existing allocations are invalid and must be reconstructed if the program is to continue using CUDA.
</dd>
<dt><span class="enum-member-name-def">cudaErrorTooManyPeers = <span class="ph ph apiData">60</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">61</span></span></dt>
<dd>This error indicates that the memory range passed to <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1g36b9fe28f547f28d23742e8c7cd18141" 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">62</span></span></dt>
<dd>This error indicates that the pointer passed to <a class="xref" href="group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gc07b1312c60ca36c118e2ed71b192afe" 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">cudaErrorOperatingSystem = <span class="ph ph apiData">63</span></span></dt>
<dd>This error indicates that an OS call failed. </dd>
<dt><span class="enum-member-name-def">cudaErrorPeerAccessUnsupported = <span class="ph ph apiData">64</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">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_1g32bdc6229081137acd3cba5da2897779" 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_1g32bdc6229081137acd3cba5da2897779" 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_1gb8a22e29cc297634b0702db0b69f59e7" 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_1gb8a22e29cc297634b0702db0b69f59e7" 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">cudaErrorNotPermitted = <span class="ph ph apiData">70</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">71</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">cudaErrorStartupFailure = <span class="ph ph apiData">0x7f</span></span></dt>
<dd>This indicates an internal startup failure in the CUDA runtime. </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_deprecated000051" 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_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_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/fprintf 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>
</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>Default based unified virtual address space </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">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>
</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_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_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>
<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>)
-
CUDA Toolkit v5.5
(<a href="https://developer.nvidia.com/cuda-toolkit-archive">older</a>)
-
Last updated
July 19, 2013
-
<a href="mailto:cudatools@nvidia.com?subject=CUDA Tools Documentation Feedback: cuda-runtime-api">Send Feedback</a></div>
</article>
<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>
<nav id="site-nav">
<div class="category closed"><span class="twiddle">▷</span><a href="../index.html" title="The root of the site.">CUDA Toolkit</a></div>
<ul class="closed">
<li><a href="../cuda-toolkit-release-notes/index.html" title="The Release Notes for the CUDA Toolkit from v4.0 to today.">Release Notes</a></li>
<li><a href="../eula/index.html" title="The End User License Agreements for the NVIDIA CUDA Toolkit, the NVIDIA CUDA Samples, the NVIDIA Display Driver, and NVIDIA NSight (Visual Studio Edition).">EULA</a></li>
<li><a href="../cuda-getting-started-guide-for-linux/index.html" title="This guide discusses how to install and check for correct operation of the CUDA Development Tools on GNU/Linux systems.">Getting Started Linux</a></li>
<li><a href="../cuda-getting-started-guide-for-mac-os-x/index.html" title="This guide discusses how to install and check for correct operation of the CUDA Development Tools on Mac OS X systems.">Getting Started Mac OS X</a></li>
<li><a href="../cuda-getting-started-guide-for-microsoft-windows/index.html" title="This guide discusses how to install and check for correct operation of the CUDA Development Tools on Microsoft Windows systems.">Getting Started Windows</a></li>
<li><a href="../cuda-c-programming-guide/index.html" title="This guide provides a detailed discussion of the CUDA programming model and programming interface. It then describes the hardware implementation, and provides guidance on how to achieve maximum performance. The Appendixes include a list of all CUDA-enabled devices, detailed description of all extensions to the C language, listings of supported mathematical functions, C++ features supported in host and device code, details on texture fetching, technical specifications of various devices, and concludes by introducing the low-level driver API.">Programming Guide</a></li>
<li><a href="../cuda-c-best-practices-guide/index.html" title="This guide presents established parallelization and optimization techniques and explains coding metaphors and idioms that can greatly simplify programming for CUDA-capable GPU architectures. The intent is to provide guidelines for obtaining the best performance from NVIDIA GPUs using the CUDA Toolkit.">Best Practices Guide</a></li>
<li><a href="../kepler-compatibility-guide/index.html" title="This application note is intended to help developers ensure that their NVIDIA CUDA applications will run effectively on GPUs based on the NVIDIA Kepler Architecture. This document provides guidance to ensure that your software applications are compatible with Kepler.">Kepler Compatibility Guide</a></li>
<li><a href="../kepler-tuning-guide/index.html" title="Kepler is NVIDIA's next-generation architecture for CUDA compute applications. Applications that follow the best practices for the Fermi architecture should typically see speedups on the Kepler architecture without any code changes. This guide summarizes the ways that an application can be fine-tuned to gain additional speedups by leveraging Kepler architectural features.">Kepler Tuning Guide</a></li>
<li><a href="../parallel-thread-execution/index.html" title="This guide provides detailed instructions on the use of PTX, a low-level parallel thread execution virtual machine and instruction set architecture (ISA). PTX exposes the GPU as a data-parallel computing device.">PTX ISA</a></li>
<li><a href="../optimus-developer-guide/index.html" title="This document explains how CUDA APIs can be used to query for GPU capabilities in NVIDIA Optimus systems.">Developer Guide for Optimus</a></li>
<li><a href="../video-decoder/index.html" title="This document provides the video decoder API specification and the format conversion and display using DirectX or OpenGL following decode.">Video Decoder</a></li>
<li><a href="../video-encoder/index.html" title="This document provides the CUDA video encoder specifications, including the C-library API functions and encoder query parameters.">Video Encoder</a></li>
<li><a href="../inline-ptx-assembly/index.html" title="This document shows how to inline PTX (parallel thread execution) assembly language statements into CUDA code. It describes available assembler statement parameters and constraints, and the document also provides a list of some pitfalls that you may encounter.">Inline PTX Assembly</a></li>
<li><a href="../cuda-runtime-api/index.html" title="The CUDA runtime API.">CUDA Runtime API</a></li>
<li><a href="../cuda-driver-api/index.html" title="The CUDA driver API.">CUDA Driver API</a></li>
<li><a href="../cuda-math-api/index.html" title="The CUDA math API.">CUDA Math API</a></li>
<li><a href="../cublas/index.html" title="The CUBLAS library is an implementation of BLAS (Basic Linear Algebra Subprograms) on top of the NVIDIA CUDA runtime. It allows the user to access the computational resources of NVIDIA Graphical Processing Unit (GPU), but does not auto-parallelize across multiple GPUs.">CUBLAS</a></li>
<li><a href="../cufft/index.html" title="The CUFFT library user guide.">CUFFT</a></li>
<li><a href="../curand/index.html" title="The CURAND library user guide.">CURAND</a></li>
<li><a href="../cusparse/index.html" title="The CUSPARSE library user guide.">CUSPARSE</a></li>
<li><a href="../npp/index.html" title="NVIDIA NPP is a library of functions for performing CUDA accelerated processing. The initial set of functionality in the library focuses on imaging and video processing and is widely applicable for developers in these areas. NPP will evolve over time to encompass more of the compute heavy tasks in a variety of problem domains. The NPP library is written to maximize flexibility, while maintaining high performance.">NPP</a></li>
<li><a href="../thrust/index.html" title="The Thrust getting started guide.">Thrust</a></li>
<li><a href="../cuda-samples/index.html" title="This document contains a complete listing of the code samples that are included with the NVIDIA CUDA Toolkit. It describes each code sample, lists the minimum GPU specification, and provides links to the source code and white papers if available.">CUDA Samples</a></li>
<li><a href="../cuda-compiler-driver-nvcc/index.html" title="This document is a reference guide on the use of the CUDA compiler driver nvcc. Instead of being a specific CUDA compilation driver, nvcc mimics the behavior of the GNU compiler gcc, accepting a range of conventional compiler options, such as for defining macros and include/library paths, and for steering the compilation process.">NVCC</a></li>
<li><a href="../cuda-gdb/index.html" title="The NVIDIA tool for debugging CUDA applications running on Linux and Mac, providing developers with a mechanism for debugging CUDA applications running on actual hardware. CUDA-GDB is an extension to the x86-64 port of GDB, the GNU Project debugger.">CUDA-GDB</a></li>
<li><a href="../cuda-memcheck/index.html" title="CUDA-MEMCHECK is a suite of run time tools capable of precisely detecting out of bounds and misaligned memory access errors, checking device allocation leaks, reporting hardware errors and identifying shared memory data access hazards.">CUDA-MEMCHECK</a></li>
<li><a href="../nsight-eclipse-edition-getting-started-guide/index.html" title="Nsight Eclipse Edition getting started guide">Nsight Eclipse Edition</a></li>
<li><a href="../profiler-users-guide/index.html" title="This is the guide to the Profiler.">Profiler</a></li>
<li><a href="../cuda-binary-utilities/index.html" title="The application notes for cuobjdump and nvdisasm.">CUDA Binary Utilities</a></li>
<li><a href="../floating-point/index.html" title="A number of issues related to floating point accuracy and compliance are a frequent source of confusion on both CPUs and GPUs. The purpose of this white paper is to discuss the most common issues related to NVIDIA GPUs and to supplement the documentation in the CUDA C Programming Guide.">Floating Point and IEEE 754</a></li>
<li><a href="../incomplete-lu-cholesky/index.html" title="In this white paper we show how to use the CUSPARSE and CUBLAS libraries to achieve a 2x speedup over CPU in the incomplete-LU and Cholesky preconditioned iterative methods. We focus on the Bi-Conjugate Gradient Stabilized and Conjugate Gradient iterative methods, that can be used to solve large sparse nonsymmetric and symmetric positive definite linear systems, respectively. Also, we comment on the parallel sparse triangular solve, which is an essential building block in these algorithms.">Incomplete-LU and Cholesky Preconditioned Iterative Methods</a></li>
<li><a href="../libnvvm-api/index.html" title="The libNVVM API.">libNVVM API</a></li>
<li><a href="../libdevice-users-guide/index.html" title="The libdevice library is an LLVM bitcode library that implements common functions for GPU kernels.">libdevice User's Guide</a></li>
<li><a href="../nvvm-ir-spec/index.html" title="NVVM IR is a compiler IR (internal representation) based on the LLVM IR. The NVVM IR is designed to represent GPU compute kernels (for example, CUDA kernels). High-level language front-ends, like the CUDA C compiler front-end, can generate NVVM IR.">NVVM IR</a></li>
<li><a href="../cupti/index.html" title="The CUPTI API.">CUPTI</a></li>
<li><a href="../debugger-api/index.html" title="The CUDA debugger API.">Debugger API</a></li>
<li><a href="../gpudirect-rdma/index.html" title="A tool for Kepler-class GPUs and CUDA 5.0 enabling a direct path for communication between the GPU and a peer device on the PCI Express bus when the devices share the same upstream root complex using standard features of PCI Express. This document introduces the technology and describes the steps necessary to enable a RDMA for GPUDirect connection to NVIDIA GPUs within the Linux device driver model.">RDMA for GPUDirect</a></li>
</ul>
<div class="category"><span class="twiddle">▼</span><a href="index.html" title="CUDA Runtime API">CUDA Runtime API</a></div>
<ul>
<li><a href="api-sync-behavior.html#api-sync-behavior">1. API synchronization behavior </a></li>
<li><a href="modules.html#modules">2. Modules</a><ul>
<li><a href="group__CUDART__DEVICE.html#group__CUDART__DEVICE">2.1. Device Management</a></li>
<li><a href="group__CUDART__THREAD__DEPRECATED.html#group__CUDART__THREAD__DEPRECATED">2.2. Thread Management [DEPRECATED]</a></li>
<li><a href="group__CUDART__ERROR.html#group__CUDART__ERROR">2.3. Error Handling</a></li>
<li><a href="group__CUDART__STREAM.html#group__CUDART__STREAM">2.4. Stream Management</a></li>
<li><a href="group__CUDART__EVENT.html#group__CUDART__EVENT">2.5. Event Management</a></li>
<li><a href="group__CUDART__EXECUTION.html#group__CUDART__EXECUTION">2.6. Execution Control</a></li>
<li><a href="group__CUDART__MEMORY.html#group__CUDART__MEMORY">2.7. Memory Management</a></li>
<li><a href="group__CUDART__UNIFIED.html#group__CUDART__UNIFIED">2.8. Unified Addressing</a></li>
<li><a href="group__CUDART__PEER.html#group__CUDART__PEER">2.9. Peer Device Memory Access</a></li>
<li><a href="group__CUDART__OPENGL.html#group__CUDART__OPENGL">2.10. OpenGL Interoperability</a></li>
<li><a href="group__CUDART__OPENGL__DEPRECATED.html#group__CUDART__OPENGL__DEPRECATED">2.11. OpenGL Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__D3D9.html#group__CUDART__D3D9">2.12. Direct3D 9 Interoperability</a></li>
<li><a href="group__CUDART__D3D9__DEPRECATED.html#group__CUDART__D3D9__DEPRECATED">2.13. Direct3D 9 Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__D3D10.html#group__CUDART__D3D10">2.14. Direct3D 10 Interoperability</a></li>
<li><a href="group__CUDART__D3D10__DEPRECATED.html#group__CUDART__D3D10__DEPRECATED">2.15. Direct3D 10 Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__D3D11.html#group__CUDART__D3D11">2.16. Direct3D 11 Interoperability</a></li>
<li><a href="group__CUDART__D3D11__DEPRECATED.html#group__CUDART__D3D11__DEPRECATED">2.17. Direct3D 11 Interoperability [DEPRECATED]</a></li>
<li><a href="group__CUDART__VDPAU.html#group__CUDART__VDPAU">2.18. VDPAU Interoperability</a></li>
<li><a href="group__CUDART__INTEROP.html#group__CUDART__INTEROP">2.19. Graphics Interoperability</a></li>
<li><a href="group__CUDART__TEXTURE.html#group__CUDART__TEXTURE">2.20. Texture Reference Management</a></li>
<li><a href="group__CUDART__SURFACE.html#group__CUDART__SURFACE">2.21. Surface Reference Management</a></li>
<li><a href="group__CUDART__TEXTURE__OBJECT.html#group__CUDART__TEXTURE__OBJECT">2.22. Texture Object Management</a></li>
<li><a href="group__CUDART__SURFACE__OBJECT.html#group__CUDART__SURFACE__OBJECT">2.23. Surface Object Management</a></li>
<li><a href="group__CUDART____VERSION.html#group__CUDART____VERSION">2.24. Version Management</a></li>
<li><a href="group__CUDART__HIGHLEVEL.html#group__CUDART__HIGHLEVEL">2.25. C++ API Routines</a></li>
<li><a href="group__CUDART__DRIVER.html#group__CUDART__DRIVER">2.26. Interactions with the CUDA Driver API</a></li>
<li><a href="group__CUDART__PROFILER.html#group__CUDART__PROFILER">2.27. Profiler Control</a></li>
<li><a href="group__CUDART__TYPES.html#group__CUDART__TYPES">2.28. Data types used by CUDA Runtime</a></li>
</ul>
</li>
<li><a href="annotated.html#annotated">3. Data Structures</a><ul>
<li><a href="structcudaChannelFormatDesc.html#structcudaChannelFormatDesc">3.1. cudaChannelFormatDesc</a></li>
<li><a href="structcudaDeviceProp.html#structcudaDeviceProp">3.2. cudaDeviceProp</a></li>
<li><a href="structcudaExtent.html#structcudaExtent">3.3. cudaExtent</a></li>
<li><a href="structcudaFuncAttributes.html#structcudaFuncAttributes">3.4. cudaFuncAttributes</a></li>
<li><a href="structcudaIpcEventHandle__t.html#structcudaIpcEventHandle__t">3.5. cudaIpcEventHandle_t</a></li>
<li><a href="structcudaIpcMemHandle__t.html#structcudaIpcMemHandle__t">3.6. cudaIpcMemHandle_t</a></li>
<li><a href="structcudaMemcpy3DParms.html#structcudaMemcpy3DParms">3.7. cudaMemcpy3DParms</a></li>
<li><a href="structcudaMemcpy3DPeerParms.html#structcudaMemcpy3DPeerParms">3.8. cudaMemcpy3DPeerParms</a></li>
<li><a href="structcudaPitchedPtr.html#structcudaPitchedPtr">3.9. cudaPitchedPtr</a></li>
<li><a href="structcudaPointerAttributes.html#structcudaPointerAttributes">3.10. cudaPointerAttributes</a></li>
<li><a href="structcudaPos.html#structcudaPos">3.11. cudaPos</a></li>
<li><a href="structcudaResourceDesc.html#structcudaResourceDesc">3.12. cudaResourceDesc</a></li>
<li><a href="structcudaResourceViewDesc.html#structcudaResourceViewDesc">3.13. cudaResourceViewDesc</a></li>
<li><a href="structcudaTextureDesc.html#structcudaTextureDesc">3.14. cudaTextureDesc</a></li>
<li><a href="structsurfaceReference.html#structsurfaceReference">3.15. surfaceReference</a></li>
<li><a href="structtextureReference.html#structtextureReference">3.16. textureReference</a></li>
</ul>
</li>
<li><a href="functions.html#functions">4. Data Fields</a></li>
<li><a href="deprecated.html#deprecated">5. Deprecated List</a></li>
<li><a href="notices-header.html#notices-header">Notices</a><ul></ul>
</li>
</ul>
</nav>
<nav id="search-results">
<h2>Search Results</h2>
<ol></ol>
</nav>
<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/omniture/s_code_us_dev_aut1-nolinktrackin.js"></script>
<script language="JavaScript" type="text/javascript" charset="utf-8" src="../common/scripts/omniture/omniture.js"></script>
<noscript><a href="http://www.omniture.com" title="Web Analytics"><img src="http://omniture.nvidia.com/b/ss/nvidiacudadocs/1/H.17--NS/0" height="1" width="1" border="0" alt=""></img></a></noscript>
<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>
</body>
</html>
