Viewing file:  mve_load_memory_modes.c (4.67 KB) -rw-r--r--
Select action/file-type:
 (+) |  (+) |  (+) | Code (+) | Session (+) |  (+) | SDB (+) |  (+) |  (+) |  (+) |  (+) |  (+) |
/* { dg-require-effective-target arm_v8_1m_mve_fp_ok } */
/* { dg-add-options arm_v8_1m_mve_fp } */
/* { dg-additional-options "-O2" } */
/* { dg-final { check-function-bodies "**" "" } } */
#include "arm_mve.h"
/*
**off_load8_0:
** ...
** vldrb.8 q0, \[r0, #16\]
** ...
*/
int8x16_t off_load8_0 (int8_t * a)
{
return vld1q_s8 (a + 16);
}
/*
**off_load8_1:
** ...
** vldrb.u16 q0, \[r0, #1\]
** ...
*/
uint16x8_t off_load8_1 (uint8_t * a)
{
return vldrbq_u16 (a + 1);
}
/*
**off_load8_2:
** ...
** vldrb.s32 q0, \[r0, #127\]
** ...
*/
int32x4_t off_load8_2 (int8_t * a)
{
return vldrbq_s32 (a + 127);
}
/*
**off_load8_3:
** ...
** vldrb.8 q0, \[r0, #-127\]
** ...
*/
uint8x16_t off_load8_3 (uint8_t * a)
{
return vldrbq_u8 (a - 127);
}
/*
**not_off_load8_0:
** ...
** vldrb.8 q0, \[r[0-9]+\]
** ...
*/
int8x16_t not_off_load8_0 (int8_t * a)
{
return vld1q_s8 (a + 128);
}
/*
**off_loadfp16_0:
** ...
** vldrh.16 q0, \[r0, #-244\]
** ...
*/
float16x8_t off_loadfp16_0 (float16_t *a)
{
return vld1q_f16 (a - 122);
}
/*
**off_load16_0:
** ...
** vldrh.16 q0, \[r0, #-2\]
** ...
*/
uint16x8_t off_load16_0 (uint16_t * a)
{
return vld1q_u16 (a - 1);
}
/*
**off_load16_1:
** ...
** vldrh.u32 q0, \[r0, #254\]
** ...
*/
uint32x4_t off_load16_1 (uint16_t * a)
{
return vldrhq_u32 (a + 127);
}
/*
**not_off_load16_0:
** ...
** vldrh.16 q0, \[r[0-9]+\]
** ...
*/
int16x8_t not_off_load16_0 (int8_t * a)
{
return vld1q_s16 ((int16_t *)(a + 1));
}
/*
**not_off_load16_1:
** ...
** vldrh.u32 q0, \[r[0-9]+\]
** ...
*/
uint32x4_t not_off_load16_1 (uint16_t * a)
{
return vldrhq_u32 ((a - 128));
}
/*
**off_loadfp32_0:
** ...
** vldrw.32 q0, \[r0, #24\]
** ...
*/
float32x4_t off_loadfp32_0 (float32_t *a)
{
return vld1q_f32 (a + 6);
}
/*
**off_load32_0:
** ...
** vldrw.32 q0, \[r0, #4\]
** ...
*/
uint32x4_t off_load32_0 (uint32_t * a)
{
return vld1q_u32 (a + 1);
}
/*
**off_load32_1:
** ...
** vldrw.32 q0, \[r0, #-508\]
** ...
*/
int32x4_t off_load32_1 (int32_t * a)
{
return vldrwq_s32 (a - 127);
}
/*
**pre_load8_0:
** ...
** vldrb.8 q[0-9]+, \[r0, #16\]!
** ...
*/
int8_t* pre_load8_0 (int8_t * a, int8x16_t *v)
{
a += 16;
*v = vld1q_s8 (a);
return a;
}
/*
**pre_load8_1:
** ...
** vldrb.u16 q[0-9]+, \[r0, #4\]!
** ...
*/
uint8_t* pre_load8_1 (uint8_t * a, uint16x8_t *v)
{
a += 4;
*v = vldrbq_u16 (a);
return a;
}
/*
**pre_loadfp16_0:
** ...
** vldrh.16 q[0-9]+, \[r0, #128\]!
** ...
*/
float16_t* pre_loadfp16_0 (float16_t *a, float16x8_t *v)
{
a += 64;
*v = vld1q_f16 (a);
return a;
}
/*
**pre_load16_0:
** ...
** vldrh.16 q[0-9]+, \[r0, #-254\]!
** ...
*/
int16_t* pre_load16_0 (int16_t * a, int16x8_t *v)
{
a -= 127;
*v = vldrhq_s16 (a);
return a;
}
/*
**pre_load16_1:
** ...
** vldrh.s32 q[0-9]+, \[r0, #52\]!
** ...
*/
int16_t* pre_load16_1 (int16_t * a, int32x4_t *v)
{
a += 26;
*v = vldrhq_s32 (a);
return a;
}
/*
**pre_loadfp32_0:
** ...
** vldrw.32 q[0-9]+, \[r0, #-72\]!
** ...
*/
float32_t* pre_loadfp32_0 (float32_t *a, float32x4_t *v)
{
a -= 18;
*v = vld1q_f32 (a);
return a;
}
/*
**pre_load32_0:
** ...
** vldrw.32 q[0-9]+, \[r0, #-4\]!
** ...
*/
uint32_t* pre_load32_0 (uint32_t * a, uint32x4_t *v)
{
a -= 1;
*v = vld1q_u32 (a);
return a;
}
/*
**post_load8_0:
** ...
** vldrb.8 q[0-9]+, \[r0\], #26
** ...
*/
uint8_t* post_load8_0 (uint8_t * a, uint8x16_t *v)
{
*v = vld1q_u8 (a);
a += 26;
return a;
}
/*
**post_load8_1:
** ...
** vldrb.s16 q[0-9]+, \[r0\], #-1
** ...
*/
int8_t* post_load8_1 (int8_t * a, int16x8_t *v)
{
*v = vldrbq_s16 (a);
a--;
return a;
}
/*
**post_load8_2:
** ...
** vldrb.8 q[0-9]+, \[r0\], #26
** ...
*/
uint8_t* post_load8_2 (uint8_t * a, uint8x16_t *v)
{
*v = vld1q_u8 (a);
a += 26;
return a;
}
/*
**post_load8_3:
** ...
** vldrb.s16 q[0-9]+, \[r0\], #-1
** ...
*/
int8_t* post_load8_3 (int8_t * a, int16x8_t *v)
{
*v = vldrbq_s16 (a);
a--;
return a;
}
/*
**post_loadfp16_0:
** ...
** vldrh.16 q[0-9]+, \[r0\], #-24
** ...
*/
float16_t* post_loadfp16_0 (float16_t *a, float16x8_t *v)
{
*v = vld1q_f16 (a);
a -= 12;
return a;
}
/*
**post_load16_0:
** ...
** vldrh.16 q[0-9]+, \[r0\], #-126
** ...
*/
uint16_t* post_load16_0 (uint16_t * a, uint16x8_t *v)
{
*v = vldrhq_u16 (a);
a -= 63;
return a;
}
/*
**post_load16_1:
** ...
** vldrh.u32 q[0-9]+, \[r0\], #16
** ...
*/
uint16_t* post_load16_1 (uint16_t * a, uint32x4_t *v)
{
*v = vldrhq_u32 (a);
a += 8;
return a;
}
/*
**post_loadfp32_0:
** ...
** vldrw.32 q[0-9]+, \[r0\], #4
** ...
*/
float32_t* post_loadfp32_0 (float32_t *a, float32x4_t *v)
{
*v = vld1q_f32 (a);
a++;
return a;
}
/*
**post_load32_0:
** ...
** vldrw.32 q[0-9]+, \[r0\], #-16
** ...
*/
int32_t* post_load32_0 (int32_t * a, int32x4_t *v)
{
*v = vld1q_s32 (a);
a -= 4;
return a;
}
|
