Re: [PATCH] arm64: kexec: add support for kexec with spin-table
by kernel test robot
Hi Henry,
Thank you for the patch! Yet something to improve:
[auto build test ERROR on arm64/for-next/core]
[also build test ERROR on v5.14-rc1 next-20210714]
[If your patch is applied to the wrong git tree, kindly drop us a note.
And when submitting patch, we suggest to use '--base' as documented in
https://git-scm.com/docs/git-format-patch]
url: https://github.com/0day-ci/linux/commits/Henry-Willard/arm64-kexec-add-su...
base: https://git.kernel.org/pub/scm/linux/kernel/git/arm64/linux.git for-next/core
config: arm64-randconfig-r025-20210714 (attached as .config)
compiler: clang version 13.0.0 (https://github.com/llvm/llvm-project 8d69635ed9ecf36fd0ca85906bfde17949671cbe)
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
# install arm64 cross compiling tool for clang build
# apt-get install binutils-aarch64-linux-gnu
# https://github.com/0day-ci/linux/commit/3dd4112e1b67732182a5e12891867db4e...
git remote add linux-review https://github.com/0day-ci/linux
git fetch --no-tags linux-review Henry-Willard/arm64-kexec-add-support-for-kexec-with-spin-table/20210715-014204
git checkout 3dd4112e1b67732182a5e12891867db4e139980c
# save the attached .config to linux build tree
mkdir build_dir
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=clang make.cross O=build_dir ARCH=arm64 SHELL=/bin/bash arch/arm64/kernel/
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All errors (new ones prefixed by >>):
>> arch/arm64/kernel/smp_spin_table.c:235:3: error: field designator 'cpu_die' does not refer to any field in type 'const struct cpu_operations'
.cpu_die = smp_spin_table_cpu_die,
^
>> arch/arm64/kernel/smp_spin_table.c:236:3: error: field designator 'cpu_kill' does not refer to any field in type 'const struct cpu_operations'
.cpu_kill = smp_spin_table_cpu_kill,
^
>> arch/arm64/kernel/smp_spin_table.c:237:3: error: field designator 'cpu_disable' does not refer to any field in type 'const struct cpu_operations'
.cpu_disable = smp_spin_table_cpu_disable,
^
3 errors generated.
vim +235 arch/arm64/kernel/smp_spin_table.c
229
230 const struct cpu_operations smp_spin_table_ops = {
231 .name = "spin-table",
232 .cpu_init = smp_spin_table_cpu_init,
233 .cpu_prepare = smp_spin_table_cpu_prepare,
234 .cpu_boot = smp_spin_table_cpu_boot,
> 235 .cpu_die = smp_spin_table_cpu_die,
> 236 .cpu_kill = smp_spin_table_cpu_kill,
> 237 .cpu_disable = smp_spin_table_cpu_disable,
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
[frank-w-bpi-r2-4.14:5.14-hdmilarb 8/45] drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:191:6: error: no previous prototype for function 'mtk_wcn_consys_power_on'
by kernel test robot
tree: https://github.com/frank-w/BPI-R2-4.14 5.14-hdmilarb
head: a11fbee1b23c2d5f7c177ced2043eb54c53a5d50
commit: daf840cab15926e075953cf836e903114868c074 [8/45] mt6625l: add changes outside driver dir
config: arm-randconfig-r033-20210714 (attached as .config)
compiler: clang version 13.0.0 (https://github.com/llvm/llvm-project 8d69635ed9ecf36fd0ca85906bfde17949671cbe)
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
# install arm cross compiling tool for clang build
# apt-get install binutils-arm-linux-gnueabi
# https://github.com/frank-w/BPI-R2-4.14/commit/daf840cab15926e075953cf836e...
git remote add frank-w-bpi-r2-4.14 https://github.com/frank-w/BPI-R2-4.14
git fetch --no-tags frank-w-bpi-r2-4.14 5.14-hdmilarb
git checkout daf840cab15926e075953cf836e903114868c074
# save the attached .config to linux build tree
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=clang make.cross ARCH=arm
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All errors (new ones prefixed by >>):
>> drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:191:6: error: no previous prototype for function 'mtk_wcn_consys_power_on' [-Werror,-Wmissing-prototypes]
VOID mtk_wcn_consys_power_on(VOID)
^
drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:191:1: note: declare 'static' if the function is not intended to be used outside of this translation unit
VOID mtk_wcn_consys_power_on(VOID)
^
static
>> drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:207:6: error: no previous prototype for function 'mtk_wcn_consys_power_off' [-Werror,-Wmissing-prototypes]
VOID mtk_wcn_consys_power_off(VOID)
^
drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:207:1: note: declare 'static' if the function is not intended to be used outside of this translation unit
VOID mtk_wcn_consys_power_off(VOID)
^
static
>> drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:224:7: error: no previous prototype for function 'mtk_wcn_consys_hw_reg_ctrl' [-Werror,-Wmissing-prototypes]
INT32 mtk_wcn_consys_hw_reg_ctrl(UINT32 on, UINT32 co_clock_type)
^
drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:224:1: note: declare 'static' if the function is not intended to be used outside of this translation unit
INT32 mtk_wcn_consys_hw_reg_ctrl(UINT32 on, UINT32 co_clock_type)
^
static
>> drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:335:7: error: no previous prototype for function 'mtk_wcn_consys_hw_gpio_ctrl' [-Werror,-Wmissing-prototypes]
INT32 mtk_wcn_consys_hw_gpio_ctrl(UINT32 on)
^
drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:335:1: note: declare 'static' if the function is not intended to be used outside of this translation unit
INT32 mtk_wcn_consys_hw_gpio_ctrl(UINT32 on)
^
static
>> drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:539:7: error: no previous prototype for function 'mtk_wcn_consys_hw_restore' [-Werror,-Wmissing-prototypes]
INT32 mtk_wcn_consys_hw_restore(struct device *device)
^
drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:539:1: note: declare 'static' if the function is not intended to be used outside of this translation unit
INT32 mtk_wcn_consys_hw_restore(struct device *device)
^
static
>> drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:592:5: error: no previous prototype for function 'reserve_memory_consys_fn' [-Werror,-Wmissing-prototypes]
int reserve_memory_consys_fn(struct reserved_mem *rmem)
^
drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c:592:1: note: declare 'static' if the function is not intended to be used outside of this translation unit
int reserve_memory_consys_fn(struct reserved_mem *rmem)
^
static
6 errors generated.
Kconfig warnings: (for reference only)
WARNING: unmet direct dependencies detected for MTK_GPS
Depends on ARM && GPS
Selected by
- MTK_GPS_SUPPORT && ARM
vim +/mtk_wcn_consys_power_on +191 drivers/misc/mediatek/connectivity/common/conn_soc/mt7623/mtk_wcn_consys_hw.c
2b190f4faaa462 Frank Wunderlich 2021-07-12 190
2b190f4faaa462 Frank Wunderlich 2021-07-12 @191 VOID mtk_wcn_consys_power_on(VOID)
2b190f4faaa462 Frank Wunderlich 2021-07-12 192 {
2b190f4faaa462 Frank Wunderlich 2021-07-12 193 INT32 iRet = -1;
2b190f4faaa462 Frank Wunderlich 2021-07-12 194 iRet = pm_runtime_get_sync(&my_pdev->dev);
2b190f4faaa462 Frank Wunderlich 2021-07-12 195 if (iRet)
2b190f4faaa462 Frank Wunderlich 2021-07-12 196 WMT_PLAT_ERR_FUNC("pm_runtime_get_sync() fail(%d)\n", iRet);
2b190f4faaa462 Frank Wunderlich 2021-07-12 197 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 198 WMT_PLAT_INFO_FUNC("pm_runtime_get_sync() CONSYS ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 199
2b190f4faaa462 Frank Wunderlich 2021-07-12 200 iRet = device_init_wakeup(&my_pdev->dev, true);
2b190f4faaa462 Frank Wunderlich 2021-07-12 201 if (iRet)
2b190f4faaa462 Frank Wunderlich 2021-07-12 202 WMT_PLAT_ERR_FUNC("device_init_wakeup(true) fail.\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 203 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 204 WMT_PLAT_INFO_FUNC("device_init_wakeup(true) CONSYS ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 205 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 206
2b190f4faaa462 Frank Wunderlich 2021-07-12 @207 VOID mtk_wcn_consys_power_off(VOID)
2b190f4faaa462 Frank Wunderlich 2021-07-12 208 {
2b190f4faaa462 Frank Wunderlich 2021-07-12 209 INT32 iRet = -1;
2b190f4faaa462 Frank Wunderlich 2021-07-12 210
2b190f4faaa462 Frank Wunderlich 2021-07-12 211 iRet = pm_runtime_put_sync(&my_pdev->dev);
2b190f4faaa462 Frank Wunderlich 2021-07-12 212 if (iRet)
2b190f4faaa462 Frank Wunderlich 2021-07-12 213 WMT_PLAT_ERR_FUNC("pm_runtime_put_sync() fail.\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 214 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 215 WMT_PLAT_INFO_FUNC("pm_runtime_put_sync() CONSYS ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 216
2b190f4faaa462 Frank Wunderlich 2021-07-12 217 iRet = device_init_wakeup(&my_pdev->dev, false);
2b190f4faaa462 Frank Wunderlich 2021-07-12 218 if (iRet)
2b190f4faaa462 Frank Wunderlich 2021-07-12 219 WMT_PLAT_ERR_FUNC("device_init_wakeup(false) fail.\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 220 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 221 WMT_PLAT_INFO_FUNC("device_init_wakeup(false) CONSYS ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 222 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 223
2b190f4faaa462 Frank Wunderlich 2021-07-12 @224 INT32 mtk_wcn_consys_hw_reg_ctrl(UINT32 on, UINT32 co_clock_type)
2b190f4faaa462 Frank Wunderlich 2021-07-12 225 {
2b190f4faaa462 Frank Wunderlich 2021-07-12 226 UINT32 retry = 10;
2b190f4faaa462 Frank Wunderlich 2021-07-12 227 UINT32 consysHwChipId = 0;
2b190f4faaa462 Frank Wunderlich 2021-07-12 228
2b190f4faaa462 Frank Wunderlich 2021-07-12 229 WMT_PLAT_DBG_FUNC("CONSYS-HW-REG-CTRL(0x%08x),start\n", on);
2b190f4faaa462 Frank Wunderlich 2021-07-12 230 if (on) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 231 WMT_PLAT_DBG_FUNC("++\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 232 /*need PMIC driver provide new API protocol */
2b190f4faaa462 Frank Wunderlich 2021-07-12 233 /*1.AP power on VCN_1V8 LDO (with PMIC_WRAP API) VCN_1V8 */
2b190f4faaa462 Frank Wunderlich 2021-07-12 234 regulator_set_mode(reg_VCN18, REGULATOR_MODE_STANDBY);
2b190f4faaa462 Frank Wunderlich 2021-07-12 235 /* VOL_DEFAULT, VOL_1200, VOL_1300, VOL_1500, VOL_1800... */
2b190f4faaa462 Frank Wunderlich 2021-07-12 236 if (reg_VCN18) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 237 regulator_set_voltage(reg_VCN18, 1800000, 1800000);
2b190f4faaa462 Frank Wunderlich 2021-07-12 238 if (regulator_enable(reg_VCN18))
2b190f4faaa462 Frank Wunderlich 2021-07-12 239 WMT_PLAT_ERR_FUNC("enable VCN18 fail\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 240 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 241 WMT_PLAT_DBG_FUNC("enable VCN18 ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 242 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 243 udelay(150);
2b190f4faaa462 Frank Wunderlich 2021-07-12 244 if (co_clock_type) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 245 /*step0,clk buf ctrl */
2b190f4faaa462 Frank Wunderlich 2021-07-12 246 WMT_PLAT_INFO_FUNC("co clock type(%d),turn on clk buf\n", co_clock_type);
2b190f4faaa462 Frank Wunderlich 2021-07-12 247 #if CONSYS_CLOCK_BUF_CTRL
2b190f4faaa462 Frank Wunderlich 2021-07-12 248 clk_buf_ctrl(CLK_BUF_CONN, 1);
2b190f4faaa462 Frank Wunderlich 2021-07-12 249 #endif
2b190f4faaa462 Frank Wunderlich 2021-07-12 250 /*if co-clock mode: */
2b190f4faaa462 Frank Wunderlich 2021-07-12 251 /*2.set VCN28 to SW control mode (with PMIC_WRAP API) */
2b190f4faaa462 Frank Wunderlich 2021-07-12 252 /*turn on VCN28 LDO only when FMSYS is activated" */
2b190f4faaa462 Frank Wunderlich 2021-07-12 253 regmap_update_bits(pmic_regmap, 0x41C, 0x1 << 14, 0x0 << 14);/*V28*/
2b190f4faaa462 Frank Wunderlich 2021-07-12 254 } else {
2b190f4faaa462 Frank Wunderlich 2021-07-12 255 /*if NOT co-clock: */
2b190f4faaa462 Frank Wunderlich 2021-07-12 256 /*2.1.switch VCN28 to HW control mode (with PMIC_WRAP API) */
2b190f4faaa462 Frank Wunderlich 2021-07-12 257 regmap_update_bits(pmic_regmap, 0x41C, 0x1 << 14, 0x1 << 14);/*V28*/
2b190f4faaa462 Frank Wunderlich 2021-07-12 258 /*2.2.turn on VCN28 LDO (with PMIC_WRAP API)" */
2b190f4faaa462 Frank Wunderlich 2021-07-12 259 /*fix vcn28 not balance warning */
2b190f4faaa462 Frank Wunderlich 2021-07-12 260 if (reg_VCN28) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 261 regulator_set_voltage(reg_VCN28, 2800000, 2800000);
2b190f4faaa462 Frank Wunderlich 2021-07-12 262 if (regulator_enable(reg_VCN28))
2b190f4faaa462 Frank Wunderlich 2021-07-12 263 WMT_PLAT_ERR_FUNC("enable VCN_2V8 fail!\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 264 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 265 WMT_PLAT_DBG_FUNC("enable VCN_2V8 ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 266 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 267 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 268
2b190f4faaa462 Frank Wunderlich 2021-07-12 269 /*3.assert CONNSYS CPU SW reset 0x10007018 "[12]=1'b1 [31:24]=8'h88 (key)" */
2b190f4faaa462 Frank Wunderlich 2021-07-12 270 reset_control_reset(rstc);
2b190f4faaa462 Frank Wunderlich 2021-07-12 271 mtk_wcn_consys_power_on();
2b190f4faaa462 Frank Wunderlich 2021-07-12 272 /*11.26M is ready now, delay 10us for mem_pd de-assert */
2b190f4faaa462 Frank Wunderlich 2021-07-12 273 udelay(10);
2b190f4faaa462 Frank Wunderlich 2021-07-12 274 /*enable AP bus clock : connmcu_bus_pd API: enable_clock() ++?? */
2b190f4faaa462 Frank Wunderlich 2021-07-12 275 clk_prepare_enable(clk_infra_conn_main);
2b190f4faaa462 Frank Wunderlich 2021-07-12 276 WMT_PLAT_DBG_FUNC("[CCF]enable clk_infra_conn_main\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 277 /*12.poll CONNSYS CHIP ID until chipid is returned 0x18070008 */
2b190f4faaa462 Frank Wunderlich 2021-07-12 278 while (retry-- > 0) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 279 consysHwChipId = CONSYS_REG_READ(conn_reg.mcu_base + CONSYS_CHIP_ID_OFFSET) - 0xf6d;
2b190f4faaa462 Frank Wunderlich 2021-07-12 280
2b190f4faaa462 Frank Wunderlich 2021-07-12 281 if ((consysHwChipId == 0x0321) || (consysHwChipId == 0x0335) || (consysHwChipId == 0x0337)) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 282 WMT_PLAT_INFO_FUNC("retry(%d)consys chipId(0x%08x)\n", retry, consysHwChipId);
2b190f4faaa462 Frank Wunderlich 2021-07-12 283 break;
2b190f4faaa462 Frank Wunderlich 2021-07-12 284 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 285 if ((consysHwChipId == 0x8163) || (consysHwChipId == 0x8127) || (consysHwChipId == 0x7623)) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 286 WMT_PLAT_INFO_FUNC("retry(%d)consys chipId(0x%08x)\n", retry, consysHwChipId);
2b190f4faaa462 Frank Wunderlich 2021-07-12 287 break;
2b190f4faaa462 Frank Wunderlich 2021-07-12 288 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 289
2b190f4faaa462 Frank Wunderlich 2021-07-12 290 WMT_PLAT_ERR_FUNC("Read CONSYS chipId(0x%08x)", consysHwChipId);
2b190f4faaa462 Frank Wunderlich 2021-07-12 291 msleep(20);
2b190f4faaa462 Frank Wunderlich 2021-07-12 292 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 293
2b190f4faaa462 Frank Wunderlich 2021-07-12 294 if ((0 == retry) || (0 == consysHwChipId))
2b190f4faaa462 Frank Wunderlich 2021-07-12 295 WMT_PLAT_ERR_FUNC("Maybe has a consys power on issue,(0x%08x)\n", consysHwChipId);
2b190f4faaa462 Frank Wunderlich 2021-07-12 296
2b190f4faaa462 Frank Wunderlich 2021-07-12 297 msleep(40);
2b190f4faaa462 Frank Wunderlich 2021-07-12 298
2b190f4faaa462 Frank Wunderlich 2021-07-12 299 } else {
2b190f4faaa462 Frank Wunderlich 2021-07-12 300
2b190f4faaa462 Frank Wunderlich 2021-07-12 301 clk_disable_unprepare(clk_infra_conn_main);
2b190f4faaa462 Frank Wunderlich 2021-07-12 302 WMT_PLAT_DBG_FUNC("[CCF] clk_disable_unprepare(clk_infra_conn_main) calling\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 303 mtk_wcn_consys_power_off();
2b190f4faaa462 Frank Wunderlich 2021-07-12 304
2b190f4faaa462 Frank Wunderlich 2021-07-12 305 if (co_clock_type) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 306 /*VCN28 has been turned off by GPS OR FM */
2b190f4faaa462 Frank Wunderlich 2021-07-12 307 #if CONSYS_CLOCK_BUF_CTRL
2b190f4faaa462 Frank Wunderlich 2021-07-12 308 clk_buf_ctrl(CLK_BUF_CONN, 0);
2b190f4faaa462 Frank Wunderlich 2021-07-12 309 #endif
2b190f4faaa462 Frank Wunderlich 2021-07-12 310 } else {
2b190f4faaa462 Frank Wunderlich 2021-07-12 311 regmap_update_bits(pmic_regmap, 0x41C, 0x1 << 14, 0x0 << 14);/*V28*/
2b190f4faaa462 Frank Wunderlich 2021-07-12 312 /*turn off VCN28 LDO (with PMIC_WRAP API)" */
2b190f4faaa462 Frank Wunderlich 2021-07-12 313 if (reg_VCN28) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 314 if (regulator_disable(reg_VCN28))
2b190f4faaa462 Frank Wunderlich 2021-07-12 315 WMT_PLAT_ERR_FUNC("disable VCN_2V8 fail!\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 316 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 317 WMT_PLAT_DBG_FUNC("disable VCN_2V8 ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 318 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 319 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 320
2b190f4faaa462 Frank Wunderlich 2021-07-12 321 /*AP power off MT6625L VCN_1V8 LDO */
2b190f4faaa462 Frank Wunderlich 2021-07-12 322 regulator_set_mode(reg_VCN18, REGULATOR_MODE_STANDBY);
2b190f4faaa462 Frank Wunderlich 2021-07-12 323 if (reg_VCN18) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 324 if (regulator_disable(reg_VCN18))
2b190f4faaa462 Frank Wunderlich 2021-07-12 325 WMT_PLAT_ERR_FUNC("disable VCN_1V8 fail!\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 326 else
2b190f4faaa462 Frank Wunderlich 2021-07-12 327 WMT_PLAT_DBG_FUNC("disable VCN_1V8 ok\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 328 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 329
2b190f4faaa462 Frank Wunderlich 2021-07-12 330 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 331 WMT_PLAT_DBG_FUNC("CONSYS-HW-REG-CTRL(0x%08x),finish\n", on);
2b190f4faaa462 Frank Wunderlich 2021-07-12 332 return 0;
2b190f4faaa462 Frank Wunderlich 2021-07-12 333 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 334
2b190f4faaa462 Frank Wunderlich 2021-07-12 @335 INT32 mtk_wcn_consys_hw_gpio_ctrl(UINT32 on)
2b190f4faaa462 Frank Wunderlich 2021-07-12 336 {
2b190f4faaa462 Frank Wunderlich 2021-07-12 337 INT32 iRet = 0;
2b190f4faaa462 Frank Wunderlich 2021-07-12 338
2b190f4faaa462 Frank Wunderlich 2021-07-12 339 WMT_PLAT_DBG_FUNC("CONSYS-HW-GPIO-CTRL(0x%08x), start\n", on);
2b190f4faaa462 Frank Wunderlich 2021-07-12 340
2b190f4faaa462 Frank Wunderlich 2021-07-12 341 if (on) {
2b190f4faaa462 Frank Wunderlich 2021-07-12 342
2b190f4faaa462 Frank Wunderlich 2021-07-12 343 /* TODO: [FixMe][GeorgeKuo] double check if BGF_INT is implemented ok */
2b190f4faaa462 Frank Wunderlich 2021-07-12 344 /* iRet += wmt_plat_gpio_ctrl(PIN_BGF_EINT, PIN_STA_MUX); */
2b190f4faaa462 Frank Wunderlich 2021-07-12 345 iRet += wmt_plat_eirq_ctrl(PIN_BGF_EINT, PIN_STA_INIT);
2b190f4faaa462 Frank Wunderlich 2021-07-12 346 iRet += wmt_plat_eirq_ctrl(PIN_BGF_EINT, PIN_STA_EINT_DIS);
2b190f4faaa462 Frank Wunderlich 2021-07-12 347 WMT_PLAT_DBG_FUNC("CONSYS-HW, BGF IRQ registered and disabled\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 348
2b190f4faaa462 Frank Wunderlich 2021-07-12 349 } else {
2b190f4faaa462 Frank Wunderlich 2021-07-12 350
2b190f4faaa462 Frank Wunderlich 2021-07-12 351 /* set bgf eint/all eint to deinit state, namely input low state */
2b190f4faaa462 Frank Wunderlich 2021-07-12 352 iRet += wmt_plat_eirq_ctrl(PIN_BGF_EINT, PIN_STA_EINT_DIS);
2b190f4faaa462 Frank Wunderlich 2021-07-12 353 iRet += wmt_plat_eirq_ctrl(PIN_BGF_EINT, PIN_STA_DEINIT);
2b190f4faaa462 Frank Wunderlich 2021-07-12 354 WMT_PLAT_DBG_FUNC("CONSYS-HW, BGF IRQ unregistered and disabled\n");
2b190f4faaa462 Frank Wunderlich 2021-07-12 355 /* iRet += wmt_plat_gpio_ctrl(PIN_BGF_EINT, PIN_STA_DEINIT); */
2b190f4faaa462 Frank Wunderlich 2021-07-12 356 }
2b190f4faaa462 Frank Wunderlich 2021-07-12 357 WMT_PLAT_DBG_FUNC("CONSYS-HW-GPIO-CTRL(0x%08x), finish\n", on);
2b190f4faaa462 Frank Wunderlich 2021-07-12 358 return iRet;
2b190f4faaa462 Frank Wunderlich 2021-07-12 359
:::::: The code at line 191 was first introduced by commit
:::::: 2b190f4faaa462e17cc35e26250875142e239187 mt6625l: add driver folder from 5.13
:::::: TO: Frank Wunderlich <frank-w(a)public-files.de>
:::::: CC: Frank Wunderlich <frank-w(a)public-files.de>
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
undefined reference to `__irqentry_text_start'
by kernel test robot
tree: https://git.kernel.org/pub/scm/linux/kernel/git/torvalds/linux.git master
head: 8096acd7442e613fad0354fc8dfdb2003cceea0b
commit: 788691464c29455346dc613a3b43c2fb9e5757a4 mm/slub: use stackdepot to save stack trace in objects
date: 6 days ago
config: arc-randconfig-r023-20210714 (attached as .config)
compiler: arceb-elf-gcc (GCC) 9.3.0
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
# https://git.kernel.org/pub/scm/linux/kernel/git/torvalds/linux.git/commit...
git remote add linus https://git.kernel.org/pub/scm/linux/kernel/git/torvalds/linux.git
git fetch --no-tags linus master
git checkout 788691464c29455346dc613a3b43c2fb9e5757a4
# save the attached .config to linux build tree
mkdir build_dir
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=gcc-9.3.0 make.cross O=build_dir ARCH=arc SHELL=/bin/bash
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All errors (new ones prefixed by >>):
arceb-elf-ld: lib/stackdepot.o: in function `filter_irq_stacks':
>> (.text+0x18): undefined reference to `__irqentry_text_start'
>> arceb-elf-ld: (.text+0x18): undefined reference to `__irqentry_text_start'
>> arceb-elf-ld: (.text+0x34): undefined reference to `__irqentry_text_end'
>> arceb-elf-ld: (.text+0x34): undefined reference to `__irqentry_text_end'
>> arceb-elf-ld: (.text+0x64): undefined reference to `__softirqentry_text_start'
>> arceb-elf-ld: (.text+0x64): undefined reference to `__softirqentry_text_start'
>> arceb-elf-ld: (.text+0x6c): undefined reference to `__softirqentry_text_end'
>> arceb-elf-ld: (.text+0x6c): undefined reference to `__softirqentry_text_end'
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
Re: [Intel-gfx] [PATCH v3 4/5] drm/print: move conditional deref into macro defn
by kernel test robot
Hi Jim,
I love your patch! Yet something to improve:
[auto build test ERROR on drm-intel/for-linux-next]
[also build test ERROR on drm-tip/drm-tip linus/master v5.14-rc1 next-20210714]
[If your patch is applied to the wrong git tree, kindly drop us a note.
And when submitting patch, we suggest to use '--base' as documented in
https://git-scm.com/docs/git-format-patch]
url: https://github.com/0day-ci/linux/commits/Jim-Cromie/drm-use-dyndbg-in-drm...
base: git://anongit.freedesktop.org/drm-intel for-linux-next
config: arm-randconfig-r004-20210714 (attached as .config)
compiler: clang version 13.0.0 (https://github.com/llvm/llvm-project 8d69635ed9ecf36fd0ca85906bfde17949671cbe)
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
# install arm cross compiling tool for clang build
# apt-get install binutils-arm-linux-gnueabi
# https://github.com/0day-ci/linux/commit/4a3dcdd418da090977ab9fa225818e5ad...
git remote add linux-review https://github.com/0day-ci/linux
git fetch --no-tags linux-review Jim-Cromie/drm-use-dyndbg-in-drm_print/20210715-015347
git checkout 4a3dcdd418da090977ab9fa225818e5ad142288d
# save the attached .config to linux build tree
mkdir build_dir
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=clang make.cross O=build_dir ARCH=arm SHELL=/bin/bash drivers/gpu/drm/bridge/
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All errors (new ones prefixed by >>):
>> drivers/gpu/drm/bridge/nwl-dsi.c:229:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "DSI Lanes %d\n", dsi->lanes);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:242:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_t_pre: 0x%x\n", cycles);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:245:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_tx_gap (pre): 0x%x\n", cycles);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:247:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_t_post: 0x%x\n", cycles);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:250:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_tx_gap: 0x%x\n", cycles);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:259:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_twakeup: 0x%x\n", cycles);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:281:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "hfront_porch = %d\n", hfront_porch);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:282:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "hback_porch = %d\n", hback_porch);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
^
include/drm/drm_print.h:330:30: note: expanded from macro 'drm_dev_dbg'
_drm_dev_dbg((drm) ? (drm)->dev : NULL, cls, fmt, ##__VA_ARGS__)
^
include/linux/device.h:544:10: note: 'devt' declared here
dev_t devt; /* dev_t, creates the sysfs "dev" */
^
drivers/gpu/drm/bridge/nwl-dsi.c:283:2: error: no member named 'dev' in 'struct device'; did you mean 'devt'?
DRM_DEV_DEBUG_DRIVER(dsi->dev, "hsync_len = %d\n", hsync_len);
^
include/drm/drm_print.h:439:2: note: expanded from macro 'DRM_DEV_DEBUG_DRIVER'
drm_dev_dbg(dev, cDRM_UT_DRIVER, fmt, ##__VA_ARGS__)
vim +229 drivers/gpu/drm/bridge/nwl-dsi.c
44cfc6233447cb Guido Günther 2020-04-09 220
44cfc6233447cb Guido Günther 2020-04-09 221 static int nwl_dsi_config_host(struct nwl_dsi *dsi)
44cfc6233447cb Guido Günther 2020-04-09 222 {
44cfc6233447cb Guido Günther 2020-04-09 223 u32 cycles;
44cfc6233447cb Guido Günther 2020-04-09 224 struct phy_configure_opts_mipi_dphy *cfg = &dsi->phy_cfg.mipi_dphy;
44cfc6233447cb Guido Günther 2020-04-09 225
44cfc6233447cb Guido Günther 2020-04-09 226 if (dsi->lanes < 1 || dsi->lanes > 4)
44cfc6233447cb Guido Günther 2020-04-09 227 return -EINVAL;
44cfc6233447cb Guido Günther 2020-04-09 228
44cfc6233447cb Guido Günther 2020-04-09 @229 DRM_DEV_DEBUG_DRIVER(dsi->dev, "DSI Lanes %d\n", dsi->lanes);
44cfc6233447cb Guido Günther 2020-04-09 230 nwl_dsi_write(dsi, NWL_DSI_CFG_NUM_LANES, dsi->lanes - 1);
44cfc6233447cb Guido Günther 2020-04-09 231
44cfc6233447cb Guido Günther 2020-04-09 232 if (dsi->dsi_mode_flags & MIPI_DSI_CLOCK_NON_CONTINUOUS) {
44cfc6233447cb Guido Günther 2020-04-09 233 nwl_dsi_write(dsi, NWL_DSI_CFG_NONCONTINUOUS_CLK, 0x01);
44cfc6233447cb Guido Günther 2020-04-09 234 nwl_dsi_write(dsi, NWL_DSI_CFG_AUTOINSERT_EOTP, 0x01);
44cfc6233447cb Guido Günther 2020-04-09 235 } else {
44cfc6233447cb Guido Günther 2020-04-09 236 nwl_dsi_write(dsi, NWL_DSI_CFG_NONCONTINUOUS_CLK, 0x00);
44cfc6233447cb Guido Günther 2020-04-09 237 nwl_dsi_write(dsi, NWL_DSI_CFG_AUTOINSERT_EOTP, 0x00);
44cfc6233447cb Guido Günther 2020-04-09 238 }
44cfc6233447cb Guido Günther 2020-04-09 239
44cfc6233447cb Guido Günther 2020-04-09 240 /* values in byte clock cycles */
44cfc6233447cb Guido Günther 2020-04-09 241 cycles = ui2bc(dsi, cfg->clk_pre);
44cfc6233447cb Guido Günther 2020-04-09 242 DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_t_pre: 0x%x\n", cycles);
44cfc6233447cb Guido Günther 2020-04-09 243 nwl_dsi_write(dsi, NWL_DSI_CFG_T_PRE, cycles);
44cfc6233447cb Guido Günther 2020-04-09 244 cycles = ps2bc(dsi, cfg->lpx + cfg->clk_prepare + cfg->clk_zero);
44cfc6233447cb Guido Günther 2020-04-09 245 DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_tx_gap (pre): 0x%x\n", cycles);
44cfc6233447cb Guido Günther 2020-04-09 246 cycles += ui2bc(dsi, cfg->clk_pre);
44cfc6233447cb Guido Günther 2020-04-09 247 DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_t_post: 0x%x\n", cycles);
44cfc6233447cb Guido Günther 2020-04-09 248 nwl_dsi_write(dsi, NWL_DSI_CFG_T_POST, cycles);
44cfc6233447cb Guido Günther 2020-04-09 249 cycles = ps2bc(dsi, cfg->hs_exit);
44cfc6233447cb Guido Günther 2020-04-09 250 DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_tx_gap: 0x%x\n", cycles);
44cfc6233447cb Guido Günther 2020-04-09 251 nwl_dsi_write(dsi, NWL_DSI_CFG_TX_GAP, cycles);
44cfc6233447cb Guido Günther 2020-04-09 252
44cfc6233447cb Guido Günther 2020-04-09 253 nwl_dsi_write(dsi, NWL_DSI_CFG_EXTRA_CMDS_AFTER_EOTP, 0x01);
44cfc6233447cb Guido Günther 2020-04-09 254 nwl_dsi_write(dsi, NWL_DSI_CFG_HTX_TO_COUNT, 0x00);
44cfc6233447cb Guido Günther 2020-04-09 255 nwl_dsi_write(dsi, NWL_DSI_CFG_LRX_H_TO_COUNT, 0x00);
44cfc6233447cb Guido Günther 2020-04-09 256 nwl_dsi_write(dsi, NWL_DSI_CFG_BTA_H_TO_COUNT, 0x00);
44cfc6233447cb Guido Günther 2020-04-09 257 /* In LP clock cycles */
44cfc6233447cb Guido Günther 2020-04-09 258 cycles = us2lp(cfg->lp_clk_rate, cfg->wakeup);
44cfc6233447cb Guido Günther 2020-04-09 259 DRM_DEV_DEBUG_DRIVER(dsi->dev, "cfg_twakeup: 0x%x\n", cycles);
44cfc6233447cb Guido Günther 2020-04-09 260 nwl_dsi_write(dsi, NWL_DSI_CFG_TWAKEUP, cycles);
44cfc6233447cb Guido Günther 2020-04-09 261
44cfc6233447cb Guido Günther 2020-04-09 262 return nwl_dsi_clear_error(dsi);
44cfc6233447cb Guido Günther 2020-04-09 263 }
44cfc6233447cb Guido Günther 2020-04-09 264
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
[tegra-drm:drm/tegra/for-next 9/14] drivers/gpu/drm/tegra/uapi.c:278:5: warning: no previous prototype for 'tegra_drm_ioctl_gem_create'
by kernel test robot
tree: git://anongit.freedesktop.org/tegra/linux.git drm/tegra/for-next
head: b19502d1a683c11f6f2c92ad63c61288b0fbe1a1
commit: cdf631031f3e574b76afed51bda0ccc9d71d4a4e [9/14] drm/tegra: Implement new UAPI
config: arm-defconfig (attached as .config)
compiler: arm-linux-gnueabi-gcc (GCC) 9.3.0
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
git remote add tegra-drm git://anongit.freedesktop.org/tegra/linux.git
git fetch --no-tags tegra-drm drm/tegra/for-next
git checkout cdf631031f3e574b76afed51bda0ccc9d71d4a4e
# save the attached .config to linux build tree
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=gcc-9.3.0 make.cross ARCH=arm
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All warnings (new ones prefixed by >>):
>> drivers/gpu/drm/tegra/uapi.c:278:5: warning: no previous prototype for 'tegra_drm_ioctl_gem_create' [-Wmissing-prototypes]
278 | int tegra_drm_ioctl_gem_create(struct drm_device *drm, void *data,
| ^~~~~~~~~~~~~~~~~~~~~~~~~~
>> drivers/gpu/drm/tegra/uapi.c:295:5: warning: no previous prototype for 'tegra_drm_ioctl_gem_mmap' [-Wmissing-prototypes]
295 | int tegra_drm_ioctl_gem_mmap(struct drm_device *drm, void *data,
| ^~~~~~~~~~~~~~~~~~~~~~~~
vim +/tegra_drm_ioctl_gem_create +278 drivers/gpu/drm/tegra/uapi.c
277
> 278 int tegra_drm_ioctl_gem_create(struct drm_device *drm, void *data,
279 struct drm_file *file)
280 {
281 struct drm_tegra_gem_create *args = data;
282 struct tegra_bo *bo;
283
284 if (args->flags)
285 return -EINVAL;
286
287 bo = tegra_bo_create_with_handle(file, drm, args->size, args->flags,
288 &args->handle);
289 if (IS_ERR(bo))
290 return PTR_ERR(bo);
291
292 return 0;
293 }
294
> 295 int tegra_drm_ioctl_gem_mmap(struct drm_device *drm, void *data,
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
[xlnx:xlnx_rebase_v5.10 711/1756] drivers/remoteproc/ingenic_rproc.c:144:14: error: incompatible function pointer types initializing 'void *(*)(struct rproc *, u64, int)' (aka 'void *(*)(struct rproc *, unsigned long long, int)') with an expression of type 'void *(struct rproc *, u64, siz...
by kernel test robot
tree: https://github.com/Xilinx/linux-xlnx xlnx_rebase_v5.10
head: f6f032f82f0a13def702a0154df535db88f43391
commit: dbb49124cb3ba0ebd03cca4efa2c91cf0164d071 [711/1756] remoteproc: Add support for peek from remote and acking kick from remote
config: mips-randconfig-r004-20210714 (attached as .config)
compiler: clang version 13.0.0 (https://github.com/llvm/llvm-project 8d69635ed9ecf36fd0ca85906bfde17949671cbe)
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
# install mips cross compiling tool for clang build
# apt-get install binutils-mips-linux-gnu
# https://github.com/Xilinx/linux-xlnx/commit/dbb49124cb3ba0ebd03cca4efa2c9...
git remote add xlnx https://github.com/Xilinx/linux-xlnx
git fetch --no-tags xlnx xlnx_rebase_v5.10
git checkout dbb49124cb3ba0ebd03cca4efa2c91cf0164d071
# save the attached .config to linux build tree
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=clang make.cross ARCH=mips
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All errors (new ones prefixed by >>):
>> drivers/remoteproc/ingenic_rproc.c:144:14: error: incompatible function pointer types initializing 'void *(*)(struct rproc *, u64, int)' (aka 'void *(*)(struct rproc *, unsigned long long, int)') with an expression of type 'void *(struct rproc *, u64, size_t)' (aka 'void *(struct rproc *, unsigned long long, unsigned long)') [-Werror,-Wincompatible-function-pointer-types]
.da_to_va = ingenic_rproc_da_to_va,
^~~~~~~~~~~~~~~~~~~~~~
1 error generated.
vim +144 drivers/remoteproc/ingenic_rproc.c
48f0a1bbb7586c Paul Cercueil 2020-05-15 137
48f0a1bbb7586c Paul Cercueil 2020-05-15 138 static struct rproc_ops ingenic_rproc_ops = {
4605ad8f458198 Mathieu Poirier 2020-06-30 139 .prepare = ingenic_rproc_prepare,
4605ad8f458198 Mathieu Poirier 2020-06-30 140 .unprepare = ingenic_rproc_unprepare,
48f0a1bbb7586c Paul Cercueil 2020-05-15 141 .start = ingenic_rproc_start,
48f0a1bbb7586c Paul Cercueil 2020-05-15 142 .stop = ingenic_rproc_stop,
48f0a1bbb7586c Paul Cercueil 2020-05-15 143 .kick = ingenic_rproc_kick,
48f0a1bbb7586c Paul Cercueil 2020-05-15 @144 .da_to_va = ingenic_rproc_da_to_va,
48f0a1bbb7586c Paul Cercueil 2020-05-15 145 };
48f0a1bbb7586c Paul Cercueil 2020-05-15 146
:::::: The code at line 144 was first introduced by commit
:::::: 48f0a1bbb7586c94e0f15116b06f8179df2fd60f remoteproc: ingenic: Added remoteproc driver
:::::: TO: Paul Cercueil <paul(a)crapouillou.net>
:::::: CC: Bjorn Andersson <bjorn.andersson(a)linaro.org>
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
lib/raid6/neon1.c:27:10: fatal error: 'arm_neon.h' file not found
by kernel test robot
Hi Alexey,
First bad commit (maybe != root cause):
tree: https://github.com/0day-ci/linux/commits/UPDATE-20210715-014555/Alexey-Do...
head: f189675c22efc0acc3b1d1d15220c37aa3cb4fe3
commit: f189675c22efc0acc3b1d1d15220c37aa3cb4fe3 Decouple build from userspace headers
date: 4 hours ago
config: arm64-randconfig-r025-20210714 (attached as .config)
compiler: clang version 13.0.0 (https://github.com/llvm/llvm-project 8d69635ed9ecf36fd0ca85906bfde17949671cbe)
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
# install arm64 cross compiling tool for clang build
# apt-get install binutils-aarch64-linux-gnu
# https://github.com/0day-ci/linux/commit/f189675c22efc0acc3b1d1d15220c37aa...
git remote add linux-review https://github.com/0day-ci/linux
git fetch --no-tags linux-review UPDATE-20210715-014555/Alexey-Dobriyan/Decouple-build-from-userspace-headers/20210714-034924
git checkout f189675c22efc0acc3b1d1d15220c37aa3cb4fe3
# save the attached .config to linux build tree
mkdir build_dir
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=clang make.cross O=build_dir ARCH=arm64 SHELL=/bin/bash arch/arm64/kernel/ lib/raid6/
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All errors (new ones prefixed by >>):
>> lib/raid6/neon1.c:27:10: fatal error: 'arm_neon.h' file not found
#include <arm_neon.h>
^~~~~~~~~~~~
1 error generated.
--
>> lib/raid6/neon2.c:27:10: fatal error: 'arm_neon.h' file not found
#include <arm_neon.h>
^~~~~~~~~~~~
1 error generated.
--
>> lib/raid6/neon4.c:27:10: fatal error: 'arm_neon.h' file not found
#include <arm_neon.h>
^~~~~~~~~~~~
1 error generated.
--
>> lib/raid6/neon8.c:27:10: fatal error: 'arm_neon.h' file not found
#include <arm_neon.h>
^~~~~~~~~~~~
1 error generated.
--
>> lib/raid6/recov_neon_inner.c:7:10: fatal error: 'arm_neon.h' file not found
#include <arm_neon.h>
^~~~~~~~~~~~
1 error generated.
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
Re: [PATCH v2 02/16] soc: qcom: apr: make code more reuseable
by kernel test robot
Hi Srinivas,
I love your patch! Perhaps something to improve:
[auto build test WARNING on asoc/for-next]
[also build test WARNING on robh/for-next sound/for-next linus/master v5.14-rc1 next-20210714]
[If your patch is applied to the wrong git tree, kindly drop us a note.
And when submitting patch, we suggest to use '--base' as documented in
https://git-scm.com/docs/git-format-patch]
url: https://github.com/0day-ci/linux/commits/Srinivas-Kandagatla/ASoC-qcom-Ad...
base: https://git.kernel.org/pub/scm/linux/kernel/git/broonie/sound.git for-next
config: mips-randconfig-r004-20210714 (attached as .config)
compiler: clang version 13.0.0 (https://github.com/llvm/llvm-project 8d69635ed9ecf36fd0ca85906bfde17949671cbe)
reproduce (this is a W=1 build):
wget https://raw.githubusercontent.com/intel/lkp-tests/master/sbin/make.cross -O ~/bin/make.cross
chmod +x ~/bin/make.cross
# install mips cross compiling tool for clang build
# apt-get install binutils-mips-linux-gnu
# https://github.com/0day-ci/linux/commit/16cc55dede1767dd253072173a72dcc8c...
git remote add linux-review https://github.com/0day-ci/linux
git fetch --no-tags linux-review Srinivas-Kandagatla/ASoC-qcom-Add-AudioReach-support/20210714-233339
git checkout 16cc55dede1767dd253072173a72dcc8c7a88a34
# save the attached .config to linux build tree
COMPILER_INSTALL_PATH=$HOME/0day COMPILER=clang make.cross ARCH=mips
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All warnings (new ones prefixed by >>):
>> drivers/soc/qcom/apr.c:446:6: warning: variable 'ret' is used uninitialized whenever 'if' condition is false [-Wsometimes-uninitialized]
if (of_device_is_compatible(dev->of_node, "qcom,apr")) {
^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
drivers/soc/qcom/apr.c:451:6: note: uninitialized use occurs here
if (ret) {
^~~
drivers/soc/qcom/apr.c:446:2: note: remove the 'if' if its condition is always true
if (of_device_is_compatible(dev->of_node, "qcom,apr")) {
^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
drivers/soc/qcom/apr.c:440:9: note: initialize the variable 'ret' to silence this warning
int ret;
^
= 0
1 warning generated.
vim +446 drivers/soc/qcom/apr.c
435
436 static int apr_probe(struct rpmsg_device *rpdev)
437 {
438 struct device *dev = &rpdev->dev;
439 struct packet_router *apr;
440 int ret;
441
442 apr = devm_kzalloc(dev, sizeof(*apr), GFP_KERNEL);
443 if (!apr)
444 return -ENOMEM;
445
> 446 if (of_device_is_compatible(dev->of_node, "qcom,apr")) {
447 ret = of_property_read_u32(dev->of_node, "qcom,apr-domain", &apr->dest_domain_id);
448 apr->type = PR_TYPE_APR;
449 }
450
451 if (ret) {
452 dev_err(dev, "Domain ID not specified in DT\n");
453 return ret;
454 }
455
456 dev_set_drvdata(dev, apr);
457 apr->ch = rpdev->ept;
458 apr->dev = dev;
459 apr->rxwq = create_singlethread_workqueue("qcom_apr_rx");
460 if (!apr->rxwq) {
461 dev_err(apr->dev, "Failed to start Rx WQ\n");
462 return -ENOMEM;
463 }
464 INIT_WORK(&apr->rx_work, apr_rxwq);
465
466 apr->pdr = pdr_handle_alloc(apr_pd_status, apr);
467 if (IS_ERR(apr->pdr)) {
468 dev_err(dev, "Failed to init PDR handle\n");
469 ret = PTR_ERR(apr->pdr);
470 goto destroy_wq;
471 }
472
473 INIT_LIST_HEAD(&apr->rx_list);
474 spin_lock_init(&apr->rx_lock);
475 spin_lock_init(&apr->svcs_lock);
476 idr_init(&apr->svcs_idr);
477
478 ret = of_apr_add_pd_lookups(dev);
479 if (ret)
480 goto handle_release;
481
482 of_register_apr_devices(dev, NULL);
483
484 return 0;
485
486 handle_release:
487 pdr_handle_release(apr->pdr);
488 destroy_wq:
489 destroy_workqueue(apr->rxwq);
490 return ret;
491 }
492
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months
[xlnx:xlnx_rebase_v5.10 1042/1756] ./usr/include/linux/videodev2.h:2380:20: error: field 'timestamp' has incomplete type
by kernel test robot
tree: https://github.com/Xilinx/linux-xlnx xlnx_rebase_v5.10
head: f6f032f82f0a13def702a0154df535db88f43391
commit: 87134cbd0bfd3a28abc5747ce98d0c2098bdda1a [1042/1756] staging: xlnxsync: Fix the uapi header license
config: i386-allyesconfig (attached as .config)
compiler: gcc-10 (Debian 10.2.1-6) 10.2.1 20210110
reproduce (this is a W=1 build):
# https://github.com/Xilinx/linux-xlnx/commit/87134cbd0bfd3a28abc5747ce98d0...
git remote add xlnx https://github.com/Xilinx/linux-xlnx
git fetch --no-tags xlnx xlnx_rebase_v5.10
git checkout 87134cbd0bfd3a28abc5747ce98d0c2098bdda1a
# save the attached .config to linux build tree
mkdir build_dir
make W=1 O=build_dir ARCH=i386 SHELL=/bin/bash
If you fix the issue, kindly add following tag as appropriate
Reported-by: kernel test robot <lkp(a)intel.com>
All errors (new ones prefixed by >>):
In file included from ./usr/include/linux/xilinx-hls.h:8,
from <command-line>:32:
>> ./usr/include/linux/videodev2.h:2380:20: error: field 'timestamp' has incomplete type
2380 | struct timespec timestamp;
| ^~~~~~~~~
--
In file included from <command-line>:32:
>> ./usr/include/linux/xlnxsync.h:44:2: error: unknown type name 'u64'
44 | u64 hdr_ver;
| ^~~
./usr/include/linux/xlnxsync.h:45:2: error: unknown type name 'u64'
45 | u64 luma_start_offset[XLNXSYNC_IO];
| ^~~
./usr/include/linux/xlnxsync.h:46:2: error: unknown type name 'u64'
46 | u64 chroma_start_offset[XLNXSYNC_IO];
| ^~~
./usr/include/linux/xlnxsync.h:47:2: error: unknown type name 'u64'
47 | u64 luma_end_offset[XLNXSYNC_IO];
| ^~~
./usr/include/linux/xlnxsync.h:48:2: error: unknown type name 'u64'
48 | u64 chroma_end_offset[XLNXSYNC_IO];
| ^~~
>> ./usr/include/linux/xlnxsync.h:49:2: error: unknown type name 'u32'
49 | u32 luma_margin;
| ^~~
./usr/include/linux/xlnxsync.h:50:2: error: unknown type name 'u32'
50 | u32 chroma_margin;
| ^~~
./usr/include/linux/xlnxsync.h:51:2: error: unknown type name 'u32'
51 | u32 luma_core_offset[XLNXSYNC_MAX_CORES];
| ^~~
./usr/include/linux/xlnxsync.h:52:2: error: unknown type name 'u32'
52 | u32 chroma_core_offset[XLNXSYNC_MAX_CORES];
| ^~~
./usr/include/linux/xlnxsync.h:53:2: error: unknown type name 'u32'
53 | u32 dma_fd;
| ^~~
>> ./usr/include/linux/xlnxsync.h:54:2: error: unknown type name 'u8'
54 | u8 fb_id[XLNXSYNC_IO];
| ^~
./usr/include/linux/xlnxsync.h:55:2: error: unknown type name 'u8'
55 | u8 ismono[XLNXSYNC_IO];
| ^~
./usr/include/linux/xlnxsync.h:67:2: error: unknown type name 'u64'
67 | u64 hdr_ver;
| ^~~
./usr/include/linux/xlnxsync.h:68:2: error: unknown type name 'u8'
68 | u8 sync_err;
| ^~
./usr/include/linux/xlnxsync.h:69:2: error: unknown type name 'u8'
69 | u8 wdg_err;
| ^~
./usr/include/linux/xlnxsync.h:70:2: error: unknown type name 'u8'
70 | u8 ldiff_err;
| ^~
./usr/include/linux/xlnxsync.h:71:2: error: unknown type name 'u8'
71 | u8 cdiff_err;
| ^~
./usr/include/linux/xlnxsync.h:80:2: error: unknown type name 'u64'
80 | u64 hdr_ver;
| ^~~
./usr/include/linux/xlnxsync.h:81:2: error: unknown type name 'u8'
81 | u8 status[XLNXSYNC_BUF_PER_CHAN][XLNXSYNC_IO];
| ^~
./usr/include/linux/xlnxsync.h:93:2: error: unknown type name 'u64'
93 | u64 hdr_ver;
| ^~~
./usr/include/linux/xlnxsync.h:94:2: error: unknown type name 'u8'
94 | u8 encode;
| ^~
./usr/include/linux/xlnxsync.h:95:2: error: unknown type name 'u8'
95 | u8 max_channels;
| ^~
./usr/include/linux/xlnxsync.h:96:2: error: unknown type name 'u8'
96 | u8 active_channels;
| ^~
./usr/include/linux/xlnxsync.h:97:2: error: unknown type name 'u8'
97 | u8 reserved_id;
| ^~
./usr/include/linux/xlnxsync.h:98:2: error: unknown type name 'u32'
98 | u32 reserved[10];
| ^~~
./usr/include/linux/xlnxsync.h:112:2: error: unknown type name 'u64'
112 | u64 hdr_ver;
| ^~~
./usr/include/linux/xlnxsync.h:113:2: error: unknown type name 'u8'
113 | u8 fbdone[XLNXSYNC_BUF_PER_CHAN][XLNXSYNC_IO];
| ^~
./usr/include/linux/xlnxsync.h:114:2: error: unknown type name 'u8'
114 | u8 enable;
| ^~
./usr/include/linux/xlnxsync.h:115:2: error: unknown type name 'u8'
115 | u8 sync_err;
| ^~
./usr/include/linux/xlnxsync.h:116:2: error: unknown type name 'u8'
116 | u8 wdg_err;
| ^~
./usr/include/linux/xlnxsync.h:117:2: error: unknown type name 'u8'
117 | u8 ldiff_err;
| ^~
./usr/include/linux/xlnxsync.h:118:2: error: unknown type name 'u8'
118 | u8 cdiff_err;
| ^~
--
In file included from <command-line>:32:
>> ./usr/include/linux/xlnx_mpg2tsmux_interface.h:58:2: error: unknown type name 'u8'
58 | u8 stream_id;
| ^~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:59:2: error: unknown type name 'u8'
59 | u8 extended_stream_id;
| ^~
>> ./usr/include/linux/xlnx_mpg2tsmux_interface.h:60:2: error: unknown type name 'bool'
60 | bool is_pcr_stream;
| ^~~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:61:2: error: unknown type name 'bool'
61 | bool is_valid_pts;
| ^~~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:62:2: error: unknown type name 'bool'
62 | bool is_valid_dts;
| ^~~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:63:2: error: unknown type name 'bool'
63 | bool is_dmabuf;
| ^~~~
>> ./usr/include/linux/xlnx_mpg2tsmux_interface.h:64:2: error: unknown type name 'u16'
64 | u16 pid;
| ^~~
>> ./usr/include/linux/xlnx_mpg2tsmux_interface.h:65:2: error: unknown type name 'u64'
65 | u64 size_data_in;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:66:2: error: unknown type name 'u64'
66 | u64 pts;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:67:2: error: unknown type name 'u64'
67 | u64 dts;
| ^~~
>> ./usr/include/linux/xlnx_mpg2tsmux_interface.h:68:2: error: unknown type name 'u32'
68 | u32 srcbuf_id;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:69:2: error: unknown type name 'bool'
69 | bool insert_pcr;
| ^~~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:70:2: error: unknown type name 'u16'
70 | u16 pcr_extension;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:71:2: error: unknown type name 'u64'
71 | u64 pcr_base;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:81:2: error: unknown type name 'bool'
81 | bool is_dmabuf;
| ^~~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:82:2: error: unknown type name 'u32'
82 | u32 dstbuf_id;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:83:2: error: unknown type name 'u32'
83 | u32 dmabuf_size;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:104:2: error: unknown type name 'u32'
104 | u32 num_buf;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:105:2: error: unknown type name 'u32'
105 | u32 buf_size;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:114:2: error: unknown type name 'u32'
114 | u32 buf_id;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:115:2: error: unknown type name 'u32'
115 | u32 buf_write;
| ^~~
./usr/include/linux/xlnx_mpg2tsmux_interface.h:137:2: error: unknown type name 'u16'
137 | u16 pid;
| ^~~
---
0-DAY CI Kernel Test Service, Intel Corporation
https://lists.01.org/hyperkitty/list/kbuild-all@lists.01.org
1 year, 2 months