Enflame Documents
Version: TopsPlatform_v1.0.6
安装部署
快速开始
1. 环境配置
1.1. 组件列表
1.2. TopsPlatform 安装
1.3. 加载环境
加载驱动
配置环境变量
其他变量
适配平台
适配平台
1. 适配平台
用户手册
Tops C++ 编程指南
1. 版权声明
2. 简介
2.1. TopsRider® ：加速计算平台及编程模型
2.2. 文档结构
3. 硬件架构
3.1. GCU210和GCU300的架构 (GCU210 & GCU300 Architecture)
SIP架构 (SIP Architecture)
计算单元集群
芯片的架构 (Chip Architecture)
4. 执行模型
4.1. 主机端程序 (Host Program)
4.2. 核函数 (Kernel Function)
5. 线程模型
5.1. 线程层次结构 (Thread Hierarchy)
5.2. 软硬件映射 (Software to Hardware Mapping)
6. 内存模型
6.1. 内存空间（Memory Space）
6.2. 内存空间的映射（Memory Mapping）
6.3. 地址空间（Address Space）
6.4. 异步内存分配 (Asynchronous Memory Allocation)
7. 编程接口
7.1. 内存管理（Memory Management）
7.2. 执行流（Stream）
7.3. 事件（Event）
7.4. 默认执行流（Default Stream）
8. C++语言扩展
8.1. 函数执行空间指示符 (Function Execution Space Specifiers)
__global__
__device__
__host__
__cooperative__
8.2. 变量内存空间指示符（Variable Memory Space Specifiers）
__device__
__constant__
__shared__
__local__
__restrict__
转换规则
8.3. 内置向量类型和操作 (Built-in Vector Types & Operators)
内置向量类型 (Built-in Vector Types)
向量运算符 (Built-in vector Operators)
8.4. 数学函数 (Mathmatical Functions)
8.5. 内置变量 (Built-in Variables)
gridDim
blockIdx
blockDim
threadIdx
8.6. 内置宏定义 (Built-in Macro Definitions)
GCU_ARCH
AGCU_ARCH
8.7. 数据变换引擎 (Data Transformation Engine)
DTE上下文 (DTE Context)
DTE的数据参数 (DTE Parameters)
DTE的操作 (DTE Operations)
8.8. 同步机制 (Synchronization Mechanism)
线程组同步
计数同步
9. C++语言支持
9.1. 支持的标量类型 (Supported Scalar Type)
10. 错误处理机制
11. 兼容性
11.1. AGCU计算能力 (AGCU Compute Capability)
AGCU功能支持 (Feature Supported per AGCU Capability)
AGCU技术参数（Technical Specifications per AGCU Capability）
11.2. 二进制兼容 (Binary Compatibility)
11.3. 汇编指令兼容 (Assembly Compability)
12. 性能优化
12.1. 总体优化策略 (Overall Performance Optimization Strategies)
12.2. 利用率分析 (Utilization Analysis)
算力利用率分析
带宽利用率分析
算术密度和瓶颈分析
12.3. 编译优化（Compilation Optimization）
指定循环的属性
13. 术语定义
14. 变更历史
14.1. 1.1.0的变更 (2024-06-26)
14.2. 1.0.1的变更 (2024-03-22)
14.3. 0.9.0的变更 (2023-12-26)
TopsCC命令行使用手册
1. 引言/Preface
1.1. 目的/Purpose
1.2. 术语/Glossary
1.3. 版本/Revision History
1.4. 参考/Reference
2. 概述/Overview
2.1. 系统结构图/Architecture
2.2. 功能概述/Function Description
2.3. 安装方法/Installation
3. 详细设计/Detail Design
3.1. clang
命令行接口/Command Interface
使用范例/Use Case
3.2. topscc
命令行接口/Command Interface
使用范例/Use Case
3.3. llc
命令行接口/Command Interface
使用范例/Use Case
3.4. lld
命令行接口/Command Interface
使用范例/Use Case
3.5. fatbinary
命令行接口/Command Interface
使用范例/Use Case
3.6. llvm-mc
命令行接口/Command Interface
使用范例/Use Case
3.7. llvm-objdump
命令行接口/Command Interface
使用范例/Use Case
3.8. llvm-dis
命令行接口/Command Interface
使用范例/Use Case
KMD 用户使用手册
1. 简介
2. 前提
3. KMD安装
4. KMD模块签名
5. 修改KMD的模块参数
6. 卸载kmd
7. 整卡透传虚拟化
7.1. GCU Qemu quirk patch功能介绍
7.2. GCU Qemu quirk patch源文件
7.3. Qemu的编译和安装
7.4. 检查是否安装GCU Qemu Quirk Patch
7.5. Security寄存器访问控制配置文件
7.6. GCU Qemu qurk patch log开关
7.7. S60系列加速卡透传的Reset操作
7.8. S60系列加速卡透传/SRIOV VF透传/SRIOV使能时的限制
8. 常用调试功能
8.1. 查看当前KMD的版本
8.2. 查看当前KMD的模块参数
8.3. 查看所有GCU设备的PCI设备号
8.4. 查看GCU上各个firmware的版本
8.5. 查看KMD日志
8.6. 防火墙相关
8.7. KMD standby相关
8.8. power stock相关
8.9. 运行时低功耗（RPM）相关
8.10. 替换run包中固件
9. GCU虚拟化用户向导
9.1. GCU各种虚拟化方法概要
9.2. S60系列加速卡 SR-IOV支持
9.3. 各种reset
9.4. VF管理
9.5. VF的典型应用
9.6. 限制
10. FAQ
10.1. KMD编译失败
10.2. 模块正在使用而无法卸载
10.3. enflame_peer_mem驱动加载失败
10.4. KMD device id与PCI bdf对应关系
10.5. KMD ioctl版本号使用说明
10.6. 设备整卡透传到Qemu虚拟机后，执行hot reset失败
11. 相关参考
11.1. reset种类
11.2. Reset GCU的几种方法
11.3. 关闭Gcu Reset
EFSMI 用户使用手册
工具简介
参考文献
词汇表
分发包
支持的OS类型
安装包内容
安装步骤
RPM
DEB
驱动
使用须知
在宿主机中运行
在容器中运行
赋予容器特权模式
不赋予特权模式
在虚拟机中运行
EFSMI 命令
信息概览
信息查询
设备监控
PCIE 拓扑
ECC 状态
EFML - Enflame 管理库
EFML包含的文件
C/C++ 示例
Script Bindings
Python
Go
其他脚本支持
API 参考
pyefml
Module Contents
样例
TopsCC 使用样例
TopsCC Samples
1. 版权声明
2. TopsCC Samples
2.1. Get Started
2.2. Build the Samples with TopsCC
3. Samples List
3.1. Introduction
3.2. Utilities
3.3. Concepts and Techniques
3.4. TOPS Features
4. References
开发者工具
可视化性能分析工具
TopsVisualProfiler 用户使用手册
1. 前言
1.1. 版权声明
1.2. 文档综述
1.3. 专有名词解释
2. 原理说明
2.1. 软件的作用和意义
2.2. 软件实现的原理
3. 安装使用说明
3.1. 软件版本对应关系
3.2. 安装方式说明
3.3. 卸载方式说明
3.4. 版本升降级
4. 用户使用说明
4.1. 快速开始
4.2. 使用工具栏快速Profiling
4.3. 打开Timeline文件
4.4. 拖拽Timeline文件快速打开
4.5. VPD文件的兼容性
4.6. 打开VPD文件所在位置
4.7. 过滤Timeline文件
5. TopsVisualProfiler菜单
5.1. 文件
5.2. 运行
5.3. 窗口
5.4. 帮助
6. TopsVisualProfiler工具栏
7. TopsVisualProfiler视图
7.1. Timeline视图
7.2. 选择视图
7.3. 事件视图
7.4. 分析报告视图
7.5. SystemInfo视图
7.6. Summary视图
7.7. 调用关系视图
7.8. OP Compare视图
7.9. 进程视图
7.10. 控制台视图
8. 首选项配置
8.1. 外观
8.2. 远程连接
8.3. 网络连接
9. FAQ
9.1. 使用信息汇总
10. 引用说明
命令行性能分析工具
TopsProf 用户使用手册
1. 前言
1.1. 版权声明
1.2. 版本记录
1.3. 名词解释
1.4. 概述
1.5. 使用方法
2. 命令行选项
2.1. GCU 采集选项
2.2. CPU 采集选项
2.3. 打印选项
2.4. 输入输出选项
2.5. 控制选项
2.6. 插件选项
2.7. 高级选项
2.8. 选项说明
3. 采集模式
3.1. 统计模式
3.2. 跟踪模式
3.3. Event/metric 统计模式(Experimental T20 only)
4. 采集控制
4.1. Session
4.2. 查询采集项
4.3. 使用字符串控制
4.4. 使用json文件控制
4.5. Event/metric项的控制
4.6. 采集控制
5. 输出
5.1. Export/Import
5.2. 打印应用输出
6. 分布式
6.1. 分布式启动采集
6.2. 合并输出结果
7. 附录
7.1. perf工具说明
7.2. release note
TOPSPTI API参考
1. Attribute
1.1. Prof
1.2. Misc
TOPSTX C/C++ API Reference
1. Attribute
1.1. TOPSTX C API
1.2. TOPSTX C++ API
接口文档
Host Runtime API参考
1. Attribute
1.1. GlobalDefs
1.2. GlobalDefsExt
enum topsDeviceAttribute_t
enum topsComputeMode
enum topsMemoryAdvise
enum topsMemRangeCoherencyMode
enum topsMemRangeAttribute
enum topsMemPoolAttr
enum topsMemLocationType
enum topsMemAccessFlags
enum topsMemAllocationType
enum topsMemAllocationHandleType
enum topsJitOption
enum topsFuncAttribute
enum topsFuncCache_t
enum topsSharedMemConfig
enum topsLaunchAttributeID
enum topsSchedulingPolicy
enum topsClusterSchedulingPolicy
enum topsAccessProperty
enum topsSynchronizationPolicy
enum topsLaunchMemSyncDomain
enum topsExternalMemoryHandleType_enum
enum topsExternalSemaphoreHandleType_enum
enum topsGLDeviceList
typedef struct topsMemLocation topsMemLocation
typedef struct topsMemAccessDesc topsMemAccessDesc
typedef struct topsMemPoolProps topsMemPoolProps
typedef struct topsMemPoolPtrExportData topsMemPoolPtrExportData
typedef struct dim3 dim3
typedef enum topsLaunchAttributeID topsLaunchAttributeID_t
typedef enum topsSchedulingPolicy topsSchedulingPolicy_t
typedef enum topsClusterSchedulingPolicy topsClusterSchedulingPolicy_t
typedef enum topsSynchronizationPolicy topsSynchronizationPolicy_t
typedef enum topsLaunchMemSyncDomain topsLaunchMemSyncDomain_t
typedef struct topsAccessPolicyWindow topsAccessPolicyWindow
typedef struct topsLaunchMemSyncDomainMap topsLaunchMemSyncDomainMap_t
typedef union topsLaunchAttributeValue topsLaunchAttributeValue_t
typedef struct topsLaunchAttribute topsLaunchAttribute_t
typedef struct topsLaunchConfig topsLaunchConfig_t
typedef struct topsLaunchParams_t topsLaunchParams
typedef enum topsExternalMemoryHandleType_enum topsExternalMemoryHandleType
typedef struct topsExternalMemoryHandleDesc_st topsExternalMemoryHandleDesc
typedef struct topsExternalMemoryBufferDesc_st topsExternalMemoryBufferDesc
typedef void *topsExternalMemory_t
typedef enum topsExternalSemaphoreHandleType_enum topsExternalSemaphoreHandleType
typedef struct topsExternalSemaphoreHandleDesc_st topsExternalSemaphoreHandleDesc
typedef void *topsExternalSemaphore_t
typedef struct topsExternalSemaphoreSignalParams_st topsExternalSemaphoreSignalParams
typedef struct topsExternalSemaphoreWaitParams_st topsExternalSemaphoreWaitParams
typedef struct _topsGraphicsResource topsGraphicsResource
typedef topsGraphicsResource *topsGraphicsResource_t
__TOPS_NODISCARD
topsStreamDefault
topsStreamNonBlocking
topsStreamCallbackBlocking
topsStreamNonMerging
topsEventDefault
topsEventBlockingSync
topsEventDisableTiming
topsEventInterprocess
topsEventRecordOnce
topsEventStrongOrder
topsEventDisableQueryAndSync
topsEventReleaseToDevice
topsEventReleaseToSystem
topsHostMallocDefault
topsHostMallocPortable
topsHostMallocMapped
topsHostMallocWriteCombined
topsHostMallocNumaUser
topsHostMallocCoherent
topsHostMallocNonCoherent
topsMemAttachGlobal
topsMemAttachHost
topsMemAttachSingle
topsDeviceMallocDefault
topsDeviceMallocFinegrained
topsMallocSignalMemory
topsMallocTopDown
topsMallocForbidMergeMove
topsMallocPreferHighSpeedMem
topsMallocHostAccessable
topsHostRegisterDefault
topsHostRegisterPortable
topsHostRegisterMapped
topsHostRegisterIoMemory
topsExtHostRegisterCoarseGrained
topsDeviceScheduleAuto
topsDeviceScheduleSpin
topsDeviceScheduleYield
topsDeviceScheduleBlockingSync
topsDeviceScheduleMask
topsDeviceMapHost
topsDeviceLmemResizeToMax
topsArrayDefault
topsArrayLayered
topsArraySurfaceLoadStore
topsArrayCubemap
topsArrayTextureGather
topsOccupancyDefault
topsCooperativeLaunchMultiDeviceNoPreSync
topsCooperativeLaunchMultiDeviceNoPostSync
topsCpuDeviceId
topsInvalidDeviceId
topsExtAnyOrderLaunch
topsStreamWaitValueGte
topsStreamWaitValueEq
topsStreamWaitValueAnd
topsStreamWaitValueNor
topsStreamPerThread
struct itopsStream_t
struct itopsEvent_t
struct itopsExecutable_t
struct itopsResource_t
struct itopsCtx_t
struct itopsTensor_t
union uint3
struct topsLaunchMemSyncDomainMap
union topsLaunchAttributeValue
struct topsLaunchAttribute
struct topsLaunchConfig
struct topsLaunchParams_t
struct topsExternalMemoryHandleDesc_st
struct topsExternalMemoryBufferDesc_st
struct topsExternalSemaphoreHandleDesc_st
struct topsExternalSemaphoreSignalParams_st
struct topsExternalSemaphoreWaitParams_st
enum topsResLocMode
enum topsHbmPolicy
enum topsResBundlMode
enum topsExecutableInfoType
enum topsResourceBundleInfoType
enum topsReduceOpType
enum topsReduceDataType
enum topsExtExecutableSectionHeaderType
typedef struct itopsExecutable_t *topsExecutable_t
typedef struct itopsResource_t *topsResource_t
typedef struct topsResourceBundle topsResourceBundle_t
typedef struct topsResourceRequest topsResourceRequest_t
typedef struct topsResourceReservation topsResourceReservation_t
typedef enum topsExecutableInfoType topsExecutableInfoType_t
typedef enum topsResourceBundleInfoType topsResourceBundleInfoType_t
typedef struct topsKernelDescriptor topsKernelDescriptor_t
typedef struct topsExtLaunchParams topsExtLaunchParams_t
typedef enum topsReduceOpType topsReduceOpType_t
typedef enum topsReduceDataType topsReduceDataType_t
typedef struct topsExtExecutableSectionInfo topsExtExecutableSectionInfo_t
typedef enum topsExtExecutableSectionHeaderType topsExtExecutableSectionHeaderType_t
typedef struct topsShape topsShape_t
MAX_CDMA_ENGINE_NUM_ON_20
TOPS_SHAPE_INFER_MAX_DIMS
struct topsResourceBundle
struct topsResourceRequest
struct topsResourceReservation
struct topsKernelDescriptor
struct topsExtLaunchParams
struct topsExtExecutableSectionInfo
struct topsHighspeedMemConfig_t
struct topsShape
2. API Function
2.1. Driver
2.2. Device
2.3. Error
2.4. Stream
2.5. Event
2.6. Memory
2.7. PeerToPeer
2.8. Module
2.9. Clang
2.10. Runtime
2.11. Extension
TOPS_PUBLIC_API topsError_t topsInit
TOPS_PUBLIC_API topsError_t topsDriverGetVersion
TOPS_PUBLIC_API topsError_t topsRuntimeGetVersion
TOPS_PUBLIC_API topsError_t topsDeviceGet
TOPS_PUBLIC_API topsError_t topsDeviceComputeCapability
TOPS_PUBLIC_API topsError_t topsDeviceGetName
TOPS_PUBLIC_API topsError_t topsDeviceGetPCIBusId
TOPS_PUBLIC_API topsError_t topsDeviceGetByPCIBusId
TOPS_PUBLIC_API topsError_t topsDeviceTotalMem
TOPS_PUBLIC_API topsError_t topsDeviceSynchronize
TOPS_PUBLIC_API topsError_t topsDeviceReset
TOPS_PUBLIC_API topsError_t topsSetDevice
TOPS_PUBLIC_API topsError_t topsGetDevice
TOPS_PUBLIC_API topsError_t topsGetDeviceCount
TOPS_PUBLIC_API topsError_t topsDeviceGetAttribute
TOPS_PUBLIC_API topsError_t topsGetDeviceProperties
TOPS_PUBLIC_API topsError_t topsResourceReservationGetAttribute
TOPS_PUBLIC_API topsError_t topsDeviceGetLimit
TOPS_PUBLIC_API topsError_t topsGetDeviceFlags
TOPS_PUBLIC_API topsError_t topsSetDeviceFlags
TOPS_PUBLIC_API topsError_t topsChooseDevice
TOPS_PUBLIC_API topsError_t topsIpcGetMemHandle
TOPS_PUBLIC_API topsError_t topsIpcOpenMemHandle
TOPS_PUBLIC_API topsError_t topsIpcCloseMemHandle
TOPS_PUBLIC_API topsError_t topsIpcGetEventHandle
TOPS_PUBLIC_API topsError_t topsIpcOpenEventHandle
TOPS_PUBLIC_API topsError_t topsIpcOpenEventHandleExt
TOPS_PUBLIC_API topsError_t topsOpenEventHandle
TOPS_PUBLIC_API topsError_t topsOpenEventHandleExt
TOPS_PUBLIC_API topsError_t topsGetLastError
TOPS_PUBLIC_API topsError_t topsPeekAtLastError
TOPS_PUBLIC_API const char *topsGetErrorName
TOPS_PUBLIC_API const char *topsGetErrorString
typedef void
TOPS_PUBLIC_API topsError_t topsStreamCreate
TOPS_PUBLIC_API topsError_t topsStreamCreateWithFlags
TOPS_PUBLIC_API topsError_t topsStreamDestroy
TOPS_PUBLIC_API topsError_t topsStreamQuery
TOPS_PUBLIC_API topsError_t topsStreamSynchronize
TOPS_PUBLIC_API topsError_t topsStreamWaitEvent
TOPS_PUBLIC_API topsError_t topsStreamAddCallback
TOPS_PUBLIC_API topsError_t topsStreamWriteValue32
TOPS_PUBLIC_API topsError_t topsStreamWaitValue32
TOPS_PUBLIC_API topsError_t topsEventCreateWithFlags
TOPS_PUBLIC_API topsError_t topsEventCreate
TOPS_PUBLIC_API topsError_t topsEventRecord
TOPS_PUBLIC_API topsError_t topsEventDestroy
TOPS_PUBLIC_API topsError_t topsEventSynchronize
TOPS_PUBLIC_API topsError_t topsEventElapsedTime
TOPS_PUBLIC_API topsError_t topsEventQuery
TOPS_PUBLIC_API topsError_t topsPointerGetAttributes
TOPS_PUBLIC_API topsError_t topsPointerGetAttribute
TOPS_PUBLIC_API topsError_t topsDrvPointerGetAttributes
TOPS_PUBLIC_API topsError_t topsMalloc
TOPS_PUBLIC_API topsError_t topsExtCodecMemHandle
TOPS_PUBLIC_API topsError_t topsExtMallocWithFlags
TOPS_PUBLIC_API topsError_t topsHostMalloc
TOPS_PUBLIC_API topsError_t topsHostGetDevicePointer
TOPS_PUBLIC_API topsError_t topsHostGetFlags
TOPS_PUBLIC_API topsError_t topsHostRegister
TOPS_PUBLIC_API topsError_t topsHostUnregister
TOPS_PUBLIC_API topsError_t topsFree
TOPS_PUBLIC_API topsError_t topsHostFree
TOPS_PUBLIC_API topsError_t topsMemcpy
TOPS_PUBLIC_API topsError_t topsMemcpyWithStream
TOPS_PUBLIC_API topsError_t topsMemcpyHtoD
TOPS_PUBLIC_API topsError_t topsMemcpyDtoH
TOPS_PUBLIC_API topsError_t topsMemcpyDtoD
TOPS_PUBLIC_API topsError_t topsMemcpyHtoDAsync
TOPS_PUBLIC_API topsError_t topsMemcpyDtoHAsync
TOPS_PUBLIC_API topsError_t topsMemcpyDtoDAsync
TOPS_PUBLIC_API topsError_t topsModuleGetGlobal
TOPS_PUBLIC_API topsError_t topsGetSymbolAddress
TOPS_PUBLIC_API topsError_t topsGetSymbolSize
TOPS_PUBLIC_API topsError_t topsMemset
TOPS_PUBLIC_API topsError_t topsMemsetD8
TOPS_PUBLIC_API topsError_t topsMemsetD16
TOPS_PUBLIC_API topsError_t topsMemsetD32
TOPS_PUBLIC_API topsError_t topsMemGetInfo
TOPS_PUBLIC_API topsError_t topsMemPtrGetInfo
TOPS_PUBLIC_API topsError_t topsMemGetAddressRange
TOPS_PUBLIC_API topsError_t topsDeviceCanAccessPeer
TOPS_PUBLIC_API topsError_t topsDeviceEnablePeerAccess
TOPS_PUBLIC_API topsError_t topsDeviceEnablePeerAccessRegion
TOPS_PUBLIC_API topsError_t topsDeviceDisablePeerAccessRegion
TOPS_PUBLIC_API topsError_t topsMemcpyPeer
TOPS_PUBLIC_API topsError_t topsMemcpyPeerAsync
TOPS_PUBLIC_API topsError_t topsMemcpyPeerExt
TOPS_PUBLIC_API topsError_t topsMemcpyPeerExtAsync
TOPS_PUBLIC_API topsError_t topsModuleLoad
TOPS_PUBLIC_API topsError_t topsModuleUnload
TOPS_PUBLIC_API topsError_t topsModuleGetFunction
TOPS_PUBLIC_API topsError_t topsFuncGetAttributes
TOPS_PUBLIC_API topsError_t topsFuncGetAttribute
TOPS_PUBLIC_API topsError_t topsModuleLoadData
TOPS_PUBLIC_API topsError_t topsModuleLoadDataEx
TOPS_PUBLIC_API topsError_t topsModuleLaunchKernel
TOPS_PUBLIC_API topsError_t topsLaunchCooperativeKernel
TOPS_PUBLIC_API topsError_t topsSetupArgument
TOPS_PUBLIC_API topsError_t topsLaunchByPtr
TOPS_PUBLIC_API topsError_t __topsPopCallConfiguration
TOPS_PUBLIC_API topsError_t topsLaunchKernelExC
enum topsrtcResult
typedef struct _topsrtcProgram *topsrtcProgram
TOPS_PUBLIC_API const char *topsrtcGetErrorString
TOPS_PUBLIC_API topsrtcResult topsrtcVersion
TOPS_PUBLIC_API topsrtcResult topsrtcAddNameExpression
TOPS_PUBLIC_API topsrtcResult topsrtcCompileProgram
TOPS_PUBLIC_API topsrtcResult topsrtcCreateProgram
TOPS_PUBLIC_API topsrtcResult topsrtcDestroyProgram
TOPS_PUBLIC_API topsrtcResult topsrtcGetLoweredName
TOPS_PUBLIC_API topsrtcResult topsrtcGetProgramLog
TOPS_PUBLIC_API topsrtcResult topsrtcGetProgramLogSize
TOPS_PUBLIC_API topsrtcResult topsrtcGetCode
TOPS_PUBLIC_API topsrtcResult topsrtcGetCodeSize
TOPS_PUBLIC_API topsError_t topsMemorySetDims
TOPS_PUBLIC_API topsError_t topsMemoryGetDims
TOPS_PUBLIC_API topsError_t topsCreateExecutable
TOPS_PUBLIC_API topsError_t topsCreateExecutableFromFile
TOPS_PUBLIC_API topsError_t topsDestroyExecutable
TOPS_PUBLIC_API topsError_t topsCreateResource
TOPS_PUBLIC_API topsError_t topsCreateResourceForExecutable
TOPS_PUBLIC_API topsError_t topsDestroyResource
TOPS_PUBLIC_API topsError_t topsResourceBundleGetAttribute
TOPS_PUBLIC_API topsError_t topsMallocForResource
TOPS_PUBLIC_API topsError_t topsLaunchExecutableV2
TOPS_PUBLIC_API topsError_t topsLaunchExecutableV3
TOPS_PUBLIC_API topsError_t topsLaunchExecutableV4
TOPS_PUBLIC_API topsError_t topsLaunchExecutable
TOPS_PUBLIC_API topsError_t topsLaunchExecutableWithConstData
TOPS_PUBLIC_API topsError_t topsLaunchExecutableWithConstDataV2
TOPS_PUBLIC_API topsError_t topsLaunchExecutableWithConstDataV3
TOPS_PUBLIC_API topsError_t topsLaunchExecutableWithConstDataV4
TOPS_PUBLIC_API topsError_t topsExecutableGetConstManagedData
TOPS_PUBLIC_API topsError_t topsExecutableGetConstManagedDataV2
TOPS_PUBLIC_API topsError_t topsExecutableUpdateConstantKey
TOPS_PUBLIC_API topsError_t topsExecutableUpdateRuntimeResource
TOPS_PUBLIC_API topsError_t topsExecutableLoadConstData
TOPS_PUBLIC_API topsError_t topsExecutableLoadConstDataV2
TOPS_PUBLIC_API topsError_t topsExecutableGetRuntimeOutputShape
TOPS_PUBLIC_API topsError_t topsExecutableGetSubFuncInfo
TOPS_PUBLIC_API topsError_t topsExecutableGetRefitFlag
TOPS_PUBLIC_API topsError_t topsExecutableCallSubFunc
TOPS_PUBLIC_API topsError_t topsDeviceSetResource
TOPS_PUBLIC_API topsError_t topsConstBufferGet
TOPS_PUBLIC_API topsError_t topsConstBufferPut
TOPS_PUBLIC_API topsError_t topsExecutableQueryInfo
TOPS_PUBLIC_API topsError_t topsExecutableQueryInfoV2
TOPS_PUBLIC_API topsError_t topsExecutableQueryInfoV3
TOPS_PUBLIC_API topsError_t topsExecutableQueryInputName
TOPS_PUBLIC_API topsError_t topsExecutableQueryOutputName
TOPS_PUBLIC_API topsError_t topsExecutableSaveToFile
TOPS_PUBLIC_API topsError_t topsExtMallocWithBank
TOPS_PUBLIC_API topsError_t topsExtMallocWithBankV2
TOPS_PUBLIC_API topsError_t topsExtMallocWithAffinity
TOPS_PUBLIC_API topsError_t topsExtLaunchCooperativeKernelMultiCluster
TOPS_PUBLIC_API topsError_t topsExtSetProfileMeta
TOPS_PUBLIC_API topsError_t topsExtSetProfileMetas
TOPS_PUBLIC_API topsError_t topsScatterMemoryGetInfo
TOPS_PUBLIC_API topsError_t topsScatterMemoryGetSubNum
TOPS_PUBLIC_API topsError_t topsMallocScatter
TOPS_PUBLIC_API topsError_t topsScatterPopulateSub
TOPS_PUBLIC_API topsError_t topsScatterInplace
TOPS_PUBLIC_API topsError_t topsScatterGetSubMem
TOPS_PUBLIC_API topsError_t topsMemoryReduceAsync
TOPS_PUBLIC_API topsError_t topsMemCachePrefetch
TOPS_PUBLIC_API topsError_t topsMemCacheInvalidate
TOPS_PUBLIC_API topsError_t topsMemCacheInvalidateAll
TOPS_PUBLIC_API topsError_t topsMemCacheFlushAll
TOPS_PUBLIC_API topsError_t topsExtGetMcAvailableMemSize
TOPS_PUBLIC_API topsError_t topsExecutableGetSectionCount
TOPS_PUBLIC_API topsError_t topsExecutableGetStackSize
TOPS_PUBLIC_API topsError_t topsExecutableGetSectionInfo
TOPS_PUBLIC_API topsError_t topsGetMemUsageInfo
TOPS_PUBLIC_API topsError_t topsGetAffinityBankList
TOPS_PUBLIC_API topsError_t topsGetAffinityBankListV2
TOPS_PUBLIC_API topsError_t topsMemGetInfoExt
TOPS_PUBLIC_API topsError_t topsKernelSignalMaxNumGet
TOPS_PUBLIC_API topsError_t topsKernelSignalAvailableNumGet
TOPS_PUBLIC_API topsError_t topsKernelSignalAlloc
TOPS_PUBLIC_API topsError_t topsKernelSignalFree
TOPS_PUBLIC_API topsError_t topsKernelSignalRead
TOPS_PUBLIC_API topsError_t topsKernelSignalWrite
TOPS_PUBLIC_API topsError_t topsRoceCreateQueue
TOPS_PUBLIC_API topsError_t topsRoceQueryQueue
TOPS_PUBLIC_API topsError_t topsRoceBindQueuePair
TOPS_PUBLIC_API topsError_t topsRoceDeleteQueue
TOPS_PUBLIC_API topsError_t topsRoceWriteQueue
TOPS_PUBLIC_API topsError_t topsGetGlobalRandomSeed
TOPS_PUBLIC_API topsError_t topsSetGlobalRandomSeed
TOPS_PUBLIC_API topsError_t topsSetDeviceAndResourceReservation
Library Kernel API参考
1. Attribute
1.1. BuiltinType
tops::bfloat
tops::half
1.2. VectorTypes
vchar
vuchar
vshort
vushort
vint
vuint
vhalf
vbfloat
vfloat
vfloatx2
2. API Function
2.1. Builtins
2.2. Event
2.3. DTE
2.4. Math
Scalar
Vector
2.5. Synchronization
__device__ __forceinline__ tops_implicit_params_t *__tops_get_implicit_params_ptr
__device__ __forceinline__ tops_amos_sip_interface_t *__tops_get_amos_sip_params_ptr
__device__ __forceinline__ void *__tops_private_heap_pointer
__device__ __forceinline__ void *__tops_block_shared_memory_pointer
__device__ __forceinline__ void tops_halt
__constant__
__private__
__shared__
__local__
__device__
__global__
__cooperative__
)
__host__
__sp__
__shared_dte__
__private_dte__
__scalar_only__
__mmu_pointer__
__noinline__
__forceinline__
__valigned__
__block_tile__
__KRT_ARCH__
AS5_TASK_NODE_T_PTR
AS5_DTE_CTX_T_PTR
threadIdx
blockIdx
blockDim
gridDim
struct __tops_builtin_threadDim_t
__device__ __forceinline__ void wait
__device__ __forceinline__ void wait
struct tops::event
enum AddrSpace
enum tops_directions
inline __device__ __forceinline__ dte_scope
inline __device__ __forceinline__ ~dte_scope
__device__ __forceinline__ void memcpy
__device__ __forceinline__ void memcpy
__device__ __forceinline__ void memcpy
__device__ __forceinline__ tops::event memcpy_async
__device__ __forceinline__ tops::event memcpy_async
__device__ __forceinline__ tops::event memcpy_async
template<typename T = int> __device__ __forceinline__ void slice
template<typename T = int> __device__ __forceinline__ void slice
template<typename T = int> __device__ __forceinline__ tops::event slice_async
template<typename T = int> __device__ __forceinline__ tops::event slice_async
__device__ __forceinline__ void deslice
__device__ __forceinline__ void deslice
__device__ __forceinline__ tops::event deslice_async
__device__ __forceinline__ tops::event deslice_async
__device__ __forceinline__ void transpose
__device__ __forceinline__ void transpose
__device__ __forceinline__ tops::event transpose_async
__device__ __forceinline__ tops::event transpose_async
template<typename T> __device__ __forceinline__ void pad
template<typename T> __device__ __forceinline__ tops::event pad_async
template<typename T> __device__ __forceinline__ void memset
template<typename T> __device__ __forceinline__ tops::event memset_async
__device__ __forceinline__ void mirror_lr
__device__ __forceinline__ tops::event mirror_lr_async
__device__ __forceinline__ void mirror_tb
__device__ __forceinline__ tops::event mirror_tb_async
__device__ __forceinline__ void broadcast
__device__ __forceinline__ tops::event broadcast_async
__device__ __forceinline__ void slice_transpose
__device__ __forceinline__ void slice_transpose
__device__ __forceinline__ tops::event slice_transpose_async
__device__ __forceinline__ tops::event slice_transpose_async
__device__ __forceinline__ void transpose_deslice
__device__ __forceinline__ void transpose_deslice
__device__ __forceinline__ tops::event transpose_deslice_async
__device__ __forceinline__ tops::event transpose_deslice_async
template<typename T> __device__ __forceinline__ void slice_pad
template<typename T> __device__ __forceinline__ tops::event slice_pad_async
__device__ __forceinline__ void slice_deslice
__device__ __forceinline__ tops::event slice_deslice_async
__device__ __forceinline__ void slice_broadcast
__device__ __forceinline__ tops::event slice_broadcast_async
__device__ __forceinline__ void slice_expand
__device__ __forceinline__ tops::event slice_expand_async
__device__ __forceinline__ void shrink_deslice
__device__ __forceinline__ tops::event shrink_deslice_async
template<typename T> __device__ __forceinline__ void memset_deslice
template<typename T> __device__ __forceinline__ tops::event memset_deslice_async
template<typename T> __device__ __forceinline__ void mirror_lr_pad
template<typename T> __device__ __forceinline__ tops::event mirror_lr_pad_async
template<typename T> __device__ __forceinline__ void mirror_tb_pad
template<typename T> __device__ __forceinline__ tops::event mirror_tb_pad_async
__device__ __forceinline__ void mirror_lr_deslice
__device__ __forceinline__ tops::event mirror_lr_deslice_async
__device__ __forceinline__ void mirror_tb_deslice
__device__ __forceinline__ tops::event mirror_tb_deslice_async
template<typename T> __device__ __forceinline__ void sub_sample
template<typename T> __device__ __forceinline__ tops::event sub_sample_async
__device__ __forceinline__ void wait
__TOPS_ADJUST_ADDR
__TOPS_SHARED_CDTE_COUNT
__TOPS_BLOCK_SHARED_EDTE_COUNT
__TOPS_LOCAL_EDTE_COUNT
__TOPS_PRIVATE_EDTE_COUNT
__TOPS_LOCALSHARED_SDTE_COUNT
__TOPS_EOF_BLOCK_SHARED_CDTE
__TOPS_EOF_SHARED_CDTE
__TOPS_EOF_PRIVATE_CDTE
__TOPS_EOF_LOCALSHARED_SDTE
__TOPS_EOF_BLOCK_SHARED_EDTE
__TOPS_EOF_SHARED_EDTE
__TOPS_EOF_PRIVATE_EDTE
__TOPS_GET_CDTE_VC_START
struct tops::mdspan_base
struct tops::mdspan : public tops::mdspan_base
struct tops_dte_ctx_s
struct tops::dte_scope
__device__ __forceinline__ void __syncsubthreads
__device__ __forceinline__ void __syncthreads
__device__ __forceinline__ void __syncblocks
合规声明
文档法律声明
版本信息
版本须知
TopsPlatform 1.0.2
新增
变更
修复
已知问题
TopsPlatform 0.9.0
新增
变更
修复
已知问题
TopsPlatform 0.8.1
新增
变更
修复
已知问题
TopsPlatform
»
TopsCC 使用样例
TopsCC 使用样例
¶
TopsCC 使用样例
TopsCC 使用样例