void test_vld1Q_laneu32 (void) { uint32x4_t out_uint32x4_t; uint32x4_t arg1_uint32x4_t; out_uint32x4_t = vld1q_lane_u32 (0, arg1_uint32x4_t, 1); }
/* Expands a palettized row into RGBA. */ int png_do_expand_palette_neon_rgba(png_structrp png_ptr, png_row_infop row_info, png_const_bytep row, png_bytepp ssp, png_bytepp ddp) { png_uint_32 row_width = row_info->width; const png_uint_32 *riffled_palette = (const png_uint_32 *)png_ptr->riffled_palette; const png_int_32 pixels_per_chunk = 4; int i; if (row_width < pixels_per_chunk) return 0; /* This function originally gets the last byte of the output row. * The NEON part writes forward from a given position, so we have * to seek this back by 4 pixels x 4 bytes. */ *ddp = *ddp - ((pixels_per_chunk * sizeof(png_uint_32)) - 1); for (i = 0; i < row_width; i += pixels_per_chunk) { uint32x4_t cur; png_bytep sp = *ssp - i, dp = *ddp - (i << 2); cur = vld1q_dup_u32 (riffled_palette + *(sp - 3)); cur = vld1q_lane_u32(riffled_palette + *(sp - 2), cur, 1); cur = vld1q_lane_u32(riffled_palette + *(sp - 1), cur, 2); cur = vld1q_lane_u32(riffled_palette + *(sp - 0), cur, 3); vst1q_u32((void *)dp, cur); } if (i != row_width) { /* Remove the amount that wasn't processed. */ i -= pixels_per_chunk; } /* Decrement output pointers. */ *ssp = *ssp - i; *ddp = *ddp - (i << 2); return i; }