cann/asc-devkit bfloat16除法函数

发布时间:2026/7/17 13:09:35
cann/asc-devkit bfloat16除法函数 __hdiv【免费下载链接】asc-devkit本项目是CANN 推出的昇腾AI处理器专用的算子程序开发语言原生支持C和C标准规范主要由类库和语言扩展层构成提供多层级API满足多维场景算子开发诉求。项目地址: https://gitcode.com/cann/asc-devkit产品支持情况Ascend 950PR/Ascend 950DT支持Atlas A3 训练系列产品/Atlas A3 推理系列产品不支持Atlas A2 训练系列产品/Atlas A2 推理系列产品不支持Atlas 200I/500 A2 推理产品不支持Atlas 推理系列产品AI Core不支持Atlas 推理系列产品Vector Core不支持Atlas 训练系列产品不支持功能说明计算两个bfloat16类型数据相除的结果并遵循CAST_RINT模式对结果进行舍入。函数原型bfloat16_t __hdiv(const bfloat16_t x, const bfloat16_t y)参数说明表1参数说明参数名输入/输出描述x输入源操作数。y输入源操作数。返回值说明输入数据相除的结果。本接口受全局饱和模式影响特殊值如下x值y值非饱和模式返回值饱和模式返回值±0±0nan0±inf±infnan0有限值±inf符号由x和y的符号异或决定值为0符号由x和y的符号异或决定值为0inf正有限值infASCRT_MAX_NORMAL_BF16inf负有限值-inf-ASCRT_MAX_NORMAL_BF16-inf正有限值-inf-ASCRT_MAX_NORMAL_BF16-inf负有限值infASCRT_MAX_NORMAL_BF1600infASCRT_MAX_NORMAL_BF1600-inf-ASCRT_MAX_NORMAL_BF160-0-inf-ASCRT_MAX_NORMAL_BF160-0infASCRT_MAX_NORMAL_BF16±0非0符号由x和y的符号异或决定值为0符号由x和y的符号异或决定值为0xy任意一个为nannan0约束说明针对Ascend 950PR/Ascend 950DT本接口不支持Subnormal场景处于Subnormal范围内的输入和输出值都会被刷新为保留符号的0。需要包含的头文件使用该接口需要包含simt_api/asc_bf16.h头文件。#include simt_api/asc_bf16.h调用示例SIMT编程场景__global__ __launch_bounds__(1024) void KernelHdiv(bfloat16_t* dst, bfloat16_t* x, bfloat16_t* y) { int idx threadIdx.x blockIdx.x * blockDim.x; dst[idx] __hdiv(x[idx], y[idx]); }SIMD与SIMT混合编程场景__simt_vf__ __launch_bounds__(1024) inline void KernelHdiv(__gm__ bfloat16_t* dst, __gm__ bfloat16_t* x, __gm__ bfloat16_t* y) { int idx threadIdx.x blockIdx.x * blockDim.x; dst[idx] __hdiv(x[idx], y[idx]); }【免费下载链接】asc-devkit本项目是CANN 推出的昇腾AI处理器专用的算子程序开发语言原生支持C和C标准规范主要由类库和语言扩展层构成提供多层级API满足多维场景算子开发诉求。项目地址: https://gitcode.com/cann/asc-devkit创作声明:本文部分内容由AI辅助生成(AIGC),仅供参考