Logo
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
  • »
  • Search

Copyright © 2024 上海燧原科技股份有限公司 | 备案/许可证编号：沪ICP备18023946号-1沪公网安备 31011502008689号.

Built with Sphinx using a theme provided by Read the Docs.