SME demo用例运行失败，报错Illegal instruction

**【缺陷描述】：请补充详细的缺陷问题现象描述**

SME demo用例运行失败，Illegal instruction（核心已转储）

**一、缺陷信息**

**【缺陷所属的os版本】（如openEuler-22.03-LTS，参考命令"cat /etc/os-release"结果）**

NAME="openEuler"
VERSION="22.03 (LTS-SP4)"
ID="openEuler"
VERSION_ID="22.03"
PRETTY_NAME="openEuler 22.03 (LTS-SP4)"
ANSI_COLOR="0;31"

**【内核版本】（如kernel-5.10.0-60.138.0.165，参考命令"uname -r"结果）**

5.10.0-216.0.0.115.oe2203sp4.aarch64

**【缺陷所属软件及版本号】（如kernel-5.10.0-60.138.0.165，参考命令"rpm -q 包名"结果）**

https://gitee.com/openeuler/gcc/tree/master/  最新源码

**【环境信息】**
硬件信息

支持SME指令集机型

软件信息

https://gitee.com/openeuler/gcc/tree/master/  最新源码构建的编译器

**【问题复现步骤】：请描述具体的操作步骤**

用例如下，
```
#include <stdlib.h>
#include <stdio.h>
#include <arm_sme.h>
#include <arm_sve.h>

#define PRECISION_TYPE double

#define M 8
#define N 8

// __arm_new("za")
void example(PRECISION_TYPE *data_c, PRECISION_TYPE *data_d) __arm_streaming __arm_inout("za");

// __arm_new("za")
void example0(PRECISION_TYPE *data_e) __arm_streaming __arm_in("za");

// #define SME_ON()              \
//     __asm__ volatile(         \
//         "msr SVCRSMZA, # 1\n" \
//         "isb\n"               \
//         :                     \
//         :                     \
//         : "memory");
// #define SME_OFF()             \
//     __asm__ volatile(         \
//         "msr SVCRSMZA, # 0\n" \
//         "isb\n"               \
//         :                     \
//         :                     \
//         : "memory");

__arm_new("za")
int main(int argc, char **argv)
{
    PRECISION_TYPE *data_c = (PRECISION_TYPE*)malloc(sizeof(PRECISION_TYPE) * M * N);
    PRECISION_TYPE *data_d = (PRECISION_TYPE*)malloc(sizeof(PRECISION_TYPE) * M * N);
    PRECISION_TYPE *data_e = (PRECISION_TYPE*)malloc(sizeof(PRECISION_TYPE) * M * N);
    for (int i = 0; i < N * M; i++) {
        data_c[i] = i;
        data_d[i] = 0;
        data_e[i] = 0;
    }

for (int i = 0; i < N * M; i++) {
        printf("before: %d --- data_c = %lf --- data_d = %lf\n", i, data_c[i], data_d[i]);
    }

// SME_ON();

example(data_c, data_d);

example0(data_e);

// SME_OFF();

for (int i = 0; i < N * M; i++) {
        printf("after: %d --- data_c = %lf --- data_d = %lf\n", i, data_c[i], data_d[i]);
    }

for (int i = 0; i < N * M; i++) {
        printf("after: %d --- data_e = %lf\n", i, data_e[i]);
    }

free(data_c);
    free(data_d);
    free(data_e);

return 0;
}

// __arm_new("za")
void example(PRECISION_TYPE *data_c, PRECISION_TYPE *data_d) __arm_streaming __arm_inout("za")
{
    // __asm__ volatile("smstart sm");
    // __asm__ volatile("smstart za");
    svbool_t pn = svwhilelt_b64(0, 8);

svfloat64_t vc;
    PRECISION_TYPE *matc = data_c;
    for (int t = 0; t < M; t++) {
        vc = svld1_f64(pn, matc);
        svwrite_hor_za64_m(0, t, pn, vc);
        matc += N;
    }

PRECISION_TYPE *matd = data_d;
    for (int t = 0; t < M; t++) {
        svst1_hor_za64(0, t, pn, matd);
        matd += N;
    }
    // __asm__ volatile("smstop sm");
    // __asm__ volatile("smstop za");
}

// __arm_new("za")
void example0(PRECISION_TYPE *data_e) __arm_streaming __arm_in("za")
{
    // __asm__ volatile("smstart sm");
    // __asm__ volatile("smstart za");
    svbool_t pn = svwhilelt_b64(0, 8);

PRECISION_TYPE *mate = data_e;
    for (int t = 0; t < M; t++) {
        svst1_hor_za64(0, t, pn, mate);
        mate += N;
    }
    // __asm__ volatile("smstop sm");
    // __asm__ volatile("smstop za");
}
```

编译方式，
```
gcc test.c  -O2    -march=armv9-a+sve+sve2+sme -static
```

**【实际结果】**

正常运行结束

**【期望结果】**

Illegal instruction（核心已转储）

**【其他相关附件信息】**

**【缺陷详情及分析指导参考链接】**

**二、缺陷分析结构反馈**
影响性分析说明：

缺陷严重等级:(Critical/High/Moderate/Low)

缺陷根因说明:

受影响版本排查(受影响/不受影响):
openEuler-20.03-LTS-SP4
openEuler-22.03-LTS-SP3
openEuler-22.03-LTS-SP4
openEuler-24.03-LTS
openEuler-24.03-LTS-SP1

修复是否涉及abi变化(是/否):
openEuler-20.03-LTS-SP4
openEuler-22.03-LTS-SP3
openEuler-22.03-LTS-SP4
openEuler-24.03-LTS
openEuler-24.03-LTS-SP1

src-openEuler/gcc
关闭

内容风险标识

评论 (3)

src-openEuler/gcc关闭 .gitee-modal { width: 500px !important; }

内容风险标识